[SYCL][CUDA] Make piextKernelSetArgMemObj setting an error message (#6521)

This patch makes `cuda_piextKernelSetArgMemObj` setting an error message
instead of `std::terminate` in case of the image format is not
supported. This error message is encapsulated in an exception thrown by
the RT.

This allows to continue the SYCL-CTS execution in case of tests using
unsupported channel types, see
#2119 (comment).

Author: pgorlani

sycl/plugins/cuda/pi_cuda.cpp

@@ -2834,9 +2834,10 @@ pi_result cuda_piextKernelSetArgMemObj(pi_kernel kernel, pi_uint32 arg_index,
           arrayDesc.Format != CU_AD_FORMAT_SIGNED_INT32 &&
           arrayDesc.Format != CU_AD_FORMAT_HALF &&
           arrayDesc.Format != CU_AD_FORMAT_FLOAT) {
-        sycl::detail::pi::die(
-            "PI CUDA kernels only support images with channel types int32, "
-            "uint32, float, and half.");
+        setErrorMessage("PI CUDA kernels only support images with channel "
+                        "types int32, uint32, float, and half.",
+                        PI_ERROR_PLUGIN_SPECIFIC_ERROR);
+        return PI_ERROR_PLUGIN_SPECIFIC_ERROR;
       }
       CUsurfObject cuSurf = arg_mem->mem_.surface_mem_.get_surface();
       kernel->set_kernel_arg(arg_index, sizeof(cuSurf), (void *)&cuSurf);