[NFC][SYCL] Prepare backend.cpp for getSyclObjImpl to return raw ref (#19248)

I'm planning to change `getSyclObjImpl` to return a raw reference in a
later patch, uploading a bunch of PRs in preparation to that to make the
subsequent review easier.

Author: aelovikov-intel

sycl/source/backend.cpp

@@ -172,15 +172,15 @@ __SYCL_EXPORT event make_event(ur_native_handle_t NativeHandle,
                                const context &Context, bool KeepOwnership,
                                backend Backend) {
   const adapter_impl &Adapter = getAdapter(Backend);
-  const auto &ContextImpl = getSyclObjImpl(Context);
+  context_impl &ContextImpl = *getSyclObjImpl(Context);
 
   ur_event_handle_t UrEvent = nullptr;
   ur_event_native_properties_t Properties{};
   Properties.stype = UR_STRUCTURE_TYPE_EVENT_NATIVE_PROPERTIES;
   Properties.isNativeHandleOwned = !KeepOwnership;
 
   Adapter.call<UrApiKind::urEventCreateWithNativeHandle>(
-      NativeHandle, ContextImpl->getHandleRef(), &Properties, &UrEvent);
+      NativeHandle, ContextImpl.getHandleRef(), &Properties, &UrEvent);
   event Event = detail::createSyclObjFromImpl<event>(
       event_impl::create_from_handle(UrEvent, Context));
 
@@ -194,21 +194,21 @@ make_kernel_bundle(ur_native_handle_t NativeHandle,
                    const context &TargetContext, bool KeepOwnership,
                    bundle_state State, backend Backend) {
   const adapter_impl &Adapter = getAdapter(Backend);
-  const auto &ContextImpl = getSyclObjImpl(TargetContext);
+  context_impl &ContextImpl = *getSyclObjImpl(TargetContext);
 
   ur_program_handle_t UrProgram = nullptr;
   ur_program_native_properties_t Properties{};
   Properties.stype = UR_STRUCTURE_TYPE_PROGRAM_NATIVE_PROPERTIES;
   Properties.isNativeHandleOwned = !KeepOwnership;
 
   Adapter.call<UrApiKind::urProgramCreateWithNativeHandle>(
-      NativeHandle, ContextImpl->getHandleRef(), &Properties, &UrProgram);
+      NativeHandle, ContextImpl.getHandleRef(), &Properties, &UrProgram);
   if (UrProgram == nullptr)
     throw sycl::exception(
         sycl::make_error_code(sycl::errc::invalid),
         "urProgramCreateWithNativeHandle resulted in a null program handle.");
 
-  if (ContextImpl->getBackend() == backend::opencl)
+  if (ContextImpl.getBackend() == backend::opencl)
     __SYCL_OCL_CALL(clRetainProgram, ur::cast<cl_program>(NativeHandle));
 
   std::vector<ur_device_handle_t> ProgramDevices;
@@ -234,7 +234,7 @@ make_kernel_bundle(ur_native_handle_t NativeHandle,
             UrProgram, 1, &Dev, nullptr);
         if (Res == UR_RESULT_ERROR_UNSUPPORTED_FEATURE) {
           Res = Adapter.call_nocheck<UrApiKind::urProgramCompile>(
-              ContextImpl->getHandleRef(), UrProgram, nullptr);
+              ContextImpl.getHandleRef(), UrProgram, nullptr);
         }
         Adapter.checkUrResult<errc::build>(Res);
       }
@@ -244,7 +244,7 @@ make_kernel_bundle(ur_native_handle_t NativeHandle,
             UrProgram, 1, &Dev, nullptr);
         if (Res == UR_RESULT_ERROR_UNSUPPORTED_FEATURE) {
           Res = Adapter.call_nocheck<UrApiKind::urProgramBuild>(
-              ContextImpl->getHandleRef(), UrProgram, nullptr);
+              ContextImpl.getHandleRef(), UrProgram, nullptr);
         }
         Adapter.checkUrResult<errc::build>(Res);
       }
@@ -260,11 +260,11 @@ make_kernel_bundle(ur_native_handle_t NativeHandle,
       if (State == bundle_state::executable) {
         ur_program_handle_t UrLinkedProgram = nullptr;
         auto Res = Adapter.call_nocheck<UrApiKind::urProgramLinkExp>(
-            ContextImpl->getHandleRef(), 1, &Dev, 1, &UrProgram, nullptr,
+            ContextImpl.getHandleRef(), 1, &Dev, 1, &UrProgram, nullptr,
             &UrLinkedProgram);
         if (Res == UR_RESULT_ERROR_UNSUPPORTED_FEATURE) {
           Res = Adapter.call_nocheck<UrApiKind::urProgramLink>(
-              ContextImpl->getHandleRef(), 1, &UrProgram, nullptr,
+              ContextImpl.getHandleRef(), 1, &UrProgram, nullptr,
               &UrLinkedProgram);
         }
         Adapter.checkUrResult<errc::build>(Res);
@@ -322,7 +322,7 @@ kernel make_kernel(const context &TargetContext,
                    ur_native_handle_t NativeHandle, bool KeepOwnership,
                    backend Backend) {
   const auto &Adapter = getAdapter(Backend);
-  const auto &ContextImpl = getSyclObjImpl(TargetContext);
+  context_impl &ContextImpl = *getSyclObjImpl(TargetContext);
   kernel_bundle_impl &KernelBundleImpl = *getSyclObjImpl(KernelBundle);
 
   // For Level-Zero expect exactly one device image in the bundle. This is
@@ -342,8 +342,8 @@ kernel make_kernel(const context &TargetContext,
 
     const device_image<bundle_state::executable> &DeviceImage =
         *KernelBundle.begin();
-    const auto &DeviceImageImpl = getSyclObjImpl(DeviceImage);
-    UrProgram = DeviceImageImpl->get_ur_program_ref();
+    device_image_impl &DeviceImageImpl = *getSyclObjImpl(DeviceImage);
+    UrProgram = DeviceImageImpl.get_ur_program_ref();
   }
 
   // Create UR kernel first.
@@ -352,15 +352,15 @@ kernel make_kernel(const context &TargetContext,
   Properties.stype = UR_STRUCTURE_TYPE_KERNEL_NATIVE_PROPERTIES;
   Properties.isNativeHandleOwned = !KeepOwnership;
   Adapter.call<UrApiKind::urKernelCreateWithNativeHandle>(
-      NativeHandle, ContextImpl->getHandleRef(), UrProgram, &Properties,
+      NativeHandle, ContextImpl.getHandleRef(), UrProgram, &Properties,
       &UrKernel);
 
   if (Backend == backend::opencl)
     __SYCL_OCL_CALL(clRetainKernel, ur::cast<cl_kernel>(NativeHandle));
 
   // Construct the SYCL queue from UR queue.
   return detail::createSyclObjFromImpl<kernel>(
-      std::make_shared<kernel_impl>(UrKernel, *ContextImpl, &KernelBundleImpl));
+      std::make_shared<kernel_impl>(UrKernel, ContextImpl, &KernelBundleImpl));
 }
 
 kernel make_kernel(ur_native_handle_t NativeHandle,