Use clang-format tool(default llvm style)

pwisniewskimobica · pwisniewskimobica · commit b40bd2975ab8 · 2023-06-20T18:13:11.000+02:00
diff --git a/sycl/source/backend.cpp b/sycl/source/backend.cpp
@@ -38,7 +38,8 @@ static const PluginPtr &getPlugin(backend Backend) {
   case backend::ext_oneapi_cuda:
     return pi::getPlugin<backend::ext_oneapi_cuda>();
   default:
-    throw sycl::exception(sycl::errc::runtime, "getPlugin: Unsupported backend");
+    throw sycl::exception(sycl::make_error_code(sycl::errc::runtime),
+                          "getPlugin: Unsupported backend");
   }
 }
 
@@ -195,15 +196,17 @@ make_kernel_bundle(pi_native_handle NativeHandle, const context &TargetContext,
     case (PI_PROGRAM_BINARY_TYPE_COMPILED_OBJECT):
     case (PI_PROGRAM_BINARY_TYPE_LIBRARY):
       if (State == bundle_state::input)
-        throw sycl::exception(sycl::errc::runtime, "Program and kernel_bundle state mismatch");
+        throw sycl::exception(sycl::make_error_code(sycl::errc::runtime),
+                              "Program and kernel_bundle state mismatch");
       if (State == bundle_state::executable)
         Plugin->call<errc::build, PiApiKind::piProgramLink>(
             ContextImpl->getHandleRef(), 1, &Dev, nullptr, 1, &PiProgram,
             nullptr, nullptr, &PiProgram);
       break;
     case (PI_PROGRAM_BINARY_TYPE_EXECUTABLE):
       if (State == bundle_state::input || State == bundle_state::object)
-        throw sycl::exception(sycl::errc::runtime, "Program and kernel_bundle state mismatch");
+        throw sycl::exception(sycl::make_error_code(sycl::errc::runtime),
+                              "Program and kernel_bundle state mismatch");
       break;
     }
   }
@@ -257,7 +260,9 @@ kernel make_kernel(const context &TargetContext,
   pi::PiProgram PiProgram = nullptr;
   if (Backend == backend::ext_oneapi_level_zero) {
     if (KernelBundleImpl->size() != 1)
-      throw sycl::exception(sycl::errc::runtime, "make_kernel: kernel_bundle must have single program image");
+      throw sycl::exception(
+          sycl::make_error_code(sycl::errc::runtime),
+          "make_kernel: kernel_bundle must have single program image");
 
     const device_image<bundle_state::executable> &DeviceImage =
         *KernelBundle.begin();
diff --git a/sycl/source/detail/allowlist.cpp b/sycl/source/detail/allowlist.cpp
@@ -72,7 +72,7 @@ AllowListParsedT parseAllowList(const std::string &AllowListRaw) {
   const char DelimiterBtwDeviceDescs = '|';
 
   if (AllowListRaw.find(DelimiterBtwKeyAndValue, KeyStart) == std::string::npos)
-    throw sycl::exception(sycl::errc::runtime,
+    throw sycl::exception(sycl::make_error_code(sycl::errc::runtime),
                           "SYCL_DEVICE_ALLOWLIST has incorrect format. For "
                           "details, please refer to "
                           "https://github.com/intel/llvm/blob/sycl/sycl/"
@@ -95,7 +95,8 @@ AllowListParsedT parseAllowList(const std::string &AllowListRaw) {
     if (std::find(SupportedAllowListKeyNames.begin(),
                   SupportedAllowListKeyNames.end(),
                   Key) == SupportedAllowListKeyNames.end()) {
-      throw sycl::exception(sycl::errc::runtime,
+      throw sycl::exception(
+          sycl::make_error_code(sycl::errc::runtime),
           "Unrecognized key in SYCL_DEVICE_ALLOWLIST. For details, please "
           "refer to "
           "https://github.com/intel/llvm/blob/sycl/sycl/doc/"
@@ -148,7 +149,8 @@ AllowListParsedT parseAllowList(const std::string &AllowListRaw) {
                 break;
               }
             if (!ValueIsValid)
-              throw sycl::exception( sycl::errc::runtime,
+              throw sycl::exception(
+                  sycl::make_error_code(sycl::errc::runtime),
                   "Value " + Value + " for key " + Key +
                       " is not valid in "
                       "SYCL_DEVICE_ALLOWLIST. For details, please refer to "
@@ -167,7 +169,7 @@ AllowListParsedT parseAllowList(const std::string &AllowListRaw) {
           // DeviceVendorId should have hex format
           if (!std::regex_match(Value, std::regex("0[xX][0-9a-fA-F]+"))) {
             throw sycl::exception(
-                sycl::errc::runtime,
+                sycl::make_error_code(sycl::errc::runtime),
                 "Value " + Value + " for key " + Key +
                     " is not valid in "
                     "SYCL_DEVICE_ALLOWLIST. It should have the hex format. For "
@@ -185,7 +187,7 @@ AllowListParsedT parseAllowList(const std::string &AllowListRaw) {
         // TODO: can be changed to string_view::starts_with after switching
         // DPC++ RT to C++20
         if (Prefix != AllowListRaw.substr(ValueStart, Prefix.length())) {
-          throw sycl::exception(sycl::errc::runtime,
+          throw sycl::exception(sycl::make_error_code(sycl::errc::runtime),
                                 "Key " + Key +
                                     " of SYCL_DEVICE_ALLOWLIST should have "
                                     "value which starts with " +
@@ -203,7 +205,7 @@ AllowListParsedT parseAllowList(const std::string &AllowListRaw) {
           // if it is the last iteration and next 2 symbols are not a postfix,
           // throw exception
           if (ValueEnd == AllowListRaw.length() - Postfix.length())
-            throw sycl::exception(sycl::errc::runtime,
+            throw sycl::exception(sycl::make_error_code(sycl::errc::runtime),
                                   "Key " + Key +
                                       " of SYCL_DEVICE_ALLOWLIST should have "
                                       "value which ends with " +
@@ -217,7 +219,7 @@ AllowListParsedT parseAllowList(const std::string &AllowListRaw) {
              DelimiterBtwItemsInDeviceDesc) &&
             (AllowListRaw[NextExpectedDelimiterPos] != DelimiterBtwDeviceDescs))
           throw sycl::exception(
-              sycl::errc::runtime,
+              sycl::make_error_code(sycl::errc::runtime),
               "Unexpected symbol on position " +
                   std::to_string(NextExpectedDelimiterPos) + ": " +
                   AllowListRaw[NextExpectedDelimiterPos] +
@@ -238,7 +240,7 @@ AllowListParsedT parseAllowList(const std::string &AllowListRaw) {
       // add key and value to the map
       DeviceDescMap.emplace(Key, Value);
     } else
-      throw sycl::exception(sycl::errc::runtime, "Re-definition of key " + Key +
+      throw sycl::exception(sycl::make_error_code(sycl::errc::runtime), "Re-definition of key " + Key +
                                                      " is not allowed in "
                                                      "SYCL_DEVICE_ALLOWLIST");
 
diff --git a/sycl/source/detail/event_impl.cpp b/sycl/source/detail/event_impl.cpp
@@ -127,21 +127,25 @@ event_impl::event_impl(RT::PiEvent Event, const context &SyclContext)
       MIsFlushed(true), MState(HES_Complete) {
 
   if (MContext->is_host()) {
-    throw sycl::exception(sycl::errc::invalid, "The syclContext must match the OpenCL context associated with the clEvent.");
+    throw sycl::exception(sycl::make_error_code(sycl::errc::invalid),
+                          "The syclContext must match the OpenCL context "
+                          "associated with the clEvent.");
   }
 
   RT::PiContext TempContext;
   getPlugin()->call<PiApiKind::piEventGetInfo>(MEvent, PI_EVENT_INFO_CONTEXT,
                                                sizeof(RT::PiContext),
                                                &TempContext, nullptr);
   if (MContext->getHandleRef() != TempContext) {
-    throw sycl::exception(sycl::errc::invalid, "The syclContext must match the OpenCL context associated with the clEvent.");
+    throw sycl::exception(sycl::make_error_code(sycl::errc::invalid),
+                          "The syclContext must match the OpenCL context "
+                          "associated with the clEvent.");
   }
 }
 
 event_impl::event_impl(const QueueImplPtr &Queue)
-    : MQueue{Queue},
-      MIsProfilingEnabled{Queue->is_host() || Queue->MIsProfilingEnabled},
+    : MQueue{Queue}, MIsProfilingEnabled{Queue->is_host() ||
+                                         Queue->MIsProfilingEnabled},
       MLimitedProfiling{MIsProfilingEnabled && Queue->isProfilingLimited()} {
   this->setContextImpl(Queue->getContextImplPtr());
 
@@ -151,7 +155,7 @@ event_impl::event_impl(const QueueImplPtr &Queue)
     if (Queue->has_property<property::queue::enable_profiling>()) {
       MHostProfilingInfo.reset(new HostProfilingInfo());
       if (!MHostProfilingInfo)
-        throw sycl::exception(sycl::errc::runtime, "Out of host memory");
+        throw sycl::exception(sycl::make_error_code(sycl::errc::runtime), "Out of host memory");
     }
     return;
   }
@@ -281,7 +285,8 @@ event_impl::get_profiling_info<info::event_profiling::command_start>() {
     return 0;
   }
   if (!MHostProfilingInfo)
-    throw sycl::exception(0,sycl::errc::invalid, "Profiling info is not available.");
+    throw sycl::exception(0, sycl::errc::invalid,
+                          "Profiling info is not available.");
   return MHostProfilingInfo->getStartTime();
 }
 
@@ -295,7 +300,8 @@ uint64_t event_impl::get_profiling_info<info::event_profiling::command_end>() {
     return 0;
   }
   if (!MHostProfilingInfo)
-    throw sycl::exception(sycl::errc::invalid, "Profiling info is not available.");
+    throw sycl::exception(sycl::make_error_code(sycl::errc::invalid),
+                          "Profiling info is not available.");
   return MHostProfilingInfo->getEndTime();
 }
 
diff --git a/sycl/source/detail/scheduler/commands.cpp b/sycl/source/detail/scheduler/commands.cpp
@@ -1526,7 +1526,8 @@ AllocaCommandBase *ExecCGCommand::getAllocaForReq(Requirement *Req) {
     if (Dep.MDepRequirement == Req)
       return Dep.MAllocaCmd;
   }
-  throw sycl::exception(sycl::errc::runtime,"Alloca for command not found");
+  throw sycl::exception(sycl::make_error_code(sycl::errc::runtime),
+                        "Alloca for command not found");
 }
 
 std::vector<std::shared_ptr<const void>>
@@ -2230,7 +2231,7 @@ static pi_result SetKernelParamsAndLaunch(
     case kernel_param_kind_t::kind_specialization_constants_buffer: {
       if (Queue->is_host()) {
         throw sycl::exception(
-            sycl::errc::feature_not_supported,
+            sycl::make_error_code(sycl::errc::feature_not_supported),
             "SYCL2020 specialization constants are not yet supported on host "
             "device");
       }
@@ -2244,7 +2245,8 @@ static pi_result SetKernelParamsAndLaunch(
       break;
     }
     case kernel_param_kind_t::kind_invalid:
-      throw sycl::exception(sycl::errc::runtime, "Invalid kernel param kind");
+      throw sycl::exception(sycl::make_error_code(sycl::errc::runtime),
+                            "Invalid kernel param kind");
       break;
     }
   };
@@ -2491,7 +2493,7 @@ pi_int32 ExecCGCommand::enqueueImp() {
   switch (MCommandGroup->getType()) {
 
   case CG::CGTYPE::UpdateHost: {
-    throw sycl::exception(sycl::errc::runtime,
+    throw sycl::exception(sycl::make_error_code(sycl::errc::runtime),
                           "Update host should be handled by the Scheduler.");
   }
   case CG::CGTYPE::CopyAccToPtr: {
@@ -2630,12 +2632,12 @@ pi_int32 ExecCGCommand::enqueueImp() {
 
     switch (Error) {
     case PI_ERROR_INVALID_OPERATION:
-      throw sycl::exception(sycl::errc::runtime,
-          "Device doesn't support run_on_host_intel tasks.");
+      throw sycl::exception(sycl::make_error_code(sycl::errc::runtime),
+                            "Device doesn't support run_on_host_intel tasks.");
     case PI_SUCCESS:
       return Error;
     default:
-      throw sycl::exception(sycl::errc::runtime,
+      throw sycl::exception(sycl::make_error_code(sycl::errc::runtime),
                             "Enqueueing run_on_host_intel task has failed.");
     }
   }
@@ -2794,7 +2796,8 @@ pi_int32 ExecCGCommand::enqueueImp() {
         break;
       }
       default:
-        throw sycl::exception(sycl::errc::runtime, "Unsupported arg type");
+        throw sycl::exception(sycl::make_error_code(sycl::errc::runtime),
+                              "Unsupported arg type");
       }
     }
 
@@ -2803,7 +2806,8 @@ pi_int32 ExecCGCommand::enqueueImp() {
     if (HostTask->MHostTask->isInteropTask()) {
       // Extract the Mem Objects for all Requirements, to ensure they are
       // available if a user asks for them inside the interop task scope
-      const std::vector<Requirement *> &HandlerReq = HostTask->getRequirements();
+      const std::vector<Requirement *> &HandlerReq =
+          HostTask->getRequirements();
       auto ReqToMemConv = [&ReqToMem, HostTask](Requirement *Req) {
         const std::vector<AllocaCommandBase *> &AllocaCmds =
             Req->MSYCLMemObj->MRecord->MAllocaCommands;
@@ -2822,7 +2826,7 @@ pi_int32 ExecCGCommand::enqueueImp() {
                "Can't get memory object due to no allocation available");
 
         throw sycl::exception(
-            sycl::errc::runtime,
+            sycl::make_error_code(sycl::errc::runtime),
             "Can't get memory object due to no allocation available");
       };
       std::for_each(std::begin(HandlerReq), std::end(HandlerReq), ReqToMemConv);
@@ -2901,7 +2905,8 @@ pi_int32 ExecCGCommand::enqueueImp() {
                                     typeSize, RawEvents, Event, read);
   }
   case CG::CGTYPE::None:
-    throw sycl::exception(sycl::errc::runtime, "CG type not implemented.");
+    throw sycl::exception(sycl::make_error_code(sycl::errc::runtime),
+                          "CG type not implemented.");
   }
   return PI_ERROR_INVALID_OPERATION;
 }
