[SYCL][local_accessor] std::abort instead of throwing from noexcept (#17146)

Author: aelovikov-intel

sycl/include/sycl/accessor.hpp

@@ -229,6 +229,18 @@ class accessor;
 
 namespace detail {
 
+template <typename... Ts>
+#ifndef __SYCL_DEVICE_ONLY__
+[[noreturn]]
+#endif
+void cannot_be_called_on_host([[maybe_unused]] const char *API,
+                              Ts &&.../* ignore */) {
+#ifndef __SYCL_DEVICE_ONLY__
+  std::fprintf(stderr, "%s cannot be called on host!\n", API);
+  std::abort();
+#endif
+}
+
 // A helper structure which is shared between buffer accessor and accessor_impl
 // TODO: Unify with AccessorImplDevice?
 struct AccHostDataT {
@@ -2564,22 +2576,20 @@ class __SYCL_EBO __SYCL_SPECIAL_CLASS __SYCL_TYPE(local_accessor) local_accessor
   __SYCL2020_DEPRECATED(
       "local_accessor::get_pointer() is deprecated, please use get_multi_ptr()")
   local_ptr<DataT> get_pointer() const noexcept {
-#ifndef __SYCL_DEVICE_ONLY__
-    throw sycl::exception(
-        make_error_code(errc::invalid),
-        "get_pointer must not be called on the host for a local accessor");
-#endif
+#if __SYCL_DEVICE_ONLY__
     return local_ptr<DataT>(local_acc::getQualifiedPtr());
+#else
+    detail::cannot_be_called_on_host("local_accessor::get_pointer");
+#endif
   }
 
   template <access::decorated IsDecorated>
   accessor_ptr<IsDecorated> get_multi_ptr() const noexcept {
-#ifndef __SYCL_DEVICE_ONLY__
-    throw sycl::exception(
-        make_error_code(errc::invalid),
-        "get_multi_ptr must not be called on the host for a local accessor");
-#endif
+#if __SYCL_DEVICE_ONLY__
     return accessor_ptr<IsDecorated>(local_acc::getQualifiedPtr());
+#else
+    detail::cannot_be_called_on_host("local_accessor::get_multi_ptr");
+#endif
   }
 
   template <typename Property> bool has_property() const noexcept {