From 88eb0bbad0bb375219471624a4bfbce28bfaa9a1 Mon Sep 17 00:00:00 2001 From: tapplencourt Date: Wed, 1 Apr 2026 18:16:20 +0000 Subject: [PATCH 1/6] Constify prefetch and mem advice --- test_plans/queue-shortcut-functions.asciidoc | 12 ++++++------ tests/queue/queue_shortcuts_usm.h | 10 ++++++---- tests/usm/usm_api.h | 4 ++-- 3 files changed, 14 insertions(+), 12 deletions(-) diff --git a/test_plans/queue-shortcut-functions.asciidoc b/test_plans/queue-shortcut-functions.asciidoc index 744b320ca..b79f88281 100644 --- a/test_plans/queue-shortcut-functions.asciidoc +++ b/test_plans/queue-shortcut-functions.asciidoc @@ -80,16 +80,16 @@ The below functions are called to set some USM zero-initialized buffer `ptr` to ==== Prefetch Each of the below functions is called with some USM buffer. It is checked whether the return type of the functions is `event`. The USM buffers are allocation type `shared`. If the used device lacks this capability (aspect `aspect::usm_shared_allocations`), this test is skipped. -* `event prefetch(void* ptr, size_t numBytes)` -* `event prefetch(void* ptr, size_t numBytes, event depEvent)` -* `event prefetch(void* ptr, size_t numBytes, const std::vector& depEvents)` +* `event prefetch(const void* ptr, size_t numBytes)` +* `event prefetch(const void* ptr, size_t numBytes, event depEvent)` +* `event prefetch(const void* ptr, size_t numBytes, const std::vector& depEvents)` ==== Memory advise Each of the below functions is called with some USM buffer. It is checked whether the return type of the functions is `event`. The value of `advice` is `0`. The USM buffers are allocation type `device`. If the used device lacks this capability (aspect `aspect::usm_device_allocations`), this test is skipped. -* `event mem_advise(void* ptr, size_t numBytes, int advice)` -* `event mem_advise(void* ptr, size_t numBytes, int advice, event depEvent)` -* `event mem_advise(void* ptr, size_t numBytes, int advice, const std::vector& depEvents)` +* `event mem_advise(const void* ptr, size_t numBytes, int advice)` +* `event mem_advise(const void* ptr, size_t numBytes, int advice, event depEvent)` +* `event mem_advise(const void* ptr, size_t numBytes, int advice, const std::vector& depEvents)` === Explicit copy All accessors used are one-dimensional. diff --git a/tests/queue/queue_shortcuts_usm.h b/tests/queue/queue_shortcuts_usm.h index 1291f569d..997efc29d 100644 --- a/tests/queue/queue_shortcuts_usm.h +++ b/tests/queue/queue_shortcuts_usm.h @@ -237,7 +237,8 @@ void test_unified_shared_memory(sycl::queue q, unsigned int element_count) { // prefetch if (has_usm_shared_allocations) { - T* ptr = sycl::malloc_shared(element_count, q); + const T* ptr = + static_cast(sycl::malloc_shared(element_count, q)); sycl::event prefetch_no_events = q.prefetch(ptr, element_count * sizeof(T)); sycl::event prefetch_single_event = q.prefetch(ptr, element_count * sizeof(T), prefetch_no_events); @@ -246,7 +247,7 @@ void test_unified_shared_memory(sycl::queue q, unsigned int element_count) { {prefetch_no_events, prefetch_single_event}); prefetch_multiple_events.wait(); prefetch_no_events.wait(); - sycl::free(ptr, q); + sycl::free(const_cast(ptr), q); } else { WARN( "Device does not support USM shared allocations. " @@ -255,7 +256,8 @@ void test_unified_shared_memory(sycl::queue q, unsigned int element_count) { // advise if (has_usm_device_allocations) { - T* ptr = sycl::malloc_device(element_count, q); + const T* ptr = + static_cast(sycl::malloc_device(element_count, q)); constexpr int advice = 0; sycl::event advise_no_events = q.mem_advise(ptr, element_count * sizeof(T), advice); @@ -266,7 +268,7 @@ void test_unified_shared_memory(sycl::queue q, unsigned int element_count) { {advise_no_events, advise_single_event}); advise_multiple_events.wait(); advise_no_events.wait(); - sycl::free(ptr, q); + sycl::free(const_cast(ptr), q); } else { WARN( "Device does not support USM device allocations. " diff --git a/tests/usm/usm_api.h b/tests/usm/usm_api.h index 3093cd039..6dbf7230a 100644 --- a/tests/usm/usm_api.h +++ b/tests/usm/usm_api.h @@ -416,7 +416,7 @@ class prefetch : public detail::noAdditionalDeviceRequirements { } template - auto call(parentT &parent, T *ptr, depEventsT &&... events) const { + auto call(parentT &parent, const T *ptr, depEventsT &&... events) const { return parent.prefetch(ptr, size, std::forward(events)...); } @@ -444,7 +444,7 @@ class mem_advise : public detail::noAdditionalDeviceRequirements { } template - auto call(parentT &parent, T *ptr, depEventsT &&... events) const { + auto call(parentT &parent, const T *ptr, depEventsT &&... events) const { const int advice = 0; // Reset to defaults according to the SYCL 2020 spec return parent.mem_advise(ptr, size, advice, std::forward(events)...); From 26c8e8e701acc45adcd4eb74c7f9cbb60ba14ece Mon Sep 17 00:00:00 2001 From: tapplencourt Date: Wed, 1 Apr 2026 20:19:54 +0000 Subject: [PATCH 2/6] Let try clang-format by hand --- tests/usm/usm_api.h | 4 ++-- 1 file changed, 2 insertions(+), 2 deletions(-) diff --git a/tests/usm/usm_api.h b/tests/usm/usm_api.h index 6dbf7230a..e672b0d95 100644 --- a/tests/usm/usm_api.h +++ b/tests/usm/usm_api.h @@ -416,7 +416,7 @@ class prefetch : public detail::noAdditionalDeviceRequirements { } template - auto call(parentT &parent, const T *ptr, depEventsT &&... events) const { + auto call(parentT& parent, const T* ptr, depEventsT&&... events) const { return parent.prefetch(ptr, size, std::forward(events)...); } @@ -444,7 +444,7 @@ class mem_advise : public detail::noAdditionalDeviceRequirements { } template - auto call(parentT &parent, const T *ptr, depEventsT &&... events) const { + auto call(parentT& parent, const T* ptr, depEventsT&&... events) const { const int advice = 0; // Reset to defaults according to the SYCL 2020 spec return parent.mem_advise(ptr, size, advice, std::forward(events)...); From ea2c0c11e8fc667269aa6f5430dd2d82867cf902 Mon Sep 17 00:00:00 2001 From: tapplencourt Date: Wed, 29 Apr 2026 14:48:03 +0000 Subject: [PATCH 3/6] Split and conditional --- tests/queue/queue_shortcuts_usm.h | 46 ++++++++++++++++++------------- 1 file changed, 27 insertions(+), 19 deletions(-) diff --git a/tests/queue/queue_shortcuts_usm.h b/tests/queue/queue_shortcuts_usm.h index 997efc29d..48c63af71 100644 --- a/tests/queue/queue_shortcuts_usm.h +++ b/tests/queue/queue_shortcuts_usm.h @@ -235,25 +235,6 @@ void test_unified_shared_memory(sycl::queue q, unsigned int element_count) { "Skipping the test case."); } - // prefetch - if (has_usm_shared_allocations) { - const T* ptr = - static_cast(sycl::malloc_shared(element_count, q)); - sycl::event prefetch_no_events = q.prefetch(ptr, element_count * sizeof(T)); - sycl::event prefetch_single_event = - q.prefetch(ptr, element_count * sizeof(T), prefetch_no_events); - sycl::event prefetch_multiple_events = - q.prefetch(ptr, element_count * sizeof(T), - {prefetch_no_events, prefetch_single_event}); - prefetch_multiple_events.wait(); - prefetch_no_events.wait(); - sycl::free(const_cast(ptr), q); - } else { - WARN( - "Device does not support USM shared allocations. " - "Skipping the test case."); - } - // advise if (has_usm_device_allocations) { const T* ptr = @@ -276,6 +257,30 @@ void test_unified_shared_memory(sycl::queue q, unsigned int element_count) { } } +template +void test_prefetch(sycl::queue q, unsigned int element_count) { + const bool has_usm_shared_allocations = + q.get_device().has(sycl::aspect::usm_shared_allocations); + + if (has_usm_shared_allocations) { + const T* ptr = + static_cast(sycl::malloc_shared(element_count, q)); + sycl::event prefetch_no_events = q.prefetch(ptr, element_count * sizeof(T)); + sycl::event prefetch_single_event = + q.prefetch(ptr, element_count * sizeof(T), prefetch_no_events); + sycl::event prefetch_multiple_events = + q.prefetch(ptr, element_count * sizeof(T), + {prefetch_no_events, prefetch_single_event}); + prefetch_multiple_events.wait(); + prefetch_no_events.wait(); + sycl::free(const_cast(ptr), q); + } else { + WARN( + "Device does not support USM shared allocations. " + "Skipping the test case."); + } +} + template class check_queue_shortcuts_usm_for_type { static constexpr unsigned int element_count = 10; @@ -285,6 +290,9 @@ class check_queue_shortcuts_usm_for_type { INFO("for type \"" << type_name << "\": "); test_unified_shared_memory(queue, element_count); +#if !SYCL_CTS_COMPILING_WITH_SIMSYCL + test_prefetch(queue, element_count); +#endif } }; From 243b817c98a84d0ff3cfb58aef87ff7ba9877d52 Mon Sep 17 00:00:00 2001 From: tapplencourt Date: Wed, 29 Apr 2026 15:06:53 +0000 Subject: [PATCH 4/6] Memadvice too... --- tests/queue/queue_shortcuts_usm.h | 50 +++++++++++++++++-------------- 1 file changed, 27 insertions(+), 23 deletions(-) diff --git a/tests/queue/queue_shortcuts_usm.h b/tests/queue/queue_shortcuts_usm.h index 48c63af71..0507db063 100644 --- a/tests/queue/queue_shortcuts_usm.h +++ b/tests/queue/queue_shortcuts_usm.h @@ -162,8 +162,6 @@ template void test_unified_shared_memory(sycl::queue q, unsigned int element_count) { const bool has_usm_device_allocations = q.get_device().has(sycl::aspect::usm_device_allocations); - const bool has_usm_shared_allocations = - q.get_device().has(sycl::aspect::usm_shared_allocations); runner_memcpy runner(q, element_count); @@ -234,27 +232,6 @@ void test_unified_shared_memory(sycl::queue q, unsigned int element_count) { "Device does not support USM device allocations. " "Skipping the test case."); } - - // advise - if (has_usm_device_allocations) { - const T* ptr = - static_cast(sycl::malloc_device(element_count, q)); - constexpr int advice = 0; - sycl::event advise_no_events = - q.mem_advise(ptr, element_count * sizeof(T), advice); - sycl::event advise_single_event = - q.mem_advise(ptr, element_count * sizeof(T), advice, advise_no_events); - sycl::event advise_multiple_events = - q.mem_advise(ptr, element_count * sizeof(T), advice, - {advise_no_events, advise_single_event}); - advise_multiple_events.wait(); - advise_no_events.wait(); - sycl::free(const_cast(ptr), q); - } else { - WARN( - "Device does not support USM device allocations. " - "Skipping the test case."); - } } template @@ -281,6 +258,32 @@ void test_prefetch(sycl::queue q, unsigned int element_count) { } } +template +void test_mem_advise(sycl::queue q, unsigned int element_count) { + const bool has_usm_device_allocations = + q.get_device().has(sycl::aspect::usm_device_allocations); + + if (has_usm_device_allocations) { + const T* ptr = + static_cast(sycl::malloc_device(element_count, q)); + constexpr int advice = 0; + sycl::event advise_no_events = + q.mem_advise(ptr, element_count * sizeof(T), advice); + sycl::event advise_single_event = + q.mem_advise(ptr, element_count * sizeof(T), advice, advise_no_events); + sycl::event advise_multiple_events = + q.mem_advise(ptr, element_count * sizeof(T), advice, + {advise_no_events, advise_single_event}); + advise_multiple_events.wait(); + advise_no_events.wait(); + sycl::free(const_cast(ptr), q); + } else { + WARN( + "Device does not support USM device allocations. " + "Skipping the test case."); + } +} + template class check_queue_shortcuts_usm_for_type { static constexpr unsigned int element_count = 10; @@ -292,6 +295,7 @@ class check_queue_shortcuts_usm_for_type { test_unified_shared_memory(queue, element_count); #if !SYCL_CTS_COMPILING_WITH_SIMSYCL test_prefetch(queue, element_count); + test_mem_advise(queue, element_count); #endif } }; From 0de39ff9ae582434cb3377433c69209064ada2c5 Mon Sep 17 00:00:00 2001 From: tapplencourt Date: Wed, 29 Apr 2026 15:27:28 +0000 Subject: [PATCH 5/6] Move to catch --- .../usm_api_mem_advise_handler_no_events.cpp | 34 +++++-------------- ...m_api_mem_advise_queue_multiple_events.cpp | 34 +++++-------------- .../usm_api_mem_advise_queue_no_events.cpp | 34 +++++-------------- .../usm_api_mem_advise_queue_single_event.cpp | 34 +++++-------------- 4 files changed, 32 insertions(+), 104 deletions(-) diff --git a/tests/usm/usm_api_mem_advise_handler_no_events.cpp b/tests/usm/usm_api_mem_advise_handler_no_events.cpp index 1284982c7..61bd75cd4 100644 --- a/tests/usm/usm_api_mem_advise_handler_no_events.cpp +++ b/tests/usm/usm_api_mem_advise_handler_no_events.cpp @@ -8,34 +8,16 @@ *******************************************************************************/ #include "../common/common.h" +#include "../common/disabled_for_test_case.h" #include "usm_api.h" -#define TEST_NAME usm_api_mem_advise_handler_no_events - -namespace TEST_NAMESPACE { +namespace usm_api_mem_advise_handler_no_events { using namespace usm_api; -template -using run_tests = run_all_tests; - -/** Test instance - */ -class TEST_NAME : public sycl_cts::util::test_base { - public: - /** return information about this test - */ - void get_info(test_base::info &out) const override { - set_test_info(out, TOSTRING(TEST_NAME), TEST_FILE); - } - - /** execute the test - */ - void run(sycl_cts::util::logger &log) override { - run_tests{}(log); - } -}; - -// construction of this proxy will register the above test -sycl_cts::util::test_proxy proxy; +DISABLED_FOR_TEST_CASE(SimSYCL) +("usm_api_mem_advise_handler_no_events", "[usm]")({ + sycl_cts::util::logger log; + run_all_tests{}(log); +}); -} // namespace TEST_NAMESPACE +} // namespace usm_api_mem_advise_handler_no_events diff --git a/tests/usm/usm_api_mem_advise_queue_multiple_events.cpp b/tests/usm/usm_api_mem_advise_queue_multiple_events.cpp index e5df3d6cf..ef441a2a1 100644 --- a/tests/usm/usm_api_mem_advise_queue_multiple_events.cpp +++ b/tests/usm/usm_api_mem_advise_queue_multiple_events.cpp @@ -8,34 +8,16 @@ *******************************************************************************/ #include "../common/common.h" +#include "../common/disabled_for_test_case.h" #include "usm_api.h" -#define TEST_NAME usm_api_mem_advise_queue_multiple_events - -namespace TEST_NAMESPACE { +namespace usm_api_mem_advise_queue_multiple_events { using namespace usm_api; -template -using run_tests = run_all_tests; - -/** Test instance - */ -class TEST_NAME : public sycl_cts::util::test_base { - public: - /** return information about this test - */ - void get_info(test_base::info &out) const override { - set_test_info(out, TOSTRING(TEST_NAME), TEST_FILE); - } - - /** execute the test - */ - void run(sycl_cts::util::logger &log) override { - run_tests{}(log); - } -}; - -// construction of this proxy will register the above test -sycl_cts::util::test_proxy proxy; +DISABLED_FOR_TEST_CASE(SimSYCL) +("usm_api_mem_advise_queue_multiple_events", "[usm]")({ + sycl_cts::util::logger log; + run_all_tests{}(log); +}); -} // namespace TEST_NAMESPACE +} // namespace usm_api_mem_advise_queue_multiple_events diff --git a/tests/usm/usm_api_mem_advise_queue_no_events.cpp b/tests/usm/usm_api_mem_advise_queue_no_events.cpp index 720139d52..9e2aa287c 100644 --- a/tests/usm/usm_api_mem_advise_queue_no_events.cpp +++ b/tests/usm/usm_api_mem_advise_queue_no_events.cpp @@ -7,34 +7,16 @@ *******************************************************************************/ #include "../common/common.h" +#include "../common/disabled_for_test_case.h" #include "usm_api.h" -#define TEST_NAME usm_api_mem_advise_queue_no_events - -namespace TEST_NAMESPACE { +namespace usm_api_mem_advise_queue_no_events { using namespace usm_api; -template -using run_tests = run_all_tests; - -/** Test instance - */ -class TEST_NAME : public sycl_cts::util::test_base { - public: - /** return information about this test - */ - void get_info(test_base::info &out) const override { - set_test_info(out, TOSTRING(TEST_NAME), TEST_FILE); - } - - /** execute the test - */ - void run(sycl_cts::util::logger &log) override { - run_tests{}(log); - } -}; - -// construction of this proxy will register the above test -sycl_cts::util::test_proxy proxy; +DISABLED_FOR_TEST_CASE(SimSYCL) +("usm_api_mem_advise_queue_no_events", "[usm]")({ + sycl_cts::util::logger log; + run_all_tests{}(log); +}); -} // namespace TEST_NAMESPACE +} // namespace usm_api_mem_advise_queue_no_events diff --git a/tests/usm/usm_api_mem_advise_queue_single_event.cpp b/tests/usm/usm_api_mem_advise_queue_single_event.cpp index b45ac0d32..3237ab96d 100644 --- a/tests/usm/usm_api_mem_advise_queue_single_event.cpp +++ b/tests/usm/usm_api_mem_advise_queue_single_event.cpp @@ -7,34 +7,16 @@ *******************************************************************************/ #include "../common/common.h" +#include "../common/disabled_for_test_case.h" #include "usm_api.h" -#define TEST_NAME usm_api_mem_advise_queue_single_event - -namespace TEST_NAMESPACE { +namespace usm_api_mem_advise_queue_single_event { using namespace usm_api; -template -using run_tests = run_all_tests; - -/** Test instance - */ -class TEST_NAME : public sycl_cts::util::test_base { - public: - /** return information about this test - */ - void get_info(test_base::info &out) const override { - set_test_info(out, TOSTRING(TEST_NAME), TEST_FILE); - } - - /** execute the test - */ - void run(sycl_cts::util::logger &log) override { - run_tests{}(log); - } -}; - -// construction of this proxy will register the above test -sycl_cts::util::test_proxy proxy; +DISABLED_FOR_TEST_CASE(SimSYCL) +("usm_api_mem_advise_queue_single_event", "[usm]")({ + sycl_cts::util::logger log; + run_all_tests{}(log); +}); -} // namespace TEST_NAMESPACE +} // namespace usm_api_mem_advise_queue_single_event From 4472553fb70a3fe9d0105131ed88b42eb2c7ebd4 Mon Sep 17 00:00:00 2001 From: tapplencourt Date: Wed, 29 Apr 2026 15:33:49 +0000 Subject: [PATCH 6/6] Forgot one as usual... --- .../usm_api_prefetch_handler_no_events.cpp | 34 +++++-------------- ...usm_api_prefetch_queue_multiple_events.cpp | 34 +++++-------------- .../usm/usm_api_prefetch_queue_no_events.cpp | 34 +++++-------------- .../usm_api_prefetch_queue_single_event.cpp | 34 +++++-------------- 4 files changed, 32 insertions(+), 104 deletions(-) diff --git a/tests/usm/usm_api_prefetch_handler_no_events.cpp b/tests/usm/usm_api_prefetch_handler_no_events.cpp index 9472b275a..6d34ed7cb 100644 --- a/tests/usm/usm_api_prefetch_handler_no_events.cpp +++ b/tests/usm/usm_api_prefetch_handler_no_events.cpp @@ -8,34 +8,16 @@ *******************************************************************************/ #include "../common/common.h" +#include "../common/disabled_for_test_case.h" #include "usm_api.h" -#define TEST_NAME usm_api_prefetch_handler_no_events - -namespace TEST_NAMESPACE { +namespace usm_api_prefetch_handler_no_events { using namespace usm_api; -template -using run_tests = run_all_tests; - -/** Test instance - */ -class TEST_NAME : public sycl_cts::util::test_base { - public: - /** return information about this test - */ - void get_info(test_base::info &out) const override { - set_test_info(out, TOSTRING(TEST_NAME), TEST_FILE); - } - - /** execute the test - */ - void run(sycl_cts::util::logger &log) override { - run_tests{}(log); - } -}; - -// construction of this proxy will register the above test -sycl_cts::util::test_proxy proxy; +DISABLED_FOR_TEST_CASE(SimSYCL) +("usm_api_prefetch_handler_no_events", "[usm]")({ + sycl_cts::util::logger log; + run_all_tests{}(log); +}); -} // namespace TEST_NAMESPACE +} // namespace usm_api_prefetch_handler_no_events diff --git a/tests/usm/usm_api_prefetch_queue_multiple_events.cpp b/tests/usm/usm_api_prefetch_queue_multiple_events.cpp index 5233b2bb7..6ab24fc0a 100644 --- a/tests/usm/usm_api_prefetch_queue_multiple_events.cpp +++ b/tests/usm/usm_api_prefetch_queue_multiple_events.cpp @@ -8,34 +8,16 @@ *******************************************************************************/ #include "../common/common.h" +#include "../common/disabled_for_test_case.h" #include "usm_api.h" -#define TEST_NAME usm_api_prefetch_queue_multiple_events - -namespace TEST_NAMESPACE { +namespace usm_api_prefetch_queue_multiple_events { using namespace usm_api; -template -using run_tests = run_all_tests; - -/** Test instance - */ -class TEST_NAME : public sycl_cts::util::test_base { - public: - /** return information about this test - */ - void get_info(test_base::info &out) const override { - set_test_info(out, TOSTRING(TEST_NAME), TEST_FILE); - } - - /** execute the test - */ - void run(sycl_cts::util::logger &log) override { - run_tests{}(log); - } -}; - -// construction of this proxy will register the above test -sycl_cts::util::test_proxy proxy; +DISABLED_FOR_TEST_CASE(SimSYCL) +("usm_api_prefetch_queue_multiple_events", "[usm]")({ + sycl_cts::util::logger log; + run_all_tests{}(log); +}); -} // namespace TEST_NAMESPACE +} // namespace usm_api_prefetch_queue_multiple_events diff --git a/tests/usm/usm_api_prefetch_queue_no_events.cpp b/tests/usm/usm_api_prefetch_queue_no_events.cpp index fa02a5f06..e70cfdae7 100644 --- a/tests/usm/usm_api_prefetch_queue_no_events.cpp +++ b/tests/usm/usm_api_prefetch_queue_no_events.cpp @@ -7,34 +7,16 @@ *******************************************************************************/ #include "../common/common.h" +#include "../common/disabled_for_test_case.h" #include "usm_api.h" -#define TEST_NAME usm_api_prefetch_queue_no_events - -namespace TEST_NAMESPACE { +namespace usm_api_prefetch_queue_no_events { using namespace usm_api; -template -using run_tests = run_all_tests; - -/** Test instance - */ -class TEST_NAME : public sycl_cts::util::test_base { - public: - /** return information about this test - */ - void get_info(test_base::info &out) const override { - set_test_info(out, TOSTRING(TEST_NAME), TEST_FILE); - } - - /** execute the test - */ - void run(sycl_cts::util::logger &log) override { - run_tests{}(log); - } -}; - -// construction of this proxy will register the above test -sycl_cts::util::test_proxy proxy; +DISABLED_FOR_TEST_CASE(SimSYCL) +("usm_api_prefetch_queue_no_events", "[usm]")({ + sycl_cts::util::logger log; + run_all_tests{}(log); +}); -} // namespace TEST_NAMESPACE +} // namespace usm_api_prefetch_queue_no_events diff --git a/tests/usm/usm_api_prefetch_queue_single_event.cpp b/tests/usm/usm_api_prefetch_queue_single_event.cpp index b5b2da55e..3d6657f88 100644 --- a/tests/usm/usm_api_prefetch_queue_single_event.cpp +++ b/tests/usm/usm_api_prefetch_queue_single_event.cpp @@ -7,34 +7,16 @@ *******************************************************************************/ #include "../common/common.h" +#include "../common/disabled_for_test_case.h" #include "usm_api.h" -#define TEST_NAME usm_api_prefetch_queue_single_event - -namespace TEST_NAMESPACE { +namespace usm_api_prefetch_queue_single_event { using namespace usm_api; -template -using run_tests = run_all_tests; - -/** Test instance - */ -class TEST_NAME : public sycl_cts::util::test_base { - public: - /** return information about this test - */ - void get_info(test_base::info &out) const override { - set_test_info(out, TOSTRING(TEST_NAME), TEST_FILE); - } - - /** execute the test - */ - void run(sycl_cts::util::logger &log) override { - run_tests{}(log); - } -}; - -// construction of this proxy will register the above test -sycl_cts::util::test_proxy proxy; +DISABLED_FOR_TEST_CASE(SimSYCL) +("usm_api_prefetch_queue_single_event", "[usm]")({ + sycl_cts::util::logger log; + run_all_tests{}(log); +}); -} // namespace TEST_NAMESPACE +} // namespace usm_api_prefetch_queue_single_event