addressed sycl deprecation warnings. Changes DPCTL aspect enum to align with SYCL aspect renaming: usm_system_allocators->usm_system_allocations

Author: oleksandr-pavlyk

libsyclinterface/helper/source/dpctl_error_handlers.cpp

@@ -39,7 +39,7 @@ void DPCTL_AsyncErrorHandler::operator()(
             std::rethrow_exception(e);
         } catch (sycl::exception const &e) {
             error_handler(e, __FILE__, __func__, __LINE__);
-            auto err_code = e.get_cl_code();
+            auto err_code = e.code();
             handler_(static_cast<int>(err_code));
         }
     }

libsyclinterface/helper/source/dpctl_utils_helper.cpp

@@ -221,8 +221,8 @@ std::string DPCTL_AspectToStr(aspect aspectTy)
     case aspect::usm_restricted_shared_allocations:
         ss << "usm_restricted_shared_allocations";
         break;
-    case aspect::usm_system_allocator:
-        ss << "usm_system_allocator";
+    case aspect::usm_system_allocations:
+        ss << "usm_system_allocations";
         break;
     default:
         throw std::runtime_error("Unsupported aspect type");
@@ -287,8 +287,8 @@ aspect DPCTL_StrToAspectType(const std::string &aspectTyStr)
     else if (aspectTyStr == "usm_restricted_shared_allocations") {
         aspectTy = aspect::usm_restricted_shared_allocations;
     }
-    else if (aspectTyStr == "usm_system_allocator") {
-        aspectTy = aspect::usm_system_allocator;
+    else if (aspectTyStr == "usm_system_allocations") {
+        aspectTy = aspect::usm_system_allocations;
     }
     else {
         // \todo handle the error
@@ -334,8 +334,8 @@ aspect DPCTL_DPCTLAspectTypeToSyclAspect(DPCTLSyclAspectType AspectTy)
         return aspect::usm_shared_allocations;
     case DPCTLSyclAspectType::usm_restricted_shared_allocations:
         return aspect::usm_restricted_shared_allocations;
-    case DPCTLSyclAspectType::usm_system_allocator:
-        return aspect::usm_system_allocator;
+    case DPCTLSyclAspectType::usm_system_allocations:
+        return aspect::usm_system_allocations;
     default:
         throw std::runtime_error("Unsupported aspect type");
     }
@@ -378,8 +378,8 @@ DPCTLSyclAspectType DPCTL_SyclAspectToDPCTLAspectType(aspect Aspect)
         return DPCTLSyclAspectType::usm_shared_allocations;
     case aspect::usm_restricted_shared_allocations:
         return DPCTLSyclAspectType::usm_restricted_shared_allocations;
-    case aspect::usm_system_allocator:
-        return DPCTLSyclAspectType::usm_system_allocator;
+    case aspect::usm_system_allocations:
+        return DPCTLSyclAspectType::usm_system_allocations;
     default:
         throw std::runtime_error("Unsupported aspect type");
     }

libsyclinterface/include/dpctl_sycl_enum_types.h

@@ -119,7 +119,7 @@ typedef enum
     usm_host_allocations,
     usm_shared_allocations,
     usm_restricted_shared_allocations,
-    usm_system_allocator
+    usm_system_allocations
 } DPCTLSyclAspectType;
 
 /*!

libsyclinterface/source/dpctl_sycl_program_interface.cpp

@@ -223,7 +223,7 @@ DPCTLProgram_CreateFromSpirv(__dpctl_keep const DPCTLSyclContextRef CtxRef,
     case backend::opencl:
         Pref = createOpenCLInterOpProgram(*SyclCtx, IL, length, CompileOpts);
         break;
-    case backend::level_zero:
+    case backend::ext_oneapi_level_zero:
 #ifdef DPCTL_ENABLE_LO_PROGRAM_CREATION
         Pref = createLevelZeroInterOpProgram(*SyclCtx, IL, length, CompileOpts);
 #endif
@@ -274,7 +274,7 @@ DPCTLProgram_CreateFromOCLSource(__dpctl_keep const DPCTLSyclContextRef Ctx,
             return nullptr;
         }
         break;
-    case backend::level_zero:
+    case backend::ext_oneapi_level_zero:
         error_handler("CreateFromSource is not supported in Level Zero.",
                       __FILE__, __func__, __LINE__);
         delete SyclProgram;

libsyclinterface/source/dpctl_sycl_queue_interface.cpp

@@ -530,7 +530,7 @@ DPCTLSyclEventRef DPCTLQueue_MemAdvise(__dpctl_keep DPCTLSyclQueueRef QRef,
     if (Q) {
         sycl::event ev;
         try {
-            ev = Q->mem_advise(Ptr, Count, static_cast<pi_mem_advice>(Advice));
+            ev = Q->mem_advise(Ptr, Count, Advice);
         } catch (std::exception const &e) {
             error_handler(e, __FILE__, __func__, __LINE__);
             return nullptr;
@@ -592,7 +592,7 @@ __dpctl_give DPCTLSyclEventRef DPCTLQueue_SubmitBarrierForEvents(
                     for (auto i = 0ul; i < NDepEvents; ++i)
                         cgh.depends_on(*unwrap(DepEvents[i]));
 
-                cgh.barrier();
+                cgh.ext_oneapi_barrier();
             });
         } catch (std::exception const &e) {
             error_handler(e, __FILE__, __func__, __LINE__);