11// Fails with opencl non-cpu, enable when fixed.
22// XFAIL: (opencl && !cpu && !accelerator)
3- // RUN: %{build} -I . -o %t.out %if any-device-is-cuda %{ -Xsycl-target-backend=nvptx64-nvidia-cuda --cuda-gpu-arch=sm_70 %} -Wno-deprecated-declarations
3+ // XFAIL-TRACKER: https://github.com/intel/llvm/issues/14641
4+
5+ // RUN: %{build} -I . -o %t.out %if any-device-is-cuda %{ -Xsycl-target-backend=nvptx64-nvidia-cuda --cuda-gpu-arch=sm_70 %}
46// RUN: %{run} %t.out
57
68// Disabled temporarily while investigation into the failure is ongoing.
1416#include < sycl/detail/core.hpp>
1517#include < sycl/ext/oneapi/experimental/root_group.hpp>
1618#include < sycl/group_barrier.hpp>
19+ #include < sycl/kernel_bundle.hpp>
1720
1821static constexpr int WorkGroupSize = 32 ;
1922
@@ -27,13 +30,18 @@ void testQueriesAndProperties() {
2730 const auto bundle =
2831 sycl::get_kernel_bundle<sycl::bundle_state::executable>(q.get_context ());
2932 const auto kernel = bundle.get_kernel <class QueryKernel >();
30- const auto maxWGs = kernel.ext_oneapi_get_info <
31- sycl::ext::oneapi::experimental::info::kernel_queue_specific::
32- max_num_work_group_sync>(q);
33- const auto wgRange = sycl::range{WorkGroupSize, 1 , 1 };
34- const auto maxWGsWithLimits = kernel.ext_oneapi_get_info <
35- sycl::ext::oneapi::experimental::info::kernel_queue_specific::
36- max_num_work_group_sync>(q, wgRange, wgRange.size () * sizeof (int ));
33+ const auto local_range = sycl::range<1 >(1 );
34+ const auto maxWGs =
35+ kernel
36+ .ext_oneapi_get_info <sycl::ext::oneapi::experimental::info::
37+ kernel_queue_specific::max_num_work_groups>(
38+ q, local_range, 0 );
39+ const auto wgRange = sycl::range<3 >{WorkGroupSize, 1 , 1 };
40+ const auto maxWGsWithLimits =
41+ kernel
42+ .ext_oneapi_get_info <sycl::ext::oneapi::experimental::info::
43+ kernel_queue_specific::max_num_work_groups>(
44+ q, wgRange, wgRange.size () * sizeof (int ));
3745 const auto props = sycl::ext::oneapi::experimental::properties{
3846 sycl::ext::oneapi::experimental::use_root_sync};
3947 q.single_task <class QueryKernel >(props, []() {});
@@ -52,9 +60,11 @@ void testRootGroup() {
5260 const auto bundle =
5361 sycl::get_kernel_bundle<sycl::bundle_state::executable>(q.get_context ());
5462 const auto kernel = bundle.get_kernel <class RootGroupKernel >();
55- const auto maxWGs = kernel.ext_oneapi_get_info <
56- sycl::ext::oneapi::experimental::info::kernel_queue_specific::
57- max_num_work_group_sync>(q);
63+ const auto maxWGs =
64+ kernel
65+ .ext_oneapi_get_info <sycl::ext::oneapi::experimental::info::
66+ kernel_queue_specific::max_num_work_groups>(
67+ q, WorkGroupSize, 0 );
5868 const auto props = sycl::ext::oneapi::experimental::properties{
5969 sycl::ext::oneapi::experimental::use_root_sync};
6070 sycl::buffer<int > dataBuf{sycl::range{maxWGs * WorkGroupSize}};
@@ -94,9 +104,11 @@ void testRootGroupFunctions() {
94104 const auto bundle =
95105 sycl::get_kernel_bundle<sycl::bundle_state::executable>(q.get_context ());
96106 const auto kernel = bundle.get_kernel <class RootGroupFunctionsKernel >();
97- const auto maxWGs = kernel.ext_oneapi_get_info <
98- sycl::ext::oneapi::experimental::info::kernel_queue_specific::
99- max_num_work_group_sync>(q);
107+ const auto maxWGs =
108+ kernel
109+ .ext_oneapi_get_info <sycl::ext::oneapi::experimental::info::
110+ kernel_queue_specific::max_num_work_groups>(
111+ q, WorkGroupSize, 0 );
100112 const auto props = sycl::ext::oneapi::experimental::properties{
101113 sycl::ext::oneapi::experimental::use_root_sync};
102114
0 commit comments