[SYCL][L0] Fix absence of zeInit in Level Zero LIT e2e tests

sycl/test-e2e/Adapters/level_zero/interop-thread.cpp

@@ -61,7 +61,10 @@ ze_event_pool_handle_t event_pool = {};
 std::vector<operation> 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(0);
+  assert(result == ZE_RESULT_SUCCESS);
 
   uint32_t driverCount = 0;
   assert(zeDriverGet(&driverCount, nullptr) == 0);

sycl/test-e2e/Adapters/level_zero/uuid.cpp

@@ -25,6 +25,15 @@ 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;
+
+  // 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)

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;

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();

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 {

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];

sycl/test-e2e/Regression/cache_test.cpp

@@ -151,6 +151,14 @@ int queryFromNativeHandle(std::vector<sycl::platform> *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.