[SYCL][Bindless][E2E] Match UUID when searching for Vulkan device (#18562)

Currently the Vulkan interop tests create a Vulkan device based on the
name of the SYCL device. This only works for very simple cases where the
Vulkan driver
and the SYCL backend driver report a similar enough name.

With this patch, a Vulkan device is created from a SYCL one by matching
the device UUID, which guarantees the same device.

Author: ProGTX

sycl/test-e2e/bindless_images/vulkan_interop/buffer_usm.cpp

@@ -299,8 +299,7 @@ int main() {
 
   sycl::device syclDevice;
 
-  if (vkutil::setupDevice(syclDevice.get_info<sycl::info::device::name>()) !=
-      VK_SUCCESS) {
+  if (vkutil::setupDevice(syclDevice) != VK_SUCCESS) {
     std::cerr << "Device setup failed!\n";
     return EXIT_FAILURE;
   }

sycl/test-e2e/bindless_images/vulkan_interop/depth_format.cpp

@@ -363,8 +363,7 @@ int main() {
 
   sycl::device syclDevice;
 
-  if (vkutil::setupDevice(syclDevice.get_info<sycl::info::device::name>()) !=
-      VK_SUCCESS) {
+  if (vkutil::setupDevice(syclDevice) != VK_SUCCESS) {
     std::cerr << "Device setup failed!\n";
     return EXIT_FAILURE;
   }

sycl/test-e2e/bindless_images/vulkan_interop/mipmaps.cpp

@@ -447,8 +447,7 @@ int main() {
 
   sycl::device dev;
 
-  if (vkutil::setupDevice(dev.get_info<sycl::info::device::name>()) !=
-      VK_SUCCESS) {
+  if (vkutil::setupDevice(dev) != VK_SUCCESS) {
     std::cerr << "Device setup failed!\n";
     return EXIT_FAILURE;
   }

sycl/test-e2e/bindless_images/vulkan_interop/sampled_images.cpp

@@ -578,8 +578,7 @@ int main() {
 
   sycl::device dev;
 
-  if (vkutil::setupDevice(dev.get_info<sycl::info::device::name>()) !=
-      VK_SUCCESS) {
+  if (vkutil::setupDevice(dev) != VK_SUCCESS) {
     std::cerr << "Device setup failed!\n";
     return EXIT_FAILURE;
   }

sycl/test-e2e/bindless_images/vulkan_interop/sampled_images_USM.cpp

@@ -328,8 +328,7 @@ int main() {
 
   sycl::device dev;
 
-  if (vkutil::setupDevice(dev.get_info<sycl::info::device::name>()) !=
-      VK_SUCCESS) {
+  if (vkutil::setupDevice(dev) != VK_SUCCESS) {
     std::cerr << "Device setup failed!\n";
     return EXIT_FAILURE;
   }

sycl/test-e2e/bindless_images/vulkan_interop/unsampled_images.cpp

@@ -677,8 +677,7 @@ int main() {
 
   sycl::device dev;
 
-  if (vkutil::setupDevice(dev.get_info<sycl::info::device::name>()) !=
-      VK_SUCCESS) {
+  if (vkutil::setupDevice(dev) != VK_SUCCESS) {
     std::cerr << "Device setup failed!\n";
     return EXIT_FAILURE;
   }

sycl/test-e2e/bindless_images/vulkan_interop/unsampled_images_timeline_semaphore.cpp

@@ -480,8 +480,7 @@ int main() {
 
   sycl::device dev;
 
-  if (vkutil::setupDevice(dev.get_info<sycl::info::device::name>()) !=
-      VK_SUCCESS) {
+  if (vkutil::setupDevice(dev) != VK_SUCCESS) {
     std::cerr << "Device setup failed!\n";
     return EXIT_FAILURE;
   }

sycl/test-e2e/bindless_images/vulkan_interop/vulkan_common.hpp

@@ -207,8 +207,8 @@ getSupportedDeviceExtensions(std::vector<VkExtensionProperties> &extensions,
   return VK_SUCCESS;
 }
 
-// Set up the Vulkan device.
-VkResult setupDevice(std::string device) {
+// Set up the Vulkan device from the SYCL one
+VkResult setupDevice(const sycl::device &dev) {
   uint32_t physicalDeviceCount = 0;
   // Get all physical devices.
   VK_CHECK_CALL_RET(
@@ -237,24 +237,25 @@ VkResult setupDevice(std::string device) {
 #endif
   };
 
-  // Make lowercase to fix inconsistent capitalization between SYCL and Vulkan
-  // device naming.
-  std::transform(device.begin(), device.end(), device.begin(),
-                 [](unsigned char c) { return std::tolower(c); });
+  const auto UUID = dev.get_info<sycl::ext::intel::info::device::uuid>();
 
-  // From all physical devices, find the first one that supports all our
-  // required device extensions.
+  // From all physical devices, find the first one with a matching UUID
+  // that also supports all our required device extensions
   for (int i = 0; i < physicalDeviceCount; i++) {
     vk_physical_device = physicalDevices[i];
-    VkPhysicalDeviceProperties props;
-    vkGetPhysicalDeviceProperties(vk_physical_device, &props);
-    std::string name(props.deviceName);
 
-    // Make lowercase for comparision.
-    std::transform(name.begin(), name.end(), name.begin(),
-                   [](unsigned char c) { return std::tolower(c); });
+    VkPhysicalDeviceIDProperties devIDProps = {
+        .sType = VK_STRUCTURE_TYPE_PHYSICAL_DEVICE_ID_PROPERTIES};
 
-    if (name.find(device) == std::string::npos) {
+    VkPhysicalDeviceProperties2 devProps2 = {
+        .sType = VK_STRUCTURE_TYPE_PHYSICAL_DEVICE_PROPERTIES_2,
+        .pNext = &devIDProps};
+
+    vkGetPhysicalDeviceProperties2(vk_physical_device, &devProps2);
+
+    if (!std::equal(std::begin(UUID), std::end(UUID),
+                    std::begin(devIDProps.deviceUUID),
+                    std::begin(devIDProps.deviceUUID) + VK_UUID_SIZE)) {
       continue;
     }
 
@@ -275,8 +276,8 @@ VkResult setupDevice(std::string device) {
     }
 
     foundDevice = true;
-    std::cout << "Found suitable Vulkan device: " << props.deviceName
-              << std::endl;
+    std::cout << "Found suitable Vulkan device: "
+              << devProps2.properties.deviceName << std::endl;
     break;
   }