Added size_t DPCTLDevice_Hash(DRef)

Author: oleksandr-pavlyk

dpctl-capi/include/dpctl_sycl_device_interface.h

@@ -555,3 +555,13 @@ uint32_t DPCTLDevice_GetPreferredVectorWidthHalf(
 DPCTL_API
 __dpctl_give DPCTLSyclDeviceRef
 DPCTLDevice_GetParentDevice(__dpctl_keep const DPCTLSyclDeviceRef DRef);
+
+/*!
+ * @brief Wrapper over
+ * std::hash<sycl::device>'s operator()
+ *
+ * @param    DRef           Opaque pointer to a sycl::device
+ * @return   Returns hash value.
+ */
+DPCTL_API
+size_t DPCTLDevice_Hash(__dpctl_keep const DPCTLSyclDeviceRef DRef);

dpctl-capi/source/dpctl_sycl_device_interface.cpp

@@ -690,3 +690,18 @@ __dpctl_give DPCTLDeviceVectorRef DPCTLDevice_CreateSubDevicesByAffinity(
     }
     return wrap(Devices);
 }
+
+size_t DPCTLDevice_Hash(__dpctl_keep const DPCTLSyclDeviceRef DRef)
+{
+    if (DRef) {
+        auto D = unwrap(DRef);
+        std::hash<device> hash_fn;
+        return hash_fn(*D);
+    }
+    else {
+        // todo: log error
+        std::cerr << "Argument DRef is null"
+                  << "/n";
+        return 0;
+    }
+}

dpctl-capi/tests/test_sycl_device_interface.cpp

@@ -68,6 +68,8 @@ TEST_P(TestDPCTLSyclDeviceInterface, ChkCopy)
     DPCTLSyclDeviceRef Copied_DRef = nullptr;
     EXPECT_NO_FATAL_FAILURE(Copied_DRef = DPCTLDevice_Copy(DRef));
     EXPECT_TRUE(bool(Copied_DRef));
+    EXPECT_TRUE(DPCTLDevice_AreEq(DRef, Copied_DRef));
+    EXPECT_TRUE(DPCTLDevice_Hash(DRef) == DPCTLDevice_Hash(Copied_DRef));
     EXPECT_NO_FATAL_FAILURE(DPCTLDevice_Delete(Copied_DRef));
 }