[SYCL] Report an error for using "sycl::program::create_program_with_source" with Level-Zero/CUDA (#3212)

Level-Zero and CUDA backends do not support create_program_with_source. This is to report an error message from SYCL RT if that is requested.

Signed-off-by: rbegam <[email protected]>

Author: rbegam

sycl/plugins/cuda/pi_cuda.cpp

@@ -289,6 +289,11 @@ namespace pi {
   std::terminate();
 }
 
+// Reports error messages
+void cuPrint(const char *Message) {
+  std::cerr << "pi_print: " << Message << std::endl;
+}
+
 void assertion(bool Condition, const char *Message) {
   if (!Condition)
     die(Message);
@@ -2649,8 +2654,9 @@ pi_result cuda_piclProgramCreateWithSource(pi_context context, pi_uint32 count,
                                            const char **strings,
                                            const size_t *lengths,
                                            pi_program *program) {
-  cl::sycl::detail::pi::die("cuda_piclProgramCreateWithSource not implemented");
-  return {};
+  cl::sycl::detail::pi::cuPrint(
+      "cuda_piclProgramCreateWithSource not implemented");
+  return PI_INVALID_OPERATION;
 }
 
 /// Loads the images from a PI program into a CUmodule that can be

sycl/source/detail/program_impl.cpp

@@ -358,8 +358,15 @@ void program_impl::create_cl_program_with_source(const string_class &Source) {
   const char *Src = Source.c_str();
   size_t Size = Source.size();
   const detail::plugin &Plugin = getPlugin();
-  Plugin.call<PiApiKind::piclProgramCreateWithSource>(
-      MContext->getHandleRef(), 1, &Src, &Size, &MProgram);
+  RT::PiResult Err =
+      Plugin.call_nocheck<PiApiKind::piclProgramCreateWithSource>(
+          MContext->getHandleRef(), 1, &Src, &Size, &MProgram);
+
+  if (Err == PI_INVALID_OPERATION) {
+    throw feature_not_supported(
+        "program::compile_with_source is not supported by the selected backend",
+        PI_INVALID_OPERATION);
+  }
 }
 
 void program_impl::compile(const string_class &Options) {