diff --git a/SYCL/BFloat16/bfloat16_type.hpp b/SYCL/BFloat16/bfloat16_type.hpp index 17742fb5dc..97e1ccb7fc 100644 --- a/SYCL/BFloat16/bfloat16_type.hpp +++ b/SYCL/BFloat16/bfloat16_type.hpp @@ -169,7 +169,7 @@ void verify_logic(queue &q, buffer &a, buffer &b, } int run_tests() { - device dev{default_selector()}; + device dev{default_selector_v}; // TODO: replace is_gpu check with extension check when the appropriate part // of implementation ready (aspect) diff --git a/SYCL/Basic/barrier_order.cpp b/SYCL/Basic/barrier_order.cpp index 1d4d0769ba..ad492086a4 100644 --- a/SYCL/Basic/barrier_order.cpp +++ b/SYCL/Basic/barrier_order.cpp @@ -8,7 +8,7 @@ #include int main() { - sycl::device dev{sycl::default_selector{}}; + sycl::device dev{sycl::default_selector_v}; sycl::queue q{dev}; int *x = sycl::malloc_shared(1, q); diff --git a/SYCL/Basic/buffer/buffer_dev_to_dev.cpp b/SYCL/Basic/buffer/buffer_dev_to_dev.cpp index b9773412ee..aab4596dc7 100644 --- a/SYCL/Basic/buffer/buffer_dev_to_dev.cpp +++ b/SYCL/Basic/buffer/buffer_dev_to_dev.cpp @@ -25,8 +25,7 @@ int main() { buffer Buffer(Data, range<1>(10), {property::buffer::use_host_ptr()}); - default_selector Selector; - device Device(Selector); + device Device(default_selector_v); context FirstContext(Device); context SecondContext(Device); diff --git a/SYCL/Basic/buffer/buffer_migrate.cpp b/SYCL/Basic/buffer/buffer_migrate.cpp index 715106a97b..087f5d439f 100644 --- a/SYCL/Basic/buffer/buffer_migrate.cpp +++ b/SYCL/Basic/buffer/buffer_migrate.cpp @@ -21,7 +21,7 @@ int main() { buffer Buffer(&Data, range<1>(1)); const auto &Devices = - platform(gpu_selector{}).get_devices(info::device_type::gpu); + platform(gpu_selector_v).get_devices(info::device_type::gpu); std::cout << Devices.size() << " devices found" << std::endl; context C(Devices); diff --git a/SYCL/Basic/build_log.cpp b/SYCL/Basic/build_log.cpp index ebfc651d22..60d245f2f0 100644 --- a/SYCL/Basic/build_log.cpp +++ b/SYCL/Basic/build_log.cpp @@ -7,7 +7,7 @@ #include int main() { - sycl::queue Q{sycl::default_selector()}; + sycl::queue Q{sycl::default_selector_v}; auto *I = sycl::malloc_device(1, Q); Q.single_task([=]() { I[0] = 42; }); diff --git a/SYCL/Basic/enqueue_barrier.cpp b/SYCL/Basic/enqueue_barrier.cpp index 225dda44e6..fc911ad230 100644 --- a/SYCL/Basic/enqueue_barrier.cpp +++ b/SYCL/Basic/enqueue_barrier.cpp @@ -12,7 +12,7 @@ int main() { sycl::context Context; - sycl::queue Q1(Context, sycl::default_selector{}); + sycl::queue Q1(Context, sycl::default_selector_v); Q1.submit( [&](sycl::handler &cgh) { cgh.single_task([]() {}); }); @@ -30,8 +30,8 @@ int main() { // call queue::ext_oneapi_submit_barrier() Q1.ext_oneapi_submit_barrier(); - sycl::queue Q2(Context, sycl::default_selector{}); - sycl::queue Q3(Context, sycl::default_selector{}); + sycl::queue Q2(Context, sycl::default_selector_v); + sycl::queue Q3(Context, sycl::default_selector_v); auto Event1 = Q1.submit( [&](sycl::handler &cgh) { cgh.single_task([]() {}); }); diff --git a/SYCL/Basic/fpga_tests/Inputs/fpga_host.cpp b/SYCL/Basic/fpga_tests/Inputs/fpga_host.cpp index 727edf6beb..cd143d5256 100644 --- a/SYCL/Basic/fpga_tests/Inputs/fpga_host.cpp +++ b/SYCL/Basic/fpga_tests/Inputs/fpga_host.cpp @@ -14,7 +14,7 @@ using namespace sycl; void foo(double &, queue q, int x); int main(void) { - queue q(accelerator_selector{}); + queue q(accelerator_selector_v); double result; foo(result, q, 3); diff --git a/SYCL/Basic/get_backend.cpp b/SYCL/Basic/get_backend.cpp index ed5407d4bc..6c696119b1 100644 --- a/SYCL/Basic/get_backend.cpp +++ b/SYCL/Basic/get_backend.cpp @@ -43,8 +43,7 @@ int main() { return_fail(); } - default_selector sel; - queue q(c, sel); + queue q(c, default_selector_v); if (q.get_backend() != plt.get_backend()) { return_fail(); } diff --git a/SYCL/Basic/group_local_id.cpp b/SYCL/Basic/group_local_id.cpp index db70924295..47849f93ca 100644 --- a/SYCL/Basic/group_local_id.cpp +++ b/SYCL/Basic/group_local_id.cpp @@ -8,7 +8,7 @@ using namespace sycl; int main() { - queue q(cpu_selector{}); + queue q(cpu_selector_v); const int sz = 16; q.submit([&](handler &h) { diff --git a/SYCL/Basic/half_type.cpp b/SYCL/Basic/half_type.cpp index c46649411e..004ef340ac 100644 --- a/SYCL/Basic/half_type.cpp +++ b/SYCL/Basic/half_type.cpp @@ -237,7 +237,7 @@ int main() { constexpr_verify_mul(); constexpr_verify_div(); - device dev{default_selector()}; + device dev{default_selector_v}; if (!dev.has(sycl::aspect::fp16)) { std::cout << "This device doesn't support the extension cl_khr_fp16" << std::endl; diff --git a/SYCL/Basic/handler/interop_task.cpp b/SYCL/Basic/handler/interop_task.cpp index cf56b8126c..2cde2698d6 100644 --- a/SYCL/Basic/handler/interop_task.cpp +++ b/SYCL/Basic/handler/interop_task.cpp @@ -27,7 +27,7 @@ int main() { sycl::buffer DstBuf(sycl::range<1>{BufSize}); sycl::buffer DstBuf2(sycl::range<1>{BufSize}); - TestQueue Queue{sycl::default_selector{}}; + TestQueue Queue{sycl::default_selector_v}; Queue.submit([&](sycl::handler &CGH) { auto DstAcc = DstBuf.get_access(CGH); diff --git a/SYCL/Basic/handler/run_on_host_intel.cpp b/SYCL/Basic/handler/run_on_host_intel.cpp index 1b63c811b5..8f0d7d39f6 100644 --- a/SYCL/Basic/handler/run_on_host_intel.cpp +++ b/SYCL/Basic/handler/run_on_host_intel.cpp @@ -26,7 +26,7 @@ int main() { sycl::buffer SrcBuf(data1, sycl::range<1>{BufSize}); sycl::buffer DstBuf(sycl::range<1>{BufSize}); - TestQueue Queue{sycl::default_selector{}}; + TestQueue Queue{sycl::default_selector_v}; Queue.submit([&](sycl::handler &CGH) { auto SrcAcc = SrcBuf.get_access(CGH); auto DstAcc = DstBuf.get_access(CGH); diff --git a/SYCL/Basic/image/image.cpp b/SYCL/Basic/image/image.cpp index 8180d4e6f8..1b48bcc541 100644 --- a/SYCL/Basic/image/image.cpp +++ b/SYCL/Basic/image/image.cpp @@ -34,7 +34,7 @@ int main() { { sycl::image<2> Img1(Img1HostData.data(), ChanOrder, ChanType, Img1Size); sycl::image<2> Img2(Img2HostData.data(), ChanOrder, ChanType, Img2Size); - TestQueue Q{sycl::default_selector()}; + TestQueue Q{sycl::default_selector_v}; Q.submit([&](sycl::handler &CGH) { auto Img1Acc = Img1.get_access(CGH); auto Img2Acc = Img2.get_access(CGH); @@ -63,7 +63,7 @@ int main() { { const sycl::range<1> ImgPitch(4 * 4 * 4 * 2); sycl::image<2> Img(ChanOrder, ChanType, Img1Size, ImgPitch); - TestQueue Q{sycl::default_selector()}; + TestQueue Q{sycl::default_selector_v}; Q.submit([&](sycl::handler &CGH) { auto ImgAcc = Img.get_access(CGH); CGH.single_task([=]() { ImgAcc.get_range(); }); @@ -74,7 +74,7 @@ int main() { const sycl::range<1> ImgPitch(4 * 4 * 4 * 2); sycl::image<2> Img(Img1HostData.data(), ChanOrder, ChanType, Img1Size, ImgPitch); - TestQueue Q{sycl::default_selector()}; + TestQueue Q{sycl::default_selector_v}; Q.submit([&](sycl::handler &CGH) { auto ImgAcc = Img.get_access(CGH); CGH.single_task([=] { ImgAcc.get_range(); }); diff --git a/SYCL/Basic/image/image_accessor_readwrite_half.cpp b/SYCL/Basic/image/image_accessor_readwrite_half.cpp index 305e6d03bf..83a9f32691 100644 --- a/SYCL/Basic/image/image_accessor_readwrite_half.cpp +++ b/SYCL/Basic/image/image_accessor_readwrite_half.cpp @@ -146,7 +146,7 @@ void check_half4(char *HostPtr) { int main() { // Checking if default selected device supports half datatype. // Same device will be selected in the write/read functions. - s::device Dev{s::default_selector()}; + s::device Dev{s::default_selector_v}; if (!Dev.has(sycl::aspect::fp16)) { std::cout << "This device doesn't support the extension cl_khr_fp16" << std::endl; diff --git a/SYCL/Basic/image/image_array.cpp b/SYCL/Basic/image/image_array.cpp index 520c3047f3..9494705e14 100644 --- a/SYCL/Basic/image/image_array.cpp +++ b/SYCL/Basic/image/image_array.cpp @@ -46,7 +46,7 @@ int main() { sycl::buffer ResBuf(ResBufData.data(), {ResBufSize}); - TestQueue Q{sycl::default_selector()}; + TestQueue Q{sycl::default_selector_v}; constexpr auto SYCLRead = sycl::access::mode::read; constexpr auto SYCLWrite = sycl::access::mode::write; diff --git a/SYCL/Basic/image/image_read.cpp b/SYCL/Basic/image/image_read.cpp index 1edb1ca3f9..9d94a1378a 100644 --- a/SYCL/Basic/image/image_read.cpp +++ b/SYCL/Basic/image/image_read.cpp @@ -7,8 +7,7 @@ int main() { - s::default_selector selector; - s::queue myQueue(selector); + s::queue myQueue(s::default_selector_v); bool passed = true; diff --git a/SYCL/Basic/image/image_read_fp16.cpp b/SYCL/Basic/image/image_read_fp16.cpp index a40b31bedb..beee757400 100644 --- a/SYCL/Basic/image/image_read_fp16.cpp +++ b/SYCL/Basic/image/image_read_fp16.cpp @@ -6,8 +6,7 @@ #include "image_read.h" int main() { - s::default_selector selector; - s::queue myQueue(selector); + s::queue myQueue(s::default_selector_v); // Device doesn't support cl_khr_fp16 extension - skip. if (!myQueue.get_device().has(sycl::aspect::fp16)) diff --git a/SYCL/Basic/image/image_sample.cpp b/SYCL/Basic/image/image_sample.cpp index fe9f153716..1e54b8e13b 100644 --- a/SYCL/Basic/image/image_sample.cpp +++ b/SYCL/Basic/image/image_sample.cpp @@ -43,8 +43,6 @@ bool test1d_coord(dataT *hostPtr, coordT coord, dataT expectedColour) { s::sampler testSampler(s::coordinate_normalization_mode::unnormalized, s::addressing_mode::clamp, s::filtering_mode::linear); - s::default_selector selector; - { // Scope everything to force destruction s::image<1> image(hostPtr, s::image_channel_order::rgba, channelType, s::range<1>{3}); @@ -52,7 +50,7 @@ bool test1d_coord(dataT *hostPtr, coordT coord, dataT expectedColour) { s::buffer resultDataBuf(&resultData, s::range<1>(1)); // Do the test by reading a single pixel from the image - s::queue myQueue(selector); + s::queue myQueue(s::default_selector_v); myQueue.submit([&](s::handler &cgh) { auto imageAcc = image.get_access(cgh); s::accessor resultDataAcc(resultDataBuf, @@ -80,8 +78,6 @@ bool test2d_coord(dataT *hostPtr, coordT coord, dataT expectedColour) { s::sampler testSampler(s::coordinate_normalization_mode::unnormalized, s::addressing_mode::clamp, s::filtering_mode::linear); - s::default_selector selector; - { // Scope everything to force destruction s::image<2> image(hostPtr, s::image_channel_order::rgba, channelType, s::range<2>{3, 3}); @@ -89,7 +85,7 @@ bool test2d_coord(dataT *hostPtr, coordT coord, dataT expectedColour) { s::buffer resultDataBuf(&resultData, s::range<1>(1)); // Do the test by reading a single pixel from the image - s::queue myQueue(selector); + s::queue myQueue(s::default_selector_v); myQueue.submit([&](s::handler &cgh) { auto imageAcc = image.get_access(cgh); s::accessor resultDataAcc(resultDataBuf, @@ -117,8 +113,6 @@ bool test3d_coord(dataT *hostPtr, coordT coord, dataT expectedColour) { s::sampler testSampler(s::coordinate_normalization_mode::unnormalized, s::addressing_mode::clamp, s::filtering_mode::linear); - s::default_selector selector; - { // Scope everything to force destruction s::image<3> image(hostPtr, s::image_channel_order::rgba, channelType, s::range<3>{3, 3, 3}); @@ -126,7 +120,7 @@ bool test3d_coord(dataT *hostPtr, coordT coord, dataT expectedColour) { s::buffer resultDataBuf(&resultData, s::range<1>(1)); // Do the test by reading a single pixel from the image - s::queue myQueue(selector); + s::queue myQueue(s::default_selector_v); myQueue.submit([&](s::handler &cgh) { auto imageAcc = image.get_access(cgh); s::accessor resultDataAcc(resultDataBuf, diff --git a/SYCL/Basic/image/image_write.cpp b/SYCL/Basic/image/image_write.cpp index 852fa13a17..d5680dd57c 100644 --- a/SYCL/Basic/image/image_write.cpp +++ b/SYCL/Basic/image/image_write.cpp @@ -11,8 +11,7 @@ int main() { - s::default_selector selector; - s::queue myQueue(selector); + s::queue myQueue(s::default_selector_v); bool passed = true; diff --git a/SYCL/Basic/image/image_write.h b/SYCL/Basic/image/image_write.h index 0ebadcf599..6a87a63925 100644 --- a/SYCL/Basic/image/image_write.h +++ b/SYCL/Basic/image/image_write.h @@ -119,8 +119,6 @@ bool test3d_coord(s::queue myQueue, dataT *hostPtr, coordT coord, dataT colour) { dataT resultData; - s::default_selector selector; - { // Scope everything to force destruction s::image<3> image(hostPtr, s::image_channel_order::rgba, channelType, s::range<3>{3, 3, 3}); diff --git a/SYCL/Basic/image/image_write_fp16.cpp b/SYCL/Basic/image/image_write_fp16.cpp index 091782a8d8..559cae990c 100644 --- a/SYCL/Basic/image/image_write_fp16.cpp +++ b/SYCL/Basic/image/image_write_fp16.cpp @@ -6,8 +6,7 @@ #include "image_write.h" int main() { - s::default_selector selector; - s::queue myQueue(selector); + s::queue myQueue(s::default_selector_v); // Device doesn't support cl_khr_fp16 extension - skip. if (!myQueue.get_device().has(sycl::aspect::fp16)) diff --git a/SYCL/Basic/interop/construction_ocl.cpp b/SYCL/Basic/interop/construction_ocl.cpp index 91912ace44..95313a839b 100644 --- a/SYCL/Basic/interop/construction_ocl.cpp +++ b/SYCL/Basic/interop/construction_ocl.cpp @@ -10,7 +10,7 @@ constexpr auto BE = sycl::backend::opencl; int main() { - sycl::device Dev{sycl::default_selector{}}; + sycl::device Dev{sycl::default_selector_v}; auto NativeDev = sycl::get_native(Dev); sycl::device NewDev = sycl::make_device(NativeDev); diff --git a/SYCL/Basic/interop/construction_ze.cpp b/SYCL/Basic/interop/construction_ze.cpp index 345499338f..6c6ee2f3fa 100644 --- a/SYCL/Basic/interop/construction_ze.cpp +++ b/SYCL/Basic/interop/construction_ze.cpp @@ -10,7 +10,7 @@ constexpr auto BE = sycl::backend::ext_oneapi_level_zero; int main() { - sycl::device Dev{sycl::default_selector{}}; + sycl::device Dev{sycl::default_selector_v}; sycl::queue Q{Dev}; diff --git a/SYCL/Basic/kernel_bundle/kernel_bundle_api.cpp b/SYCL/Basic/kernel_bundle/kernel_bundle_api.cpp index b7321230a4..cb4e59c8a1 100644 --- a/SYCL/Basic/kernel_bundle/kernel_bundle_api.cpp +++ b/SYCL/Basic/kernel_bundle/kernel_bundle_api.cpp @@ -34,8 +34,8 @@ void checkException(TryBodyT TryBody, const std::string &ExpectedErrMsg) { } int main() { - const sycl::device Dev{sycl::default_selector{}}; - const sycl::device Dev2{sycl::default_selector{}}; + const sycl::device Dev{sycl::default_selector_v}; + const sycl::device Dev2{sycl::default_selector_v}; const sycl::context Ctx{Dev}; const sycl::context Ctx2{Dev2}; diff --git a/SYCL/Basic/partition_supported.cpp b/SYCL/Basic/partition_supported.cpp index a8e0a4d678..0786a0ac3c 100644 --- a/SYCL/Basic/partition_supported.cpp +++ b/SYCL/Basic/partition_supported.cpp @@ -53,7 +53,7 @@ supports_partition_property(const sycl::device &dev, int main() { - auto dev = sycl::device(sycl::default_selector()); + auto dev = sycl::device(sycl::default_selector_v); // 1 - check exceed max_compute_units sycl::info::partition_property partitionEqually = diff --git a/SYCL/Basic/stream/stream.cpp b/SYCL/Basic/stream/stream.cpp index 0d3587e65b..ebdd3c9458 100644 --- a/SYCL/Basic/stream/stream.cpp +++ b/SYCL/Basic/stream/stream.cpp @@ -20,8 +20,7 @@ using namespace sycl; int main() { { - default_selector Selector; - queue Queue(Selector); + queue Queue(default_selector_v); context Context = Queue.get_context(); // Check constructor and getters diff --git a/SYCL/Basic/subdevice_pi.cpp b/SYCL/Basic/subdevice_pi.cpp index 5a2adbeb13..5544d06170 100644 --- a/SYCL/Basic/subdevice_pi.cpp +++ b/SYCL/Basic/subdevice_pi.cpp @@ -194,8 +194,7 @@ int main(int argc, const char **argv) { std::string test(argv[1]); std::string partition_type(argv[2]); - default_selector selector; - device dev(selector); + device dev(default_selector_v); std::vector host_mem(1024, 1); buffer buf(&host_mem[0], host_mem.size()); diff --git a/SYCL/Basic/submit_barrier.cpp b/SYCL/Basic/submit_barrier.cpp index 815f7105c6..034abf4106 100755 --- a/SYCL/Basic/submit_barrier.cpp +++ b/SYCL/Basic/submit_barrier.cpp @@ -8,7 +8,7 @@ int main() { - sycl::device dev{sycl::default_selector{}}; + sycl::device dev{sycl::default_selector_v}; sycl::queue q{dev}; q.submit( diff --git a/SYCL/Config/select_device.cpp b/SYCL/Config/select_device.cpp index 7364841e43..d47701d163 100644 --- a/SYCL/Config/select_device.cpp +++ b/SYCL/Config/select_device.cpp @@ -180,6 +180,9 @@ int main() { fs.open("select_device_config.txt"); if (fs.is_open()) { for (const auto &plt : platform::get_platforms()) { + if (passed) { + break; + } // no need to write more than one match for (const auto &dev : plt.get_devices()) { if (dev.has(aspect::gpu)) { std::string name = dev.get_info(); @@ -226,7 +229,7 @@ int main() { std::vector components(getAllowListDesc(allowlist)); std::cout << "SYCL_DEVICE_ALLOWLIST=" << allowlist << std::endl; - sycl::queue deviceQueue(gpu_selector{}); + sycl::queue deviceQueue(gpu_selector_v); device dev = deviceQueue.get_device(); for (const DevDescT &desc : components) { if ((std::regex_match(dev.get_info(), @@ -284,7 +287,7 @@ int main() { std::vector components(getAllowListDesc(allowlist)); std::cout << "SYCL_DEVICE_ALLOWLIST=" << allowlist << std::endl; - sycl::queue deviceQueue(gpu_selector{}); + sycl::queue deviceQueue(gpu_selector_v); device dev = deviceQueue.get_device(); const auto &plt = dev.get_platform(); for (const DevDescT &desc : components) { @@ -310,6 +313,9 @@ int main() { fs.open("select_device_config.txt"); if (fs.is_open()) { for (const auto &plt : platform::get_platforms()) { + if (passed) { + break; + } // no need for additional entries for (const auto &dev : plt.get_devices()) { if (dev.has(aspect::gpu)) { std::string name = dev.get_info(); @@ -345,12 +351,12 @@ int main() { std::cout << "SYCL_DEVICE_ALLOWLIST=" << allowlist << std::endl; try { - sycl::queue deviceQueue(gpu_selector{}); + sycl::queue deviceQueue(gpu_selector_v); device dev = deviceQueue.get_device(); const auto &plt = dev.get_platform(); - } catch (sycl::runtime_error &E) { + } catch (sycl::exception &E) { const std::string expectedMsg( - "No device of requested type available"); + "No device of requested type 'info::device_type::gpu' available"); const std::string gotMessage(E.what()); if (gotMessage.find(expectedMsg) != std::string::npos) { passed = true; @@ -417,12 +423,12 @@ int main() { std::cout << "SYCL_DEVICE_ALLOWLIST=" << allowlist << std::endl; try { - sycl::queue deviceQueue(gpu_selector{}); + sycl::queue deviceQueue(gpu_selector_v); device dev = deviceQueue.get_device(); const auto &plt = dev.get_platform(); - } catch (sycl::runtime_error &E) { + } catch (sycl::exception &E) { const std::string expectedMsg( - "No device of requested type available"); + "No device of requested type 'info::device_type::gpu' available"); const std::string gotMessage(E.what()); if (gotMessage.find(expectedMsg) != std::string::npos) { passed = true; @@ -441,6 +447,9 @@ int main() { fs.open("select_device_config.txt"); if (fs.is_open()) { for (const auto &plt : platform::get_platforms()) { + if (passed) { + break; + } // no need for additional entries for (const auto &dev : plt.get_devices()) { if (dev.has(aspect::gpu)) { std::string name = dev.get_info(); @@ -491,7 +500,7 @@ int main() { std::vector components(getAllowListDesc(allowlist)); std::cout << "SYCL_DEVICE_ALLOWLIST=" << allowlist << std::endl; - sycl::queue deviceQueue(gpu_selector{}); + sycl::queue deviceQueue(gpu_selector_v); device dev = deviceQueue.get_device(); for (const DevDescT &desc : components) { if ((std::regex_match(dev.get_info(), @@ -517,6 +526,9 @@ int main() { fs.open("select_device_config.txt"); if (fs.is_open()) { for (const auto &plt : platform::get_platforms()) { + if (passed) { + break; + } // no need for additional entries for (const auto &dev : plt.get_devices()) { if (dev.has(aspect::gpu)) { std::string name = dev.get_info(); @@ -549,7 +561,7 @@ int main() { std::vector components(getAllowListDesc(allowlist)); std::cout << "SYCL_DEVICE_ALLOWLIST=" << allowlist << std::endl; - sycl::queue deviceQueue(gpu_selector{}); + sycl::queue deviceQueue(gpu_selector_v); device dev = deviceQueue.get_device(); for (const DevDescT &desc : components) { if (std::regex_match(dev.get_info(), @@ -600,7 +612,7 @@ int main() { std::vector components(getAllowListDesc(allowlist)); std::cout << "SYCL_DEVICE_ALLOWLIST=" << allowlist << std::endl; - sycl::queue deviceQueue(gpu_selector{}); + sycl::queue deviceQueue(gpu_selector_v); device dev = deviceQueue.get_device(); const auto &plt = dev.get_platform(); for (const DevDescT &desc : components) { @@ -663,7 +675,7 @@ int main() { std::vector components(getAllowListDesc(allowlist)); std::cout << "SYCL_DEVICE_ALLOWLIST=" << allowlist << std::endl; - sycl::queue deviceQueue(gpu_selector{}); + sycl::queue deviceQueue(gpu_selector_v); device dev = deviceQueue.get_device(); for (const DevDescT &desc : components) { if ((std::regex_match(dev.get_info(), @@ -722,10 +734,10 @@ int main() { std::cout << "SYCL_DEVICE_ALLOWLIST=" << allowlist << std::endl; try { - sycl::queue deviceQueue(gpu_selector{}); + sycl::queue deviceQueue(gpu_selector_v); device dev = deviceQueue.get_device(); const auto &plt = dev.get_platform(); - } catch (sycl::runtime_error &E) { + } catch (sycl::exception &E) { // Workaround to make CI pass. // TODO: after the submission of PR intel/llvm:3826, create PR to // intel/llvm-test-suite with removal of 1st parameter of the vector, @@ -785,10 +797,10 @@ int main() { std::cout << "SYCL_DEVICE_ALLOWLIST=" << allowlist << std::endl; try { - sycl::queue deviceQueue(gpu_selector{}); + sycl::queue deviceQueue(gpu_selector_v); device dev = deviceQueue.get_device(); const auto &plt = dev.get_platform(); - } catch (sycl::runtime_error &E) { + } catch (sycl::exception &E) { // Workaround to make CI pass. // TODO: after the submission of PR intel/llvm:3826, create PR to // intel/llvm-test-suite with removal of 1st parameter of the vector, @@ -852,10 +864,10 @@ int main() { std::cout << "SYCL_DEVICE_ALLOWLIST=" << allowlist << std::endl; try { - sycl::queue deviceQueue(gpu_selector{}); + sycl::queue deviceQueue(gpu_selector_v); device dev = deviceQueue.get_device(); const auto &plt = dev.get_platform(); - } catch (sycl::runtime_error &E) { + } catch (sycl::exception &E) { // Workaround to make CI pass. // TODO: after the submission of PR intel/llvm:3826, create PR to // intel/llvm-test-suite with removal of 1st parameter of the vector, @@ -917,10 +929,10 @@ int main() { std::cout << "SYCL_DEVICE_ALLOWLIST=" << allowlist << std::endl; try { - sycl::queue deviceQueue(gpu_selector{}); + sycl::queue deviceQueue(gpu_selector_v); device dev = deviceQueue.get_device(); const auto &plt = dev.get_platform(); - } catch (sycl::runtime_error &E) { + } catch (sycl::exception &E) { // Workaround to make CI pass. // TODO: after the submission of PR intel/llvm:3826, create PR to // intel/llvm-test-suite with removal of 1st parameter of the vector, diff --git a/SYCL/DeprecatedFeatures/deprecated.cpp b/SYCL/DeprecatedFeatures/deprecated.cpp index 434910ddf3..5bb41824a1 100644 --- a/SYCL/DeprecatedFeatures/deprecated.cpp +++ b/SYCL/DeprecatedFeatures/deprecated.cpp @@ -16,8 +16,8 @@ using namespace sycl; int main() { - device Device{default_selector()}; - platform Platform{default_selector()}; + device Device{default_selector_v}; + platform Platform{default_selector_v}; bool b = Device.has_extension("cl_intel_subgroups"); b = Platform.has_extension("some_extension"); diff --git a/SYCL/DeprecatedFeatures/device_platform_interop.cpp b/SYCL/DeprecatedFeatures/device_platform_interop.cpp index ad72e159e7..8938af2d28 100644 --- a/SYCL/DeprecatedFeatures/device_platform_interop.cpp +++ b/SYCL/DeprecatedFeatures/device_platform_interop.cpp @@ -22,21 +22,20 @@ using namespace sycl; int main() { - default_selector device_selector; - device D1(device_selector); + device D1(default_selector_v); cl_device_id cl_device; { - device D2(device_selector); + device D2(default_selector_v); cl_device = get_native(D2); } device D3(cl_device); assert(D1 == D3 && "Device impls are different"); - platform P1(device_selector); + platform P1(default_selector_v); cl_platform_id cl_platform; { - platform P2(device_selector); + platform P2(default_selector_v); cl_platform = get_native(P2); } platform P3(cl_platform); diff --git a/SYCL/DeviceLib/built-ins/printf.cpp b/SYCL/DeviceLib/built-ins/printf.cpp index fd94fb101d..5afc03f565 100644 --- a/SYCL/DeviceLib/built-ins/printf.cpp +++ b/SYCL/DeviceLib/built-ins/printf.cpp @@ -34,9 +34,8 @@ static const CONSTANT char format_vec[] = "%d,%d,%d,%d\n"; const CONSTANT char format_hello_world_2[] = "%lu: Hello, World!\n"; int main() { - default_selector Selector; { - queue Queue(Selector); + queue Queue(default_selector_v); Queue.submit([&](handler &CGH) { CGH.single_task([=]() { @@ -109,7 +108,7 @@ int main() { } { - queue Queue(Selector); + queue Queue(default_selector_v); // printf in parallel_for Queue.submit([&](handler &CGH) { CGH.parallel_for(range<1>(10), [=](id<1> i) { diff --git a/SYCL/DeviceLib/imf_simd_emulate_test.cpp b/SYCL/DeviceLib/imf_simd_emulate_test.cpp index e7088867db..a76ddaf6b9 100644 --- a/SYCL/DeviceLib/imf_simd_emulate_test.cpp +++ b/SYCL/DeviceLib/imf_simd_emulate_test.cpp @@ -1810,8 +1810,7 @@ void run_vgtle_2_4_test(s::queue &queue) { } int main(int, char **) { - s::default_selector device_selector; - s::queue device_queue(device_selector); + s::queue device_queue(s::default_selector_v); std::cout << "Running on " << device_queue.get_device().get_info() << "\n"; diff --git a/SYCL/ESIMD/BitonicSortK.cpp b/SYCL/ESIMD/BitonicSortK.cpp index d63a068ba3..d47db53661 100644 --- a/SYCL/ESIMD/BitonicSortK.cpp +++ b/SYCL/ESIMD/BitonicSortK.cpp @@ -700,7 +700,7 @@ int main(int argc, char *argv[]) { int size = 1 << LOG2_ELEMENTS; cout << "BitonicSort (" << size << ") Start..." << std::endl; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler(), + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler(), property::queue::enable_profiling{}); BitonicSort bitonicSort; diff --git a/SYCL/ESIMD/BitonicSortKv2.cpp b/SYCL/ESIMD/BitonicSortKv2.cpp index f0e12f3c37..6f9347ee90 100644 --- a/SYCL/ESIMD/BitonicSortKv2.cpp +++ b/SYCL/ESIMD/BitonicSortKv2.cpp @@ -620,7 +620,7 @@ int main(int argc, char *argv[]) { sycl::property_list props{sycl::property::queue::enable_profiling{}, sycl::property::queue::in_order()}; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler(), + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler(), props); BitonicSort bitonicSort; diff --git a/SYCL/ESIMD/PrefixSum.cpp b/SYCL/ESIMD/PrefixSum.cpp index 72b54c88b2..11e2f9a252 100644 --- a/SYCL/ESIMD/PrefixSum.cpp +++ b/SYCL/ESIMD/PrefixSum.cpp @@ -391,7 +391,7 @@ int main(int argc, char *argv[]) { sycl::range<2> LocalRange{1, 1}; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler(), + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler(), property::queue::in_order()); auto dev = q.get_device(); diff --git a/SYCL/ESIMD/Prefix_Local_sum1.cpp b/SYCL/ESIMD/Prefix_Local_sum1.cpp index 5295461681..e4845af050 100644 --- a/SYCL/ESIMD/Prefix_Local_sum1.cpp +++ b/SYCL/ESIMD/Prefix_Local_sum1.cpp @@ -125,7 +125,7 @@ int main(int argc, char *argv[]) { sycl::range<2> LocalRange{1, 1}; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler(), + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler(), property::queue::enable_profiling{}); auto dev = q.get_device(); diff --git a/SYCL/ESIMD/Prefix_Local_sum2.cpp b/SYCL/ESIMD/Prefix_Local_sum2.cpp index 1a0f911016..02557f4f76 100644 --- a/SYCL/ESIMD/Prefix_Local_sum2.cpp +++ b/SYCL/ESIMD/Prefix_Local_sum2.cpp @@ -120,7 +120,7 @@ int main(int argc, char *argv[]) { sycl::range<2> LocalRange{1, 1}; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler(), + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler(), property::queue::enable_profiling{}); auto dev = q.get_device(); diff --git a/SYCL/ESIMD/Prefix_Local_sum3.cpp b/SYCL/ESIMD/Prefix_Local_sum3.cpp index 8860c3e1b2..9f98f43f0d 100644 --- a/SYCL/ESIMD/Prefix_Local_sum3.cpp +++ b/SYCL/ESIMD/Prefix_Local_sum3.cpp @@ -324,7 +324,7 @@ int main(int argc, char *argv[]) { sycl::range<2> LocalRange{1, 1}; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler(), + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler(), property::queue::enable_profiling{}); auto dev = q.get_device(); diff --git a/SYCL/ESIMD/Stencil.cpp b/SYCL/ESIMD/Stencil.cpp index 38b22dbcda..632c1935ad 100644 --- a/SYCL/ESIMD/Stencil.cpp +++ b/SYCL/ESIMD/Stencil.cpp @@ -88,7 +88,7 @@ int main(int argc, char *argv[]) { << std::endl; sycl::range<2> LocalRange{1, 1}; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler(), + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler(), property::queue::enable_profiling{}); auto dev = q.get_device(); diff --git a/SYCL/ESIMD/acc_gather_scatter_rgba.hpp b/SYCL/ESIMD/acc_gather_scatter_rgba.hpp index fc1abbf72d..939706ede6 100644 --- a/SYCL/ESIMD/acc_gather_scatter_rgba.hpp +++ b/SYCL/ESIMD/acc_gather_scatter_rgba.hpp @@ -161,7 +161,7 @@ template bool test(queue q) { } int main(void) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() diff --git a/SYCL/ESIMD/accessor.hpp b/SYCL/ESIMD/accessor.hpp index 7075877b68..115697a86f 100644 --- a/SYCL/ESIMD/accessor.hpp +++ b/SYCL/ESIMD/accessor.hpp @@ -31,7 +31,7 @@ int main() { } try { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); buffer buf0(data0, range<1>(VL)); buffer buf1(data1, range<1>(VL)); diff --git a/SYCL/ESIMD/accessor_gather_scatter.hpp b/SYCL/ESIMD/accessor_gather_scatter.hpp index 4ea6a09817..a8a0254e96 100644 --- a/SYCL/ESIMD/accessor_gather_scatter.hpp +++ b/SYCL/ESIMD/accessor_gather_scatter.hpp @@ -108,7 +108,7 @@ template bool test(queue q) { } int main(void) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/accessor_load_store.hpp b/SYCL/ESIMD/accessor_load_store.hpp index 4dde24df1a..7bd0ff83f6 100644 --- a/SYCL/ESIMD/accessor_load_store.hpp +++ b/SYCL/ESIMD/accessor_load_store.hpp @@ -98,7 +98,7 @@ int main(int argc, char **argv) { size = size == 0 ? 128 : size; } std::cout << "Using size=" << size << "\n"; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/aot_mixed.cpp b/SYCL/ESIMD/aot_mixed.cpp index 615139278e..c299325482 100644 --- a/SYCL/ESIMD/aot_mixed.cpp +++ b/SYCL/ESIMD/aot_mixed.cpp @@ -156,7 +156,7 @@ bool test_sycl(queue q) { #endif int main(void) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/api/ballot.cpp b/SYCL/ESIMD/api/ballot.cpp index c448b6d9c5..0b45872977 100755 --- a/SYCL/ESIMD/api/ballot.cpp +++ b/SYCL/ESIMD/api/ballot.cpp @@ -88,7 +88,7 @@ template bool test(queue &Q) { } int main(void) { - queue Q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue Q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto Dev = Q.get_device(); std::cout << "Running on " << Dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/api/bin_and_cmp_ops_heavy.cpp b/SYCL/ESIMD/api/bin_and_cmp_ops_heavy.cpp index a2e0827c63..243a7b2e09 100644 --- a/SYCL/ESIMD/api/bin_and_cmp_ops_heavy.cpp +++ b/SYCL/ESIMD/api/bin_and_cmp_ops_heavy.cpp @@ -255,7 +255,7 @@ template using IDf = init_default; template using ISf = init_for_shift; int main(void) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() diff --git a/SYCL/ESIMD/api/esimd_bit_ops.cpp b/SYCL/ESIMD/api/esimd_bit_ops.cpp index 2fbaf3e96b..246d270efe 100644 --- a/SYCL/ESIMD/api/esimd_bit_ops.cpp +++ b/SYCL/ESIMD/api/esimd_bit_ops.cpp @@ -120,7 +120,7 @@ template bool test(queue q) { } int main(int argc, char **argv) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/api/esimd_merge.cpp b/SYCL/ESIMD/api/esimd_merge.cpp index 07d06fa602..3660c569c3 100644 --- a/SYCL/ESIMD/api/esimd_merge.cpp +++ b/SYCL/ESIMD/api/esimd_merge.cpp @@ -38,7 +38,7 @@ int main(void) { constexpr unsigned SUB_VL = VL / FACTOR / FACTOR; constexpr unsigned Size = VL * NUM_THREADS; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() diff --git a/SYCL/ESIMD/api/esimd_pack_unpack_mask.cpp b/SYCL/ESIMD/api/esimd_pack_unpack_mask.cpp index 8542deb73c..ecf6cf9467 100644 --- a/SYCL/ESIMD/api/esimd_pack_unpack_mask.cpp +++ b/SYCL/ESIMD/api/esimd_pack_unpack_mask.cpp @@ -111,7 +111,7 @@ template bool test(queue q) { } int main(int argc, char **argv) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/api/esimd_rgba_smoke.cpp b/SYCL/ESIMD/api/esimd_rgba_smoke.cpp index 9a9d215db6..cec697a0d0 100644 --- a/SYCL/ESIMD/api/esimd_rgba_smoke.cpp +++ b/SYCL/ESIMD/api/esimd_rgba_smoke.cpp @@ -200,7 +200,7 @@ template bool test(queue q) { } int main(void) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/api/functional/ctors/ctor_array_core.cpp b/SYCL/ESIMD/api/functional/ctors/ctor_array_core.cpp index 984969249d..feaed2f9c1 100644 --- a/SYCL/ESIMD/api/functional/ctors/ctor_array_core.cpp +++ b/SYCL/ESIMD/api/functional/ctors/ctor_array_core.cpp @@ -27,7 +27,7 @@ using namespace esimd_test::api::functional; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = true; diff --git a/SYCL/ESIMD/api/functional/ctors/ctor_array_fp_extra.cpp b/SYCL/ESIMD/api/functional/ctors/ctor_array_fp_extra.cpp index 27e9a3a568..1aa0b9f1c8 100644 --- a/SYCL/ESIMD/api/functional/ctors/ctor_array_fp_extra.cpp +++ b/SYCL/ESIMD/api/functional/ctors/ctor_array_fp_extra.cpp @@ -27,7 +27,7 @@ using namespace esimd_test::api::functional; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = true; diff --git a/SYCL/ESIMD/api/functional/ctors/ctor_broadcast_core.cpp b/SYCL/ESIMD/api/functional/ctors/ctor_broadcast_core.cpp index 02fd350d85..53a3e9aa69 100644 --- a/SYCL/ESIMD/api/functional/ctors/ctor_broadcast_core.cpp +++ b/SYCL/ESIMD/api/functional/ctors/ctor_broadcast_core.cpp @@ -28,7 +28,7 @@ using namespace sycl::ext::intel::esimd; using namespace esimd_test::api::functional; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = true; diff --git a/SYCL/ESIMD/api/functional/ctors/ctor_broadcast_fp_extra.cpp b/SYCL/ESIMD/api/functional/ctors/ctor_broadcast_fp_extra.cpp index 2f4b7c6b57..3770c48a1a 100644 --- a/SYCL/ESIMD/api/functional/ctors/ctor_broadcast_fp_extra.cpp +++ b/SYCL/ESIMD/api/functional/ctors/ctor_broadcast_fp_extra.cpp @@ -31,7 +31,7 @@ using namespace sycl::ext::intel::esimd; using namespace esimd_test::api::functional; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = true; diff --git a/SYCL/ESIMD/api/functional/ctors/ctor_converting_core.cpp b/SYCL/ESIMD/api/functional/ctors/ctor_converting_core.cpp index 69965f7580..9978df13a3 100644 --- a/SYCL/ESIMD/api/functional/ctors/ctor_converting_core.cpp +++ b/SYCL/ESIMD/api/functional/ctors/ctor_converting_core.cpp @@ -28,7 +28,7 @@ using namespace sycl::ext::intel::experimental::esimd; using namespace esimd_test::api::functional; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = true; diff --git a/SYCL/ESIMD/api/functional/ctors/ctor_converting_fp_extra.cpp b/SYCL/ESIMD/api/functional/ctors/ctor_converting_fp_extra.cpp index 39f9be9fcd..dc92626058 100644 --- a/SYCL/ESIMD/api/functional/ctors/ctor_converting_fp_extra.cpp +++ b/SYCL/ESIMD/api/functional/ctors/ctor_converting_fp_extra.cpp @@ -28,7 +28,7 @@ using namespace sycl::ext::intel::experimental::esimd; using namespace esimd_test::api::functional; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = true; diff --git a/SYCL/ESIMD/api/functional/ctors/ctor_copy_core.cpp b/SYCL/ESIMD/api/functional/ctors/ctor_copy_core.cpp index 6062f00138..564d9af4b8 100644 --- a/SYCL/ESIMD/api/functional/ctors/ctor_copy_core.cpp +++ b/SYCL/ESIMD/api/functional/ctors/ctor_copy_core.cpp @@ -27,7 +27,7 @@ using namespace esimd_test::api::functional; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = true; diff --git a/SYCL/ESIMD/api/functional/ctors/ctor_copy_fp_extra.cpp b/SYCL/ESIMD/api/functional/ctors/ctor_copy_fp_extra.cpp index 9815900eb6..253719c54d 100644 --- a/SYCL/ESIMD/api/functional/ctors/ctor_copy_fp_extra.cpp +++ b/SYCL/ESIMD/api/functional/ctors/ctor_copy_fp_extra.cpp @@ -27,7 +27,7 @@ using namespace esimd_test::api::functional; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = true; diff --git a/SYCL/ESIMD/api/functional/ctors/ctor_default_core.cpp b/SYCL/ESIMD/api/functional/ctors/ctor_default_core.cpp index fda84f942f..378cb64f6c 100644 --- a/SYCL/ESIMD/api/functional/ctors/ctor_default_core.cpp +++ b/SYCL/ESIMD/api/functional/ctors/ctor_default_core.cpp @@ -27,7 +27,7 @@ using namespace esimd_test::api::functional; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = true; diff --git a/SYCL/ESIMD/api/functional/ctors/ctor_default_fp_extra.cpp b/SYCL/ESIMD/api/functional/ctors/ctor_default_fp_extra.cpp index cdb47bfd15..36dfbb5718 100644 --- a/SYCL/ESIMD/api/functional/ctors/ctor_default_fp_extra.cpp +++ b/SYCL/ESIMD/api/functional/ctors/ctor_default_fp_extra.cpp @@ -27,7 +27,7 @@ using namespace esimd_test::api::functional; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = true; diff --git a/SYCL/ESIMD/api/functional/ctors/ctor_fill_accuracy_fp.cpp b/SYCL/ESIMD/api/functional/ctors/ctor_fill_accuracy_fp.cpp index 27393d8ade..b81c5e1831 100644 --- a/SYCL/ESIMD/api/functional/ctors/ctor_fill_accuracy_fp.cpp +++ b/SYCL/ESIMD/api/functional/ctors/ctor_fill_accuracy_fp.cpp @@ -30,7 +30,7 @@ using namespace esimd_test::api::functional; using init_val = ctors::init_val; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = true; diff --git a/SYCL/ESIMD/api/functional/ctors/ctor_fill_accuracy_fp_extra.cpp b/SYCL/ESIMD/api/functional/ctors/ctor_fill_accuracy_fp_extra.cpp index 014a1659ed..622c93aeb5 100644 --- a/SYCL/ESIMD/api/functional/ctors/ctor_fill_accuracy_fp_extra.cpp +++ b/SYCL/ESIMD/api/functional/ctors/ctor_fill_accuracy_fp_extra.cpp @@ -29,7 +29,7 @@ using namespace esimd_test::api::functional; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = true; diff --git a/SYCL/ESIMD/api/functional/ctors/ctor_fill_core.cpp b/SYCL/ESIMD/api/functional/ctors/ctor_fill_core.cpp index 96a285d392..920c09289d 100644 --- a/SYCL/ESIMD/api/functional/ctors/ctor_fill_core.cpp +++ b/SYCL/ESIMD/api/functional/ctors/ctor_fill_core.cpp @@ -27,7 +27,7 @@ using namespace esimd_test::api::functional; using init_val = ctors::init_val; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = true; diff --git a/SYCL/ESIMD/api/functional/ctors/ctor_fill_fp_extra.cpp b/SYCL/ESIMD/api/functional/ctors/ctor_fill_fp_extra.cpp index 740175f154..1d34715c86 100644 --- a/SYCL/ESIMD/api/functional/ctors/ctor_fill_fp_extra.cpp +++ b/SYCL/ESIMD/api/functional/ctors/ctor_fill_fp_extra.cpp @@ -26,7 +26,7 @@ using namespace esimd_test::api::functional; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = true; diff --git a/SYCL/ESIMD/api/functional/ctors/ctor_load_acc_core.cpp b/SYCL/ESIMD/api/functional/ctors/ctor_load_acc_core.cpp index ff2f4bb074..b7bfda4988 100644 --- a/SYCL/ESIMD/api/functional/ctors/ctor_load_acc_core.cpp +++ b/SYCL/ESIMD/api/functional/ctors/ctor_load_acc_core.cpp @@ -27,7 +27,7 @@ using namespace esimd_test::api::functional; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = true; diff --git a/SYCL/ESIMD/api/functional/ctors/ctor_load_acc_fp_extra.cpp b/SYCL/ESIMD/api/functional/ctors/ctor_load_acc_fp_extra.cpp index 797ff009c8..4349aef399 100644 --- a/SYCL/ESIMD/api/functional/ctors/ctor_load_acc_fp_extra.cpp +++ b/SYCL/ESIMD/api/functional/ctors/ctor_load_acc_fp_extra.cpp @@ -27,7 +27,7 @@ using namespace esimd_test::api::functional; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = true; diff --git a/SYCL/ESIMD/api/functional/ctors/ctor_load_usm_core.cpp b/SYCL/ESIMD/api/functional/ctors/ctor_load_usm_core.cpp index ce57ae120e..78cb139646 100644 --- a/SYCL/ESIMD/api/functional/ctors/ctor_load_usm_core.cpp +++ b/SYCL/ESIMD/api/functional/ctors/ctor_load_usm_core.cpp @@ -26,7 +26,7 @@ using namespace esimd_test::api::functional; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = true; diff --git a/SYCL/ESIMD/api/functional/ctors/ctor_load_usm_fp_extra.cpp b/SYCL/ESIMD/api/functional/ctors/ctor_load_usm_fp_extra.cpp index 4b960879c1..5d0d11b9f4 100644 --- a/SYCL/ESIMD/api/functional/ctors/ctor_load_usm_fp_extra.cpp +++ b/SYCL/ESIMD/api/functional/ctors/ctor_load_usm_fp_extra.cpp @@ -26,7 +26,7 @@ using namespace esimd_test::api::functional; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = true; diff --git a/SYCL/ESIMD/api/functional/ctors/ctor_move_core.cpp b/SYCL/ESIMD/api/functional/ctors/ctor_move_core.cpp index 7bfa6666df..3715e7917c 100644 --- a/SYCL/ESIMD/api/functional/ctors/ctor_move_core.cpp +++ b/SYCL/ESIMD/api/functional/ctors/ctor_move_core.cpp @@ -42,7 +42,7 @@ int main(int, char **) { unnamed_type_pack::generate(); - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); // Run test for all combinations possible diff --git a/SYCL/ESIMD/api/functional/ctors/ctor_move_fp_extra.cpp b/SYCL/ESIMD/api/functional/ctors/ctor_move_fp_extra.cpp index 6fcd17c450..4538173ef6 100644 --- a/SYCL/ESIMD/api/functional/ctors/ctor_move_fp_extra.cpp +++ b/SYCL/ESIMD/api/functional/ctors/ctor_move_fp_extra.cpp @@ -36,7 +36,7 @@ int main(int, char **) { unnamed_type_pack::generate(); - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); // Run test for all combinations possible diff --git a/SYCL/ESIMD/api/functional/ctors/ctor_vector_core.cpp b/SYCL/ESIMD/api/functional/ctors/ctor_vector_core.cpp index 45d044a6a2..0f47d23c77 100644 --- a/SYCL/ESIMD/api/functional/ctors/ctor_vector_core.cpp +++ b/SYCL/ESIMD/api/functional/ctors/ctor_vector_core.cpp @@ -27,7 +27,7 @@ using namespace esimd_test::api::functional; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); const auto types = get_tested_types(); diff --git a/SYCL/ESIMD/api/functional/ctors/ctor_vector_fp_extra.cpp b/SYCL/ESIMD/api/functional/ctors/ctor_vector_fp_extra.cpp index 30798ef5e2..9f469c2803 100644 --- a/SYCL/ESIMD/api/functional/ctors/ctor_vector_fp_extra.cpp +++ b/SYCL/ESIMD/api/functional/ctors/ctor_vector_fp_extra.cpp @@ -27,7 +27,7 @@ using namespace esimd_test::api::functional; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = true; diff --git a/SYCL/ESIMD/api/functional/functions/functions_select_2d_core.cpp b/SYCL/ESIMD/api/functional/functions/functions_select_2d_core.cpp index 13bc7cf562..14442c17b9 100644 --- a/SYCL/ESIMD/api/functional/functions/functions_select_2d_core.cpp +++ b/SYCL/ESIMD/api/functional/functions/functions_select_2d_core.cpp @@ -27,7 +27,7 @@ using namespace sycl::ext::intel::experimental::esimd; using namespace esimd_test::api::functional; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = functions::run_test_for_types(queue); diff --git a/SYCL/ESIMD/api/functional/functions/functions_select_2d_fp_extra.cpp b/SYCL/ESIMD/api/functional/functions/functions_select_2d_fp_extra.cpp index bdd68484f2..1619ddea47 100644 --- a/SYCL/ESIMD/api/functional/functions/functions_select_2d_fp_extra.cpp +++ b/SYCL/ESIMD/api/functional/functions/functions_select_2d_fp_extra.cpp @@ -30,7 +30,7 @@ using namespace sycl::ext::intel::experimental::esimd; using namespace esimd_test::api::functional; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = functions::run_test_for_types(queue); diff --git a/SYCL/ESIMD/api/functional/functions/functions_select_lvalue_core.cpp b/SYCL/ESIMD/api/functional/functions/functions_select_lvalue_core.cpp index 265b15a0b0..691519f9d4 100644 --- a/SYCL/ESIMD/api/functional/functions/functions_select_lvalue_core.cpp +++ b/SYCL/ESIMD/api/functional/functions/functions_select_lvalue_core.cpp @@ -30,7 +30,7 @@ using namespace sycl::ext::intel::experimental::esimd; using namespace esimd_test::api::functional; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = diff --git a/SYCL/ESIMD/api/functional/functions/functions_select_lvalue_fp_extra.cpp b/SYCL/ESIMD/api/functional/functions/functions_select_lvalue_fp_extra.cpp index ba71d3f0cf..4af233b879 100644 --- a/SYCL/ESIMD/api/functional/functions/functions_select_lvalue_fp_extra.cpp +++ b/SYCL/ESIMD/api/functional/functions/functions_select_lvalue_fp_extra.cpp @@ -27,7 +27,7 @@ using namespace sycl::ext::intel::experimental::esimd; using namespace esimd_test::api::functional; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = functions::run_test_for_types class run_test { }; int main(int, char **) { - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool passed = true; diff --git a/SYCL/ESIMD/api/replicate_smoke.cpp b/SYCL/ESIMD/api/replicate_smoke.cpp index 1ed688571c..338e52aac2 100644 --- a/SYCL/ESIMD/api/replicate_smoke.cpp +++ b/SYCL/ESIMD/api/replicate_smoke.cpp @@ -176,7 +176,7 @@ template bool test(queue q) { } int main(int argc, char **argv) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); const bool doublesSupported = dev.has(sycl::aspect::fp64); std::cout << "Running on " << dev.get_info() diff --git a/SYCL/ESIMD/api/saturation_smoke.cpp b/SYCL/ESIMD/api/saturation_smoke.cpp index 29b3b3d1a1..005cb1497e 100644 --- a/SYCL/ESIMD/api/saturation_smoke.cpp +++ b/SYCL/ESIMD/api/saturation_smoke.cpp @@ -180,7 +180,7 @@ template struct FpToFp : public DataMgr { // clang-format on int main(int argc, char **argv) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/api/simd_any_all.cpp b/SYCL/ESIMD/api/simd_any_all.cpp index 53a5e1dce0..ba0e700cc5 100644 --- a/SYCL/ESIMD/api/simd_any_all.cpp +++ b/SYCL/ESIMD/api/simd_any_all.cpp @@ -139,7 +139,7 @@ template bool test(queue q) { } int main(int argc, char **argv) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/api/simd_binop_integer_promotion.cpp b/SYCL/ESIMD/api/simd_binop_integer_promotion.cpp index f4cf221bd7..56f5951754 100644 --- a/SYCL/ESIMD/api/simd_binop_integer_promotion.cpp +++ b/SYCL/ESIMD/api/simd_binop_integer_promotion.cpp @@ -102,7 +102,7 @@ template bool test(queue q) { } int main(int argc, char **argv) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() diff --git a/SYCL/ESIMD/api/simd_copy_to_from.cpp b/SYCL/ESIMD/api/simd_copy_to_from.cpp index 18f9efdeab..1bca8708cf 100644 --- a/SYCL/ESIMD/api/simd_copy_to_from.cpp +++ b/SYCL/ESIMD/api/simd_copy_to_from.cpp @@ -226,7 +226,7 @@ template bool testAcc(queue &Q) { } int main(void) { - queue Q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue Q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto Dev = Q.get_device(); std::cout << "Running on " << Dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/api/simd_mask.cpp b/SYCL/ESIMD/api/simd_mask.cpp index e2ea377c94..7df876ca2c 100644 --- a/SYCL/ESIMD/api/simd_mask.cpp +++ b/SYCL/ESIMD/api/simd_mask.cpp @@ -328,7 +328,7 @@ template struct simd_mask_api_test { }; int main(int argc, char **argv) { - queue Q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue Q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto Dev = Q.get_device(); std::cout << "Running on " << Dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/api/simd_memory_access.cpp b/SYCL/ESIMD/api/simd_memory_access.cpp index 46363f88eb..4912d52ca9 100644 --- a/SYCL/ESIMD/api/simd_memory_access.cpp +++ b/SYCL/ESIMD/api/simd_memory_access.cpp @@ -150,7 +150,7 @@ int main(int argc, char **argv) { return 2; } std::cout << "Using size=" << size << "\n"; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() diff --git a/SYCL/ESIMD/api/simd_negation_operator.cpp b/SYCL/ESIMD/api/simd_negation_operator.cpp index 1c53914c64..5f7dd17635 100644 --- a/SYCL/ESIMD/api/simd_negation_operator.cpp +++ b/SYCL/ESIMD/api/simd_negation_operator.cpp @@ -80,7 +80,7 @@ bool test(queue q, const std::array &input, } int main(void) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/api/simd_subscript_operator.cpp b/SYCL/ESIMD/api/simd_subscript_operator.cpp index ef3dde7661..85257c7653 100644 --- a/SYCL/ESIMD/api/simd_subscript_operator.cpp +++ b/SYCL/ESIMD/api/simd_subscript_operator.cpp @@ -93,7 +93,7 @@ template bool test(queue &q) { } int main(int argc, char **argv) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() diff --git a/SYCL/ESIMD/api/simd_view_copy_move_assign.cpp b/SYCL/ESIMD/api/simd_view_copy_move_assign.cpp index 9829a89401..811605fb65 100644 --- a/SYCL/ESIMD/api/simd_view_copy_move_assign.cpp +++ b/SYCL/ESIMD/api/simd_view_copy_move_assign.cpp @@ -157,7 +157,7 @@ template bool testT(queue &q) { } int main(void) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/api/simd_view_negation_operator.cpp b/SYCL/ESIMD/api/simd_view_negation_operator.cpp index 813978f250..1b4a140500 100644 --- a/SYCL/ESIMD/api/simd_view_negation_operator.cpp +++ b/SYCL/ESIMD/api/simd_view_negation_operator.cpp @@ -81,7 +81,7 @@ bool test(queue q, const std::array &input, } int main(void) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/api/simd_view_select_2d_fp.cpp b/SYCL/ESIMD/api/simd_view_select_2d_fp.cpp index 980f32ad09..b2d326b690 100644 --- a/SYCL/ESIMD/api/simd_view_select_2d_fp.cpp +++ b/SYCL/ESIMD/api/simd_view_select_2d_fp.cpp @@ -16,7 +16,7 @@ #include "simd_view_select_2d.hpp" int main(int argc, char **argv) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/api/simd_view_select_2d_int.cpp b/SYCL/ESIMD/api/simd_view_select_2d_int.cpp index d761a6c7fd..f57b1c8d01 100644 --- a/SYCL/ESIMD/api/simd_view_select_2d_int.cpp +++ b/SYCL/ESIMD/api/simd_view_select_2d_int.cpp @@ -19,7 +19,7 @@ #include "simd_view_select_2d.hpp" int main(int argc, char **argv) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/api/simd_view_subscript_operator.cpp b/SYCL/ESIMD/api/simd_view_subscript_operator.cpp index e66bf83269..91c43a04f3 100644 --- a/SYCL/ESIMD/api/simd_view_subscript_operator.cpp +++ b/SYCL/ESIMD/api/simd_view_subscript_operator.cpp @@ -96,7 +96,7 @@ template bool test(queue &q) { } int main(int argc, char **argv) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() diff --git a/SYCL/ESIMD/api/slm_gather_scatter.cpp b/SYCL/ESIMD/api/slm_gather_scatter.cpp index 0780acd466..5e3f1960d1 100644 --- a/SYCL/ESIMD/api/slm_gather_scatter.cpp +++ b/SYCL/ESIMD/api/slm_gather_scatter.cpp @@ -121,7 +121,7 @@ template bool test(queue q) { } int main(void) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() diff --git a/SYCL/ESIMD/api/slm_gather_scatter_heavy.cpp b/SYCL/ESIMD/api/slm_gather_scatter_heavy.cpp index 92572cf706..40b95b6f1a 100644 --- a/SYCL/ESIMD/api/slm_gather_scatter_heavy.cpp +++ b/SYCL/ESIMD/api/slm_gather_scatter_heavy.cpp @@ -441,7 +441,7 @@ template bool test_vl1(queue q) { } int main(int argc, char **argv) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() diff --git a/SYCL/ESIMD/api/slm_gather_scatter_rgba.cpp b/SYCL/ESIMD/api/slm_gather_scatter_rgba.cpp index 3f06520949..232b68379b 100644 --- a/SYCL/ESIMD/api/slm_gather_scatter_rgba.cpp +++ b/SYCL/ESIMD/api/slm_gather_scatter_rgba.cpp @@ -177,7 +177,7 @@ template bool test(queue q) { } int main(void) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() diff --git a/SYCL/ESIMD/api/svm_gather_scatter.cpp b/SYCL/ESIMD/api/svm_gather_scatter.cpp index b0f355aef2..37878bec9a 100644 --- a/SYCL/ESIMD/api/svm_gather_scatter.cpp +++ b/SYCL/ESIMD/api/svm_gather_scatter.cpp @@ -74,7 +74,7 @@ template bool test(queue &Q) { } int main(void) { - queue Q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue Q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto Dev = Q.get_device(); std::cout << "Running on " << Dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/api/unary_ops_heavy.cpp b/SYCL/ESIMD/api/unary_ops_heavy.cpp index ac6c7dbd98..df14cecc0b 100644 --- a/SYCL/ESIMD/api/unary_ops_heavy.cpp +++ b/SYCL/ESIMD/api/unary_ops_heavy.cpp @@ -152,7 +152,7 @@ bool test(Ops ops, queue &q) { } int main(void) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() diff --git a/SYCL/ESIMD/dp4a.cpp b/SYCL/ESIMD/dp4a.cpp index aecd971ff1..730ad7a831 100644 --- a/SYCL/ESIMD/dp4a.cpp +++ b/SYCL/ESIMD/dp4a.cpp @@ -23,7 +23,7 @@ int main(void) { constexpr unsigned GROUPSIZE = 1; using DTYPE = unsigned int; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/dpas/dpas_bf16.cpp b/SYCL/ESIMD/dpas/dpas_bf16.cpp index 28e8f7d60b..0b73333210 100644 --- a/SYCL/ESIMD/dpas/dpas_bf16.cpp +++ b/SYCL/ESIMD/dpas/dpas_bf16.cpp @@ -15,7 +15,7 @@ #include "dpas_common.hpp" int main(int argc, const char *argv[]) { - queue Q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue Q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool Print = argc > 1 && std::string(argv[1]) == "-debug"; bool Passed = true; diff --git a/SYCL/ESIMD/dpas/dpas_fp16.cpp b/SYCL/ESIMD/dpas/dpas_fp16.cpp index e038d12e4a..41797f9877 100644 --- a/SYCL/ESIMD/dpas/dpas_fp16.cpp +++ b/SYCL/ESIMD/dpas/dpas_fp16.cpp @@ -15,7 +15,7 @@ #include "dpas_common.hpp" int main(int argc, const char *argv[]) { - queue Q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue Q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool Print = argc > 1 && std::string(argv[1]) == "-debug"; bool Passed = true; diff --git a/SYCL/ESIMD/dpas/dpas_int.cpp b/SYCL/ESIMD/dpas/dpas_int.cpp index ecf4937148..612ddd9f20 100644 --- a/SYCL/ESIMD/dpas/dpas_int.cpp +++ b/SYCL/ESIMD/dpas/dpas_int.cpp @@ -15,7 +15,7 @@ #include "dpas_common.hpp" int main(int argc, const char *argv[]) { - queue Q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue Q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); bool Print = argc > 1 && std::string(argv[1]) == "-debug"; bool Passed = true; diff --git a/SYCL/ESIMD/dpas/dpas_test1.cpp b/SYCL/ESIMD/dpas/dpas_test1.cpp index ad4d6cb63a..865241f73f 100644 --- a/SYCL/ESIMD/dpas/dpas_test1.cpp +++ b/SYCL/ESIMD/dpas/dpas_test1.cpp @@ -23,7 +23,7 @@ int main(void) { constexpr unsigned VL = 16; constexpr unsigned GroupSize = 1; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/dpas/dpas_test2.cpp b/SYCL/ESIMD/dpas/dpas_test2.cpp index ab0653ccab..53539fdea1 100644 --- a/SYCL/ESIMD/dpas/dpas_test2.cpp +++ b/SYCL/ESIMD/dpas/dpas_test2.cpp @@ -23,7 +23,7 @@ int main(void) { constexpr unsigned VL = 16; constexpr unsigned GroupSize = 1; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/dpas/dpas_test3.cpp b/SYCL/ESIMD/dpas/dpas_test3.cpp index 4c10ba08c2..68aa171cbe 100644 --- a/SYCL/ESIMD/dpas/dpas_test3.cpp +++ b/SYCL/ESIMD/dpas/dpas_test3.cpp @@ -94,7 +94,7 @@ void dpas_ker(nd_item<1> &idx, BF16 *matA, BF16 *matB, float *matC) { int main() { // A [8][16] * B[16][16]= C[8][16] - queue q(gpu_selector{}); + queue q(gpu_selector_v); nd_range<1> Range(range<1>{1}, range<1>{1}); constexpr int MB = 8; constexpr int NB = 16; // KB = NB = 16 in pvc diff --git a/SYCL/ESIMD/dpas/dpas_tf32.cpp b/SYCL/ESIMD/dpas/dpas_tf32.cpp index b9ee59a9d9..00da75d225 100644 --- a/SYCL/ESIMD/dpas/dpas_tf32.cpp +++ b/SYCL/ESIMD/dpas/dpas_tf32.cpp @@ -24,7 +24,7 @@ using namespace sycl::ext::intel::esimd; using namespace sycl::ext::intel::experimental::esimd; int main() { - queue Q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue Q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); constexpr int REPEAT_COUNT = 8; constexpr int SYSTOLIC_DEPTH = 8; diff --git a/SYCL/ESIMD/dpas/dpasw_test.cpp b/SYCL/ESIMD/dpas/dpasw_test.cpp index e1bfda68c0..1a8892ff6d 100644 --- a/SYCL/ESIMD/dpas/dpasw_test.cpp +++ b/SYCL/ESIMD/dpas/dpasw_test.cpp @@ -23,7 +23,7 @@ int main(void) { constexpr unsigned VL = 16; constexpr unsigned GroupSize = 2; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/esimd_check_vc_codegen.cpp b/SYCL/ESIMD/esimd_check_vc_codegen.cpp index 73c3473531..fbf60a2482 100644 --- a/SYCL/ESIMD/esimd_check_vc_codegen.cpp +++ b/SYCL/ESIMD/esimd_check_vc_codegen.cpp @@ -44,7 +44,7 @@ int main(void) { // We need that many threads in each group range<1> LocalRange{1}; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/esimd_test_utils.hpp b/SYCL/ESIMD/esimd_test_utils.hpp index b72f2d8a9b..99c7517f6f 100644 --- a/SYCL/ESIMD/esimd_test_utils.hpp +++ b/SYCL/ESIMD/esimd_test_utils.hpp @@ -26,30 +26,27 @@ using namespace sycl; namespace esimd_test { -// This is the class provided to SYCL runtime by the application to decide +// This is function provided to SYCL runtime by the application to decide // on which device to run, or whether to run at all. // When selecting a device, SYCL runtime first takes (1) a selector provided by // the program or a default one and (2) the set of all available devices. Then -// it passes each device to the '()' operator of the selector. Device, for -// which '()' returned the highest number, is selected. If a negative number -// was returned for all devices, then the selection process will cause an -// exception. -class ESIMDSelector : public device_selector { - // Require GPU device - virtual int operator()(const device &device) const { - if (const char *dev_filter = getenv("SYCL_DEVICE_FILTER")) { - std::string filter_string(dev_filter); - if (filter_string.find("gpu") != std::string::npos) - return device.is_gpu() ? 1000 : -1; - std::cerr - << "Supported 'SYCL_DEVICE_FILTER' env var values is 'gpu' and '" - << filter_string << "' does not contain such substrings.\n"; - return -1; - } - // If "SYCL_DEVICE_FILTER" not defined, only allow gpu device - return device.is_gpu() ? 1000 : -1; +// it passes each device to the selector. A device for which the highest number +// is returned is selected. If a negative number was returned for all devices, +// then the selection process will cause an exception. +inline int ESIMDSelector(const device &device) { + if (const char *dev_filter = getenv("SYCL_DEVICE_FILTER")) { + std::string filter_string(dev_filter); + if (filter_string.find("gpu") != std::string::npos) + return device.is_gpu() ? 1000 : -1; + + std::cerr + << "Supported 'SYCL_DEVICE_FILTER' env var device type is 'gpu' and " + << filter_string << "' does not contain that.\n"; + return -1; } -}; + // If "SYCL_DEVICE_FILTER" not defined, only allow gpu device + return device.is_gpu() ? 1000 : -1; +} inline auto createExceptionHandler() { return [](exception_list l) { diff --git a/SYCL/ESIMD/ext_math.cpp b/SYCL/ESIMD/ext_math.cpp index 89bf7a4923..691b5e2b67 100644 --- a/SYCL/ESIMD/ext_math.cpp +++ b/SYCL/ESIMD/ext_math.cpp @@ -463,7 +463,7 @@ template bool testSYCL(queue &Q) { // --- The entry point int main(void) { - queue Q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue Q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto Dev = Q.get_device(); std::cout << "Running on " << Dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/fp_args_size/Inputs/fp_args_size_common.hpp b/SYCL/ESIMD/fp_args_size/Inputs/fp_args_size_common.hpp index 17b759c1b5..242a44cfe9 100644 --- a/SYCL/ESIMD/fp_args_size/Inputs/fp_args_size_common.hpp +++ b/SYCL/ESIMD/fp_args_size/Inputs/fp_args_size_common.hpp @@ -36,7 +36,7 @@ ESIMD_NOINLINE TC add(TA A, TB B) { } int main(void) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/fp_call_from_func.cpp b/SYCL/ESIMD/fp_call_from_func.cpp index 153c62c2d1..cfaadd17ec 100644 --- a/SYCL/ESIMD/fp_call_from_func.cpp +++ b/SYCL/ESIMD/fp_call_from_func.cpp @@ -39,7 +39,7 @@ template ESIMD_NOINLINE void test(AccTy acc, int A, int B) { } int main(int argc, char **argv) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/fp_call_recursive.cpp b/SYCL/ESIMD/fp_call_recursive.cpp index f772581b4e..fc3a62adf7 100644 --- a/SYCL/ESIMD/fp_call_recursive.cpp +++ b/SYCL/ESIMD/fp_call_recursive.cpp @@ -33,7 +33,7 @@ ESIMD_NOINLINE unsigned add(unsigned A, unsigned B, unsigned C) { } int main(int argc, char **argv) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/fp_in_phi.cpp b/SYCL/ESIMD/fp_in_phi.cpp index 4ffc857fa3..8089b460ad 100644 --- a/SYCL/ESIMD/fp_in_phi.cpp +++ b/SYCL/ESIMD/fp_in_phi.cpp @@ -83,7 +83,7 @@ bool test(queue q, bool flag) { } int main(int argc, char **argv) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/fp_in_select.cpp b/SYCL/ESIMD/fp_in_select.cpp index b050f0989c..e0f54db788 100644 --- a/SYCL/ESIMD/fp_in_select.cpp +++ b/SYCL/ESIMD/fp_in_select.cpp @@ -71,7 +71,7 @@ bool test(queue q, bool flag) { } int main(int argc, char **argv) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/histogram.cpp b/SYCL/ESIMD/histogram.cpp index ef3bdd2ac1..5a393c9a11 100644 --- a/SYCL/ESIMD/histogram.cpp +++ b/SYCL/ESIMD/histogram.cpp @@ -78,7 +78,7 @@ int main(int argc, char *argv[]) { // Read in image luma plane // Allocate Input Buffer - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler(), + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler(), property::queue::enable_profiling{}); auto dev = q.get_device(); diff --git a/SYCL/ESIMD/histogram_256_slm.cpp b/SYCL/ESIMD/histogram_256_slm.cpp index 85092d5671..27d1cd7ea5 100644 --- a/SYCL/ESIMD/histogram_256_slm.cpp +++ b/SYCL/ESIMD/histogram_256_slm.cpp @@ -104,7 +104,7 @@ int CheckHistogram(unsigned int *cpu_histogram, unsigned int *gpu_histogram) { } int main() { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler(), + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler(), sycl::property::queue::enable_profiling{}); const char *input_file = nullptr; diff --git a/SYCL/ESIMD/histogram_256_slm_spec_2020.cpp b/SYCL/ESIMD/histogram_256_slm_spec_2020.cpp index 29db543127..4d3b673dba 100644 --- a/SYCL/ESIMD/histogram_256_slm_spec_2020.cpp +++ b/SYCL/ESIMD/histogram_256_slm_spec_2020.cpp @@ -104,7 +104,7 @@ class NumBlocksConst; class histogram_slm; int main(int argc, char **argv) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler(), + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler(), sycl::property::queue::enable_profiling{}); auto dev = q.get_device(); auto ctxt = q.get_context(); diff --git a/SYCL/ESIMD/histogram_2d.cpp b/SYCL/ESIMD/histogram_2d.cpp index 3d44cac9d8..7d0ff309d8 100644 --- a/SYCL/ESIMD/histogram_2d.cpp +++ b/SYCL/ESIMD/histogram_2d.cpp @@ -78,7 +78,7 @@ int main(int argc, char *argv[]) { // Read in image luma plane // Allocate Input Buffer - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler(), + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler(), property::queue::enable_profiling{}); auto dev = q.get_device(); diff --git a/SYCL/ESIMD/histogram_raw_send.cpp b/SYCL/ESIMD/histogram_raw_send.cpp index 5c0246d8b7..eedc2df141 100644 --- a/SYCL/ESIMD/histogram_raw_send.cpp +++ b/SYCL/ESIMD/histogram_raw_send.cpp @@ -109,7 +109,7 @@ int main(int argc, char *argv[]) { // Read in image luma plane // Allocate Input Buffer - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler(), + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler(), sycl::property::queue::enable_profiling{}); auto dev = q.get_device(); diff --git a/SYCL/ESIMD/kmeans/kmeans.cpp b/SYCL/ESIMD/kmeans/kmeans.cpp index 76e43c874b..ab80459742 100644 --- a/SYCL/ESIMD/kmeans/kmeans.cpp +++ b/SYCL/ESIMD/kmeans/kmeans.cpp @@ -127,7 +127,7 @@ int main(int argc, char *argv[]) { sycl::property_list props{property::queue::enable_profiling{}, property::queue::in_order()}; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler(), + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler(), props); auto points4 = malloc_shared(NUM_POINTS / SIMD_SIZE, q); diff --git a/SYCL/ESIMD/linear/linear.cpp b/SYCL/ESIMD/linear/linear.cpp index 6cff4a1459..8892c0741b 100644 --- a/SYCL/ESIMD/linear/linear.cpp +++ b/SYCL/ESIMD/linear/linear.cpp @@ -79,7 +79,7 @@ int main(int argc, char *argv[]) { // Number of workitems in a workgroup range<2> LocalRange{1, 1}; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler(), + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler(), property::queue::enable_profiling{}); auto dev = q.get_device(); diff --git a/SYCL/ESIMD/lsc/Inputs/lsc_block_load.hpp b/SYCL/ESIMD/lsc/Inputs/lsc_block_load.hpp index 101a83a17e..5cf4bebbfd 100644 --- a/SYCL/ESIMD/lsc/Inputs/lsc_block_load.hpp +++ b/SYCL/ESIMD/lsc/Inputs/lsc_block_load.hpp @@ -99,8 +99,7 @@ bool test(unsigned SurfaceWidth, unsigned SurfaceHeight, unsigned SurfacePitch, T old_val = get_rand(); - auto GPUSelector = gpu_selector{}; - auto q = queue{GPUSelector}; + auto q = queue{gpu_selector_v}; auto dev = q.get_device(); std::cout << "Running case #" << case_num << " on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/lsc/Inputs/lsc_block_store.hpp b/SYCL/ESIMD/lsc/Inputs/lsc_block_store.hpp index 5cba736c93..262fe43199 100644 --- a/SYCL/ESIMD/lsc/Inputs/lsc_block_store.hpp +++ b/SYCL/ESIMD/lsc/Inputs/lsc_block_store.hpp @@ -36,7 +36,7 @@ bool test(unsigned SurfaceWidth, unsigned SurfaceHeight, unsigned SurfacePitch, T old_val = get_rand(); T new_val = get_rand(); - auto GPUSelector = gpu_selector{}; + auto GPUSelector = gpu_selector_v; auto q = queue{GPUSelector}; auto dev = q.get_device(); std::cout << "Running case #" << case_num << " on " diff --git a/SYCL/ESIMD/lsc/Inputs/lsc_slm_load.hpp b/SYCL/ESIMD/lsc/Inputs/lsc_slm_load.hpp index 61e0f87b13..9500e1cdfa 100644 --- a/SYCL/ESIMD/lsc/Inputs/lsc_slm_load.hpp +++ b/SYCL/ESIMD/lsc/Inputs/lsc_slm_load.hpp @@ -43,7 +43,7 @@ bool test(uint32_t PMask = ~0) { else if constexpr (DS == lsc_data_size::u16u32h) VMask = static_cast(0xffff0000); - queue Q(gpu_selector{}); + queue Q(gpu_selector_v); auto D = Q.get_device(); std::cout << "Running case #" << CaseNum << " on " << D.get_info() << std::endl; diff --git a/SYCL/ESIMD/lsc/Inputs/lsc_slm_store.hpp b/SYCL/ESIMD/lsc/Inputs/lsc_slm_store.hpp index 021dd48cc4..0db95b3499 100644 --- a/SYCL/ESIMD/lsc/Inputs/lsc_slm_store.hpp +++ b/SYCL/ESIMD/lsc/Inputs/lsc_slm_store.hpp @@ -36,7 +36,7 @@ bool test(uint32_t PMask = ~0) { else if constexpr (DS == lsc_data_size::u16u32h) VMask = static_cast(0xffff0000); - queue Q(gpu_selector{}); + queue Q(gpu_selector_v); auto D = Q.get_device(); std::cout << "Running case #" << CaseNum << " on " << D.get_info() << std::endl; diff --git a/SYCL/ESIMD/lsc/Inputs/lsc_surf.hpp b/SYCL/ESIMD/lsc/Inputs/lsc_surf.hpp index 2e1f7302e7..5a953950b5 100644 --- a/SYCL/ESIMD/lsc/Inputs/lsc_surf.hpp +++ b/SYCL/ESIMD/lsc/Inputs/lsc_surf.hpp @@ -22,7 +22,7 @@ int main() { auto constexpr SIMDSize = unsigned{4}; auto q = - queue{esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()}; + queue{esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()}; auto device = q.get_device(); std::cout << "Device name: " << device.get_info() << std::endl; diff --git a/SYCL/ESIMD/lsc/Inputs/lsc_surf_load.hpp b/SYCL/ESIMD/lsc/Inputs/lsc_surf_load.hpp index 523b04e05b..eec95f9f12 100644 --- a/SYCL/ESIMD/lsc/Inputs/lsc_surf_load.hpp +++ b/SYCL/ESIMD/lsc/Inputs/lsc_surf_load.hpp @@ -49,8 +49,7 @@ bool test(uint32_t pmask = 0xffffffff) { T old_val = get_rand(); - auto GPUSelector = gpu_selector{}; - auto q = queue{GPUSelector}; + auto q = queue{gpu_selector_v}; auto dev = q.get_device(); std::cout << "Running case #" << case_num << " on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/lsc/Inputs/lsc_surf_store.hpp b/SYCL/ESIMD/lsc/Inputs/lsc_surf_store.hpp index 8def84e688..264089d79f 100644 --- a/SYCL/ESIMD/lsc/Inputs/lsc_surf_store.hpp +++ b/SYCL/ESIMD/lsc/Inputs/lsc_surf_store.hpp @@ -49,8 +49,7 @@ bool test(uint32_t pmask = 0xffffffff) { T old_val = get_rand(); T new_val = get_rand(); - auto GPUSelector = gpu_selector{}; - auto q = queue{GPUSelector}; + auto q = queue{gpu_selector_v}; auto dev = q.get_device(); std::cout << "Running case #" << case_num << " on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/lsc/Inputs/lsc_usm_load.hpp b/SYCL/ESIMD/lsc/Inputs/lsc_usm_load.hpp index e9170fa6fe..670a38cc8e 100644 --- a/SYCL/ESIMD/lsc/Inputs/lsc_usm_load.hpp +++ b/SYCL/ESIMD/lsc/Inputs/lsc_usm_load.hpp @@ -50,8 +50,7 @@ bool test(uint32_t pmask = 0xffffffff) { T old_val = get_rand(); T zero_val = (T)0; - auto GPUSelector = gpu_selector{}; - auto q = queue{GPUSelector}; + auto q = queue{gpu_selector_v}; auto dev = q.get_device(); std::cout << "Running case #" << case_num << " on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/lsc/Inputs/lsc_usm_store.hpp b/SYCL/ESIMD/lsc/Inputs/lsc_usm_store.hpp index 5be20237c9..ca68299172 100644 --- a/SYCL/ESIMD/lsc/Inputs/lsc_usm_store.hpp +++ b/SYCL/ESIMD/lsc/Inputs/lsc_usm_store.hpp @@ -49,8 +49,7 @@ bool test(uint32_t pmask = 0xffffffff) { T old_val = get_rand(); T new_val = get_rand(); - auto GPUSelector = gpu_selector{}; - auto q = queue{GPUSelector}; + auto q = queue{gpu_selector_v}; auto dev = q.get_device(); std::cout << "Running case #" << case_num << " on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/lsc/atomic_smoke.cpp b/SYCL/ESIMD/lsc/atomic_smoke.cpp index e48e2905fc..2c1753d0fa 100644 --- a/SYCL/ESIMD/lsc/atomic_smoke.cpp +++ b/SYCL/ESIMD/lsc/atomic_smoke.cpp @@ -482,7 +482,7 @@ bool test_int_types(queue q, const Config &cfg) { } int main(void) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/lsc/lsc_predicate.cpp b/SYCL/ESIMD/lsc/lsc_predicate.cpp index 5f0df4672a..764996d220 100644 --- a/SYCL/ESIMD/lsc/lsc_predicate.cpp +++ b/SYCL/ESIMD/lsc/lsc_predicate.cpp @@ -170,7 +170,7 @@ template int testUSM(queue q) { int main() { auto q = - queue{esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()}; + queue{esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()}; auto device = q.get_device(); std::cout << "Device name: " << device.get_info() << std::endl; diff --git a/SYCL/ESIMD/lsc/lsc_predicate_stateless.cpp b/SYCL/ESIMD/lsc/lsc_predicate_stateless.cpp index 23ab9d3e52..9d1e8692d0 100644 --- a/SYCL/ESIMD/lsc/lsc_predicate_stateless.cpp +++ b/SYCL/ESIMD/lsc/lsc_predicate_stateless.cpp @@ -104,7 +104,7 @@ template int testAccessor(queue q) { int main() { auto q = - queue{esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()}; + queue{esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()}; auto device = q.get_device(); std::cout << "Device name: " << device.get_info() << std::endl; diff --git a/SYCL/ESIMD/lsc/lsc_slm.cpp b/SYCL/ESIMD/lsc/lsc_slm.cpp index cf050bd8b4..b435b84628 100644 --- a/SYCL/ESIMD/lsc/lsc_slm.cpp +++ b/SYCL/ESIMD/lsc/lsc_slm.cpp @@ -27,7 +27,7 @@ int main() { auto constexpr SIMDSize = unsigned{4}; auto q = - queue{esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()}; + queue{esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()}; auto device = q.get_device(); std::cout << "Device name: " << device.get_info() << std::endl; diff --git a/SYCL/ESIMD/lsc/lsc_usm.cpp b/SYCL/ESIMD/lsc/lsc_usm.cpp index 4d6e5c501a..ee3015b77f 100644 --- a/SYCL/ESIMD/lsc/lsc_usm.cpp +++ b/SYCL/ESIMD/lsc/lsc_usm.cpp @@ -27,7 +27,7 @@ int main() { auto constexpr SIMDSize = unsigned{4}; auto q = - queue{esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()}; + queue{esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()}; auto device = q.get_device(); std::cout << "Device name: " << device.get_info() << std::endl; diff --git a/SYCL/ESIMD/lsc/lsc_usm_2d.cpp b/SYCL/ESIMD/lsc/lsc_usm_2d.cpp index ff41d4f442..3289b33190 100644 --- a/SYCL/ESIMD/lsc/lsc_usm_2d.cpp +++ b/SYCL/ESIMD/lsc/lsc_usm_2d.cpp @@ -30,7 +30,7 @@ int main() { unsigned y = 0; unsigned size = data_height * data_pitch; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto device = q.get_device(); std::cout << "Device name: " << device.get_info() << std::endl; diff --git a/SYCL/ESIMD/lsc/lsc_usm_atomic_cachehint.cpp b/SYCL/ESIMD/lsc/lsc_usm_atomic_cachehint.cpp index 8d259c0fbb..356380aa67 100644 --- a/SYCL/ESIMD/lsc/lsc_usm_atomic_cachehint.cpp +++ b/SYCL/ESIMD/lsc/lsc_usm_atomic_cachehint.cpp @@ -43,7 +43,7 @@ int main(void) { constexpr size_t LocalRange = 4; constexpr size_t GlobalRange = 64; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() diff --git a/SYCL/ESIMD/mandelbrot/mandelbrot.cpp b/SYCL/ESIMD/mandelbrot/mandelbrot.cpp index 4549b3b78f..0267597713 100644 --- a/SYCL/ESIMD/mandelbrot/mandelbrot.cpp +++ b/SYCL/ESIMD/mandelbrot/mandelbrot.cpp @@ -96,7 +96,7 @@ int main(int argc, char *argv[]) { double kernel_times = 0; unsigned num_iters = 10; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler(), + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler(), property::queue::enable_profiling{}); try { diff --git a/SYCL/ESIMD/mandelbrot/mandelbrot_spec.cpp b/SYCL/ESIMD/mandelbrot/mandelbrot_spec.cpp index ac0733d723..a0b77853c6 100644 --- a/SYCL/ESIMD/mandelbrot/mandelbrot_spec.cpp +++ b/SYCL/ESIMD/mandelbrot/mandelbrot_spec.cpp @@ -119,7 +119,7 @@ int main(int argc, char *argv[]) { // Number of workitems in a workgroup sycl::range<2> LocalRange{1, 1}; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler(), + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler(), property::queue::enable_profiling{}); auto dev = q.get_device(); diff --git a/SYCL/ESIMD/matrix_transpose.cpp b/SYCL/ESIMD/matrix_transpose.cpp index ebe14bc029..499183db31 100644 --- a/SYCL/ESIMD/matrix_transpose.cpp +++ b/SYCL/ESIMD/matrix_transpose.cpp @@ -274,7 +274,7 @@ ESIMD_INLINE void transpose16(AccessorTy buf, int MZ, int block_col, bool runTest(unsigned MZ, unsigned block_size, unsigned num_iters, double &kernel_times, double &total_times) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler(), + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler(), property::queue::enable_profiling{}); int *M = new int[MZ * MZ]; diff --git a/SYCL/ESIMD/matrix_transpose2.cpp b/SYCL/ESIMD/matrix_transpose2.cpp index 6f0df0e28c..00dd924a9d 100644 --- a/SYCL/ESIMD/matrix_transpose2.cpp +++ b/SYCL/ESIMD/matrix_transpose2.cpp @@ -272,7 +272,7 @@ ESIMD_INLINE void transpose16(AccessorInTy in, AccessorOutTy out, int MZ, bool runTest(unsigned MZ, unsigned block_size, unsigned num_iters, double &kernel_times, double &total_times) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler(), + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler(), property::queue::enable_profiling{}); int *M = new int[MZ * MZ]; diff --git a/SYCL/ESIMD/matrix_transpose_glb.cpp b/SYCL/ESIMD/matrix_transpose_glb.cpp index a6c299b563..1e008f48f3 100644 --- a/SYCL/ESIMD/matrix_transpose_glb.cpp +++ b/SYCL/ESIMD/matrix_transpose_glb.cpp @@ -243,7 +243,7 @@ ESIMD_INLINE void transpose16(int *buf, int MZ, int block_col, int block_row) { bool runTest(unsigned MZ, unsigned block_size, unsigned num_iters, double &kernel_times, double &total_times) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler(), + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler(), property::queue::enable_profiling{}); int *M = malloc_shared(MZ * MZ, q); diff --git a/SYCL/ESIMD/matrix_transpose_usm.cpp b/SYCL/ESIMD/matrix_transpose_usm.cpp index 48d45b9980..babf8fa97d 100644 --- a/SYCL/ESIMD/matrix_transpose_usm.cpp +++ b/SYCL/ESIMD/matrix_transpose_usm.cpp @@ -320,7 +320,7 @@ int main(int argc, char *argv[]) { MZ = (MZ < (1U << 12)) ? MZ : (1U << 12); } - queue Q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler(), + queue Q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler(), property::queue::enable_profiling{}); unsigned num_iters = 10; diff --git a/SYCL/ESIMD/noinline_args_size/Inputs/noinline_args_size_common.hpp b/SYCL/ESIMD/noinline_args_size/Inputs/noinline_args_size_common.hpp index 781efe0320..bd6add9c8e 100644 --- a/SYCL/ESIMD/noinline_args_size/Inputs/noinline_args_size_common.hpp +++ b/SYCL/ESIMD/noinline_args_size/Inputs/noinline_args_size_common.hpp @@ -35,7 +35,7 @@ ESIMD_NOINLINE TC add(TA A, TB B) { } int main(void) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/noinline_call_from_func.cpp b/SYCL/ESIMD/noinline_call_from_func.cpp index 0d187a2623..0e1f8f150d 100644 --- a/SYCL/ESIMD/noinline_call_from_func.cpp +++ b/SYCL/ESIMD/noinline_call_from_func.cpp @@ -37,7 +37,7 @@ template ESIMD_NOINLINE void test(AccTy acc, int A, int B) { } int main(int argc, char **argv) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/noinline_call_recursive.cpp b/SYCL/ESIMD/noinline_call_recursive.cpp index c736a47659..eaa583f1d3 100644 --- a/SYCL/ESIMD/noinline_call_recursive.cpp +++ b/SYCL/ESIMD/noinline_call_recursive.cpp @@ -32,7 +32,7 @@ ESIMD_NOINLINE unsigned add(unsigned A, unsigned B, unsigned C) { } int main(int argc, char **argv) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/printf.cpp b/SYCL/ESIMD/printf.cpp index c730b3a1f5..4a65166ec5 100644 --- a/SYCL/ESIMD/printf.cpp +++ b/SYCL/ESIMD/printf.cpp @@ -45,7 +45,7 @@ const CONSTANT char format_int[] = "%d\n"; int main() { { - queue Queue(esimd_test::ESIMDSelector{}, + queue Queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); Queue.submit([&](handler &CGH) { @@ -84,7 +84,7 @@ int main() { } { - queue Q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue Q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); // printf in parallel_for constexpr int SIMD_SIZE = 16; constexpr int WORK_SIZE = SIMD_SIZE; diff --git a/SYCL/ESIMD/private_memory/Inputs/pm_common.cpp b/SYCL/ESIMD/private_memory/Inputs/pm_common.cpp index 5857c77943..fbd46806bd 100644 --- a/SYCL/ESIMD/private_memory/Inputs/pm_common.cpp +++ b/SYCL/ESIMD/private_memory/Inputs/pm_common.cpp @@ -109,7 +109,7 @@ ESIMD_INLINE void work(int *o, int offx1, int offx2, int offy1, int offy2, template class KernelID; template int test() { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/radix_sort.cpp b/SYCL/ESIMD/radix_sort.cpp index 04e703d185..ba1d05cf38 100644 --- a/SYCL/ESIMD/radix_sort.cpp +++ b/SYCL/ESIMD/radix_sort.cpp @@ -589,7 +589,7 @@ int main(int argc, char *argv[]) { cl::sycl::range<2> LocalRange{1, 1}; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler(), + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler(), property::queue::in_order()); auto dev = q.get_device(); diff --git a/SYCL/ESIMD/reduction.cpp b/SYCL/ESIMD/reduction.cpp index 118c634c4e..5be1efe9d5 100644 --- a/SYCL/ESIMD/reduction.cpp +++ b/SYCL/ESIMD/reduction.cpp @@ -27,7 +27,7 @@ int main(void) { constexpr unsigned VL = 32; constexpr unsigned GroupSize = 1; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/regression/Inputs/complex-lib-test.cpp b/SYCL/ESIMD/regression/Inputs/complex-lib-test.cpp index 9ad66fd437..532deeab29 100644 --- a/SYCL/ESIMD/regression/Inputs/complex-lib-test.cpp +++ b/SYCL/ESIMD/regression/Inputs/complex-lib-test.cpp @@ -10,7 +10,7 @@ int main(int argc, char *argv[]) { try { size_t i; size_t N = 1024; - sycl::device D(sycl::default_selector{}); + sycl::device D(sycl::default_selector_v); sycl::context Ctx(D); sycl::queue Q(Ctx, D); diff --git a/SYCL/ESIMD/regression/big_const_initializer.cpp b/SYCL/ESIMD/regression/big_const_initializer.cpp index ade56b4832..1ff20c2f0d 100644 --- a/SYCL/ESIMD/regression/big_const_initializer.cpp +++ b/SYCL/ESIMD/regression/big_const_initializer.cpp @@ -37,7 +37,7 @@ inline void foo(sycl::ext::intel::esimd::simd &k) { int main(int argc, char **argv) { size_t nsamples = N_SAMPLES; - sycl::queue queue(esimd_test::ESIMDSelector{}, + sycl::queue queue(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); std::cout << "Running on " diff --git a/SYCL/ESIMD/regression/noinline_bypointers_vadd.cpp b/SYCL/ESIMD/regression/noinline_bypointers_vadd.cpp index 799870f2b5..eabe96018c 100644 --- a/SYCL/ESIMD/regression/noinline_bypointers_vadd.cpp +++ b/SYCL/ESIMD/regression/noinline_bypointers_vadd.cpp @@ -42,7 +42,7 @@ int main(void) { constexpr unsigned Size = 1024; constexpr unsigned GroupSize = 8; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() diff --git a/SYCL/ESIMD/regression/operator_decrement.cpp b/SYCL/ESIMD/regression/operator_decrement.cpp index 1294d472fb..76d3972765 100644 --- a/SYCL/ESIMD/regression/operator_decrement.cpp +++ b/SYCL/ESIMD/regression/operator_decrement.cpp @@ -39,7 +39,7 @@ int main(void) { // We need that many threads in each group range<1> LocalRange{1}; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/regression/replicate_bug.cpp b/SYCL/ESIMD/regression/replicate_bug.cpp index 02e2e63752..e7e36283f3 100644 --- a/SYCL/ESIMD/regression/replicate_bug.cpp +++ b/SYCL/ESIMD/regression/replicate_bug.cpp @@ -74,7 +74,7 @@ template bool test(queue q, const std::vector &gold) { } int main(void) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/regression/store_zero_const.cpp b/SYCL/ESIMD/regression/store_zero_const.cpp index c4080b0398..dcb5896137 100644 --- a/SYCL/ESIMD/regression/store_zero_const.cpp +++ b/SYCL/ESIMD/regression/store_zero_const.cpp @@ -78,7 +78,7 @@ template bool test(queue Q) { } int main(void) { - queue Q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue Q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto Dev = Q.get_device(); std::cout << "Running on " << Dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/regression/usm_gather_scatter_32.cpp b/SYCL/ESIMD/regression/usm_gather_scatter_32.cpp index 1c8cd50af0..330e4edb2c 100644 --- a/SYCL/ESIMD/regression/usm_gather_scatter_32.cpp +++ b/SYCL/ESIMD/regression/usm_gather_scatter_32.cpp @@ -28,7 +28,7 @@ int main(void) { constexpr unsigned Size = 1024; constexpr unsigned VL = 32; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() diff --git a/SYCL/ESIMD/regression/variable_gather_mask.cpp b/SYCL/ESIMD/regression/variable_gather_mask.cpp index cd9b77e40c..c5cbe4a25d 100644 --- a/SYCL/ESIMD/regression/variable_gather_mask.cpp +++ b/SYCL/ESIMD/regression/variable_gather_mask.cpp @@ -129,7 +129,7 @@ template bool test(const char *msg, queue q, Command cmd) { } int main(int argc, char **argv) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() diff --git a/SYCL/ESIMD/slm_barrier.cpp b/SYCL/ESIMD/slm_barrier.cpp index 9751c22e32..5c14a7ef22 100644 --- a/SYCL/ESIMD/slm_barrier.cpp +++ b/SYCL/ESIMD/slm_barrier.cpp @@ -75,7 +75,7 @@ int main(void) { constexpr unsigned VL = 16; constexpr unsigned Size = NUM_THREADS * VL; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() diff --git a/SYCL/ESIMD/slm_split_barrier.cpp b/SYCL/ESIMD/slm_split_barrier.cpp index 2603a6f78d..d256488370 100644 --- a/SYCL/ESIMD/slm_split_barrier.cpp +++ b/SYCL/ESIMD/slm_split_barrier.cpp @@ -79,7 +79,7 @@ int main(void) { constexpr unsigned VL = 16; constexpr unsigned Size = NUM_THREADS * VL; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() diff --git a/SYCL/ESIMD/spec_const/Inputs/spec-const-2020-common.hpp b/SYCL/ESIMD/spec_const/Inputs/spec-const-2020-common.hpp index 61e300701b..8c15561771 100644 --- a/SYCL/ESIMD/spec_const/Inputs/spec-const-2020-common.hpp +++ b/SYCL/ESIMD/spec_const/Inputs/spec-const-2020-common.hpp @@ -36,7 +36,7 @@ class TestKernel; constexpr specialization_id ConstID(DEF_VAL); int main(int argc, char **argv) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); if (std::is_same_v && !dev.has(aspect::fp64)) diff --git a/SYCL/ESIMD/stencil2.cpp b/SYCL/ESIMD/stencil2.cpp index 94ee136272..ede181b9c7 100644 --- a/SYCL/ESIMD/stencil2.cpp +++ b/SYCL/ESIMD/stencil2.cpp @@ -90,7 +90,7 @@ int main(int argc, char *argv[]) { << std::endl; sycl::range<2> LocalRange{1, 1}; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler(), + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler(), property::queue::enable_profiling{}); auto dev = q.get_device(); diff --git a/SYCL/ESIMD/sycl_esimd_mix.cpp b/SYCL/ESIMD/sycl_esimd_mix.cpp index d5d724fc6e..5f08c1b07c 100644 --- a/SYCL/ESIMD/sycl_esimd_mix.cpp +++ b/SYCL/ESIMD/sycl_esimd_mix.cpp @@ -63,7 +63,7 @@ int main(void) { // We need that many threads in each group sycl::range<1> LocalRange{1}; - queue q(gpu_selector{}, esimd_test::createExceptionHandler()); + queue q(gpu_selector_v, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; @@ -94,7 +94,7 @@ int main(void) { // We need that many threads in each group sycl::range<1> LocalRange{1}; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/test_id_3d.cpp b/SYCL/ESIMD/test_id_3d.cpp index 7935f3c71a..875530f3c8 100644 --- a/SYCL/ESIMD/test_id_3d.cpp +++ b/SYCL/ESIMD/test_id_3d.cpp @@ -31,7 +31,7 @@ int main(void) { size_t Y = GlobalRange[1]; size_t X = GlobalRange[2]; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/usm_gather_scatter_rgba.cpp b/SYCL/ESIMD/usm_gather_scatter_rgba.cpp index a6e998eae4..6e1c7f713b 100644 --- a/SYCL/ESIMD/usm_gather_scatter_rgba.cpp +++ b/SYCL/ESIMD/usm_gather_scatter_rgba.cpp @@ -162,7 +162,7 @@ template bool test(queue q) { } int main(void) { - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/vadd_1d.cpp b/SYCL/ESIMD/vadd_1d.cpp index c6b2c1db51..dfd898343a 100644 --- a/SYCL/ESIMD/vadd_1d.cpp +++ b/SYCL/ESIMD/vadd_1d.cpp @@ -42,7 +42,7 @@ int main(void) { // We need that many threads in each group range<1> LocalRange{1}; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/vadd_2d.cpp b/SYCL/ESIMD/vadd_2d.cpp index ce58008f61..cc40bec6bf 100644 --- a/SYCL/ESIMD/vadd_2d.cpp +++ b/SYCL/ESIMD/vadd_2d.cpp @@ -48,7 +48,7 @@ int main(void) { // Number of workitems in a workgroup range<1> LocalRange{GroupSize}; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/vadd_2d_acc.cpp b/SYCL/ESIMD/vadd_2d_acc.cpp index d42239e8ad..78d6f32a0d 100644 --- a/SYCL/ESIMD/vadd_2d_acc.cpp +++ b/SYCL/ESIMD/vadd_2d_acc.cpp @@ -48,7 +48,7 @@ int main(void) { sycl::nd_range<2> Range(GlobalRange, LocalRange); - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); auto ctxt = q.get_context(); diff --git a/SYCL/ESIMD/vadd_half.cpp b/SYCL/ESIMD/vadd_half.cpp index 1ca24dabe4..1482aae505 100644 --- a/SYCL/ESIMD/vadd_half.cpp +++ b/SYCL/ESIMD/vadd_half.cpp @@ -54,7 +54,7 @@ int main(int argc, char **argv) { } std::cout << "Using start value = " << start_val << "\n"; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/ESIMD/vadd_raw_send.cpp b/SYCL/ESIMD/vadd_raw_send.cpp index 8479c44431..8790c09f72 100644 --- a/SYCL/ESIMD/vadd_raw_send.cpp +++ b/SYCL/ESIMD/vadd_raw_send.cpp @@ -109,7 +109,7 @@ int main(void) { // We need that many threads in each group range<1> LocalRange{1}; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() diff --git a/SYCL/ESIMD/vadd_usm.cpp b/SYCL/ESIMD/vadd_usm.cpp index 61836fbe04..1246538b14 100644 --- a/SYCL/ESIMD/vadd_usm.cpp +++ b/SYCL/ESIMD/vadd_usm.cpp @@ -23,7 +23,7 @@ int main(void) { constexpr unsigned VL = 32; constexpr unsigned GroupSize = 8; - queue q(esimd_test::ESIMDSelector{}, esimd_test::createExceptionHandler()); + queue q(esimd_test::ESIMDSelector, esimd_test::createExceptionHandler()); auto dev = q.get_device(); std::cout << "Running on " << dev.get_info() << "\n"; diff --git a/SYCL/GroupAlgorithm/SYCL2020/sort.cpp b/SYCL/GroupAlgorithm/SYCL2020/sort.cpp index 1a513d726f..13d9463c8c 100644 --- a/SYCL/GroupAlgorithm/SYCL2020/sort.cpp +++ b/SYCL/GroupAlgorithm/SYCL2020/sort.cpp @@ -343,7 +343,7 @@ void test_sort_by_type(sycl::queue &q, std::size_t dataSize) { } int main(int argc, char *argv[]) { - sycl::queue q(sycl::default_selector{}, async_handler_); + sycl::queue q(sycl::default_selector_v, async_handler_); if (!isSupportedDevice(q.get_device())) { std::cout << "Skipping test\n"; return 0; diff --git a/SYCL/InlineAsm/include/asmhelper.h b/SYCL/InlineAsm/include/asmhelper.h index 35c8c68b5f..4cf9b4362d 100644 --- a/SYCL/InlineAsm/include/asmhelper.h +++ b/SYCL/InlineAsm/include/asmhelper.h @@ -92,7 +92,7 @@ auto exception_handler = [](sycl::exception_list exceptions) { template bool launchInlineASMTestImpl(F &f, bool requires_particular_sg_size = true) { - sycl::queue deviceQueue(sycl::gpu_selector{}, exception_handler); + sycl::queue deviceQueue(sycl::gpu_selector_v, exception_handler); sycl::device device = deviceQueue.get_device(); if (!isInlineASMSupported(device)) { diff --git a/SYCL/InorderQueue/prop.cpp b/SYCL/InorderQueue/prop.cpp index 773f7bd373..3b641a3186 100644 --- a/SYCL/InorderQueue/prop.cpp +++ b/SYCL/InorderQueue/prop.cpp @@ -51,7 +51,7 @@ int main() { if (res != 0) return res; - device dev{sycl::default_selector{}}; + device dev{sycl::default_selector_v}; context ctx{dev}; auto exception_handler = [](sycl::exception_list exceptions) {}; diff --git a/SYCL/Plugin/enqueue-arg-order-buffer.cpp b/SYCL/Plugin/enqueue-arg-order-buffer.cpp index aa3660be64..bca144a582 100644 --- a/SYCL/Plugin/enqueue-arg-order-buffer.cpp +++ b/SYCL/Plugin/enqueue-arg-order-buffer.cpp @@ -237,7 +237,7 @@ void testcopyH2DBuffer() { buffer buffer_from_1D(data_from_1D.data(), range<1>(width)); buffer buffer_to_1D(data_to_1D.data(), range<1>(width)); - device Dev{default_selector{}}; + device Dev{default_selector_v}; context myCtx{Dev}; context otherCtx{Dev}; diff --git a/SYCL/Plugin/enqueue-arg-order-image.cpp b/SYCL/Plugin/enqueue-arg-order-image.cpp index fec4b94ce7..8329792b2e 100644 --- a/SYCL/Plugin/enqueue-arg-order-image.cpp +++ b/SYCL/Plugin/enqueue-arg-order-image.cpp @@ -206,7 +206,7 @@ void testcopyH2DImage() { ImgSize_2D); sycl::image<2> image_to_2D(data_to_2D.data(), ChanOrder, ChanType, ImgSize_2D); - device Dev{default_selector{}}; + device Dev{default_selector_v}; context Ctx{Dev}; context otherCtx{Dev}; @@ -245,7 +245,7 @@ void testcopyH2DImage() { ImgSize_3D); sycl::image<3> image_to_3D(data_to_3D.data(), ChanOrder, ChanType, ImgSize_3D); - device Dev{default_selector{}}; + device Dev{default_selector_v}; context Ctx{Dev}; context otherCtx{Dev}; diff --git a/SYCL/Plugin/interop-buffer-cuda.cpp b/SYCL/Plugin/interop-buffer-cuda.cpp index 7b72bbd034..11e063ae0d 100644 --- a/SYCL/Plugin/interop-buffer-cuda.cpp +++ b/SYCL/Plugin/interop-buffer-cuda.cpp @@ -17,7 +17,7 @@ int main() { int Data[1] = {0}; sycl::buffer Buffer(&Data[0], sycl::range<1>(1)); { - sycl::queue Queue{sycl::gpu_selector()}; + sycl::queue Queue{sycl::gpu_selector_v}; Queue.submit([&](sycl::handler &cgh) { auto Acc = Buffer.get_access(cgh); cgh.single_task([=]() { (void)Acc; }); diff --git a/SYCL/Plugin/interop-cuda-experimental.cpp b/SYCL/Plugin/interop-cuda-experimental.cpp index 13b1c97be1..f5c1fac18c 100644 --- a/SYCL/Plugin/interop-cuda-experimental.cpp +++ b/SYCL/Plugin/interop-cuda-experimental.cpp @@ -55,7 +55,7 @@ int main() { // Create sycl queue with queue construct from Q's native types and submit // some work { - sycl::queue new_Q(Q_sycl_ctx, sycl::default_selector()); + sycl::queue new_Q(Q_sycl_ctx, sycl::default_selector_v); assert(check_queue(new_Q)); } @@ -92,7 +92,7 @@ int main() { // Create sycl queue with new queue and submit some work { - sycl::queue new_Q(sycl_ctx, sycl::default_selector()); + sycl::queue new_Q(sycl_ctx, sycl::default_selector_v); assert(check_queue(new_Q)); } @@ -112,7 +112,7 @@ int main() { // Check sycl queue with sycl_ctx still works { - sycl::queue new_Q(sycl_ctx, sycl::default_selector()); + sycl::queue new_Q(sycl_ctx, sycl::default_selector_v); assert(check_queue(new_Q)); } diff --git a/SYCL/Plugin/interop-level-zero-buffer-multi-dim.cpp b/SYCL/Plugin/interop-level-zero-buffer-multi-dim.cpp index 442ef5c6c7..87cf6cc339 100644 --- a/SYCL/Plugin/interop-level-zero-buffer-multi-dim.cpp +++ b/SYCL/Plugin/interop-level-zero-buffer-multi-dim.cpp @@ -16,7 +16,7 @@ using namespace sycl; int main() { #ifdef SYCL_EXT_ONEAPI_BACKEND_LEVEL_ZERO try { - platform Plt{gpu_selector{}}; + platform Plt{gpu_selector_v}; auto Devices = Plt.get_devices(); diff --git a/SYCL/Plugin/interop-level-zero-buffer-ownership.cpp b/SYCL/Plugin/interop-level-zero-buffer-ownership.cpp index 852e605237..742554c879 100644 --- a/SYCL/Plugin/interop-level-zero-buffer-ownership.cpp +++ b/SYCL/Plugin/interop-level-zero-buffer-ownership.cpp @@ -108,7 +108,7 @@ void test_copyback_and_free( int main() { #ifdef SYCL_EXT_ONEAPI_BACKEND_LEVEL_ZERO try { - platform Plt{gpu_selector{}}; + platform Plt{gpu_selector_v}; auto Devices = Plt.get_devices(); diff --git a/SYCL/Plugin/interop-level-zero-buffer.cpp b/SYCL/Plugin/interop-level-zero-buffer.cpp index 60ac2187cf..1bf2d3538f 100644 --- a/SYCL/Plugin/interop-level-zero-buffer.cpp +++ b/SYCL/Plugin/interop-level-zero-buffer.cpp @@ -139,7 +139,7 @@ int main() { // Test case #3 // Use buffer in two different contexts context Context1; - queue Queue1(Context1, default_selector{}); + queue Queue1(Context1, default_selector_v); Queue1.submit([&](sycl::handler &CGH) { auto Acc = HostBufferInterop2.get_access(CGH); @@ -151,7 +151,7 @@ int main() { }); context Context2; - queue Queue2(Context2, default_selector{}); + queue Queue2(Context2, default_selector_v); Queue2.submit([&](sycl::handler &CGH) { auto Acc = HostBufferInterop2.get_access(CGH); diff --git a/SYCL/Plugin/interop-level-zero-get-native-mem.cpp b/SYCL/Plugin/interop-level-zero-get-native-mem.cpp index 513f99e668..41381d1ec0 100644 --- a/SYCL/Plugin/interop-level-zero-get-native-mem.cpp +++ b/SYCL/Plugin/interop-level-zero-get-native-mem.cpp @@ -22,7 +22,7 @@ constexpr size_t SIZE = 16; int main() { #ifdef SYCL_EXT_ONEAPI_BACKEND_LEVEL_ZERO try { - platform Plt{gpu_selector{}}; + platform Plt{gpu_selector_v}; auto Devices = Plt.get_devices(); diff --git a/SYCL/Plugin/interop-level-zero-keep-ownership.cpp b/SYCL/Plugin/interop-level-zero-keep-ownership.cpp index 6fd5307a1e..eeeb60cb32 100644 --- a/SYCL/Plugin/interop-level-zero-keep-ownership.cpp +++ b/SYCL/Plugin/interop-level-zero-keep-ownership.cpp @@ -16,7 +16,7 @@ using namespace sycl; int main() { // Creat SYCL platform/device - device Device(gpu_selector{}); + device Device(gpu_selector_v); platform Platform = Device.get_info(); // Create native Level-Zero context diff --git a/SYCL/Plugin/level-zero-usm-capabilities.cpp b/SYCL/Plugin/level-zero-usm-capabilities.cpp index 1170f6e033..fa25287fb8 100644 --- a/SYCL/Plugin/level-zero-usm-capabilities.cpp +++ b/SYCL/Plugin/level-zero-usm-capabilities.cpp @@ -18,7 +18,7 @@ using namespace sycl; int main() { - auto D = device(gpu_selector()); + auto D = device(gpu_selector_v); std::cout << "name = " << D.get_info() << std::endl; std::cout << " usm_host_allocations: " << D.has(aspect::usm_host_allocations) diff --git a/SYCL/Plugin/level_zero_batch_event_status.cpp b/SYCL/Plugin/level_zero_batch_event_status.cpp index a87d63eccc..073b099ee0 100644 --- a/SYCL/Plugin/level_zero_batch_event_status.cpp +++ b/SYCL/Plugin/level_zero_batch_event_status.cpp @@ -48,8 +48,7 @@ #include int main(void) { - sycl::default_selector ds{}; - sycl::queue q{ds}; + sycl::queue q{sycl::default_selector_v}; std::vector events(10); sycl::event ev1 = q.submit([&](sycl::handler &cgh) { diff --git a/SYCL/Plugin/level_zero_batch_test.cpp b/SYCL/Plugin/level_zero_batch_test.cpp index 9f93141de2..8533a49d91 100644 --- a/SYCL/Plugin/level_zero_batch_test.cpp +++ b/SYCL/Plugin/level_zero_batch_test.cpp @@ -297,7 +297,7 @@ int main(int argc, char *argv[]) { #else sycl::property_list Props{}; #endif - sycl::queue q(sycl::default_selector{}, Props); + sycl::queue q(sycl::default_selector_v, Props); auto ctx = q.get_context(); auto dev = q.get_device(); diff --git a/SYCL/Plugin/level_zero_batch_test_copy_with_compute.cpp b/SYCL/Plugin/level_zero_batch_test_copy_with_compute.cpp index 3afbc83a01..46dbd6f137 100644 --- a/SYCL/Plugin/level_zero_batch_test_copy_with_compute.cpp +++ b/SYCL/Plugin/level_zero_batch_test_copy_with_compute.cpp @@ -248,7 +248,7 @@ int main(int argc, char *argv[]) { size_t N = 4; size_t AL = M * N * sizeof(uint32_t); - sycl::queue q(sycl::default_selector{}); + sycl::queue q(sycl::default_selector_v); auto ctx = q.get_context(); auto dev = q.get_device(); diff --git a/SYCL/Plugin/level_zero_device_scope_events.cpp b/SYCL/Plugin/level_zero_device_scope_events.cpp index 425b6e0eeb..4af63e06a9 100644 --- a/SYCL/Plugin/level_zero_device_scope_events.cpp +++ b/SYCL/Plugin/level_zero_device_scope_events.cpp @@ -33,8 +33,7 @@ #include int main(int argc, char **argv) { - sycl::gpu_selector device_selector; - sycl::queue queue(device_selector); + sycl::queue queue(sycl::gpu_selector_v); int N = (argc >= 2 ? std::atoi(argv[1]) : 100); std::cout << N << " kernels" << std::endl; diff --git a/SYCL/Plugin/level_zero_dynamic_batch_test.cpp b/SYCL/Plugin/level_zero_dynamic_batch_test.cpp index d5f3d7b92b..0697e5b0d5 100644 --- a/SYCL/Plugin/level_zero_dynamic_batch_test.cpp +++ b/SYCL/Plugin/level_zero_dynamic_batch_test.cpp @@ -71,7 +71,7 @@ int main(int argc, char *argv[]) { #else sycl::property_list Props{}; #endif - sycl::queue q(sycl::default_selector{}, Props); + sycl::queue q(sycl::default_selector_v, Props); auto ctx = q.get_context(); auto dev = q.get_device(); diff --git a/SYCL/Plugin/level_zero_queue_profiling.cpp b/SYCL/Plugin/level_zero_queue_profiling.cpp index dbb1816fbe..5efac0d353 100644 --- a/SYCL/Plugin/level_zero_queue_profiling.cpp +++ b/SYCL/Plugin/level_zero_queue_profiling.cpp @@ -56,12 +56,11 @@ int main(int argc, char **argv) { bool profiling = argc > 1; { - gpu_selector dev_sel; property_list propList{}; if (profiling) propList = sycl::property::queue::enable_profiling(); - queue q(dev_sel, propList); + queue q(gpu_selector_v, propList); // Perform the computation foo(q, 2); } // SYCL scope diff --git a/SYCL/Plugin/max_malloc.cpp b/SYCL/Plugin/max_malloc.cpp index a402fec64b..8bcdc9022f 100644 --- a/SYCL/Plugin/max_malloc.cpp +++ b/SYCL/Plugin/max_malloc.cpp @@ -13,7 +13,7 @@ using namespace sycl; const double Gb = 1024 * 1024 * 1024; int main() { - auto D = device(gpu_selector()); + auto D = device(gpu_selector_v); std::cout << "name = " << D.get_info() << std::endl; diff --git a/SYCL/Plugin/retain_events.cpp b/SYCL/Plugin/retain_events.cpp index d48854affa..da1b1f25b3 100644 --- a/SYCL/Plugin/retain_events.cpp +++ b/SYCL/Plugin/retain_events.cpp @@ -67,7 +67,7 @@ int test(sycl::device &D) { int main() { try { - sycl::device D1{sycl::gpu_selector{}}; + sycl::device D1{sycl::gpu_selector_v}; print_device_properties(D1); for (int i = 0; i < 10; ++i) { test(D1); diff --git a/SYCL/Plugin/sycl-targets-order.cpp b/SYCL/Plugin/sycl-targets-order.cpp index 04b8221eb1..eb0f45ad68 100644 --- a/SYCL/Plugin/sycl-targets-order.cpp +++ b/SYCL/Plugin/sycl-targets-order.cpp @@ -21,7 +21,7 @@ int main(int argc, char **argv) { // select the default SYCL device - sycl::device device{sycl::default_selector{}}; + sycl::device device{sycl::default_selector_v}; std::cout << "Running on SYCL device " << device.get_info() << ", driver version " diff --git a/SYCL/Reduction/regression_after_pr_6343.cpp b/SYCL/Reduction/regression_after_pr_6343.cpp index ab20dd64a8..2c1026528b 100644 --- a/SYCL/Reduction/regression_after_pr_6343.cpp +++ b/SYCL/Reduction/regression_after_pr_6343.cpp @@ -8,7 +8,7 @@ using namespace sycl; int main() { - device d(default_selector{}); + device d(default_selector_v); context ctx{d}; queue q{ctx, d}; diff --git a/SYCL/Regression/cache_test.cpp b/SYCL/Regression/cache_test.cpp index a485539bf2..5c6ed75a96 100644 --- a/SYCL/Regression/cache_test.cpp +++ b/SYCL/Regression/cache_test.cpp @@ -36,7 +36,7 @@ using namespace sycl::ext::oneapi; int queryFromQueue(std::vector *platform_list, std::vector *device_list) { int failures = 0; - sycl::queue Q{sycl::default_selector{}}; + sycl::queue Q{sycl::default_selector_v}; sycl::device dev = Q.get_info(); auto plt = dev.get_platform(); diff --git a/SYCL/Regression/context_is_destroyed_after_exception.cpp b/SYCL/Regression/context_is_destroyed_after_exception.cpp index 15fe32ab27..11ef3cc1ed 100644 --- a/SYCL/Regression/context_is_destroyed_after_exception.cpp +++ b/SYCL/Regression/context_is_destroyed_after_exception.cpp @@ -11,7 +11,7 @@ int main() { const auto GlobalRange = 1; const auto LocalRange = 2; - sycl::queue myQueue{sycl::gpu_selector{}, [](sycl::exception_list elist) { + sycl::queue myQueue{sycl::gpu_selector_v, [](sycl::exception_list elist) { for (auto e : elist) std::rethrow_exception(e); }}; diff --git a/SYCL/Regression/event_destruction.cpp b/SYCL/Regression/event_destruction.cpp index a3d35b4217..9e7ef70faf 100644 --- a/SYCL/Regression/event_destruction.cpp +++ b/SYCL/Regression/event_destruction.cpp @@ -20,8 +20,7 @@ const size_t ITERS = 100000; // The test checks that that event destruction does not lead to stack overflow int main() { - sycl::default_selector S; - sycl::queue Q(S); + sycl::queue Q(sycl::default_selector_v); sycl::buffer Buf(3000); for (size_t Idx = 0; Idx < ITERS; ++Idx) { auto Event = Q.submit([&](sycl::handler &cgh) { diff --git a/SYCL/Regression/kernel_bundle_ignore_sycl_external.cpp b/SYCL/Regression/kernel_bundle_ignore_sycl_external.cpp index 6e5a22981f..207a24a95d 100644 --- a/SYCL/Regression/kernel_bundle_ignore_sycl_external.cpp +++ b/SYCL/Regression/kernel_bundle_ignore_sycl_external.cpp @@ -13,7 +13,7 @@ SYCL_EXTERNAL int f(int a) { return a + 1; } int main() { - const sycl::device Dev{sycl::default_selector{}}; + const sycl::device Dev{sycl::default_selector_v}; const sycl::context Ctx{Dev}; sycl::queue Q{Ctx, Dev}; diff --git a/SYCL/Regression/usm_malloc_shared.cpp b/SYCL/Regression/usm_malloc_shared.cpp index 824080dedd..d044768398 100644 --- a/SYCL/Regression/usm_malloc_shared.cpp +++ b/SYCL/Regression/usm_malloc_shared.cpp @@ -23,7 +23,7 @@ int main(int argc, char *argv[]) { } }; - queue myQueue(default_selector{}, exception_handler); + queue myQueue(default_selector_v, exception_handler); std::cout << "Device: " << myQueue.get_device().get_info() << std::endl; diff --git a/SYCL/Scheduler/DataMovement.cpp b/SYCL/Scheduler/DataMovement.cpp index d64d119a6b..abf5333571 100644 --- a/SYCL/Scheduler/DataMovement.cpp +++ b/SYCL/Scheduler/DataMovement.cpp @@ -55,8 +55,8 @@ template class CustomAllocator { }; int main() { - TestQueue Queue1(sycl::default_selector{}); - TestQueue Queue2(sycl::default_selector{}); + TestQueue Queue1(sycl::default_selector_v); + TestQueue Queue2(sycl::default_selector_v); std::vector Data(1); diff --git a/SYCL/Scheduler/ReleaseResourcesTest.cpp b/SYCL/Scheduler/ReleaseResourcesTest.cpp index 1159e48283..acc446762e 100644 --- a/SYCL/Scheduler/ReleaseResourcesTest.cpp +++ b/SYCL/Scheduler/ReleaseResourcesTest.cpp @@ -24,12 +24,10 @@ int main() { // Checks creating of the second host accessor while first one is alive. try { - sycl::default_selector device_selector; - sycl::range<1> BufSize{1}; sycl::buffer Buf(BufSize); - TestQueue Queue(device_selector); + TestQueue Queue(sycl::default_selector_v); Queue.submit([&](sycl::handler &CGH) { auto BufAcc = Buf.get_access(CGH); diff --git a/SYCL/USM/multictxt.cpp b/SYCL/USM/multictxt.cpp index ec7e54cefd..1bb2f46b1b 100644 --- a/SYCL/USM/multictxt.cpp +++ b/SYCL/USM/multictxt.cpp @@ -20,8 +20,8 @@ using namespace sycl; // only needs to exist for this test to do its job. void GpuCpuCpu() { - queue gpu_q(gpu_selector{}); - queue cpu_q(cpu_selector{}); + queue gpu_q(gpu_selector_v); + queue cpu_q(cpu_selector_v); device dev = cpu_q.get_device(); context ctx = cpu_q.get_context(); if (dev.get_info()) { @@ -32,8 +32,8 @@ void GpuCpuCpu() { } void CpuGpuGpu() { - queue cpu_q(cpu_selector{}); - queue gpu_q(gpu_selector{}); + queue cpu_q(cpu_selector_v); + queue gpu_q(gpu_selector_v); device dev = gpu_q.get_device(); context ctx = gpu_q.get_context(); @@ -45,8 +45,8 @@ void CpuGpuGpu() { } void GpuCpuGpu() { - queue gpu_q(gpu_selector{}); - queue cpu_q(cpu_selector{}); + queue gpu_q(gpu_selector_v); + queue cpu_q(cpu_selector_v); device dev = gpu_q.get_device(); context ctx = gpu_q.get_context(); diff --git a/SYCL/XPTI/basic_event_collection.inc b/SYCL/XPTI/basic_event_collection.inc index 8eeae71c89..b23f1474e1 100644 --- a/SYCL/XPTI/basic_event_collection.inc +++ b/SYCL/XPTI/basic_event_collection.inc @@ -7,7 +7,7 @@ #include int main() { - sycl::queue Q{sycl::default_selector{}}; + sycl::queue Q{sycl::default_selector_v}; auto Ptr = sycl::malloc_device(1, Q); diff --git a/SYCL/XPTI/mem_alloc_events.inc b/SYCL/XPTI/mem_alloc_events.inc index cc23d031f5..4add70c850 100644 --- a/SYCL/XPTI/mem_alloc_events.inc +++ b/SYCL/XPTI/mem_alloc_events.inc @@ -9,7 +9,7 @@ #include int main() { - sycl::queue Q{sycl::default_selector{}}; + sycl::queue Q{sycl::default_selector_v}; sycl::buffer Buf{sycl::range{100}}; std::vector Vec; diff --git a/SYCL/helpers.hpp b/SYCL/helpers.hpp index bf27cd34d6..a51c64bd24 100644 --- a/SYCL/helpers.hpp +++ b/SYCL/helpers.hpp @@ -52,23 +52,22 @@ std::ostream &operator<<(std::ostream &Out, return Out; } +void exceptionHandlerHelper(sycl::exception_list ExceptionList) { + for (std::exception_ptr ExceptionPtr : ExceptionList) { + try { + std::rethrow_exception(ExceptionPtr); + } catch (sycl::exception &E) { + std::cerr << E.what() << std::endl; + } + } + abort(); +} + class TestQueue : public sycl::queue { public: - TestQueue(const sycl::device_selector &DevSelector, + TestQueue(const sycl::detail::DSelectorInvocableType &DevSelector, const sycl::property_list &PropList = {}) - : sycl::queue( - DevSelector, - [](sycl::exception_list ExceptionList) { - for (std::exception_ptr ExceptionPtr : ExceptionList) { - try { - std::rethrow_exception(ExceptionPtr); - } catch (sycl::exception &E) { - std::cerr << E.what() << std::endl; - } - } - abort(); - }, - PropList) {} + : sycl::queue(DevSelector, exceptionHandlerHelper, PropList) {} ~TestQueue() { wait_and_throw(); } };