Implemented DPCTLKernel_GetName

Author: ndgrigorian

dpctl/_backend.pxd

@@ -262,6 +262,7 @@ cdef extern from "syclinterface/dpctl_sycl_event_interface.h":
 
 cdef extern from "syclinterface/dpctl_sycl_kernel_interface.h":
     cdef size_t DPCTLKernel_GetNumArgs(const DPCTLSyclKernelRef KRef)
+    cdef const char *DPCTLKernel_GetName(const DPCTLSyclKernelRef KRef)
     cdef void DPCTLKernel_Delete(DPCTLSyclKernelRef KRef)
     cdef DPCTLSyclKernelRef DPCTLKernel_Copy(const DPCTLSyclKernelRef KRef)
     cdef size_t DPCTLKernel_GetWorkGroupSize(const DPCTLSyclKernelRef KRef)

dpctl/program/_program.pyx

@@ -36,6 +36,7 @@ from dpctl._backend cimport (  # noqa: E211, E402;
     DPCTLKernel_GetCompileSubGroupSize,
     DPCTLKernel_GetMaxNumSubGroups,
     DPCTLKernel_GetNumArgs,
+    DPCTLKernel_GetName,
     DPCTLKernel_GetPreferredWorkGroupSizeMultiple,
     DPCTLKernel_GetPrivateMemSize,
     DPCTLKernel_GetWorkGroupSize,
@@ -178,7 +179,9 @@ cdef api SyclKernel SyclKernel_Make(DPCTLSyclKernelRef KRef):
     instance from opaque sycl kernel reference.
     """
     cdef DPCTLSyclKernelRef copied_KRef = DPCTLKernel_Copy(KRef)
-    return SyclKernel._create(copied_KRef, "foo")
+    cdef const char *name = DPCTLKernel_GetName(copied_KRef)
+    copied_name = name.decode("UTF-8")
+    return SyclKernel._create(copied_KRef, copied_name)
 
 cdef class SyclProgram:
     """ Wraps a ``sycl::kernel_bundle<sycl::bundle_state::executable>`` object

libsyclinterface/include/dpctl_sycl_kernel_interface.h

@@ -51,6 +51,18 @@ DPCTL_C_EXTERN_C_BEGIN
 DPCTL_API
 size_t DPCTLKernel_GetNumArgs(__dpctl_keep const DPCTLSyclKernelRef KRef);
 
+/*!
+ * @brief Returns a C string for the function name.
+ *
+ * @param    KRef           DPCTLSyclKernelRef pointer to a SYCL
+ *                          interoperability kernel.
+ * @return   A C string containing the name of the function.
+ * @ingroup KernelInterface
+ */
+DPCTL_API
+__dpctl_give const char *
+DPCTLKernel_GetName(__dpctl_keep const DPCTLSyclKernelRef KRef);
+
 /*!
  * @brief Deletes the DPCTLSyclKernelRef after casting it to a
  * ``sycl::kernel``.

libsyclinterface/source/dpctl_sycl_kernel_interface.cpp

@@ -54,6 +54,21 @@ size_t DPCTLKernel_GetNumArgs(__dpctl_keep const DPCTLSyclKernelRef KRef)
     return static_cast<size_t>(num_args);
 }
 
+__dpctl_give const char *
+DPCTLKernel_GetName(__dpctl_keep const DPCTLSyclKernelRef KRef)
+{
+    if (!KRef) {
+        error_handler("Cannot get the name from "
+                      "DPCTLSyclKernelRef as input is a nullptr.",
+                      __FILE__, __func__, __LINE__);
+        return nullptr;
+    }
+
+    auto sycl_kernel = unwrap(KRef);
+    auto name = sycl_kernel->get_info<info::kernel::function_name>();
+    return dpctl::helper::cstring_from_string(name);
+}
+
 void DPCTLKernel_Delete(__dpctl_take DPCTLSyclKernelRef KRef)
 {
     delete unwrap(KRef);