Minor improvements to tests and add cuda node mask test

Author: DBDuncan

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

@@ -1,4 +1,4 @@
-// REQUIRES: aspect-ext_intel_device_info_luid
+// REQUIRES: aspect-ext_intel_device_info_node_mask
 // REQUIRES: gpu, level_zero, level_zero_dev_kit, windows
 
 // RUN: %{build} %level_zero_options -o %t.out

sycl/test-e2e/Adapters/luid-cuda.cpp

@@ -1,10 +1,10 @@
 // REQUIRES: aspect-ext_intel_device_info_luid
-// REQUIRES: gpu, cuda, cuda_dev_kit, windows
+// REQUIRES: gpu, target-nvidia, cuda_dev_kit, windows
 
 // RUN: %{build} %cuda_options -o %t.out
 // RUN: %{run} %t.out
 
-// Test that the LUID is read correctly from Level Zero.
+// Test that the LUID is read correctly from CUDA.
 
 #include <iomanip>
 #include <iostream>

sycl/test-e2e/Adapters/node_mask-cuda.cpp

@@ -0,0 +1,38 @@
+// REQUIRES: aspect-ext_intel_device_info_node_mask
+// REQUIRES: gpu, target-nvidia, cuda_dev_kit, windows
+
+// RUN: %{build} %cuda_options -o %t.out
+// RUN: %{run} %t.out
+
+// Test that the node mask is read correctly from CUDA.
+
+#include <iomanip>
+#include <iostream>
+#include <sstream>
+#define SYCL_EXT_ONEAPI_BACKEND_CUDA_EXPERIMENTAL 1
+#include <cuda.h>
+#include <sycl/backend.hpp>
+#include <sycl/detail/core.hpp>
+
+int main() {
+  sycl::device dev;
+  auto nodeMaskSYCL = dev.get_info<sycl::ext::intel::info::device::node_mask>();
+
+  std::cout << "SYCL: " << nodeMaskSYCL << std::endl;
+
+  CUdevice cudaDevice = sycl::get_native<sycl::backend::ext_oneapi_cuda>(dev);
+
+  uint32_t *nodeMaskCuda = nullptr;
+
+  cuDeviceGetLuid(nullptr, nodeMaskCuda, cudaDevice);
+
+  std::cout << "CUDA  : " << *nodeMaskCuda << std::endl;
+
+  if (nodeMaskSYCL != *nodeMaskCuda) {
+    std::cout << "FAILED" << std::endl;
+    return -1;
+  }
+
+  std::cout << "PASSED" << std::endl;
+  return 0;
+}