[SYCL] Fix KernelType definition

The KernelType definition, used to check if a kernel is using
a kernel_handler argument, should be a pure lambda type,
so remove const and reference declarations.

Author: slawekptak

sycl/include/sycl/queue.hpp

@@ -3310,7 +3310,8 @@ class __SYCL_EXPORT queue : public detail::OwnerLessBase<queue> {
                           RestT &&...Rest) {
     constexpr detail::code_location CodeLoc = getCodeLocation<KernelName>();
     detail::tls_code_loc_t TlsCodeLocCapture(CodeLoc);
-    using KernelType = std::tuple_element_t<0, std::tuple<RestT...>>;
+    using KernelType = std::remove_const_t<
+        std::remove_reference_t<std::tuple_element_t<0, std::tuple<RestT...>>>>;
 
     // TODO The handler-less path does not support reductions, and
     // kernel functions with the kernel_handler type argument yet.
@@ -3340,7 +3341,8 @@ class __SYCL_EXPORT queue : public detail::OwnerLessBase<queue> {
   parallel_for(nd_range<Dims> Range, RestT &&...Rest) {
     constexpr detail::code_location CodeLoc = getCodeLocation<KernelName>();
     detail::tls_code_loc_t TlsCodeLocCapture(CodeLoc);
-    using KernelType = std::tuple_element_t<0, std::tuple<RestT...>>;
+    using KernelType = std::remove_const_t<
+        std::remove_reference_t<std::tuple_element_t<0, std::tuple<RestT...>>>>;
 
     // TODO The handler-less path does not support reductions, and
     // kernel functions with the kernel_handler type argument yet.
@@ -3402,7 +3404,8 @@ class __SYCL_EXPORT queue : public detail::OwnerLessBase<queue> {
   parallel_for(nd_range<Dims> Range, event DepEvent, RestT &&...Rest) {
     constexpr detail::code_location CodeLoc = getCodeLocation<KernelName>();
     detail::tls_code_loc_t TlsCodeLocCapture(CodeLoc);
-    using KernelType = std::tuple_element_t<0, std::tuple<RestT...>>;
+    using KernelType = std::remove_const_t<
+        std::remove_reference_t<std::tuple_element_t<0, std::tuple<RestT...>>>>;
 
     // TODO The handler-less path does not support reductions, and
     // kernel functions with the kernel_handler type argument yet.
@@ -3469,7 +3472,8 @@ class __SYCL_EXPORT queue : public detail::OwnerLessBase<queue> {
                RestT &&...Rest) {
     constexpr detail::code_location CodeLoc = getCodeLocation<KernelName>();
     detail::tls_code_loc_t TlsCodeLocCapture(CodeLoc);
-    using KernelType = std::tuple_element_t<0, std::tuple<RestT...>>;
+    using KernelType = std::remove_const_t<
+        std::remove_reference_t<std::tuple_element_t<0, std::tuple<RestT...>>>>;
 
     // TODO The handler-less path does not support reductions, and
     // kernel functions with the kernel_handler type argument yet.