Support local_accessor kernel arguments.

    - Adds support in libsyclinterface:: dpctl_sycl_queue_interface for
      sycl::local_accessor as kernel arguments.
    - Refactoring to get rid of compiler warnings.

Author: Diptorup Deb

dpctl/enum_types.py

@@ -26,6 +26,7 @@
     "device_type",
     "backend_type",
     "event_status_type",
+    "kernel_arg_type",
 ]
 
 
@@ -113,3 +114,28 @@ class global_mem_cache_type(Enum):
     none = auto()
     read_only = auto()
     read_write = auto()
+
+
+class kernel_arg_type(Enum):
+    """
+    An enumeration of supported kernel argument types in
+    :func:`dpctl.SyclQueue.submit`
+    """
+
+    dpctl_char = auto()
+    dpctl_signed_char = auto()
+    dpctl_unsigned_char = auto()
+    dpctl_short = auto()
+    dpctl_int = auto()
+    dpctl_unsigned_int = auto()
+    dpctl_unsigned_int8 = auto()
+    dpctl_long = auto()
+    dpctl_unsigned_long = auto()
+    dpctl_long_long = auto()
+    dpctl_unsigned_long_long = auto()
+    dpctl_size_t = auto()
+    dpctl_float = auto()
+    dpctl_double = auto()
+    dpctl_long_double = auto()
+    dpctl_void_ptr = auto()
+    dpctl_local_accessor = auto()

libsyclinterface/helper/include/dpctl_error_handlers.h

@@ -20,7 +20,7 @@
 ///
 /// \file
 /// A functor to use for passing an error handler callback function to sycl
-/// context and queue contructors.
+/// context and queue constructors.
 //===----------------------------------------------------------------------===//
 
 #pragma once

libsyclinterface/include/dpctl_sycl_enum_types.h

@@ -102,7 +102,8 @@ typedef enum
     DPCTL_FLOAT,
     DPCTL_DOUBLE,
     DPCTL_LONG_DOUBLE,
-    DPCTL_VOID_PTR
+    DPCTL_VOID_PTR,
+    DPCTL_LOCAL_ACCESSOR
 } DPCTLKernelArgType;
 
 /*!

libsyclinterface/source/dpctl_sycl_kernel_bundle_interface.cpp

@@ -530,7 +530,7 @@ _GetKernel_ze_impl(const kernel_bundle<bundle_state::executable> &kb,
     else {
         error_handler("Kernel named " + std::string(kernel_name) +
                           " could not be found.",
-                      __FILE__, __func__, __LINE__);
+                      __FILE__, __func__, __LINE__, error_level::error);
         return nullptr;
     }
 }
@@ -541,7 +541,7 @@ bool _HasKernel_ze_impl(const kernel_bundle<bundle_state::executable> &kb,
     auto zeKernelCreateFn = get_zeKernelCreate();
     if (zeKernelCreateFn == nullptr) {
         error_handler("Could not load zeKernelCreate function.", __FILE__,
-                      __func__, __LINE__);
+                      __func__, __LINE__, error_level::error);
         return false;
     }
 
@@ -564,7 +564,7 @@ bool _HasKernel_ze_impl(const kernel_bundle<bundle_state::executable> &kb,
             if (ze_status != ZE_RESULT_ERROR_INVALID_KERNEL_NAME) {
                 error_handler("zeKernelCreate failed: " +
                                   _GetErrorCode_ze_impl(ze_status),
-                              __FILE__, __func__, __LINE__);
+                              __FILE__, __func__, __LINE__, error_level::error);
                 return false;
             }
         }