Added 2 descriptors: max_mem_alloc_size, max_clock_frequency

Added DPCTLDevice_GetMaxMemAllocSize, and DPCTLDevice_GetMaxClockFrequency.

Author: oleksandr-pavlyk

libsyclinterface/include/dpctl_sycl_device_interface.h

@@ -709,6 +709,28 @@ DPCTL_API
 uint32_t DPCTLDevice_GetGlobalMemCacheLineSize(
     __dpctl_keep const DPCTLSyclDeviceRef DRef);
 
+/*!
+ * @brief Wrapper over
+ * device.get_info<info::device::max_clock_frequency>
+ *
+ * @param    DRef           Opaque pointer to a sycl::device
+ * @return   Returns the maximum clock frequency in MHz as uint32_t.
+ */
+DPCTL_API
+uint32_t
+DPCTLDevice_GetMaxClockFrequency(__dpctl_keep const DPCTLSyclDeviceRef DRef);
+
+/*!
+ * @brief Wrapper over
+ * device.get_info<info::device::max_mem_alloc_size>
+ *
+ * @param    DRef           Opaque pointer to a sycl::device
+ * @return   Returns the maximum size of memory object in bytes as uint64_t.
+ */
+DPCTL_API
+uint64_t
+DPCTLDevice_GetMaxMemAllocSize(__dpctl_keep const DPCTLSyclDeviceRef DRef);
+
 /*!
  * @brief Wrapper over
  * device.get_info<info::device::global_mem_cache_size>

libsyclinterface/source/dpctl_sycl_device_interface.cpp

@@ -718,6 +718,32 @@ uint32_t DPCTLDevice_GetGlobalMemCacheLineSize(
     }
 }
 
+uint32_t
+DPCTLDevice_GetMaxClockFrequency(__dpctl_keep const DPCTLSyclDeviceRef DRef)
+{
+    if (DRef) {
+        auto D = unwrap<device>(DRef);
+        return D->get_info<info::device::max_clock_frequency>();
+    }
+    else {
+        error_handler("Argument DRef is null", __FILE__, __func__, __LINE__);
+        return 0;
+    }
+}
+
+uint64_t
+DPCTLDevice_GetMaxMemAllocSize(__dpctl_keep const DPCTLSyclDeviceRef DRef)
+{
+    if (DRef) {
+        auto D = unwrap<device>(DRef);
+        return D->get_info<info::device::max_mem_alloc_size>();
+    }
+    else {
+        error_handler("Argument DRef is null", __FILE__, __func__, __LINE__);
+        return 0;
+    }
+}
+
 uint64_t
 DPCTLDevice_GetGlobalMemCacheSize(__dpctl_keep const DPCTLSyclDeviceRef DRef)
 {

libsyclinterface/tests/test_sycl_device_interface.cpp

@@ -495,6 +495,13 @@ TEST_P(TestDPCTLSyclDeviceInterface, ChkGetProfilingTimerResolution)
     EXPECT_TRUE(res != 0);
 }
 
+TEST_P(TestDPCTLSyclDeviceInterface, ChkGetMaxMemAllocSize)
+{
+    uint64_t res = 0;
+    EXPECT_NO_FATAL_FAILURE(res = DPCTLDevice_GetMaxMemAllocSize(DRef));
+    EXPECT_TRUE(res != 0);
+}
+
 TEST_P(TestDPCTLSyclDeviceInterface, ChkGetGlobalMemCacheSize)
 {
     uint64_t res = 0;
@@ -509,6 +516,13 @@ TEST_P(TestDPCTLSyclDeviceInterface, ChkGetGlobalMemCacheLineSize)
     EXPECT_TRUE(res != 0);
 }
 
+TEST_P(TestDPCTLSyclDeviceInterface, ChkGetGetMaxClockFrequency)
+{
+    uint32_t res = 0;
+    EXPECT_NO_FATAL_FAILURE(res = DPCTLDevice_GetMaxClockFrequency(DRef));
+    EXPECT_TRUE(res != 0);
+}
+
 TEST_P(TestDPCTLSyclDeviceInterface, ChkGetGlobalMemCacheType)
 {
     DPCTLGlobalMemCacheType res = DPCTL_MEM_CACHE_TYPE_INDETERMINATE;
@@ -833,6 +847,13 @@ TEST_F(TestDPCTLSyclDeviceNullArgs, ChkGetProfilingTimerResolution)
     ASSERT_TRUE(res == 0);
 }
 
+TEST_F(TestDPCTLSyclDeviceNullArgs, ChkGetMaxMemAllocSize)
+{
+    uint64_t res = 1;
+    EXPECT_NO_FATAL_FAILURE(res = DPCTLDevice_GetMaxMemAllocSize(Null_DRef));
+    ASSERT_TRUE(res == 0);
+}
+
 TEST_F(TestDPCTLSyclDeviceNullArgs, ChkGetGlobalMemCacheSize)
 {
     uint64_t res = 1;
@@ -848,6 +869,13 @@ TEST_F(TestDPCTLSyclDeviceNullArgs, ChkGetGlobalMemCacheLineSize)
     ASSERT_TRUE(res == 0);
 }
 
+TEST_F(TestDPCTLSyclDeviceNullArgs, ChkGetMaxClockFrequency)
+{
+    uint32_t res = 1;
+    EXPECT_NO_FATAL_FAILURE(res = DPCTLDevice_GetMaxClockFrequency(Null_DRef));
+    ASSERT_TRUE(res == 0);
+}
+
 TEST_F(TestDPCTLSyclDeviceNullArgs, ChkGetGlobalMemCacheType)
 {
     DPCTLGlobalMemCacheType res = DPCTL_MEM_CACHE_TYPE_NONE;