From 026ff463cd6fad39d5cb2ad419a48d9d03e86b57 Mon Sep 17 00:00:00 2001 From: "Ptak, Slawomir" Date: Thu, 9 Oct 2025 13:45:13 +0000 Subject: [PATCH 1/3] [SYCL] Add the nd_range validation to the handler-less path --- sycl/include/sycl/queue.hpp | 3 +++ 1 file changed, 3 insertions(+) diff --git a/sycl/include/sycl/queue.hpp b/sycl/include/sycl/queue.hpp index 3a44e9504cd3b..986474c9edf23 100644 --- a/sycl/include/sycl/queue.hpp +++ b/sycl/include/sycl/queue.hpp @@ -18,6 +18,7 @@ #include // for code_location #include // for __SYCL2020_DEP... #include // for __SYCL_EXPORT +#include // for checkValueRange #include // for is_queue_info_... #include // for KernelInfo #include @@ -183,6 +184,8 @@ auto submit_kernel_direct( "must be either sycl::nd_item or be convertible from sycl::nd_item"); using TransformedArgType = sycl::nd_item; + detail::checkValueRange(Range); + detail::KernelWrapper::wrap(KernelFunc); From 2bd69907f0928a0fdc13946a5ff2fcd736338d34 Mon Sep 17 00:00:00 2001 From: "Ptak, Slawomir" Date: Thu, 9 Oct 2025 15:23:07 +0000 Subject: [PATCH 2/3] Fix compile --- sycl/include/sycl/queue.hpp | 2 ++ 1 file changed, 2 insertions(+) diff --git a/sycl/include/sycl/queue.hpp b/sycl/include/sycl/queue.hpp index 986474c9edf23..5a72029485580 100644 --- a/sycl/include/sycl/queue.hpp +++ b/sycl/include/sycl/queue.hpp @@ -184,7 +184,9 @@ auto submit_kernel_direct( "must be either sycl::nd_item or be convertible from sycl::nd_item"); using TransformedArgType = sycl::nd_item; +#ifndef __SYCL_DEVICE_ONLY__ detail::checkValueRange(Range); +#endif detail::KernelWrapper::wrap(KernelFunc); From 638784a5d5a21467ae30c9c1923c84701a2f2070 Mon Sep 17 00:00:00 2001 From: "Ptak, Slawomir" Date: Fri, 10 Oct 2025 08:47:06 +0000 Subject: [PATCH 3/3] Update sycl_detail_core.hpp.cpp --- sycl/test/include_deps/sycl_detail_core.hpp.cpp | 2 +- 1 file changed, 1 insertion(+), 1 deletion(-) diff --git a/sycl/test/include_deps/sycl_detail_core.hpp.cpp b/sycl/test/include_deps/sycl_detail_core.hpp.cpp index f4c33d1ed938f..cf98e8708254a 100644 --- a/sycl/test/include_deps/sycl_detail_core.hpp.cpp +++ b/sycl/test/include_deps/sycl_detail_core.hpp.cpp @@ -100,6 +100,7 @@ // CHECK-NEXT: kernel_handler.hpp // CHECK-NEXT: nd_item.hpp // CHECK-NEXT: nd_range.hpp +// CHECK-NEXT: detail/id_queries_fit_in_int.hpp // CHECK-NEXT: detail/optional.hpp // CHECK-NEXT: device.hpp // CHECK-NEXT: detail/string_view.hpp @@ -134,7 +135,6 @@ // CHECK-NEXT: CL/cl_ext.h // CHECK-NEXT: detail/get_device_kernel_info.hpp // CHECK-NEXT: detail/compile_time_kernel_info.hpp -// CHECK-NEXT: detail/id_queries_fit_in_int.hpp // CHECK-NEXT: detail/kernel_launch_helper.hpp // CHECK-NEXT: ext/intel/experimental/fp_control_kernel_properties.hpp // CHECK-NEXT: ext/intel/experimental/kernel_execution_properties.hpp