[SYCL][E2E] Add missing zeInit to interop tests (#17699)

Level Zero loader is now linked statically with adapters and tests. This
means that both adapters and tests need to call zeInit to initalize the
loader.

Author: igchor

sycl/test-e2e/Adapters/interop-level-zero-buffer-multi-dim.cpp

@@ -16,6 +16,14 @@ using namespace sycl;
 int main() {
 #ifdef SYCL_EXT_ONEAPI_BACKEND_LEVEL_ZERO
   try {
+    // 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;
+    }
+
     platform Plt{gpu_selector_v};
 
     auto Devices = Plt.get_devices();

sycl/test-e2e/Adapters/interop-level-zero-buffer-ownership.cpp

@@ -119,6 +119,14 @@ void test_copyback_and_free(
 int main() {
 #ifdef SYCL_EXT_ONEAPI_BACKEND_LEVEL_ZERO
   try {
+    // 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;
+    }
+
     platform Plt{gpu_selector_v};
 
     auto Devices = Plt.get_devices();

sycl/test-e2e/Adapters/interop-level-zero-buffer.cpp

@@ -36,6 +36,14 @@ class DiscreteSelector : public sycl::device_selector {
 int main() {
 #ifdef SYCL_EXT_ONEAPI_BACKEND_LEVEL_ZERO
   try {
+    // 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{};
 
     auto Context = Queue.get_info<info::queue::context>();

sycl/test-e2e/Adapters/interop-level-zero-get-native-mem.cpp

@@ -23,6 +23,14 @@ constexpr size_t SIZE = 16;
 int main() {
 #ifdef SYCL_EXT_ONEAPI_BACKEND_LEVEL_ZERO
   try {
+    // 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;
+    }
+
     platform Plt{gpu_selector_v};
 
     auto Devices = Plt.get_devices();

sycl/test-e2e/Adapters/interop-level-zero-image-get-native-mem.cpp

@@ -42,6 +42,14 @@ 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.
+  ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY);
+  if (result != ZE_RESULT_SUCCESS) {
+    std::cout << "zeInit failed\n";
+    return 1;
+  }
+
   constexpr auto BE = sycl::backend::ext_oneapi_level_zero;
   sycl::device D =
       sycl::ext::oneapi::filter_selector("level_zero:gpu").select_device();

sycl/test-e2e/Adapters/interop-level-zero-image-ownership.cpp

@@ -144,6 +144,14 @@ void test(sycl::ext::oneapi::level_zero::ownership Ownership) {
 
 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.
+  ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY);
+  if (result != ZE_RESULT_SUCCESS) {
+    std::cout << "zeInit failed\n";
+    return 1;
+  }
+
   std::cout << "test  ownership::transfer" << std::endl;
   test(sycl::ext::oneapi::level_zero::ownership::transfer);
 

sycl/test-e2e/Adapters/interop-level-zero-image.cpp

@@ -32,6 +32,14 @@ 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.
+  ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY);
+  if (result != ZE_RESULT_SUCCESS) {
+    std::cout << "zeInit failed\n";
+    return 1;
+  }
+
   constexpr auto BE = sycl::backend::ext_oneapi_level_zero;
 
   platform Plt{gpu_selector_v};

sycl/test-e2e/Adapters/interop-level-zero-keep-ownership.cpp

@@ -14,6 +14,13 @@
 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;
+  }
 
   // Creat SYCL platform/device
   device Device(gpu_selector_v);

sycl/test-e2e/Adapters/interop-level-zero.cpp

@@ -16,6 +16,14 @@ 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.
+  ze_result_t result = zeInit(ZE_INIT_FLAG_GPU_ONLY);
+  if (result != ZE_RESULT_SUCCESS) {
+    std::cout << "zeInit failed\n";
+    return 1;
+  }
+
   queue Queue{};
 
   event DefaultEvent;

sycl/test-e2e/Adapters/level_zero_batch_barrier.cpp

@@ -21,6 +21,14 @@ void submit_kernel(queue &q) {
 }
 
 int main(int argc, char *argv[]) {
+  // 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 q;
 
   submit_kernel(q); // starts a batch