[SYCL] Deprecate syclcompat

sycl/doc/syclcompat/README.md

@@ -1,3 +1,7 @@
+**⚠️ DEPRECATION NOTICE ⚠️**
+
+**SYCLcompat is deprecated and will be removed in a future release. Users are encouraged to migrate to native SYCL APIs or alternative compatibility solutions. The `syclcompat` namespace has been marked with `[[deprecated]]` attribute.**
+
 # SYCLcompat
 
 SYCLcompat is a header-only library that intends to help developers familiar

sycl/include/syclcompat/atomic.hpp

@@ -40,7 +40,7 @@
 
 #include <syclcompat/traits.hpp>
 
-namespace syclcompat {
+namespace [[deprecated("syclcompat is deprecated")]] syclcompat {
 
 /// Atomically add the value operand to the value at the addr and assign the
 /// result to the value at addr.

sycl/include/syclcompat/defs.hpp

@@ -66,7 +66,7 @@ template <int Arg> class syclcompat_kernel_scalar;
   SYCLCOMPAT_MAKE_VERSION(SYCLCOMPAT_MAJOR_VERSION, SYCLCOMPAT_MINOR_VERSION,  \
                           SYCLCOMPAT_PATCH_VERSION)
 
-namespace syclcompat {
+namespace [[deprecated("syclcompat is deprecated")]] syclcompat {
 enum error_code { success = 0, backend_error = 1, default_error = 999 };
 /// A dummy function introduced to assist auto migration.
 /// The SYCLomatic user should replace it with a real error-handling function.

sycl/include/syclcompat/device.hpp

@@ -56,7 +56,7 @@
 #include <sycl/properties/queue_properties.hpp>
 #include <sycl/queue.hpp>
 
-namespace syclcompat {
+namespace [[deprecated("syclcompat is deprecated")]] syclcompat {
 
 namespace detail {
 static void parse_version_string(const std::string &ver, int &major,

sycl/include/syclcompat/dims.hpp

@@ -26,7 +26,7 @@
 
 #include <sycl/range.hpp>
 
-namespace syclcompat {
+namespace [[deprecated("syclcompat is deprecated")]] syclcompat {
 
 class dim3 {
 public:

sycl/include/syclcompat/group_utils.hpp

@@ -38,7 +38,7 @@
 #include <syclcompat/defs.hpp>
 #include <syclcompat/math.hpp>
 
-namespace syclcompat {
+namespace [[deprecated("syclcompat is deprecated")]] syclcompat {
 namespace group {
 namespace detail {
 

sycl/include/syclcompat/id_query.hpp

@@ -25,7 +25,7 @@
 #include <sycl/ext/oneapi/free_function_queries.hpp>
 #include <sycl/nd_item.hpp>
 
-namespace syclcompat {
+namespace [[deprecated("syclcompat is deprecated")]] syclcompat {
 
 using sycl::ext::oneapi::this_work_item::get_nd_item;
 

sycl/include/syclcompat/kernel.hpp

@@ -54,7 +54,7 @@
 #include <sycl/nd_range.hpp>
 #include <sycl/queue.hpp>
 
-namespace syclcompat {
+namespace [[deprecated("syclcompat is deprecated")]] syclcompat {
 
 typedef void (*kernel_functor)(sycl::queue &, const sycl::nd_range<3> &,
                                unsigned int, void **, void **);

sycl/include/syclcompat/launch.hpp

@@ -33,7 +33,7 @@
 #include <syclcompat/dims.hpp>
 #include <syclcompat/launch_policy.hpp>
 
-namespace syclcompat {
+namespace [[deprecated("syclcompat is deprecated")]] syclcompat {
 
 namespace detail {
 
@@ -120,8 +120,8 @@ launch(const dim3 &grid, const dim3 &threads, Args... args) {
 
 } // namespace syclcompat
 
-namespace syclcompat::experimental {
-
+namespace [[deprecated("syclcompat is deprecated")]] syclcompat {
+namespace experimental {
 namespace detail {
 
 template <auto F, typename LaunchPolicy, typename... Args>
@@ -145,7 +145,6 @@ sycl::event launch(LaunchPolicy launch_policy, sycl::queue q, Args... args) {
     }
   });
 }
-
 }
 
 
@@ -161,4 +160,5 @@ sycl::event launch(LaunchPolicy launch_policy, Args... args) {
   return launch<F>(launch_policy, get_default_queue(), args...);
 }
 
-} // namespace syclcompat::experimental
+} // namespace experimental
+} // namespace syclcompat

sycl/include/syclcompat/launch_policy.hpp

@@ -34,7 +34,7 @@
 #include <syclcompat/dims.hpp>
 #include <syclcompat/traits.hpp>
 
-namespace syclcompat {
+namespace [[deprecated("syclcompat is deprecated")]] syclcompat {
 namespace experimental {
 
 namespace sycl_exp = sycl::ext::oneapi::experimental;

sycl/include/syclcompat/math.hpp

@@ -46,7 +46,7 @@
 #include <sycl/ext/oneapi/experimental/complex/complex.hpp>
 #include <syclcompat/traits.hpp>
 
-namespace syclcompat {
+namespace [[deprecated("syclcompat is deprecated")]] syclcompat {
 namespace detail {
 
 namespace complex_namespace = sycl::ext::oneapi::experimental;

sycl/include/syclcompat/memory.hpp

@@ -66,7 +66,7 @@
 #error "Only support Windows and Linux."
 #endif
 
-namespace syclcompat {
+namespace [[deprecated("syclcompat is deprecated")]] syclcompat {
 
 template <typename AllocT>
 #ifdef __SYCL_DEVICE_ONLY__

sycl/include/syclcompat/syclcompat.hpp

@@ -22,6 +22,24 @@
 
 #pragma once
 
+// MSVC ignores [[deprecated]] attribute on namespace unless compiled with
+// /W3 or above.
+#ifdef _MSC_VER
+#define __SYCLCOMPAT_STRINGIFY(x) #x
+#define __SYCLCOMPAT_TOSTRING(x) __SYCLCOMPAT_STRINGIFY(x)
+
+#define __SYCLCOMPAT_WARNING(msg)                                              \
+  __pragma(message(__FILE__                                                    \
+                   "(" __SYCLCOMPAT_TOSTRING(__LINE__) "): warning: " msg))
+
+__SYCLCOMPAT_WARNING("syclcompat is deprecated and the deprecation warnings "
+                     "are ignored unless compiled with /W3 or above.")
+
+#undef __SYCLCOMPAT_WARNING
+#undef __SYCLCOMPAT_TOSTRING
+#undef __SYCLCOMPAT_STRINGIFY
+#endif
+
 #include <syclcompat/atomic.hpp>
 #include <syclcompat/defs.hpp>
 #include <syclcompat/device.hpp>

sycl/include/syclcompat/traits.hpp

@@ -33,7 +33,7 @@
 #include <sycl/nd_range.hpp>
 #include <type_traits>
 
-namespace syclcompat {
+namespace [[deprecated("syclcompat is deprecated")]] syclcompat {
 
 // Equivalent to C++20's std::type_identity (used to create non-deduced
 // contexts)

sycl/include/syclcompat/util.hpp

@@ -65,7 +65,7 @@ __SYCL_CONVERGENT__ extern SYCL_EXTERNAL __SYCL_EXPORT
     __spirv_GroupNonUniformShuffleUp(__spv::Scope::Flag, T, unsigned) noexcept;
 #endif
 
-namespace syclcompat {
+namespace [[deprecated("syclcompat is deprecated")]] syclcompat {
 
 namespace detail {
 

sycl/test/syclcompat/warnings_deprecated.cpp

@@ -0,0 +1,50 @@
+// Test to verify that syclcompat namespace and APIs generate deprecation
+// warnings.
+
+// RUN: %clangxx -fsycl -fsyntax-only -Xclang -verify -Xclang -verify-ignore-unexpected=note,warning %s -Wall -Wextra
+
+#include <syclcompat/syclcompat.hpp>
+
+int main() {
+  // Test deprecated namespace
+  // expected-warning@+1{{'syclcompat' is deprecated}}
+  syclcompat::dim3 grid(1, 1, 1);
+
+  // expected-warning@+1{{'syclcompat' is deprecated}}
+  auto queue = syclcompat::get_default_queue();
+
+  // Test deprecated memory APIs
+  // expected-warning@+1{{'syclcompat' is deprecated}}
+  void *ptr = syclcompat::malloc(1024);
+
+  // expected-warning@+1{{'syclcompat' is deprecated}}
+  syclcompat::free(ptr);
+
+  // Test deprecated utility APIs
+  // expected-warning@+1{{'syclcompat' is deprecated}}
+  auto device_count = syclcompat::device_count();
+
+  // expected-warning@+1{{'syclcompat' is deprecated}}
+  syclcompat::wait();
+
+  // Test deprecated atomic APIs
+  int value = 42;
+  int operand = 10;
+  // expected-warning@+1{{'syclcompat' is deprecated}}
+  syclcompat::atomic_fetch_add(&value, operand);
+
+  // Test deprecated math APIs
+  // expected-warning@+1{{'syclcompat' is deprecated}}
+  auto result = syclcompat::max(1, 2);
+
+  // Test deprecated device APIs
+  // expected-warning@+1{{'syclcompat' is deprecated}}
+  syclcompat::device_info info;
+
+  // Test deprecated experimental APIs
+  // expected-warning@+1{{'syclcompat' is deprecated}}
+  syclcompat::experimental::launch_policy my_config(
+      sycl::nd_range<1>{{32}, {32}});
+
+  return 0;
+}