diff --git a/SYCL/BFloat16/bfloat16_type.hpp b/SYCL/BFloat16/bfloat16_type.hpp index 17742fb5dc10..97e1ccb7fcf0 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 1d4d0769ba4a..ad492086a49b 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 b9773412eec3..aab4596dc771 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 715106a97b1a..087f5d439f90 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 ebfc651d226b..60d245f2f0c4 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 225dda44e6e4..fc911ad2300e 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 727edf6beb99..cd143d52566e 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 ed5407d4bce0..6c696119b192 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 db709242950e..47849f93cabc 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 c46649411ebf..004ef340ac13 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 cf56b8126cd7..2cde2698d6eb 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 1b63c811b53c..8f0d7d39f6de 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 8180d4e6f86d..1b48bcc5412a 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 305e6d03bfec..83a9f3269142 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 520c3047f33e..9494705e141a 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 1edb1ca3f97b..9d94a1378a3a 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 a40b31bedb35..beee757400de 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 fe9f153716f7..1e54b8e13b90 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 852fa13a1776..d5680dd57c39 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 0ebadcf5993c..6a87a63925e9 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 091782a8d809..559cae990cb4 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 91912ace4495..95313a839b43 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 345499338fde..6c6ee2f3fad7 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 b7321230a4ea..cb4e59c8a1e0 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 a8e0a4d6784a..0786a0ac3c0e 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 0d3587e65bf0..ebdd3c945838 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 5a2adbeb1389..5544d0617059 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 815f7105c6d2..034abf4106f8 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 7364841e43be..d47701d1632e 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 434910ddf37f..5bb41824a1b7 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 ad72e159e743..8938af2d282c 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 fd94fb101dc1..5afc03f56503 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 e7088867db07..a76ddaf6b919 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 d63a068ba307..d47db53661ef 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 f0e12f3c37a3..6f9347ee90fe 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 72b54c88b294..11e2f9a25235 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 52954616814f..e4845af05014 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 1a0f911016da..02557f4f7602 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 8860c3e1b23a..9f98f43f0d5e 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 38b22dbcda2a..632c1935ad25 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 fc1abbf72dc9..939706ede685 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 7075877b68a4..115697a86f11 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 4ea6a098171f..a8a0254e9627 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 4dde24df1a43..7bd0ff83f6ac 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 615139278ef1..c29932548218 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 c448b6d9c5e3..0b4587297793 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 a2e0827c636d..243a7b2e0943 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 2fbaf3e96b98..246d270efe7e 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 07d06fa60263..3660c569c313 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 8542deb73ce5..ecf6cf9467cd 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 9a9d215db624..cec697a0d065 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 984969249d2a..feaed2f9c188 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 27e9a3a568f0..1aa0b9f1c88d 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 02fd350d857d..53a3e9aa693d 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 2f4b7c6b57f0..3770c48a1a56 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 69965f758061..9978df13a347 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 39f9be9fcdd3..dc926260587b 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 6062f0013872..564d9af4b8e2 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 9815900eb6a1..253719c54d52 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 fda84f942f12..378cb64f6c21 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 cdb47bfd15a5..36dfbb571840 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 27393d8ade7b..b81c5e183186 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 014a1659ed5d..622c93aeb56b 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 96a285d39270..920c09289da4 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 740175f1546d..1d34715c866b 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 ff2f4bb0748d..b7bfda498872 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 797ff009c8f5..4349aef39948 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 ce57ae120e34..78cb13964648 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 4b960879c105..5d0d11b9f47a 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 7bfa6666dfc1..3715e7917cf2 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 6fcd17c450e8..4538173ef6d8 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 45d044a6a262..0f47d23c7767 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 30798ef5e253..9f469c28034a 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 13bc7cf562b9..14442c17b921 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 bdd68484f2be..1619ddea477b 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 265b15a0b010..691519f9d47f 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 ba71d3f0cfc9..4af233b879de 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 1ed688571c59..338e52aac257 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 29b3b3d1a142..005cb1497e6b 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 53a5e1dce0c2..ba0e700cc57c 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 f4cf221bd710..56f595175406 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 18f9efdeabb5..1bca8708cf19 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 e2ea377c940c..7df876ca2c20 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 46363f88ebde..4912d52ca90b 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 1c53914c647e..5f7dd1763500 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 ef3dde76613a..85257c765386 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 9829a89401e8..811605fb652a 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 813978f250e6..1b4a140500f4 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 980f32ad097c..b2d326b69099 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 d761a6c7fdf2..f57b1c8d011c 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 e66bf832692f..91c43a04f344 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 0780acd46686..5e3f1960d170 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 92572cf70624..40b95b6f1a38 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 3f065209498e..232b68379b00 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 b0f355aef2d2..37878bec9acd 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 ac6c7dbd98bb..df14cecc0b12 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 aecd971ff132..730ad7a8310c 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 28e8f7d60bd4..0b73333210ec 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 e038d12e4a58..41797f987702 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 ecf493714839..612ddd9f20c2 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 ad4d6cb63af5..865241f73f8b 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 ab0653ccab45..53539fdea11d 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 4c10ba08c2c2..68aa171cbea0 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 b9ee59a9d963..00da75d225ea 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 e1bfda68c027..1a8892ff6daf 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 73c3473531fe..fbf60a248271 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 b72f2d8a9b5f..99c7517f6fd6 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 89bf7a4923bf..691b5e2b6722 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 17b759c1b528..242a44cfe90c 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 153c62c2d19a..cfaadd17ec96 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 f772581b4e6a..fc3a62adf754 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 4ffc857fa314..8089b460ad11 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 b050f0989cc7..e0f54db78858 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 ef3bdd2ac176..5a393c9a1109 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 85092d567115..27d1cd7ea583 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 29db5431272a..4d3b673dba22 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 3d44cac9d8f6..7d0ff309d8ea 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 5c0246d8b7c9..eedc2df14133 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 76e43c874b47..ab8045974248 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 6cff4a145911..8892c0741bb7 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 101a83a17efc..5cf4bebbfdca 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 5cba736c9321..262fe43199cb 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 61e0f87b135f..9500e1cdfaec 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 021dd48cc419..0db95b3499ef 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 2e1f7302e7e8..5a953950b566 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 523b04e05b30..eec95f9f1291 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 8def84e68865..264089d79f50 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 e9170fa6fe19..670a38cc8e3f 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 5be20237c918..ca682991727d 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 e48e2905fc53..2c1753d0fa33 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 5f0df4672acf..764996d2207c 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 23ab9d3e52f2..9d1e8692d0c5 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 cf050bd8b475..b435b846287d 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 4d6e5c501acb..ee3015b77f3f 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 ff41d4f44283..3289b33190f3 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 8d259c0fbb8f..356380aa675d 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 4549b3b78fae..026759771313 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 ac0733d723dd..a0b77853c631 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 ebe14bc029c7..499183db3118 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 6f0df0e28cf2..00dd924a9d1b 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 a6c299b563f9..1e008f48f394 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 48d45b9980bc..babf8fa97d36 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 781efe032009..bd6add9c8ef4 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 0d187a2623dc..0e1f8f150d4c 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 c736a47659c4..eaa583f1d348 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 c730b3a1f5b2..4a65166ec59e 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 5857c7794368..fbd46806bda6 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 04e703d18518..ba1d05cf38e9 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 118c634c4ec5..5be1efe9d5fa 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 9ad66fd4373d..532deeab29b1 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 ade56b483265..1ff20c2f0d64 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 799870f2b5cf..eabe96018c37 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 1294d472fb78..76d3972765df 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 02e2e63752d7..e7e36283f3d5 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 c4080b039865..dcb58961370d 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 1c8cd50af068..330e4edb2c9b 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 cd9b77e40cd6..c5cbe4a25d4c 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 9751c22e3205..5c14a7ef226e 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 2603a6f78d08..d2564883703e 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 61e300701b5f..8c1556177191 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 94ee136272d6..ede181b9c719 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 d5d724fc6e0e..5f08c1b07cd9 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 7935f3c71abb..875530f3c83c 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 a6e998eae48d..6e1c7f713bb0 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 c6b2c1db511e..dfd898343a35 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 ce58008f61ad..cc40bec6bf03 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 d42239e8ad56..78d6f32a0dec 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 1ca24dabe467..1482aae505c6 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 8479c4443147..8790c09f728c 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 61836fbe04a5..1246538b1404 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 1a513d726faa..13d9463c8cf5 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 35c8c68b5f27..4cf9b4362d64 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 773f7bd373e3..3b641a318690 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 aa3660be647e..bca144a58274 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 fec4b94ce743..8329792b2ea0 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 7b72bbd034ad..11e063ae0d7d 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 13b1c97be11f..f5c1fac18cd5 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 442ef5c6c789..87cf6cc33964 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 852e6052378e..742554c8795e 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 60ac2187cfba..1bf2d3538f30 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 513f99e668df..41381d1ec059 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 6fd5307a1e99..eeeb60cb326e 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 1170f6e03311..fa25287fb878 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 a87d63ecccff..073b099ee0b0 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 9f93141de237..8533a49d914f 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 3afbc83a01ed..46dbd6f137c2 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 425b6e0eeb28..4af63e06a905 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 d5f3d7b92b7e..0697e5b0d556 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 dbb1816fbefb..5efac0d3534e 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 a402fec64bb0..8bcdc9022fa4 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 d48854affa26..da1b1f25b384 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 04b8221eb1db..eb0f45ad684f 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 ab20dd64a85e..2c1026528b2f 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 a485539bf22f..5c6ed75a9650 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 15fe32ab279e..11ef3cc1eddb 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 a3d35b421763..9e7ef70faf7e 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 6e5a22981fd1..207a24a95d0e 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 824080deddd8..d04476839893 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 d64d119a6b80..abf533357173 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 1159e4828353..acc446762eca 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 ec7e54cefd12..1bb2f46b1bbe 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 8eeae71c89c2..b23f1474e1a0 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 cc23d031f5e2..4add70c85044 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 bf27cd34d63f..a51c64bd24f2 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(); } };