Addresses #587 on DPCTL-CAPI side

Adds DPCTLDevice_GetGlobalMemSize(DRef) which gives size of device
global memory in bytes as uint64_t (aka size_t)

Adds DPCTLDevice_GetLocalMemSize(DRef) which gives size of device
local memory in bytes as uint64_t

Author: oleksandr-pavlyk

dpctl-capi/include/dpctl_sycl_device_interface.h

@@ -177,6 +177,28 @@ DPCTL_API
 uint32_t
 DPCTLDevice_GetMaxComputeUnits(__dpctl_keep const DPCTLSyclDeviceRef DRef);
 
+/*!
+ * @brief Wrapper over device.get_info<info::device::global_mem_size>().
+ *
+ * @param    DRef           Opaque pointer to a ``sycl::device``
+ * @return   Returns the valid result if device exists else returns 0.
+ * @ingroup DeviceInterface
+ */
+DPCTL_API
+uint64_t
+DPCTLDevice_GetGlobalMemSize(__dpctl_keep const DPCTLSyclDeviceRef DRef);
+
+/*!
+ * @brief Wrapper over device.get_info<info::device::local_mem_size>().
+ *
+ * @param    DRef           Opaque pointer to a ``sycl::device``
+ * @return   Returns the valid result if device exists else returns 0.
+ * @ingroup DeviceInterface
+ */
+DPCTL_API
+uint64_t
+DPCTLDevice_GetLocalMemSize(__dpctl_keep const DPCTLSyclDeviceRef DRef);
+
 /*!
  * @brief Wrapper for get_info<info::device::max_work_item_dimensions>().
  *

dpctl-capi/source/dpctl_sycl_device_interface.cpp

@@ -186,6 +186,37 @@ DPCTLDevice_GetMaxComputeUnits(__dpctl_keep const DPCTLSyclDeviceRef DRef)
     return nComputeUnits;
 }
 
+uint64_t
+DPCTLDevice_GetGlobalMemSize(__dpctl_keep const DPCTLSyclDeviceRef DRef)
+{
+    uint64_t GlobalMemSize = 0;
+    auto D = unwrap(DRef);
+    if (D) {
+        try {
+            GlobalMemSize = D->get_info<info::device::global_mem_size>();
+        } catch (runtime_error const &re) {
+            // \todo log error
+            std::cerr << re.what() << '\n';
+        }
+    }
+    return GlobalMemSize;
+}
+
+uint64_t DPCTLDevice_GetLocalMemSize(__dpctl_keep const DPCTLSyclDeviceRef DRef)
+{
+    uint64_t LocalMemSize = 0;
+    auto D = unwrap(DRef);
+    if (D) {
+        try {
+            LocalMemSize = D->get_info<info::device::local_mem_size>();
+        } catch (runtime_error const &re) {
+            // \todo log error
+            std::cerr << re.what() << '\n';
+        }
+    }
+    return LocalMemSize;
+}
+
 uint32_t
 DPCTLDevice_GetMaxWorkItemDims(__dpctl_keep const DPCTLSyclDeviceRef DRef)
 {

dpctl-capi/tests/test_sycl_device_interface.cpp

@@ -132,6 +132,20 @@ TEST_P(TestDPCTLSyclDeviceInterface, ChkGetMaxComputeUnits)
     EXPECT_TRUE(n > 0);
 }
 
+TEST_P(TestDPCTLSyclDeviceInterface, ChkGetGlobalMemSize)
+{
+    size_t gm_sz = 0;
+    EXPECT_NO_FATAL_FAILURE(gm_sz = DPCTLDevice_GetGlobalMemSize(DRef));
+    EXPECT_TRUE(gm_sz > 0);
+}
+
+TEST_P(TestDPCTLSyclDeviceInterface, ChkGetLocalMemSize)
+{
+    size_t lm_sz = 0;
+    EXPECT_NO_FATAL_FAILURE(lm_sz = DPCTLDevice_GetLocalMemSize(DRef));
+    EXPECT_TRUE(lm_sz > 0);
+}
+
 TEST_P(TestDPCTLSyclDeviceInterface, ChkGetMaxWorkItemDims)
 {
     size_t n = 0;