[SYCL][L0] Fix absence of zeInit in Level Zero LIT e2e tests (#18956)

idubinov · AlexeySachkov · dm-vodopyanov · web-flow · commit 198a23ef3324 · 2025-08-13T14:33:22.000+02:00
Co-authored-by: Alexey Sachkov &lt;alexey.sachkov@intel.com&gt;
Co-authored-by: Dmitry Vodopyanov &lt;dmitry.vodopyanov@intel.com&gt;
diff --git a/sycl/test-e2e/Adapters/level_zero/batch_barrier.cpp b/sycl/test-e2e/Adapters/level_zero/batch_barrier.cpp
@@ -27,11 +27,12 @@ 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";
+    std::cout << "zeInit failed with error code: " << result << std::endl;
     return 1;
   }
 
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
@@ -25,11 +25,12 @@ 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 with error code: " << result << 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
@@ -127,11 +127,12 @@ 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 with error code: " << result << 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
@@ -45,13 +45,11 @@ int main() {
     auto ZeContext = get_native<backend::ext_oneapi_level_zero>(Context);
     auto ZeDevice = get_native<backend::ext_oneapi_level_zero>(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";
-      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/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 with error code: " << result << 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
@@ -34,11 +34,12 @@ 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 with error code: " << result << 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
@@ -46,11 +46,12 @@ 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";
+    std::cout << "zeInit failed with error code: " << result << 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
@@ -146,11 +146,12 @@ 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";
+    std::cout << "zeInit failed with error code: " << result << 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
@@ -38,11 +38,12 @@ 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";
+    std::cout << "zeInit failed with error code: " << result << 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
@@ -18,11 +18,12 @@ int main() {
   device Device(gpu_selector_v);
   platform Platform = Device.get_info<info::device::platform>();
 
-  // 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 with error code: " << result << std::endl;
     return 1;
   }
 
diff --git a/sycl/test-e2e/Adapters/level_zero/interop-thread.cpp b/sycl/test-e2e/Adapters/level_zero/interop-thread.cpp
@@ -61,7 +61,11 @@ ze_event_pool_handle_t event_pool = {};
 std::vector<operation> old_ops;
 
 void init() {
-  zeInit(0);
+  // 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);
 
   uint32_t driverCount = 0;
   assert(zeDriverGet(&driverCount, nullptr) == 0);
diff --git a/sycl/test-e2e/Adapters/level_zero/interop.cpp b/sycl/test-e2e/Adapters/level_zero/interop.cpp
@@ -16,11 +16,12 @@ 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";
+    std::cout << "zeInit failed with error code: " << result << std::endl;
     return 1;
   }
 
diff --git a/sycl/test-e2e/Adapters/level_zero/uuid.cpp b/sycl/test-e2e/Adapters/level_zero/uuid.cpp
@@ -24,6 +24,16 @@ int main() {
   auto zedev = sycl::get_native<sycl::backend::ext_oneapi_level_zero>(dev);
   ze_device_properties_t device_properties{};
   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.
+  ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY);
+  if (result != ZE_RESULT_SUCCESS) {
+    std::cout << "zeInit failed with error code: " << result << std::endl;
+    return 1;
+  }
+
   zeDeviceGetProperties(zedev, &device_properties);
   std::stringstream uuid_l0;
   for (int i = 0; i < ZE_MAX_DEVICE_UUID_SIZE; ++i)
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
@@ -9,6 +9,12 @@
 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.
+  ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY);
+  assert(result == ZE_RESULT_SUCCESS && "zeInit failed");
+
   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
@@ -1,6 +1,11 @@
 // REQUIRES: gpu,level_zero,level_zero_dev_kit
 // RUN: %{build} %level_zero_options -o %t.out
-// RUN: env UR_L0_DEBUG=1 %{run} %t.out 2>&1 | FileCheck %s
+// Because we initialize L0 driver directly in the test before UR L0 adapter
+// does that, we need to explicitly set the right environment variables instead
+// of using UR_L0_DEBUG shortcut
+// RUN: env ZEL_ENABLE_LOADER_LOGGING=1 ZEL_LOADER_LOGGING_LEVEL=trace \
+// RUN:     ZEL_LOADER_LOG_CONSOLE=1 ZE_ENABLE_VALIDATION_LAYER=1 \
+// RUN: %{run} %t.out 2>&1 | FileCheck %s
 // UNSUPPORTED: ze_debug
 
 #include <iostream>
@@ -11,6 +16,15 @@
 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.
+  ze_result_t result = zeInit(0);
+  if (result != ZE_RESULT_SUCCESS) {
+    std::cout << "zeInit failed with error code: " << result << std::endl;
+    return 1;
+  }
+
   constexpr int Size = 100;
   queue Queue;
   auto D = Queue.get_device();
diff --git a/sycl/test-e2e/Basic/interop/get_native_ze.cpp b/sycl/test-e2e/Basic/interop/get_native_ze.cpp
@@ -12,11 +12,12 @@ 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";
+    std::cout << "zeInit failed with error code: " << result << 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
@@ -93,6 +93,15 @@ 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.
+  ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY);
+  if (result != ZE_RESULT_SUCCESS) {
+    std::cout << "zeInit failed with error code: " << result << std::endl;
+    return 1;
+  }
+
   device D{gpu_selector_v};
 
   try {
diff --git 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
@@ -20,6 +20,12 @@ 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.
+  ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY);
+  assert(result == ZE_RESULT_SUCCESS);
+
   sycl::queue q;
   sycl::context ctxt = q.get_context();
   sycl::device d = ctxt.get_devices()[0];
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
@@ -21,11 +21,12 @@ 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";
+    std::cout << "zeInit failed with error code: " << result << 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
@@ -43,11 +43,12 @@ 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";
+    std::cout << "zeInit failed with error code: " << result << 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
@@ -17,11 +17,12 @@ 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";
+    std::cout << "zeInit failed with error code: " << result << 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
@@ -24,11 +24,12 @@ 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";
+    std::cout << "zeInit failed with error code: " << result << std::endl;
     return 1;
   }
 
diff --git a/sycl/test-e2e/Regression/cache_test.cpp b/sycl/test-e2e/Regression/cache_test.cpp
@@ -151,6 +151,15 @@ int queryFromNativeHandle(std::vector<sycl::platform> *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.
+  ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY);
+  if (result != ZE_RESULT_SUCCESS) {
+    std::cout << "zeInit failed with error code: " << result << std::endl;
+    return 1;
+  }
+
   int failures = 0;
 
   // Query for a list of all of the available platforms and devices.

Original file line number	Diff line number	Diff line change
`@@ -25,11 +25,12 @@ int main() {`
`25`	`25`	`return 0;`
`26`	`26`	`}`
`27`	`27`
`28`		`- // Initialize Level Zero driver is required if this test is linked`
`29`		`- // statically with Level Zero loader, the driver will not be init otherwise.`
	`28`	`+ // Initializing Level Zero driver is required if this test is linked`
	`29`	`+ // statically with Level Zero loader, otherwise the driver will not be`
	`30`	`+ // initialized.`
`30`	`31`	`ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY);`
`31`	`32`	`if (result != ZE_RESULT_SUCCESS) {`
`32`		`- std::cout << "zeInit failed\n";`
	`33`	`+ std::cout << "zeInit failed with error code: " << result << std::endl;`
`33`	`34`	`return 1;`
`34`	`35`	`}`
`35`	`36`
Original file line number	Diff line number	Diff line change
`@@ -127,11 +127,12 @@ int main() {`
`127`	`127`	`return 0;`
`128`	`128`	`}`
`129`	`129`
`130`		`- // Initialize Level Zero driver is required if this test is linked`
`131`		`- // statically with Level Zero loader, the driver will not be init otherwise.`
	`130`	`+ // Initializing Level Zero driver is required if this test is linked`
	`131`	`+ // statically with Level Zero loader, otherwise the driver will not be`
	`132`	`+ // initialized.`
`132`	`133`	`ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY);`
`133`	`134`	`if (result != ZE_RESULT_SUCCESS) {`
`134`		`- std::cout << "zeInit failed\n";`
	`135`	`+ std::cout << "zeInit failed with error code: " << result << std::endl;`
`135`	`136`	`return 1;`
`136`	`137`	`}`
`137`	`138`
Original file line number	Diff line number	Diff line change
`@@ -23,7 +23,7 @@ int main() {`
`23`	`23`	`// Init L0`
`24`	`24`	`ze_result_t result = zeInit(0);`
`25`	`25`	`if (result != ZE_RESULT_SUCCESS) {`
`26`		`- std::cout << "zeInit failed\n";`
	`26`	`+ std::cout << "zeInit failed with error code: " << result << std::endl;`
`27`	`27`	`return 1;`
`28`	`28`	`}`
`29`	`29`
Original file line number	Diff line number	Diff line change
`@@ -34,11 +34,12 @@ int main() {`
`34`	`34`	`return 0;`
`35`	`35`	`}`
`36`	`36`
`37`		`- // Initialize Level Zero driver is required if this test is linked`
`38`		`- // statically with Level Zero loader, the driver will not be init otherwise.`
	`37`	`+ // Initializing Level Zero driver is required if this test is linked`
	`38`	`+ // statically with Level Zero loader, otherwise the driver will not be`
	`39`	`+ // initialized.`
`39`	`40`	`ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY);`
`40`	`41`	`if (result != ZE_RESULT_SUCCESS) {`
`41`		`- std::cout << "zeInit failed\n";`
	`42`	`+ std::cout << "zeInit failed with error code: " << result << std::endl;`
`42`	`43`	`return 1;`
`43`	`44`	`}`
`44`	`45`