Adding runtime error conversion for Level0 backend

src/backend/Level0/CHIPBackendLevel0.cc

@@ -22,6 +22,7 @@
 
 #include "CHIPBackendLevel0.hh"
 #include "Utils.hh"
+#include "zeHipErrorConversion.hh"
 
 // Auto-generated header that lives in <build-dir>/bitcode.
 #include "rtdevlib-modules.h"
@@ -2493,7 +2494,8 @@ void CHIPModuleLevel0::compile(chipstar::Device *ChipDev) {
       KernelDesc.flags |= ZE_KERNEL_FLAG_FORCE_RESIDENCY;
 
     Status = zeKernelCreate(ZeModule_, &KernelDesc, &ZeKernel);
-    CHIPERR_CHECK_LOG_AND_THROW(Status, ZE_RESULT_SUCCESS, hipErrorTbd);
+    CHIPERR_CHECK_LOG_AND_THROW_TABLE(Status, ZE_RESULT_SUCCESS,
+                                      DEFAULT_ZE_HIP_ERROR_MAP);
     logTrace("LZ KERNEL CREATION via calling zeKernelCreate {} ", Status);
     CHIPKernelLevel0 *ChipZeKernel =
         new CHIPKernelLevel0(ZeKernel, LzDev, HostFName, FuncInfo, this);

src/backend/Level0/zeHipErrorConversion.hh

@@ -0,0 +1,69 @@
+/*
+ * Copyright (c) 2021-24 chipStar developers
+ *
+ * Permission is hereby granted, free of charge, to any person obtaining a copy
+ * of this software and associated documentation files (the "Software"), to deal
+ * in the Software without restriction, including without limitation the rights
+ * to use, copy, modify, merge, publish, distribute, sublicense, and/or sell
+ * copies of the Software, and to permit persons to whom the Software is
+ * furnished to do so, subject to the following conditions:
+ *
+ * The above copyright notice and this permission notice shall be included
+ * in all copies or substantial portions of the Software.
+ *
+ * THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR
+ * IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,
+ * FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. IN NO EVENT SHALL
+ * THE AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER
+ * LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING
+ * FROM, OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER
+ * DEALINGS IN THE SOFTWARE.
+ */
+
+#ifndef ZE_HIP_ERROR_CONVERSION_HH
+#define ZE_HIP_ERROR_CONVERSION_HH
+
+#include "../../CHIPException.hh"
+#include "ze_api.h"
+#include <string>
+#include <unordered_map>
+
+using ze_hip_error_map_t = std::unordered_map<ze_result_t, hipError_t>;
+
+// default table for ze to hip error conversion (empty map)
+#define DEFAULT_ZE_HIP_ERROR_MAP                                               \
+  ze_hip_error_map_t {}
+inline hipError_t default_ze_hip_error_convert(ze_result_t Status) {
+  switch (Status) {
+  case ZE_RESULT_ERROR_INVALID_MODULE_UNLINKED:
+    return hipErrorInvalidKernelFile;
+  default:
+    return hipErrorTbd;
+  }
+}
+
+// function converting ze_result_t into hipError_t based on provided map
+inline hipError_t hip_convert_error(ze_result_t Status,
+                                    ze_hip_error_map_t Map) {
+  if (Map.empty()) {
+    return default_ze_hip_error_convert(Status);
+  }
+  if (Map.find(Status) != Map.end()) {
+    return Map[Status];
+  }
+  return hipErrorTbd;
+}
+
+#define CHIPERR_CHECK_LOG_AND_THROW_TABLE(status, success,                     \
+                                          ze_errors_hip_errors_map, ...)       \
+  do {                                                                         \
+    if (status != success) {                                                   \
+      hipError_t err = hip_convert_error(status, ze_errors_hip_errors_map);    \
+      std::string error_msg = std::string(resultToString(status));             \
+      std::string custom_msg = std::string(__VA_ARGS__);                       \
+      std::string msg_ = error_msg + " " + custom_msg;                         \
+      CHIPERR_LOG_AND_THROW(msg_, err);                                        \
+    }                                                                          \
+  } while (0)
+
+#endif // ifdef guard