From e38f767cf5cb22b1c35354708148270c273d9a4e Mon Sep 17 00:00:00 2001 From: "Dubinov, Igor" Date: Thu, 12 Jun 2025 16:50:39 +0200 Subject: [PATCH 01/10] Fix absence of Init --- sycl/test-e2e/Adapters/level_zero/interop-thread.cpp | 8 +++++++- sycl/test-e2e/Adapters/level_zero/uuid.cpp | 9 +++++++++ 2 files changed, 16 insertions(+), 1 deletion(-) diff --git a/sycl/test-e2e/Adapters/level_zero/interop-thread.cpp b/sycl/test-e2e/Adapters/level_zero/interop-thread.cpp index cd9eb04b21ae4..ddba73ef2377e 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-thread.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-thread.cpp @@ -61,7 +61,13 @@ ze_event_pool_handle_t event_pool = {}; std::vector old_ops; void init() { - zeInit(0); + // Initialize Level Zero driver is required if this test is linked + // statically with Level Zero loader, the driver will not be init otherwise. + ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); + if (result != ZE_RESULT_SUCCESS) { + std::cout << "zeInit failed\n"; + return 1; + } uint32_t driverCount = 0; assert(zeDriverGet(&driverCount, nullptr) == 0); diff --git a/sycl/test-e2e/Adapters/level_zero/uuid.cpp b/sycl/test-e2e/Adapters/level_zero/uuid.cpp index 05e97d9447c46..379467a7e8aee 100644 --- a/sycl/test-e2e/Adapters/level_zero/uuid.cpp +++ b/sycl/test-e2e/Adapters/level_zero/uuid.cpp @@ -25,6 +25,15 @@ int main() { auto zedev = sycl::get_native(dev); ze_device_properties_t device_properties{}; device_properties.stype = ZE_STRUCTURE_TYPE_DEVICE_PROPERTIES; + + // Initialize Level Zero driver is required if this test is linked + // statically with Level Zero loader, the driver will not be init otherwise. + ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); + if (result != ZE_RESULT_SUCCESS) { + std::cout << "zeInit failed\n"; + return 1; + } + zeDeviceGetProperties(zedev, &device_properties); std::stringstream uuid_l0; for (int i = 0; i < ZE_MAX_DEVICE_UUID_SIZE; ++i) From 4fd6aaaf57caa188bb79b540518ab32581a8fa12 Mon Sep 17 00:00:00 2001 From: "Dubinov, Igor" Date: Tue, 17 Jun 2025 11:17:31 +0200 Subject: [PATCH 02/10] remove return value --- sycl/test-e2e/Adapters/level_zero/interop-thread.cpp | 5 +---- 1 file changed, 1 insertion(+), 4 deletions(-) diff --git a/sycl/test-e2e/Adapters/level_zero/interop-thread.cpp b/sycl/test-e2e/Adapters/level_zero/interop-thread.cpp index ddba73ef2377e..fd63f70129c31 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-thread.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-thread.cpp @@ -64,10 +64,7 @@ void init() { // Initialize Level Zero driver is required if this test is linked // statically with Level Zero loader, the driver will not be init otherwise. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); - if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; - return 1; - } + assert(result == ZE_RESULT_SUCCESS); uint32_t driverCount = 0; assert(zeDriverGet(&driverCount, nullptr) == 0); From 5bbe40d74c5d58af6ae7585cd777879ba4eace63 Mon Sep 17 00:00:00 2001 From: "Dubinov, Igor" Date: Tue, 17 Jun 2025 11:19:57 +0200 Subject: [PATCH 03/10] fix bitmask --- sycl/test-e2e/Adapters/level_zero/interop-thread.cpp | 2 +- 1 file changed, 1 insertion(+), 1 deletion(-) diff --git a/sycl/test-e2e/Adapters/level_zero/interop-thread.cpp b/sycl/test-e2e/Adapters/level_zero/interop-thread.cpp index fd63f70129c31..ee662114314fc 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-thread.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-thread.cpp @@ -63,7 +63,7 @@ std::vector old_ops; void init() { // Initialize Level Zero driver is required if this test is linked // statically with Level Zero loader, the driver will not be init otherwise. - ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); + ze_result_t result = zeInit(0); assert(result == ZE_RESULT_SUCCESS); uint32_t driverCount = 0; From 79d0b6a1ffdec446938a335641a290bb2d8bfc50 Mon Sep 17 00:00:00 2001 From: "Dubinov, Igor" Date: Tue, 17 Jun 2025 15:23:48 +0200 Subject: [PATCH 04/10] Update more tests with same problem --- .../AtomicRef/device_has_aspect_atomic64_level_zero.cpp | 8 ++++++++ sycl/test-e2e/Basic/buffer/buffer_create.cpp | 8 ++++++++ sycl/test-e2e/Basic/interop/make_kernel_subdevice_l0.cpp | 8 ++++++++ .../DeviceImageBackendContent/L0_interop_test.cpp | 8 ++++++++ sycl/test-e2e/Regression/cache_test.cpp | 8 ++++++++ 5 files changed, 40 insertions(+) diff --git a/sycl/test-e2e/AtomicRef/device_has_aspect_atomic64_level_zero.cpp b/sycl/test-e2e/AtomicRef/device_has_aspect_atomic64_level_zero.cpp index 1b62406094128..2b8187ad9d3c5 100644 --- a/sycl/test-e2e/AtomicRef/device_has_aspect_atomic64_level_zero.cpp +++ b/sycl/test-e2e/AtomicRef/device_has_aspect_atomic64_level_zero.cpp @@ -9,6 +9,14 @@ using namespace sycl; int main() { + // Initialize Level Zero driver is required if this test is linked + // statically with Level Zero loader, the driver will not be init otherwise. + ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); + if (result != ZE_RESULT_SUCCESS) { + std::cout << "zeInit failed\n"; + return 1; + } + queue Queue; device Dev = Queue.get_device(); bool Result; diff --git a/sycl/test-e2e/Basic/buffer/buffer_create.cpp b/sycl/test-e2e/Basic/buffer/buffer_create.cpp index 286241eeb0627..bf7faed14ffe7 100644 --- a/sycl/test-e2e/Basic/buffer/buffer_create.cpp +++ b/sycl/test-e2e/Basic/buffer/buffer_create.cpp @@ -11,6 +11,14 @@ using namespace sycl; int main() { + // Initialize Level Zero driver is required if this test is linked + // statically with Level Zero loader, the driver will not be init otherwise. + ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); + if (result != ZE_RESULT_SUCCESS) { + std::cout << "zeInit failed\n"; + return 1; + } + constexpr int Size = 100; queue Queue; auto D = Queue.get_device(); diff --git a/sycl/test-e2e/Basic/interop/make_kernel_subdevice_l0.cpp b/sycl/test-e2e/Basic/interop/make_kernel_subdevice_l0.cpp index 20a56f894dbcf..e22c7f897c542 100644 --- a/sycl/test-e2e/Basic/interop/make_kernel_subdevice_l0.cpp +++ b/sycl/test-e2e/Basic/interop/make_kernel_subdevice_l0.cpp @@ -93,6 +93,14 @@ ze_kernel_handle_t create_kernel(ze_module_handle_t module, } int main() { + // Initialize Level Zero driver is required if this test is linked + // statically with Level Zero loader, the driver will not be init otherwise. + ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); + if (result != ZE_RESULT_SUCCESS) { + std::cout << "zeInit failed\n"; + return 1; + } + device D{gpu_selector_v}; try { diff --git a/sycl/test-e2e/DeviceImageBackendContent/L0_interop_test.cpp b/sycl/test-e2e/DeviceImageBackendContent/L0_interop_test.cpp index 20dc8ee79e0f4..5705dda312dc7 100644 --- a/sycl/test-e2e/DeviceImageBackendContent/L0_interop_test.cpp +++ b/sycl/test-e2e/DeviceImageBackendContent/L0_interop_test.cpp @@ -20,6 +20,14 @@ extern "C" SYCL_EXT_ONEAPI_FUNCTION_PROPERTY( } int main() { + // Initialize Level Zero driver is required if this test is linked + // statically with Level Zero loader, the driver will not be init otherwise. + ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); + if (result != ZE_RESULT_SUCCESS) { + std::cout << "zeInit failed\n"; + return 1; + } + sycl::queue q; sycl::context ctxt = q.get_context(); sycl::device d = ctxt.get_devices()[0]; diff --git a/sycl/test-e2e/Regression/cache_test.cpp b/sycl/test-e2e/Regression/cache_test.cpp index 52cfa069f6129..c0093a3457d8a 100644 --- a/sycl/test-e2e/Regression/cache_test.cpp +++ b/sycl/test-e2e/Regression/cache_test.cpp @@ -151,6 +151,14 @@ int queryFromNativeHandle(std::vector *platform_list, } int main() { + // Initialize Level Zero driver is required if this test is linked + // statically with Level Zero loader, the driver will not be init otherwise. + ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); + if (result != ZE_RESULT_SUCCESS) { + std::cout << "zeInit failed\n"; + return 1; + } + int failures = 0; // Query for a list of all of the available platforms and devices. From b4eb835b0f02524201b74cdaac79ee04c999acbd Mon Sep 17 00:00:00 2001 From: "Dubinov, Igor" Date: Tue, 17 Jun 2025 16:28:18 +0200 Subject: [PATCH 05/10] update comment --- sycl/test-e2e/Adapters/level_zero/batch_barrier.cpp | 4 ++-- .../Adapters/level_zero/interop-buffer-multi-dim.cpp | 6 +++--- .../Adapters/level_zero/interop-buffer-ownership.cpp | 4 ++-- sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp | 4 ++-- .../test-e2e/Adapters/level_zero/interop-get-native-mem.cpp | 4 ++-- .../Adapters/level_zero/interop-image-get-native-mem.cpp | 4 ++-- .../Adapters/level_zero/interop-image-ownership.cpp | 4 ++-- sycl/test-e2e/Adapters/level_zero/interop-image.cpp | 4 ++-- .../test-e2e/Adapters/level_zero/interop-keep-ownership.cpp | 4 ++-- sycl/test-e2e/Adapters/level_zero/interop-thread.cpp | 4 ++-- sycl/test-e2e/Adapters/level_zero/interop.cpp | 4 ++-- sycl/test-e2e/Adapters/level_zero/uuid.cpp | 4 ++-- .../AtomicRef/device_has_aspect_atomic64_level_zero.cpp | 4 ++-- sycl/test-e2e/Basic/buffer/buffer_create.cpp | 4 ++-- sycl/test-e2e/Basic/interop/get_native_ze.cpp | 4 ++-- sycl/test-e2e/Basic/interop/make_kernel_subdevice_l0.cpp | 4 ++-- sycl/test-e2e/DeviceImageBackendContent/L0_interop_test.cpp | 4 ++-- .../Graph/Inputs/interop-level-zero-get-native-mem.cpp | 4 ++-- .../Graph/Inputs/interop-level-zero-launch-kernel.cpp | 4 ++-- sycl/test-e2e/Graph/NativeCommand/level-zero_usm.cpp | 4 ++-- .../Graph/NativeCommand/level-zero_usm_D2H_copy.cpp | 4 ++-- sycl/test-e2e/Regression/cache_test.cpp | 4 ++-- 22 files changed, 45 insertions(+), 45 deletions(-) diff --git a/sycl/test-e2e/Adapters/level_zero/batch_barrier.cpp b/sycl/test-e2e/Adapters/level_zero/batch_barrier.cpp index 88a51f579dc0b..ee450f897a113 100644 --- a/sycl/test-e2e/Adapters/level_zero/batch_barrier.cpp +++ b/sycl/test-e2e/Adapters/level_zero/batch_barrier.cpp @@ -27,8 +27,8 @@ int main(int argc, char *argv[]) { // CHECK: ---> urEnqueueKernelLaunch // CHECK-NOT: zeCommandQueueExecuteCommandLists - // Initialize Level Zero driver is required if this test is linked - // statically with Level Zero loader, the driver will not be init otherwise. + // Initializing Level Zero driver is required if this test is linked + // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed\n"; diff --git a/sycl/test-e2e/Adapters/level_zero/interop-buffer-multi-dim.cpp b/sycl/test-e2e/Adapters/level_zero/interop-buffer-multi-dim.cpp index 73c8a04d2f88f..853ea084d408e 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-buffer-multi-dim.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-buffer-multi-dim.cpp @@ -25,11 +25,11 @@ int main() { return 0; } - // Initialize Level Zero driver is required if this test is linked - // statically with Level Zero loader, the driver will not be init otherwise. + // Initializing Level Zero driver is required if this test is linked + // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; + std::cout << "zeInit failed" << std::endl; return 1; } diff --git a/sycl/test-e2e/Adapters/level_zero/interop-buffer-ownership.cpp b/sycl/test-e2e/Adapters/level_zero/interop-buffer-ownership.cpp index d94e8e5dab05d..e9a2b0e5174d9 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-buffer-ownership.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-buffer-ownership.cpp @@ -127,8 +127,8 @@ int main() { return 0; } - // Initialize Level Zero driver is required if this test is linked - // statically with Level Zero loader, the driver will not be init otherwise. + // Initializing Level Zero driver is required if this test is linked + // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed\n"; diff --git a/sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp b/sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp index 8f824ed113ca8..12329ce195b66 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp @@ -45,8 +45,8 @@ int main() { auto ZeContext = get_native(Context); auto ZeDevice = get_native(Device); - // Initialize Level Zero driver is required if this test is linked - // statically with Level Zero loader, the driver will not be init otherwise. + // Initializing Level Zero driver is required if this test is linked + // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed\n"; diff --git a/sycl/test-e2e/Adapters/level_zero/interop-get-native-mem.cpp b/sycl/test-e2e/Adapters/level_zero/interop-get-native-mem.cpp index d5c945feed4c4..989800b88d573 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-get-native-mem.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-get-native-mem.cpp @@ -34,8 +34,8 @@ int main() { return 0; } - // Initialize Level Zero driver is required if this test is linked - // statically with Level Zero loader, the driver will not be init otherwise. + // Initializing Level Zero driver is required if this test is linked + // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed\n"; diff --git a/sycl/test-e2e/Adapters/level_zero/interop-image-get-native-mem.cpp b/sycl/test-e2e/Adapters/level_zero/interop-image-get-native-mem.cpp index b6a48138c66d8..3d90091b7b1f0 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-image-get-native-mem.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-image-get-native-mem.cpp @@ -46,8 +46,8 @@ int main() { sycl::device D = sycl::ext::oneapi::filter_selector("level_zero:gpu").select_device(); - // Initialize Level Zero driver is required if this test is linked - // statically with Level Zero loader, the driver will not be init otherwise. + // Initializing Level Zero driver is required if this test is linked + // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed\n"; diff --git a/sycl/test-e2e/Adapters/level_zero/interop-image-ownership.cpp b/sycl/test-e2e/Adapters/level_zero/interop-image-ownership.cpp index 5a81e10f13b41..14f9c9462df6a 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-image-ownership.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-image-ownership.cpp @@ -146,8 +146,8 @@ int main() { #ifdef SYCL_EXT_ONEAPI_BACKEND_LEVEL_ZERO platform Plt{gpu_selector_v}; - // Initialize Level Zero driver is required if this test is linked - // statically with Level Zero loader, the driver will not be init otherwise. + // Initializing Level Zero driver is required if this test is linked + // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed\n"; diff --git a/sycl/test-e2e/Adapters/level_zero/interop-image.cpp b/sycl/test-e2e/Adapters/level_zero/interop-image.cpp index 2e811d155af24..3ec2d79bf457b 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-image.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-image.cpp @@ -38,8 +38,8 @@ int main() { auto Devices = Plt.get_devices(); - // Initialize Level Zero driver is required if this test is linked - // statically with Level Zero loader, the driver will not be init otherwise. + // Initializing Level Zero driver is required if this test is linked + // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed\n"; diff --git a/sycl/test-e2e/Adapters/level_zero/interop-keep-ownership.cpp b/sycl/test-e2e/Adapters/level_zero/interop-keep-ownership.cpp index d3d002ab0ed0d..7fb8e0929ba5f 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-keep-ownership.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-keep-ownership.cpp @@ -18,8 +18,8 @@ int main() { device Device(gpu_selector_v); platform Platform = Device.get_info(); - // Initialize Level Zero driver is required if this test is linked - // statically with Level Zero loader, the driver will not be init otherwise. + // Initializing Level Zero driver is required if this test is linked + // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed\n"; diff --git a/sycl/test-e2e/Adapters/level_zero/interop-thread.cpp b/sycl/test-e2e/Adapters/level_zero/interop-thread.cpp index ee662114314fc..32d40a8876c57 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-thread.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-thread.cpp @@ -61,8 +61,8 @@ ze_event_pool_handle_t event_pool = {}; std::vector old_ops; void init() { - // Initialize Level Zero driver is required if this test is linked - // statically with Level Zero loader, the driver will not be init otherwise. + // Initializing Level Zero driver is required if this test is linked + // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(0); assert(result == ZE_RESULT_SUCCESS); diff --git a/sycl/test-e2e/Adapters/level_zero/interop.cpp b/sycl/test-e2e/Adapters/level_zero/interop.cpp index 204823dd5e80b..d219dc232755c 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop.cpp @@ -16,8 +16,8 @@ using namespace sycl; int main() { #ifdef SYCL_EXT_ONEAPI_BACKEND_LEVEL_ZERO - // Initialize Level Zero driver is required if this test is linked - // statically with Level Zero loader, the driver will not be init otherwise. + // Initializing Level Zero driver is required if this test is linked + // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed\n"; diff --git a/sycl/test-e2e/Adapters/level_zero/uuid.cpp b/sycl/test-e2e/Adapters/level_zero/uuid.cpp index 379467a7e8aee..d7fd15f874a07 100644 --- a/sycl/test-e2e/Adapters/level_zero/uuid.cpp +++ b/sycl/test-e2e/Adapters/level_zero/uuid.cpp @@ -26,8 +26,8 @@ int main() { ze_device_properties_t device_properties{}; device_properties.stype = ZE_STRUCTURE_TYPE_DEVICE_PROPERTIES; - // Initialize Level Zero driver is required if this test is linked - // statically with Level Zero loader, the driver will not be init otherwise. + // Initializing Level Zero driver is required if this test is linked + // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed\n"; diff --git a/sycl/test-e2e/AtomicRef/device_has_aspect_atomic64_level_zero.cpp b/sycl/test-e2e/AtomicRef/device_has_aspect_atomic64_level_zero.cpp index 2b8187ad9d3c5..805af208ce1a4 100644 --- a/sycl/test-e2e/AtomicRef/device_has_aspect_atomic64_level_zero.cpp +++ b/sycl/test-e2e/AtomicRef/device_has_aspect_atomic64_level_zero.cpp @@ -9,8 +9,8 @@ using namespace sycl; int main() { - // Initialize Level Zero driver is required if this test is linked - // statically with Level Zero loader, the driver will not be init otherwise. + // Initializing Level Zero driver is required if this test is linked + // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed\n"; diff --git a/sycl/test-e2e/Basic/buffer/buffer_create.cpp b/sycl/test-e2e/Basic/buffer/buffer_create.cpp index bf7faed14ffe7..5dc2251342b0f 100644 --- a/sycl/test-e2e/Basic/buffer/buffer_create.cpp +++ b/sycl/test-e2e/Basic/buffer/buffer_create.cpp @@ -11,8 +11,8 @@ using namespace sycl; int main() { - // Initialize Level Zero driver is required if this test is linked - // statically with Level Zero loader, the driver will not be init otherwise. + // Initializing Level Zero driver is required if this test is linked + // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed\n"; diff --git a/sycl/test-e2e/Basic/interop/get_native_ze.cpp b/sycl/test-e2e/Basic/interop/get_native_ze.cpp index fed3afc6f29b0..4d9e7a22d0734 100644 --- a/sycl/test-e2e/Basic/interop/get_native_ze.cpp +++ b/sycl/test-e2e/Basic/interop/get_native_ze.cpp @@ -12,8 +12,8 @@ constexpr auto BE = sycl::backend::ext_oneapi_level_zero; class TestKernel; int main() { - // Initialize Level Zero driver is required if this test is linked - // statically with Level Zero loader, the driver will not be init otherwise. + // Initializing Level Zero driver is required if this test is linked + // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed\n"; diff --git a/sycl/test-e2e/Basic/interop/make_kernel_subdevice_l0.cpp b/sycl/test-e2e/Basic/interop/make_kernel_subdevice_l0.cpp index e22c7f897c542..216ffbbbd2969 100644 --- a/sycl/test-e2e/Basic/interop/make_kernel_subdevice_l0.cpp +++ b/sycl/test-e2e/Basic/interop/make_kernel_subdevice_l0.cpp @@ -93,8 +93,8 @@ ze_kernel_handle_t create_kernel(ze_module_handle_t module, } int main() { - // Initialize Level Zero driver is required if this test is linked - // statically with Level Zero loader, the driver will not be init otherwise. + // Initializing Level Zero driver is required if this test is linked + // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed\n"; diff --git a/sycl/test-e2e/DeviceImageBackendContent/L0_interop_test.cpp b/sycl/test-e2e/DeviceImageBackendContent/L0_interop_test.cpp index 5705dda312dc7..f04e9f969d59e 100644 --- a/sycl/test-e2e/DeviceImageBackendContent/L0_interop_test.cpp +++ b/sycl/test-e2e/DeviceImageBackendContent/L0_interop_test.cpp @@ -20,8 +20,8 @@ extern "C" SYCL_EXT_ONEAPI_FUNCTION_PROPERTY( } int main() { - // Initialize Level Zero driver is required if this test is linked - // statically with Level Zero loader, the driver will not be init otherwise. + // Initializing Level Zero driver is required if this test is linked + // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed\n"; diff --git a/sycl/test-e2e/Graph/Inputs/interop-level-zero-get-native-mem.cpp b/sycl/test-e2e/Graph/Inputs/interop-level-zero-get-native-mem.cpp index 641deaf4b0165..d1167a1cb0286 100644 --- a/sycl/test-e2e/Graph/Inputs/interop-level-zero-get-native-mem.cpp +++ b/sycl/test-e2e/Graph/Inputs/interop-level-zero-get-native-mem.cpp @@ -21,8 +21,8 @@ bool is_discrete(const device &Device) { } int main() { - // Initialize Level Zero driver is required if this test is linked - // statically with Level Zero loader, the driver will not be init otherwise. + // Initializing Level Zero driver is required if this test is linked + // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed\n"; diff --git a/sycl/test-e2e/Graph/Inputs/interop-level-zero-launch-kernel.cpp b/sycl/test-e2e/Graph/Inputs/interop-level-zero-launch-kernel.cpp index 94fdff8ef66dc..81f09d81124f1 100644 --- a/sycl/test-e2e/Graph/Inputs/interop-level-zero-launch-kernel.cpp +++ b/sycl/test-e2e/Graph/Inputs/interop-level-zero-launch-kernel.cpp @@ -43,8 +43,8 @@ int main(int, char **argv) { return 0; } - // Initialize Level Zero driver is required if this test is linked - // statically with Level Zero loader, the driver will not be init otherwise. + // Initializing Level Zero driver is required if this test is linked + // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed\n"; diff --git a/sycl/test-e2e/Graph/NativeCommand/level-zero_usm.cpp b/sycl/test-e2e/Graph/NativeCommand/level-zero_usm.cpp index 1bd18d5dd81ca..30133898b01ef 100644 --- a/sycl/test-e2e/Graph/NativeCommand/level-zero_usm.cpp +++ b/sycl/test-e2e/Graph/NativeCommand/level-zero_usm.cpp @@ -17,8 +17,8 @@ namespace exp_ext = sycl::ext::oneapi::experimental; using namespace sycl; int main() { - // Initialize Level Zero driver is required if this test is linked - // statically with Level Zero loader, the driver will not be init otherwise. + // Initializing Level Zero driver is required if this test is linked + // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed\n"; diff --git a/sycl/test-e2e/Graph/NativeCommand/level-zero_usm_D2H_copy.cpp b/sycl/test-e2e/Graph/NativeCommand/level-zero_usm_D2H_copy.cpp index 505faecbb9a76..b0c4e93e3afc2 100644 --- a/sycl/test-e2e/Graph/NativeCommand/level-zero_usm_D2H_copy.cpp +++ b/sycl/test-e2e/Graph/NativeCommand/level-zero_usm_D2H_copy.cpp @@ -24,8 +24,8 @@ namespace exp_ext = sycl::ext::oneapi::experimental; using namespace sycl; int main() { - // Initialize Level Zero driver is required if this test is linked - // statically with Level Zero loader, the driver will not be init otherwise. + // Initializing Level Zero driver is required if this test is linked + // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed\n"; diff --git a/sycl/test-e2e/Regression/cache_test.cpp b/sycl/test-e2e/Regression/cache_test.cpp index c0093a3457d8a..874635f5fd987 100644 --- a/sycl/test-e2e/Regression/cache_test.cpp +++ b/sycl/test-e2e/Regression/cache_test.cpp @@ -151,8 +151,8 @@ int queryFromNativeHandle(std::vector *platform_list, } int main() { - // Initialize Level Zero driver is required if this test is linked - // statically with Level Zero loader, the driver will not be init otherwise. + // Initializing Level Zero driver is required if this test is linked + // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed\n"; From ac8bb9c83a8c68f87ab5d1da23cf0041f8a78905 Mon Sep 17 00:00:00 2001 From: "Dubinov, Igor" Date: Tue, 24 Jun 2025 11:41:29 +0200 Subject: [PATCH 06/10] endl instead \n --- sycl/test-e2e/Adapters/level_zero/batch_barrier.cpp | 2 +- sycl/test-e2e/Adapters/level_zero/interop-buffer-ownership.cpp | 2 +- sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp | 2 +- sycl/test-e2e/Adapters/level_zero/interop-direct.cpp | 2 +- sycl/test-e2e/Adapters/level_zero/interop-get-native-mem.cpp | 2 +- .../Adapters/level_zero/interop-image-get-native-mem.cpp | 2 +- sycl/test-e2e/Adapters/level_zero/interop-image-ownership.cpp | 2 +- sycl/test-e2e/Adapters/level_zero/interop-image.cpp | 2 +- sycl/test-e2e/Adapters/level_zero/interop-keep-ownership.cpp | 2 +- sycl/test-e2e/Adapters/level_zero/interop.cpp | 2 +- sycl/test-e2e/Adapters/level_zero/uuid.cpp | 2 +- sycl/test-e2e/Basic/buffer/buffer_create.cpp | 2 +- sycl/test-e2e/Basic/interop/get_native_ze.cpp | 2 +- sycl/test-e2e/Basic/interop/make_kernel_subdevice_l0.cpp | 2 +- .../test-e2e/Graph/Inputs/interop-level-zero-get-native-mem.cpp | 2 +- sycl/test-e2e/Graph/Inputs/interop-level-zero-launch-kernel.cpp | 2 +- sycl/test-e2e/Graph/NativeCommand/level-zero_usm.cpp | 2 +- sycl/test-e2e/Graph/NativeCommand/level-zero_usm_D2H_copy.cpp | 2 +- sycl/test-e2e/Regression/cache_test.cpp | 2 +- 19 files changed, 19 insertions(+), 19 deletions(-) diff --git a/sycl/test-e2e/Adapters/level_zero/batch_barrier.cpp b/sycl/test-e2e/Adapters/level_zero/batch_barrier.cpp index ee450f897a113..325743958aaf9 100644 --- a/sycl/test-e2e/Adapters/level_zero/batch_barrier.cpp +++ b/sycl/test-e2e/Adapters/level_zero/batch_barrier.cpp @@ -31,7 +31,7 @@ int main(int argc, char *argv[]) { // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; + std::cout << "zeInit failed" << std::endl; return 1; } diff --git a/sycl/test-e2e/Adapters/level_zero/interop-buffer-ownership.cpp b/sycl/test-e2e/Adapters/level_zero/interop-buffer-ownership.cpp index e9a2b0e5174d9..76640df1bede3 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-buffer-ownership.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-buffer-ownership.cpp @@ -131,7 +131,7 @@ int main() { // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; + std::cout << "zeInit failed" << std::endl; return 1; } diff --git a/sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp b/sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp index 12329ce195b66..f00786cf36be0 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp @@ -49,7 +49,7 @@ int main() { // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; + std::cout << "zeInit failed" << std::endl; return 1; } diff --git a/sycl/test-e2e/Adapters/level_zero/interop-direct.cpp b/sycl/test-e2e/Adapters/level_zero/interop-direct.cpp index 8c88e559789d5..01006b7a7b694 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-direct.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-direct.cpp @@ -23,7 +23,7 @@ int main() { // Init L0 ze_result_t result = zeInit(0); if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; + std::cout << "zeInit failed" << std::endl; return 1; } diff --git a/sycl/test-e2e/Adapters/level_zero/interop-get-native-mem.cpp b/sycl/test-e2e/Adapters/level_zero/interop-get-native-mem.cpp index 989800b88d573..420fee7e40100 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-get-native-mem.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-get-native-mem.cpp @@ -38,7 +38,7 @@ int main() { // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; + std::cout << "zeInit failed" << std::endl; return 1; } diff --git a/sycl/test-e2e/Adapters/level_zero/interop-image-get-native-mem.cpp b/sycl/test-e2e/Adapters/level_zero/interop-image-get-native-mem.cpp index 3d90091b7b1f0..8539e7b663770 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-image-get-native-mem.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-image-get-native-mem.cpp @@ -50,7 +50,7 @@ int main() { // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; + std::cout << "zeInit failed" << std::endl; return 1; } diff --git a/sycl/test-e2e/Adapters/level_zero/interop-image-ownership.cpp b/sycl/test-e2e/Adapters/level_zero/interop-image-ownership.cpp index 14f9c9462df6a..6fa4191343c15 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-image-ownership.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-image-ownership.cpp @@ -150,7 +150,7 @@ int main() { // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; + std::cout << "zeInit failed" << std::endl; return 1; } diff --git a/sycl/test-e2e/Adapters/level_zero/interop-image.cpp b/sycl/test-e2e/Adapters/level_zero/interop-image.cpp index 3ec2d79bf457b..2c59a671f20b4 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-image.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-image.cpp @@ -42,7 +42,7 @@ int main() { // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; + std::cout << "zeInit failed" << std::endl; return 1; } diff --git a/sycl/test-e2e/Adapters/level_zero/interop-keep-ownership.cpp b/sycl/test-e2e/Adapters/level_zero/interop-keep-ownership.cpp index 7fb8e0929ba5f..7233547321b26 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-keep-ownership.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-keep-ownership.cpp @@ -22,7 +22,7 @@ int main() { // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; + std::cout << "zeInit failed" << std::endl; return 1; } diff --git a/sycl/test-e2e/Adapters/level_zero/interop.cpp b/sycl/test-e2e/Adapters/level_zero/interop.cpp index d219dc232755c..f559c23a7bb09 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop.cpp @@ -20,7 +20,7 @@ int main() { // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; + std::cout << "zeInit failed" << std::endl; return 1; } diff --git a/sycl/test-e2e/Adapters/level_zero/uuid.cpp b/sycl/test-e2e/Adapters/level_zero/uuid.cpp index d7fd15f874a07..60809ced5452a 100644 --- a/sycl/test-e2e/Adapters/level_zero/uuid.cpp +++ b/sycl/test-e2e/Adapters/level_zero/uuid.cpp @@ -30,7 +30,7 @@ int main() { // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; + std::cout << "zeInit failed" << std::endl; return 1; } diff --git a/sycl/test-e2e/Basic/buffer/buffer_create.cpp b/sycl/test-e2e/Basic/buffer/buffer_create.cpp index 5dc2251342b0f..06b5b2af2425b 100644 --- a/sycl/test-e2e/Basic/buffer/buffer_create.cpp +++ b/sycl/test-e2e/Basic/buffer/buffer_create.cpp @@ -15,7 +15,7 @@ int main() { // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; + std::cout << "zeInit failed" << std::endl; return 1; } diff --git a/sycl/test-e2e/Basic/interop/get_native_ze.cpp b/sycl/test-e2e/Basic/interop/get_native_ze.cpp index 4d9e7a22d0734..4794f109f0951 100644 --- a/sycl/test-e2e/Basic/interop/get_native_ze.cpp +++ b/sycl/test-e2e/Basic/interop/get_native_ze.cpp @@ -16,7 +16,7 @@ int main() { // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; + std::cout << "zeInit failed" << std::endl; return 1; } diff --git a/sycl/test-e2e/Basic/interop/make_kernel_subdevice_l0.cpp b/sycl/test-e2e/Basic/interop/make_kernel_subdevice_l0.cpp index 216ffbbbd2969..4aa2dd1ebcb81 100644 --- a/sycl/test-e2e/Basic/interop/make_kernel_subdevice_l0.cpp +++ b/sycl/test-e2e/Basic/interop/make_kernel_subdevice_l0.cpp @@ -97,7 +97,7 @@ int main() { // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; + std::cout << "zeInit failed" << std::endl; return 1; } diff --git a/sycl/test-e2e/Graph/Inputs/interop-level-zero-get-native-mem.cpp b/sycl/test-e2e/Graph/Inputs/interop-level-zero-get-native-mem.cpp index d1167a1cb0286..32e1dcd1bb6a7 100644 --- a/sycl/test-e2e/Graph/Inputs/interop-level-zero-get-native-mem.cpp +++ b/sycl/test-e2e/Graph/Inputs/interop-level-zero-get-native-mem.cpp @@ -25,7 +25,7 @@ int main() { // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; + std::cout << "zeInit failed" << std::endl; return 1; } diff --git a/sycl/test-e2e/Graph/Inputs/interop-level-zero-launch-kernel.cpp b/sycl/test-e2e/Graph/Inputs/interop-level-zero-launch-kernel.cpp index 81f09d81124f1..f4a91a9fe01ec 100644 --- a/sycl/test-e2e/Graph/Inputs/interop-level-zero-launch-kernel.cpp +++ b/sycl/test-e2e/Graph/Inputs/interop-level-zero-launch-kernel.cpp @@ -47,7 +47,7 @@ int main(int, char **argv) { // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; + std::cout << "zeInit failed" << std::endl; return 1; } diff --git a/sycl/test-e2e/Graph/NativeCommand/level-zero_usm.cpp b/sycl/test-e2e/Graph/NativeCommand/level-zero_usm.cpp index 30133898b01ef..eced58efc5373 100644 --- a/sycl/test-e2e/Graph/NativeCommand/level-zero_usm.cpp +++ b/sycl/test-e2e/Graph/NativeCommand/level-zero_usm.cpp @@ -21,7 +21,7 @@ int main() { // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; + std::cout << "zeInit failed" << std::endl; return 1; } diff --git a/sycl/test-e2e/Graph/NativeCommand/level-zero_usm_D2H_copy.cpp b/sycl/test-e2e/Graph/NativeCommand/level-zero_usm_D2H_copy.cpp index b0c4e93e3afc2..e59232c687ba8 100644 --- a/sycl/test-e2e/Graph/NativeCommand/level-zero_usm_D2H_copy.cpp +++ b/sycl/test-e2e/Graph/NativeCommand/level-zero_usm_D2H_copy.cpp @@ -28,7 +28,7 @@ int main() { // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; + std::cout << "zeInit failed" << std::endl; return 1; } diff --git a/sycl/test-e2e/Regression/cache_test.cpp b/sycl/test-e2e/Regression/cache_test.cpp index 874635f5fd987..809e1f4ddbef1 100644 --- a/sycl/test-e2e/Regression/cache_test.cpp +++ b/sycl/test-e2e/Regression/cache_test.cpp @@ -155,7 +155,7 @@ int main() { // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; + std::cout << "zeInit failed" << std::endl; return 1; } From 5a46c1d39e30997fb27ae8e6404a9a410948a0b4 Mon Sep 17 00:00:00 2001 From: "Dubinov, Igor" Date: Tue, 24 Jun 2025 11:42:22 +0200 Subject: [PATCH 07/10] assert check --- sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp | 5 +---- .../AtomicRef/device_has_aspect_atomic64_level_zero.cpp | 5 +---- sycl/test-e2e/Basic/interop/ze_context_device.cpp | 4 +++- sycl/test-e2e/DeviceImageBackendContent/L0_interop_test.cpp | 5 +---- 4 files changed, 6 insertions(+), 13 deletions(-) diff --git a/sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp b/sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp index f00786cf36be0..1daeabacd7ae2 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp @@ -48,10 +48,7 @@ int main() { // Initializing Level Zero driver is required if this test is linked // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); - if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed" << std::endl; - return 1; - } + assert(result == ZE_RESULT_SUCCESS); ze_host_mem_alloc_desc_t HostDesc = {}; HostDesc.stype = ZE_STRUCTURE_TYPE_HOST_MEM_ALLOC_DESC; diff --git a/sycl/test-e2e/AtomicRef/device_has_aspect_atomic64_level_zero.cpp b/sycl/test-e2e/AtomicRef/device_has_aspect_atomic64_level_zero.cpp index 805af208ce1a4..2d7f89e2ff219 100644 --- a/sycl/test-e2e/AtomicRef/device_has_aspect_atomic64_level_zero.cpp +++ b/sycl/test-e2e/AtomicRef/device_has_aspect_atomic64_level_zero.cpp @@ -12,10 +12,7 @@ int main() { // Initializing Level Zero driver is required if this test is linked // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); - if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; - return 1; - } + assert(result == ZE_RESULT_SUCCESS && "zeInit failed"); queue Queue; device Dev = Queue.get_device(); diff --git a/sycl/test-e2e/Basic/interop/ze_context_device.cpp b/sycl/test-e2e/Basic/interop/ze_context_device.cpp index 9dd34e93ba54d..33866c6616bb9 100644 --- a/sycl/test-e2e/Basic/interop/ze_context_device.cpp +++ b/sycl/test-e2e/Basic/interop/ze_context_device.cpp @@ -17,7 +17,9 @@ int main(int argc, char *argv[]) { int level0DriverIndex = 0; int level0DeviceIndex = 0; - zeInit(0); + ze_result_t result = zeInit(0); + assert(result == ZE_RESULT_SUCCESS); + uint32_t level0NumDrivers = 0; zeDriverGet(&level0NumDrivers, nullptr); diff --git a/sycl/test-e2e/DeviceImageBackendContent/L0_interop_test.cpp b/sycl/test-e2e/DeviceImageBackendContent/L0_interop_test.cpp index f04e9f969d59e..a2a5255a0ea7f 100644 --- a/sycl/test-e2e/DeviceImageBackendContent/L0_interop_test.cpp +++ b/sycl/test-e2e/DeviceImageBackendContent/L0_interop_test.cpp @@ -23,10 +23,7 @@ int main() { // Initializing Level Zero driver is required if this test is linked // statically with Level Zero loader, otherwise the driver will not be initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); - if (result != ZE_RESULT_SUCCESS) { - std::cout << "zeInit failed\n"; - return 1; - } + assert(result == ZE_RESULT_SUCCESS); sycl::queue q; sycl::context ctxt = q.get_context(); From ce2e3c0f8d18301dcf5455a9ca04433b4c137bc3 Mon Sep 17 00:00:00 2001 From: "Dubinov, Igor" Date: Tue, 1 Jul 2025 12:55:59 +0200 Subject: [PATCH 08/10] code format --- sycl/test-e2e/Adapters/level_zero/batch_barrier.cpp | 3 ++- sycl/test-e2e/Adapters/level_zero/interop-buffer-multi-dim.cpp | 3 ++- sycl/test-e2e/Adapters/level_zero/interop-buffer-ownership.cpp | 3 ++- sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp | 3 ++- sycl/test-e2e/Adapters/level_zero/interop-get-native-mem.cpp | 3 ++- .../Adapters/level_zero/interop-image-get-native-mem.cpp | 3 ++- sycl/test-e2e/Adapters/level_zero/interop-image-ownership.cpp | 3 ++- sycl/test-e2e/Adapters/level_zero/interop-image.cpp | 3 ++- sycl/test-e2e/Adapters/level_zero/interop-keep-ownership.cpp | 3 ++- sycl/test-e2e/Adapters/level_zero/interop-thread.cpp | 3 ++- sycl/test-e2e/Adapters/level_zero/interop.cpp | 3 ++- sycl/test-e2e/Adapters/level_zero/uuid.cpp | 3 ++- .../AtomicRef/device_has_aspect_atomic64_level_zero.cpp | 3 ++- sycl/test-e2e/Basic/buffer/buffer_create.cpp | 3 ++- sycl/test-e2e/Basic/interop/get_native_ze.cpp | 3 ++- sycl/test-e2e/Basic/interop/make_kernel_subdevice_l0.cpp | 3 ++- sycl/test-e2e/DeviceImageBackendContent/L0_interop_test.cpp | 3 ++- .../Graph/Inputs/interop-level-zero-get-native-mem.cpp | 3 ++- .../test-e2e/Graph/Inputs/interop-level-zero-launch-kernel.cpp | 3 ++- sycl/test-e2e/Graph/NativeCommand/level-zero_usm.cpp | 3 ++- sycl/test-e2e/Graph/NativeCommand/level-zero_usm_D2H_copy.cpp | 3 ++- sycl/test-e2e/Regression/cache_test.cpp | 3 ++- 22 files changed, 44 insertions(+), 22 deletions(-) diff --git a/sycl/test-e2e/Adapters/level_zero/batch_barrier.cpp b/sycl/test-e2e/Adapters/level_zero/batch_barrier.cpp index 325743958aaf9..d7993cad569f6 100644 --- a/sycl/test-e2e/Adapters/level_zero/batch_barrier.cpp +++ b/sycl/test-e2e/Adapters/level_zero/batch_barrier.cpp @@ -28,7 +28,8 @@ int main(int argc, char *argv[]) { // CHECK-NOT: zeCommandQueueExecuteCommandLists // Initializing Level Zero driver is required if this test is linked - // statically with Level Zero loader, otherwise the driver will not be initialized. + // statically with Level Zero loader, otherwise the driver will not be + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed" << std::endl; diff --git a/sycl/test-e2e/Adapters/level_zero/interop-buffer-multi-dim.cpp b/sycl/test-e2e/Adapters/level_zero/interop-buffer-multi-dim.cpp index 853ea084d408e..fbd48d8f31361 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-buffer-multi-dim.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-buffer-multi-dim.cpp @@ -26,7 +26,8 @@ int main() { } // Initializing Level Zero driver is required if this test is linked - // statically with Level Zero loader, otherwise the driver will not be initialized. + // statically with Level Zero loader, otherwise the driver will not be + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed" << std::endl; diff --git a/sycl/test-e2e/Adapters/level_zero/interop-buffer-ownership.cpp b/sycl/test-e2e/Adapters/level_zero/interop-buffer-ownership.cpp index 76640df1bede3..5e9cbae1170c1 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-buffer-ownership.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-buffer-ownership.cpp @@ -128,7 +128,8 @@ int main() { } // Initializing Level Zero driver is required if this test is linked - // statically with Level Zero loader, otherwise the driver will not be initialized. + // statically with Level Zero loader, otherwise the driver will not be + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed" << std::endl; diff --git a/sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp b/sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp index 1daeabacd7ae2..c6ca61e808f0c 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp @@ -46,7 +46,8 @@ int main() { auto ZeDevice = get_native(Device); // Initializing Level Zero driver is required if this test is linked - // statically with Level Zero loader, otherwise the driver will not be initialized. + // statically with Level Zero loader, otherwise the driver will not be + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); assert(result == ZE_RESULT_SUCCESS); diff --git a/sycl/test-e2e/Adapters/level_zero/interop-get-native-mem.cpp b/sycl/test-e2e/Adapters/level_zero/interop-get-native-mem.cpp index 420fee7e40100..b5f790272e3ed 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-get-native-mem.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-get-native-mem.cpp @@ -35,7 +35,8 @@ int main() { } // Initializing Level Zero driver is required if this test is linked - // statically with Level Zero loader, otherwise the driver will not be initialized. + // statically with Level Zero loader, otherwise the driver will not be + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed" << std::endl; diff --git a/sycl/test-e2e/Adapters/level_zero/interop-image-get-native-mem.cpp b/sycl/test-e2e/Adapters/level_zero/interop-image-get-native-mem.cpp index 8539e7b663770..25d5d8f839742 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-image-get-native-mem.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-image-get-native-mem.cpp @@ -47,7 +47,8 @@ int main() { sycl::ext::oneapi::filter_selector("level_zero:gpu").select_device(); // Initializing Level Zero driver is required if this test is linked - // statically with Level Zero loader, otherwise the driver will not be initialized. + // statically with Level Zero loader, otherwise the driver will not be + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed" << std::endl; diff --git a/sycl/test-e2e/Adapters/level_zero/interop-image-ownership.cpp b/sycl/test-e2e/Adapters/level_zero/interop-image-ownership.cpp index 6fa4191343c15..1b04e0bcd157f 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-image-ownership.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-image-ownership.cpp @@ -147,7 +147,8 @@ int main() { platform Plt{gpu_selector_v}; // Initializing Level Zero driver is required if this test is linked - // statically with Level Zero loader, otherwise the driver will not be initialized. + // statically with Level Zero loader, otherwise the driver will not be + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed" << std::endl; diff --git a/sycl/test-e2e/Adapters/level_zero/interop-image.cpp b/sycl/test-e2e/Adapters/level_zero/interop-image.cpp index 2c59a671f20b4..03d9eb8083b67 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-image.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-image.cpp @@ -39,7 +39,8 @@ int main() { auto Devices = Plt.get_devices(); // Initializing Level Zero driver is required if this test is linked - // statically with Level Zero loader, otherwise the driver will not be initialized. + // statically with Level Zero loader, otherwise the driver will not be + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed" << std::endl; diff --git a/sycl/test-e2e/Adapters/level_zero/interop-keep-ownership.cpp b/sycl/test-e2e/Adapters/level_zero/interop-keep-ownership.cpp index 7233547321b26..d225af57c0607 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-keep-ownership.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-keep-ownership.cpp @@ -19,7 +19,8 @@ int main() { platform Platform = Device.get_info(); // Initializing Level Zero driver is required if this test is linked - // statically with Level Zero loader, otherwise the driver will not be initialized. + // statically with Level Zero loader, otherwise the driver will not be + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed" << std::endl; diff --git a/sycl/test-e2e/Adapters/level_zero/interop-thread.cpp b/sycl/test-e2e/Adapters/level_zero/interop-thread.cpp index 32d40a8876c57..c3a7146a7a59f 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-thread.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-thread.cpp @@ -62,7 +62,8 @@ std::vector old_ops; void init() { // Initializing Level Zero driver is required if this test is linked - // statically with Level Zero loader, otherwise the driver will not be initialized. + // statically with Level Zero loader, otherwise the driver will not be + // initialized. ze_result_t result = zeInit(0); assert(result == ZE_RESULT_SUCCESS); diff --git a/sycl/test-e2e/Adapters/level_zero/interop.cpp b/sycl/test-e2e/Adapters/level_zero/interop.cpp index f559c23a7bb09..b37b3f7b9b1ad 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop.cpp @@ -17,7 +17,8 @@ using namespace sycl; int main() { #ifdef SYCL_EXT_ONEAPI_BACKEND_LEVEL_ZERO // Initializing Level Zero driver is required if this test is linked - // statically with Level Zero loader, otherwise the driver will not be initialized. + // statically with Level Zero loader, otherwise the driver will not be + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed" << std::endl; diff --git a/sycl/test-e2e/Adapters/level_zero/uuid.cpp b/sycl/test-e2e/Adapters/level_zero/uuid.cpp index 60809ced5452a..cbdcff8fe840b 100644 --- a/sycl/test-e2e/Adapters/level_zero/uuid.cpp +++ b/sycl/test-e2e/Adapters/level_zero/uuid.cpp @@ -27,7 +27,8 @@ int main() { device_properties.stype = ZE_STRUCTURE_TYPE_DEVICE_PROPERTIES; // Initializing Level Zero driver is required if this test is linked - // statically with Level Zero loader, otherwise the driver will not be initialized. + // statically with Level Zero loader, otherwise the driver will not be + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed" << std::endl; diff --git a/sycl/test-e2e/AtomicRef/device_has_aspect_atomic64_level_zero.cpp b/sycl/test-e2e/AtomicRef/device_has_aspect_atomic64_level_zero.cpp index 2d7f89e2ff219..93f080fdd972c 100644 --- a/sycl/test-e2e/AtomicRef/device_has_aspect_atomic64_level_zero.cpp +++ b/sycl/test-e2e/AtomicRef/device_has_aspect_atomic64_level_zero.cpp @@ -10,7 +10,8 @@ using namespace sycl; int main() { // Initializing Level Zero driver is required if this test is linked - // statically with Level Zero loader, otherwise the driver will not be initialized. + // statically with Level Zero loader, otherwise the driver will not be + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); assert(result == ZE_RESULT_SUCCESS && "zeInit failed"); diff --git a/sycl/test-e2e/Basic/buffer/buffer_create.cpp b/sycl/test-e2e/Basic/buffer/buffer_create.cpp index 06b5b2af2425b..cce80e73bdf33 100644 --- a/sycl/test-e2e/Basic/buffer/buffer_create.cpp +++ b/sycl/test-e2e/Basic/buffer/buffer_create.cpp @@ -12,7 +12,8 @@ using namespace sycl; int main() { // Initializing Level Zero driver is required if this test is linked - // statically with Level Zero loader, otherwise the driver will not be initialized. + // statically with Level Zero loader, otherwise the driver will not be + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed" << std::endl; diff --git a/sycl/test-e2e/Basic/interop/get_native_ze.cpp b/sycl/test-e2e/Basic/interop/get_native_ze.cpp index 4794f109f0951..87b9145f49abd 100644 --- a/sycl/test-e2e/Basic/interop/get_native_ze.cpp +++ b/sycl/test-e2e/Basic/interop/get_native_ze.cpp @@ -13,7 +13,8 @@ class TestKernel; int main() { // Initializing Level Zero driver is required if this test is linked - // statically with Level Zero loader, otherwise the driver will not be initialized. + // statically with Level Zero loader, otherwise the driver will not be + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed" << std::endl; diff --git a/sycl/test-e2e/Basic/interop/make_kernel_subdevice_l0.cpp b/sycl/test-e2e/Basic/interop/make_kernel_subdevice_l0.cpp index 4aa2dd1ebcb81..12b4140429186 100644 --- a/sycl/test-e2e/Basic/interop/make_kernel_subdevice_l0.cpp +++ b/sycl/test-e2e/Basic/interop/make_kernel_subdevice_l0.cpp @@ -94,7 +94,8 @@ ze_kernel_handle_t create_kernel(ze_module_handle_t module, int main() { // Initializing Level Zero driver is required if this test is linked - // statically with Level Zero loader, otherwise the driver will not be initialized. + // statically with Level Zero loader, otherwise the driver will not be + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed" << std::endl; diff --git a/sycl/test-e2e/DeviceImageBackendContent/L0_interop_test.cpp b/sycl/test-e2e/DeviceImageBackendContent/L0_interop_test.cpp index a2a5255a0ea7f..b5b550e8d6c36 100644 --- a/sycl/test-e2e/DeviceImageBackendContent/L0_interop_test.cpp +++ b/sycl/test-e2e/DeviceImageBackendContent/L0_interop_test.cpp @@ -21,7 +21,8 @@ extern "C" SYCL_EXT_ONEAPI_FUNCTION_PROPERTY( int main() { // Initializing Level Zero driver is required if this test is linked - // statically with Level Zero loader, otherwise the driver will not be initialized. + // statically with Level Zero loader, otherwise the driver will not be + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); assert(result == ZE_RESULT_SUCCESS); diff --git a/sycl/test-e2e/Graph/Inputs/interop-level-zero-get-native-mem.cpp b/sycl/test-e2e/Graph/Inputs/interop-level-zero-get-native-mem.cpp index 32e1dcd1bb6a7..aa138556b9405 100644 --- a/sycl/test-e2e/Graph/Inputs/interop-level-zero-get-native-mem.cpp +++ b/sycl/test-e2e/Graph/Inputs/interop-level-zero-get-native-mem.cpp @@ -22,7 +22,8 @@ bool is_discrete(const device &Device) { int main() { // Initializing Level Zero driver is required if this test is linked - // statically with Level Zero loader, otherwise the driver will not be initialized. + // statically with Level Zero loader, otherwise the driver will not be + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed" << std::endl; diff --git a/sycl/test-e2e/Graph/Inputs/interop-level-zero-launch-kernel.cpp b/sycl/test-e2e/Graph/Inputs/interop-level-zero-launch-kernel.cpp index f4a91a9fe01ec..3748b2265f76a 100644 --- a/sycl/test-e2e/Graph/Inputs/interop-level-zero-launch-kernel.cpp +++ b/sycl/test-e2e/Graph/Inputs/interop-level-zero-launch-kernel.cpp @@ -44,7 +44,8 @@ int main(int, char **argv) { } // Initializing Level Zero driver is required if this test is linked - // statically with Level Zero loader, otherwise the driver will not be initialized. + // statically with Level Zero loader, otherwise the driver will not be + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed" << std::endl; diff --git a/sycl/test-e2e/Graph/NativeCommand/level-zero_usm.cpp b/sycl/test-e2e/Graph/NativeCommand/level-zero_usm.cpp index eced58efc5373..4a947757a75a1 100644 --- a/sycl/test-e2e/Graph/NativeCommand/level-zero_usm.cpp +++ b/sycl/test-e2e/Graph/NativeCommand/level-zero_usm.cpp @@ -18,7 +18,8 @@ using namespace sycl; int main() { // Initializing Level Zero driver is required if this test is linked - // statically with Level Zero loader, otherwise the driver will not be initialized. + // statically with Level Zero loader, otherwise the driver will not be + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed" << std::endl; diff --git a/sycl/test-e2e/Graph/NativeCommand/level-zero_usm_D2H_copy.cpp b/sycl/test-e2e/Graph/NativeCommand/level-zero_usm_D2H_copy.cpp index e59232c687ba8..f04d9d821b46d 100644 --- a/sycl/test-e2e/Graph/NativeCommand/level-zero_usm_D2H_copy.cpp +++ b/sycl/test-e2e/Graph/NativeCommand/level-zero_usm_D2H_copy.cpp @@ -25,7 +25,8 @@ using namespace sycl; int main() { // Initializing Level Zero driver is required if this test is linked - // statically with Level Zero loader, otherwise the driver will not be initialized. + // statically with Level Zero loader, otherwise the driver will not be + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed" << std::endl; diff --git a/sycl/test-e2e/Regression/cache_test.cpp b/sycl/test-e2e/Regression/cache_test.cpp index 809e1f4ddbef1..ffdd80f5a9607 100644 --- a/sycl/test-e2e/Regression/cache_test.cpp +++ b/sycl/test-e2e/Regression/cache_test.cpp @@ -152,7 +152,8 @@ int queryFromNativeHandle(std::vector *platform_list, int main() { // Initializing Level Zero driver is required if this test is linked - // statically with Level Zero loader, otherwise the driver will not be initialized. + // statically with Level Zero loader, otherwise the driver will not be + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed" << std::endl; From 47ea7b4dadda258451e3d7b0e009ef13795faa44 Mon Sep 17 00:00:00 2001 From: "Dubinov, Igor" Date: Wed, 2 Jul 2025 09:26:32 +0200 Subject: [PATCH 09/10] code format --- sycl/test-e2e/Adapters/level_zero/interop-buffer-multi-dim.cpp | 2 +- sycl/test-e2e/Adapters/level_zero/interop-buffer-ownership.cpp | 2 +- sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp | 2 +- sycl/test-e2e/Adapters/level_zero/interop-get-native-mem.cpp | 2 +- 4 files changed, 4 insertions(+), 4 deletions(-) diff --git a/sycl/test-e2e/Adapters/level_zero/interop-buffer-multi-dim.cpp b/sycl/test-e2e/Adapters/level_zero/interop-buffer-multi-dim.cpp index fbd48d8f31361..037d218853951 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-buffer-multi-dim.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-buffer-multi-dim.cpp @@ -27,7 +27,7 @@ int main() { // Initializing Level Zero driver is required if this test is linked // statically with Level Zero loader, otherwise the driver will not be - // initialized. + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed" << std::endl; diff --git a/sycl/test-e2e/Adapters/level_zero/interop-buffer-ownership.cpp b/sycl/test-e2e/Adapters/level_zero/interop-buffer-ownership.cpp index 5e9cbae1170c1..bc121fdda7838 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-buffer-ownership.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-buffer-ownership.cpp @@ -129,7 +129,7 @@ int main() { // Initializing Level Zero driver is required if this test is linked // statically with Level Zero loader, otherwise the driver will not be - // initialized. + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed" << std::endl; diff --git a/sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp b/sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp index c6ca61e808f0c..5bfed40013b0b 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-buffer.cpp @@ -47,7 +47,7 @@ int main() { // Initializing Level Zero driver is required if this test is linked // statically with Level Zero loader, otherwise the driver will not be - // initialized. + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); assert(result == ZE_RESULT_SUCCESS); diff --git a/sycl/test-e2e/Adapters/level_zero/interop-get-native-mem.cpp b/sycl/test-e2e/Adapters/level_zero/interop-get-native-mem.cpp index b5f790272e3ed..4dc0af896aebd 100644 --- a/sycl/test-e2e/Adapters/level_zero/interop-get-native-mem.cpp +++ b/sycl/test-e2e/Adapters/level_zero/interop-get-native-mem.cpp @@ -36,7 +36,7 @@ int main() { // Initializing Level Zero driver is required if this test is linked // statically with Level Zero loader, otherwise the driver will not be - // initialized. + // initialized. ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed" << std::endl; From ec9c4e354c693ff63c4c16c98706ac364f709bc7 Mon Sep 17 00:00:00 2001 From: "Dubinov, Igor" Date: Wed, 2 Jul 2025 12:15:15 +0200 Subject: [PATCH 10/10] fix buffer create --- sycl/test-e2e/Basic/buffer/buffer_create.cpp | 2 +- 1 file changed, 1 insertion(+), 1 deletion(-) diff --git a/sycl/test-e2e/Basic/buffer/buffer_create.cpp b/sycl/test-e2e/Basic/buffer/buffer_create.cpp index cce80e73bdf33..4baa25f02c4a7 100644 --- a/sycl/test-e2e/Basic/buffer/buffer_create.cpp +++ b/sycl/test-e2e/Basic/buffer/buffer_create.cpp @@ -14,7 +14,7 @@ int main() { // Initializing Level Zero driver is required if this test is linked // statically with Level Zero loader, otherwise the driver will not be // initialized. - ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY); + ze_result_t result = zeInit(0); if (result != ZE_RESULT_SUCCESS) { std::cout << "zeInit failed" << std::endl; return 1;