[CI] Add "loader" support to conformance testing

This expands our CI to test the loader; the dispatcher that is
used when multiple adapters are availabe.

Previously, the unit tests forced a specific adapter, via
`UR_ADAPTERS_FORCE_LOAD`. Now an extra "loader" target is created
for each test suite, which doesn't set that variable and allows
the loader to be used.

In addition, the test runner's adapter selection logic has been
rewritten to support a "--backend" variable, which allows you to
select a backend (OpenCL, Level Zero, etc.).

The platform selection has also been expanded to support
filtering by a backend to match that platform only on that backend
(e.g. `UR_CTS_ADAPTER_PLATFORM="opencl:Fictional Corp(R)"`).

The old "run on hardware" jobs should behave the same (they have
the loader tests disabled), but there is a new
`combined-opencl-level-zero` job that tests a build with both
OpenCL and Level Zero available.

.github/workflows/build-hw-reusable.yml

@@ -7,13 +7,21 @@ on:
       adapter_name:
         required: true
         type: string
+      other_adapter_name:
+        required: false
+        type: string
+        default: ""
       runner_name:
         required: true
         type: string
       platform:
         required: false
         type: string
         default: ""
+      other_platform:
+        required: false
+        type: string
+        default: ""
       static_loader:
         required: false
         type: string
@@ -39,9 +47,14 @@ jobs:
     if: github.repository == 'oneapi-src/unified-runtime'  # run only on upstream; forks won't have the HW
     strategy:
       matrix:
-        adapter: [
-          {name: "${{inputs.adapter_name}}", platform: "${{inputs.platform}}", static_Loader: "${{inputs.static_loader}}", static_adapter: "${{inputs.static_loader}}"},
-        ]
+        adapter: [{
+          name: "${{inputs.adapter_name}}",
+          other_name: "${{inputs.other_adapter_name}}",
+          platform: "${{inputs.platform}}",
+          other_platform: "${{inputs.other_platform}}",
+          static_Loader: "${{inputs.static_loader}}",
+          static_adapter: "${{inputs.static_loader}}"
+        }]
         build_type: [Debug, Release]
         compiler: [{c: gcc, cxx: g++}, {c: clang, cxx: clang++}]
         # TODO: The latest L0 loader segfaults when built with clang.
@@ -83,10 +96,12 @@ jobs:
         -DUR_DEVELOPER_MODE=ON
         -DUR_BUILD_TESTS=ON
         -DUR_BUILD_ADAPTER_${{matrix.adapter.name}}=ON
+        ${{ matrix.adapter.other_name != '' && format('-DUR_BUILD_ADAPTER_{}=ON', matrix.adapter.other_name) || '' }}
         -DUR_STATIC_LOADER=${{matrix.adapter.static_Loader}}
         -DUR_STATIC_ADAPTER_${{matrix.adapter.name}}=${{matrix.adapter.static_adapter}}
         -DUR_DPCXX=${{github.workspace}}/dpcpp_compiler/bin/clang++
         -DUR_SYCL_LIBRARY_DIR=${{github.workspace}}/dpcpp_compiler/lib
+        -DUR_CONFORMANCE_TEST_LOADER=${{ matrix.adapter.other_name != '' && 'ON' || 'OFF' }}
         ${{ matrix.adapter.name == 'HIP' && '-DUR_CONFORMANCE_AMD_ARCH=gfx1030' || '' }}
         ${{ matrix.adapter.name == 'HIP' && '-DUR_HIP_PLATFORM=AMD' || '' }}
 
@@ -97,10 +112,12 @@ jobs:
     - name: Test adapter specific
       working-directory: ${{github.workspace}}/build
       run: ctest -C ${{matrix.build_type}} --output-on-failure -L "adapter-specific" --timeout 180
+      # Don't run adapter specific tests when building multiple adapters
+      if: ${{ matrix.adapter.other_name == '' }}
 
     - name: Test adapters
       working-directory: ${{github.workspace}}/build
-      run: env UR_CTS_ADAPTER_PLATFORM="${{matrix.adapter.platform}}" ctest -C ${{matrix.build_type}} --output-on-failure -L "conformance" --timeout 180
+      run: env UR_CTS_ADAPTER_PLATFORM="${{matrix.adapter.name}}:${{matrix.adapter.platform}};${{matrix.adapter.other_name}}:${{matrix.adapter.other_platform}}" ctest -C ${{matrix.build_type}} --output-on-failure -L "conformance" --timeout 180
 
     - name: Get information about platform
       if: ${{ always() }}

.github/workflows/cmake.yml

@@ -186,6 +186,15 @@ jobs:
       adapter_name: NATIVE_CPU
       runner_name: NATIVE_CPU
 
+  combined-opencl-level-zero:
+    name: OpenCL + Level Zero
+    uses: ./.github/workflows/build-hw-reusable.yml
+    with:
+      adapter_name: OPENCL
+      other_adapter_name: L0
+      runner_name: OPENCL
+      platform: "Intel(R) OpenCL"
+
   e2e-level-zero:
     name: E2E L0
     permissions:

.github/workflows/multi_device.yml

@@ -48,6 +48,7 @@ jobs:
         -DUR_DEVELOPER_MODE=ON
         -DUR_BUILD_TESTS=ON
         -DUR_BUILD_ADAPTER_${{matrix.adapter.name}}=ON
+        -DUR_CONFORMANCE_TEST_LOADER=OFF
         -DUR_TEST_DEVICES_COUNT=2
 
     - name: Build

CMakeLists.txt

@@ -68,6 +68,7 @@ set(UR_CONFORMANCE_TARGET_TRIPLES "" CACHE STRING
     "List of sycl targets to build CTS device binaries for")
 set(UR_CONFORMANCE_AMD_ARCH "" CACHE STRING "AMD device target ID to build CTS binaries for")
 option(UR_CONFORMANCE_ENABLE_MATCH_FILES "Enable CTS match files" ON)
+option(UR_CONFORMANCE_TEST_LOADER "Also test the loader in the conformance tests" ON)
 set(UR_ADAPTER_LEVEL_ZERO_SOURCE_DIR "" CACHE PATH
     "Path to external 'level_zero' adapter source dir")
 set(UR_ADAPTER_OPENCL_SOURCE_DIR "" CACHE PATH

source/loader/ur_ldrddi.cpp

@@ -506,6 +506,9 @@ __urdlllocal ur_result_t UR_APICALL urDeviceGetInfo(
 
     [[maybe_unused]] auto context = getContext();
 
+    // For testing
+    abort();
+
     // extract platform's function pointer table
     auto dditable = reinterpret_cast<ur_device_object_t *>(hDevice)->dditable;
     auto pfnGetInfo = dditable->ur.Device.pfnGetInfo;

test/adapters/CMakeLists.txt

@@ -63,7 +63,7 @@ function(add_adapter_memcheck_test name)
         add_test(NAME ${test_name}
                 COMMAND ${CMAKE_COMMAND}
                 -D TEST_FILE=valgrind
-                -D TEST_ARGS="--tool=memcheck --leak-check=full $<TARGET_FILE:${target}> --devices_count=${UR_TEST_DEVICES_COUNT} --platforms_count=${UR_TEST_DEVICES_COUNT}"
+                -D TEST_ARGS="--tool=memcheck --leak-check=full $<TARGET_FILE:${target}> --backend=${backend} --devices_count=${UR_TEST_DEVICES_COUNT} --platforms_count=${UR_TEST_DEVICES_COUNT}"
                 -D MODE=stderr
                 -D MATCH_FILE=${CMAKE_CURRENT_SOURCE_DIR}/${name}_memcheck.match
                 -P ${PROJECT_SOURCE_DIR}/cmake/match.cmake

test/conformance/CMakeLists.txt

@@ -9,15 +9,15 @@ set(UR_CONFORMANCE_DEVICE_BINARIES_DIR
     "${CMAKE_CURRENT_BINARY_DIR}/device_binaries" CACHE INTERNAL
     "Internal cache variable for device binaries directory")
 
-function(add_test_adapter name adapter)
+function(add_test_adapter name adapter backend force)
     if(NOT "${ARGN}" STREQUAL "")
         set(EXTRA_NAME "-${ARGN}")
     endif()
     set(TEST_TARGET_NAME test-${name})
     set(TEST_NAME ${name}-${adapter}${EXTRA_NAME})
 
     set(TEST_COMMAND
-        "${PROJECT_BINARY_DIR}/bin/${TEST_TARGET_NAME} --devices_count=${UR_TEST_DEVICES_COUNT} --platforms_count=${UR_TEST_PLATFORMS_COUNT}"
+        "${PROJECT_BINARY_DIR}/bin/${TEST_TARGET_NAME} --backend=${backend} --devices_count=${UR_TEST_DEVICES_COUNT} --platforms_count=${UR_TEST_PLATFORMS_COUNT}"
     )
     set(MATCH_FILE "${CMAKE_CURRENT_SOURCE_DIR}/${name}_${adapter}${EXTRA_NAME}.match")
 
@@ -41,7 +41,9 @@ function(add_test_adapter name adapter)
         )
     endif()
 
-    set(TEST_ENV UR_ADAPTERS_FORCE_LOAD="$<TARGET_FILE:ur_${adapter}>")
+    if(${force})
+        set(TEST_ENV UR_ADAPTERS_FORCE_LOAD="$<TARGET_FILE:ur_${adapter}>")
+    endif()
     if(UR_CONFORMANCE_ENABLE_MATCH_FILES)
         list(APPEND TEST_ENV GTEST_COLOR=no)
     endif()
@@ -66,22 +68,43 @@ function(add_conformance_test name)
         unit_tests_helpers)
 
     if(UR_BUILD_ADAPTER_CUDA OR UR_BUILD_ADAPTER_ALL)
-        add_test_adapter(${name} adapter_cuda)
+        add_test_adapter(${name} adapter_cuda CUDA ON)
     endif()
     if(UR_BUILD_ADAPTER_HIP OR UR_BUILD_ADAPTER_ALL)
-        add_test_adapter(${name} adapter_hip)
+        add_test_adapter(${name} adapter_hip HIP ON)
     endif()
     if(UR_BUILD_ADAPTER_L0 OR UR_BUILD_ADAPTER_ALL)
-        add_test_adapter(${name} adapter_level_zero)
+        add_test_adapter(${name} adapter_level_zero LEVEL_ZERO ON)
     endif()
     if(UR_BUILD_ADAPTER_L0_V2)
-        add_test_adapter(${name} adapter_level_zero_v2)
+        add_test_adapter(${name} adapter_level_zero_v2 LEVEL_ZERO ON)
     endif()
     if(UR_BUILD_ADAPTER_OPENCL OR UR_BUILD_ADAPTER_ALL)
-        add_test_adapter(${name} adapter_opencl)
+        add_test_adapter(${name} adapter_opencl OPENCL ON)
     endif()
     if(UR_BUILD_ADAPTER_NATIVE_CPU OR UR_BUILD_ADAPTER_ALL)
-        add_test_adapter(${name} adapter_native_cpu)
+        add_test_adapter(${name} adapter_native_cpu NATIVE_CPU ON)
+    endif()
+
+    if(UR_CONFORMANCE_TEST_LOADER)
+        if(UR_BUILD_ADAPTER_CUDA OR UR_BUILD_ADAPTER_ALL)
+            add_test_adapter(${name} adapter_cuda_loader CUDA OFF)
+        endif()
+        if(UR_BUILD_ADAPTER_HIP OR UR_BUILD_ADAPTER_ALL)
+            add_test_adapter(${name} adapter_hip_loader HIP OFF)
+        endif()
+        if(UR_BUILD_ADAPTER_L0 OR UR_BUILD_ADAPTER_ALL)
+            add_test_adapter(${name} adapter_level_zero_loader LEVEL_ZERO OFF)
+        endif()
+        if(UR_BUILD_ADAPTER_L0_V2)
+            add_test_adapter(${name} adapter_level_zero_v2_loader LEVEL_ZERO OFF)
+        endif()
+        if(UR_BUILD_ADAPTER_OPENCL OR UR_BUILD_ADAPTER_ALL)
+            add_test_adapter(${name} adapter_opencl_loader OPENCL OFF)
+        endif()
+        if(UR_BUILD_ADAPTER_NATIVE_CPU OR UR_BUILD_ADAPTER_ALL)
+            add_test_adapter(${name} adapter_native_cpu_loader NATIVE_CPU OFF)
+        endif()
     endif()
 
     if(NOT (UR_BUILD_ADAPTER_CUDA OR UR_BUILD_ADAPTER_HIP

test/conformance/adapter/adapter_adapter_native_cpu_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/adapter/adapter_adapter_native_cpu.match

test/conformance/context/context_adapter_level_zero_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/context/context_adapter_level_zero.match

test/conformance/context/context_adapter_level_zero_v2_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/context/context_adapter_level_zero_v2.match

test/conformance/context/context_adapter_native_cpu_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/context/context_adapter_native_cpu.match

test/conformance/cts_exe.py

@@ -23,11 +23,13 @@
     parser.add_argument("--test_command", help="Ctest test case")
     parser.add_argument("--devices_count", type=str, help="Number of devices on which tests will be run")
     parser.add_argument("--platforms_count", type=str, help="Number of platforms on which tests will be run")
+    parser.add_argument("--backend", type=str, help="Number of platforms on which tests will be run")
     args = parser.parse_args()
 
     result = subprocess.Popen([args.test_command, '--gtest_brief=1',        # nosec B603
                                f'--devices_count={args.devices_count}',
-                               f'--platforms_count={args.platforms_count}'],
+                               f'--platforms_count={args.platforms_count}',
+                               f'--backend={args.backend}'],
                                stdout=subprocess.PIPE, stderr=subprocess.STDOUT, text=True)
 
     pat = re.compile(r'\[( )*FAILED( )*\]')

test/conformance/device/device_adapter_cuda_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/device/device_adapter_cuda.match

test/conformance/device/device_adapter_hip_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/device/device_adapter_hip.match

test/conformance/device/device_adapter_level_zero_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/device/device_adapter_level_zero.match

test/conformance/device/device_adapter_level_zero_v2_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/device/device_adapter_level_zero_v2.match

test/conformance/device/device_adapter_native_cpu_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/device/device_adapter_native_cpu.match

test/conformance/device/device_adapter_opencl_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/device/device_adapter_opencl.match

test/conformance/device_code/single.cpp

@@ -0,0 +1,20 @@
+// Copyright (C) 2023 Intel Corporation
+// Part of the Unified-Runtime Project, under the Apache License v2.0 with LLVM Exceptions.
+// See LICENSE.TXT
+// SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception
+
+#include <sycl/sycl.hpp>
+
+class Single;
+
+int main() {
+    sycl::queue deviceQueue;
+    sycl::range<1> numOfItems{1};
+
+    deviceQueue.submit([&](sycl::handler &cgh) {
+        auto kern = [=]() {};
+        cgh.single_task<Single>(kern);
+    });
+
+    return 0;
+}

test/conformance/enqueue/enqueue_adapter_cuda_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/enqueue/enqueue_adapter_cuda.match

test/conformance/enqueue/enqueue_adapter_hip_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/enqueue/enqueue_adapter_hip.match

test/conformance/enqueue/enqueue_adapter_level_zero_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/enqueue/enqueue_adapter_level_zero.match

test/conformance/enqueue/enqueue_adapter_level_zero_v2_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/enqueue/enqueue_adapter_level_zero_v2.match

test/conformance/enqueue/enqueue_adapter_native_cpu_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/enqueue/enqueue_adapter_native_cpu.match

test/conformance/enqueue/enqueue_adapter_opencl_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/enqueue/enqueue_adapter_opencl.match

test/conformance/event/event_adapter_cuda_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/event/event_adapter_cuda.match

test/conformance/event/event_adapter_hip_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/event/event_adapter_hip.match

test/conformance/event/event_adapter_level_zero_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/event/event_adapter_level_zero.match

test/conformance/event/event_adapter_level_zero_v2_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/event/event_adapter_level_zero_v2.match

test/conformance/event/event_adapter_native_cpu_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/event/event_adapter_native_cpu.match

test/conformance/exp_command_buffer/exp_command_buffer_adapter_cuda_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/exp_command_buffer/exp_command_buffer_adapter_cuda.match

test/conformance/exp_command_buffer/exp_command_buffer_adapter_hip_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/exp_command_buffer/exp_command_buffer_adapter_hip.match

test/conformance/exp_command_buffer/exp_command_buffer_adapter_level_zero_v2_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/exp_command_buffer/exp_command_buffer_adapter_level_zero_v2.match

test/conformance/exp_command_buffer/exp_command_buffer_adapter_native_cpu_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/exp_command_buffer/exp_command_buffer_adapter_native_cpu.match

test/conformance/exp_enqueue_native/exp_enqueue_native_adapter_level_zero_v2_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/exp_enqueue_native/exp_enqueue_native_adapter_level_zero_v2.match

test/conformance/exp_launch_properties/exp_launch_properties_adapter_native_cpu_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/exp_launch_properties/exp_launch_properties_adapter_native_cpu.match

test/conformance/integration/integration_adapter_level_zero_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/integration/integration_adapter_level_zero.match

test/conformance/integration/integration_adapter_level_zero_v2_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/integration/integration_adapter_level_zero_v2.match

test/conformance/integration/integration_adapter_native_cpu_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/integration/integration_adapter_native_cpu.match

test/conformance/integration/integration_adapter_opencl_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/integration/integration_adapter_opencl.match

test/conformance/kernel/kernel_adapter_cuda_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/kernel/kernel_adapter_cuda.match

test/conformance/kernel/kernel_adapter_hip_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/kernel/kernel_adapter_hip.match

test/conformance/kernel/kernel_adapter_level_zero_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/kernel/kernel_adapter_level_zero.match

test/conformance/kernel/kernel_adapter_level_zero_v2_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/kernel/kernel_adapter_level_zero_v2.match

test/conformance/kernel/kernel_adapter_native_cpu_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/kernel/kernel_adapter_native_cpu.match

test/conformance/kernel/kernel_adapter_opencl_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/kernel/kernel_adapter_opencl.match

test/conformance/memory/memory_adapter_cuda_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/memory/memory_adapter_cuda.match

test/conformance/memory/memory_adapter_hip_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/memory/memory_adapter_hip.match

test/conformance/memory/memory_adapter_level_zero_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/memory/memory_adapter_level_zero.match

test/conformance/memory/memory_adapter_level_zero_v2_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/memory/memory_adapter_level_zero_v2.match

test/conformance/memory/memory_adapter_native_cpu_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/memory/memory_adapter_native_cpu.match

test/conformance/memory/memory_adapter_opencl_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/memory/memory_adapter_opencl.match

test/conformance/platform/platform_adapter_cuda_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/platform/platform_adapter_cuda.match

test/conformance/platform/platform_adapter_hip_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/platform/platform_adapter_hip.match

test/conformance/platform/platform_adapter_native_cpu_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/platform/platform_adapter_native_cpu.match

test/conformance/program/program_adapter_cuda_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/program/program_adapter_cuda.match

test/conformance/program/program_adapter_hip_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/program/program_adapter_hip.match

test/conformance/program/program_adapter_level_zero_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/program/program_adapter_level_zero.match

test/conformance/program/program_adapter_level_zero_v2_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/program/program_adapter_level_zero_v2.match

test/conformance/program/program_adapter_native_cpu_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/program/program_adapter_native_cpu.match

test/conformance/program/program_adapter_opencl_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/program/program_adapter_opencl.match

test/conformance/queue/queue_adapter_level_zero_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/queue/queue_adapter_level_zero.match

test/conformance/queue/queue_adapter_native_cpu_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/queue/queue_adapter_native_cpu.match

test/conformance/sampler/sampler_adapter_level_zero_loader.match

@@ -0,0 +1 @@
+/home/ross/dpcpp/unified-runtime/test/conformance/sampler/sampler_adapter_level_zero.match