Add not-implemented code for level zero & HIP plugins

Author: joeatodd

sycl/plugins/cuda/pi_cuda.cpp

@@ -2549,7 +2549,6 @@ pi_result cuda_piKernelGetGroupInfo(pi_kernel kernel, pi_device device,
                      pi_uint64(bytes));
     }
     case PI_KERNEL_GROUP_INFO_NUM_REGS: {
-      // OpenCL PRIVATE == CUDA LOCAL
       int bytes = 0;
       cl::sycl::detail::pi::assertion(
           cuFuncGetAttribute(&bytes, CU_FUNC_ATTRIBUTE_NUM_REGS,

sycl/plugins/hip/pi_hip.cpp

@@ -3129,6 +3129,12 @@ pi_result hip_piKernelGetGroupInfo(pi_kernel kernel, pi_device device,
       return getInfo(param_value_size, param_value, param_value_size_ret,
                      pi_uint64(bytes));
     }
+    case PI_KERNEL_GROUP_INFO_NUM_REGS: {
+      cl::sycl::detail::pi::die("PI_KERNEL_GROUP_INFO_NUM_REGS in "
+                                "piKernelGetGroupInfo not implemented\n");
+      return {};
+    }
+
     default:
       __SYCL_PI_HANDLE_UNKNOWN_PARAM_NAME(param_name);
     }

sycl/plugins/level_zero/pi_level_zero.cpp

@@ -4258,6 +4258,10 @@ pi_result piKernelGetGroupInfo(pi_kernel Kernel, pi_device Device,
   }
   case PI_KERNEL_GROUP_INFO_PRIVATE_MEM_SIZE:
     return ReturnValue(pi_uint32{Kernel->ZeKernelProperties->privateMemSize});
+  case PI_KERNEL_GROUP_INFO_NUM_REGS: {
+    die("PI_KERNEL_GROUP_INFO_NUM_REGS in piKernelGetGroupInfo not implemented\n");
+    break;
+  }
   default:
     zePrint("Unknown ParamName in piKernelGetGroupInfo: ParamName=%d(0x%x)\n",
             ParamName, ParamName);