[SYCL] Make the Level Zero default backend (#1883)

Signed-off-by: Artur Gainullin <[email protected]>

Author: againull

sycl/source/detail/pi.cpp

@@ -319,6 +319,11 @@ static void initializePlugins(vector_class<plugin> *Plugins) {
                PluginNames[I].first.find("cuda") != std::string::npos) {
       // Use the CUDA plugin as the GlobalPlugin
       GlobalPlugin = std::make_shared<plugin>(PluginInformation, backend::cuda);
+    } else if (InteropBE == backend::level0 &&
+               PluginNames[I].first.find("level0") != std::string::npos) {
+      // Use the LEVEL0 plugin as the GlobalPlugin
+      GlobalPlugin =
+          std::make_shared<plugin>(PluginInformation, backend::level0);
     }
     Plugins->emplace_back(plugin(PluginInformation, PluginNames[I].second));
     if (trace(TraceLevel::PI_TRACE_BASIC))

sycl/source/device_selector.cpp

@@ -19,13 +19,13 @@ __SYCL_INLINE_NAMESPACE(cl) {
 namespace sycl {
 
 // Utility function to check if device is of the preferred backend.
-// Currently preference is given to the opencl backend.
+// Currently preference is given to the level0 backend.
 static bool isDeviceOfPreferredSyclBe(const device &Device) {
   if (Device.is_host())
     return false;
 
   return detail::getSyclObjImpl(Device)->getPlugin().getBackend() ==
-         backend::opencl;
+         backend::level0;
 }
 
 device device_selector::select_device() const {

sycl/test/plugins/sycl-ls-gpu-default.cpp

@@ -0,0 +1,15 @@
+// REQUIRES: gpu, level0
+
+// RUN: sycl-ls --verbose >%t.default.out
+// RUN: FileCheck %s --check-prefixes=CHECK-GPU-BUILTIN,CHECK-GPU-CUSTOM --input-file %t.default.out
+
+// CHECK-GPU-BUILTIN: gpu_selector(){{.*}}GPU : 0.91
+// CHECK-GPU-CUSTOM: custom_selector(gpu){{.*}}GPU : 0.91
+
+//==-- sycl-ls-gpu-default.cpp - SYCL test for default selected gpu device -==//
+//
+// Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions.
+// See https://llvm.org/LICENSE.txt for license information.
+// SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception
+//
+//===----------------------------------------------------------------------===//

sycl/test/plugins/sycl-ls-gpu-opencl.cpp

@@ -1,8 +1,5 @@
 // REQUIRES: gpu, opencl
 
-// RUN: sycl-ls --verbose >%t.default.out
-// RUN: FileCheck %s --check-prefixes=CHECK-GPU-BUILTIN,CHECK-GPU-CUSTOM --input-file %t.default.out
-
 // RUN: env SYCL_BE=PI_OPENCL sycl-ls --verbose >%t.opencl.out
 // RUN: FileCheck %s --check-prefixes=CHECK-GPU-BUILTIN,CHECK-GPU-CUSTOM --input-file %t.opencl.out
 

sycl/test/scheduler/MultipleDevices.cpp

@@ -127,6 +127,8 @@ int main() {
     Result &= multidevice_test(MyQueue1, MyQueue2);
   } catch(cl::sycl::runtime_error &) {
     std::cout << "Skipping CPU and GPU" << std::endl;
+  } catch (cl::sycl::compile_program_error &) {
+    std::cout << "Skipping CPU and GPU" << std::endl;
   }
 
   try {
@@ -135,6 +137,8 @@ int main() {
     Result &= multidevice_test(MyQueue1, MyQueue2);
   } catch(cl::sycl::runtime_error &) {
     std::cout << "Skipping host and GPU" << std::endl;
+  } catch (cl::sycl::compile_program_error &) {
+    std::cout << "Skipping CPU and GPU" << std::endl;
   }
 
   try {
@@ -143,6 +147,8 @@ int main() {
     Result &= multidevice_test(MyQueue1, MyQueue2);
   } catch (cl::sycl::runtime_error &) {
     std::cout << "Skipping GPU and GPU" << std::endl;
+  } catch (cl::sycl::compile_program_error &) {
+    std::cout << "Skipping CPU and GPU" << std::endl;
   }
 
   return Result;