[SYCL] Handler-less kernel submit path (range based)

[slawekptak]

Extend the handler-less kernel submission path to sycl::range based functions. This includes:

1. A refactor of range rounding utility functions, so they can be shared between a handler and a queue
2. The actual sycl::range based submission, with range rounding logic
3. Modifications of range rounding e2e tests, which can now test both handler-based and handler-less functions.

[aelovikov-intel]

A refactor of range rounding utility functions, so they can be shared between a handler and a queue

This can/should go to a separate NFC PR.

[aelovikov-intel]

We're in ABI breaking window, just drop it.

[aelovikov-intel]

That's an extra std::shared_ptr copy. https://github.com/intel/llvm/pull/20698/files#r2561353949 is related. Can you collaborate with @lbushi25 for a better fix?

[aelovikov-intel]

llvm/sycl/include/sycl/detail/type_traits.hpp

Lines 385 to 397 in 259c433

	// Example usage:
	// using mapped = map_type<type_to_map, from0, /*->*/ to0,
	// from1, /*->*/ to1,
	// ...>
	template <typename...> struct map_type {
	using type = void;
	};
	template <typename T, typename From, typename To, typename... Rest>
	struct map_type<T, From, To, Rest...> {
	using type = std::conditional_t<std::is_same_v<From, T>, To,
	typename map_type<T, Rest...>::type>;
	};

might be helpful.

[aelovikov-intel]

Just drop it.

[aelovikov-intel]

Same comment as in #20756 (review) - use detail::nth_type_t, it's much better for compile time.

But also, this doesn't make sense because of line 3755 (AreAllButLastReductions check). Did you mean to access sizeof...(RestT) - 1's element?

[aelovikov-intel]

Would std::decay_t suffice?

[aelovikov-intel]

Isn't it use-after-move (inside the call on line 3950)?