Align proposed extension with implementation

Author: againull

sycl/doc/extensions/proposed/sycl_ext_oneapi_group_sort.asciidoc

@@ -14,7 +14,7 @@
 == Notice
 
 [%hardbreaks]
-Copyright (c) 2021-2022 Intel Corporation.  All rights reserved.
+Copyright (c) 2021-2024 Intel Corporation.  All rights reserved.
 
 Khronos(R) is a registered trademark and SYCL(TM) and SPIR(TM) are trademarks
 of The Khronos Group Inc.  OpenCL(TM) is a trademark of Apple Inc. used by
@@ -34,19 +34,16 @@ SYCL specification refer to that revision.
 
 This extension also depends on the following other SYCL extensions:
 
-* link:../experimental/sycl_ext_oneapi_properties.asciidoc[
-  sycl_ext_oneapi_properties].
+* link:../experimental/sycl_ext_oneapi_properties.asciidoc[sycl_ext_oneapi_properties]
 
 == Status
 
-This is a proposed update to an existing experimental extension.
-Interfaces defined in this
-specification may not be implemented yet or may be in a preliminary state.  The
-specification itself may also change in incompatible ways before it is
-finalized.  *Shipping software products should not rely on APIs defined in this
-specification.*  See
-link:../experimental/sycl_ext_oneapi_group_sort.asciidoc[here] for the existing
-extension, which is implemented.
+This is an experimental extension specification, intended to provide early
+access to features and gather community feedback.  Interfaces defined in this
+specification are implemented in {dpcpp}, but they are not finalized and may
+change incompatibly in future versions of {dpcpp} without prior notice.
+*Shipping software products should not rely on APIs defined in this
+specification.*
 
 == Introduction
 
@@ -963,20 +960,37 @@ Consider 2 layouts:
 |{2, 5, 8, 11}
 |===
 
-There are 2 properties that satisfy
-link:sycl_ext_oneapi_properties.asciidoc[SYCL Properties Extension]
+There are 2 compile-time properties that satisfy
+link:../experimental/sycl_ext_oneapi_properties.asciidoc[SYCL Properties Extension]
 requirements:
 
 [source,c++]
 ----
-namespace sycl::ext::oneapi::experimental::property
-{
-    template<group_algorithm_data_placement type>
-    struct input_data_placement; // (1)
+namespace sycl::ext::oneapi::experimental {
 
-    template<group_algorithm_data_placement type>
-    struct output_data_placement; // (2)
-}
+struct input_data_placement_key : /* unspecified */ {
+  template <group_algorithm_data_placement Placement>
+  using value_t =
+      property_value<input_data_placement_key,
+                     std::integral_constant<group_algorithm_data_placement, Placement>>;
+};
+
+struct output_data_placement_key : /* unspecified */ {
+  template <group_algorithm_data_placement Placement>
+  using value_t =
+      property_value<output_data_placement_key,
+                     std::integral_constant<group_algorithm_data_placement, Placement>>;
+};
+
+template <group_algorithm_data_placement Placement>
+inline constexpr input_data_placement_key::value_t<Placement>
+    input_data_placement; // (1)
+
+template <group_algorithm_data_placement Placement>
+inline constexpr output_data_placement_key::value_t<Placement>
+    output_data_placement; // (2)
+
+} // namespace sycl::ext::oneapi::experimental
 ----
 
 1. `input_data_placement` specifies the data placement for input. This is
@@ -1192,12 +1206,6 @@ because it's easy to pass different comparator types.
 overloads with `Compare` objects seems extra and overloads with sorters,
 without sorters are enough.
 
-== Non-implemented features
-Please, note that following is not inplemented yet for the open-source repo:
-
-. `radix_sorter`, `radix_order`.
-. fixed-size arrays and properties.
-
 == Revision History
 
 [cols="5,15,15,70"]
@@ -1211,4 +1219,5 @@ Please, note that following is not inplemented yet for the open-source repo:
 making the entire extension experimental
 |4|2022-11-14|Andrey Fedorov|Fixed size arrays, key-value sorting and properties
 |5|2023-11-09|Andrey Fedorov|Changed `memory_required` functions for default sorters
+|6|2024-07-17|Artur Gainullin|Align the description of data placement properties with the implementation
 |========================================

sycl/include/sycl/ext/oneapi/experimental/group_helpers_sorters.hpp

@@ -37,22 +37,22 @@ namespace sycl {
 inline namespace _V1 {
 namespace ext::oneapi::experimental {
 
-enum class group_algorithm_data_placement { blocked, striped };
+enum class group_algorithm_data_placement : std::uint8_t { blocked, striped };
 
 struct input_data_placement_key
     : detail::compile_time_property_key<detail::PropKind::InputDataPlacement> {
   template <group_algorithm_data_placement Placement>
-  using value_t =
-      property_value<input_data_placement_key,
-                     std::integral_constant<int, static_cast<int>(Placement)>>;
+  using value_t = property_value<
+      input_data_placement_key,
+      std::integral_constant<group_algorithm_data_placement, Placement>>;
 };
 
 struct output_data_placement_key
     : detail::compile_time_property_key<detail::PropKind::OutputDataPlacement> {
   template <group_algorithm_data_placement Placement>
-  using value_t =
-      property_value<output_data_placement_key,
-                     std::integral_constant<int, static_cast<int>(Placement)>>;
+  using value_t = property_value<
+      output_data_placement_key,
+      std::integral_constant<group_algorithm_data_placement, Placement>>;
 };
 
 template <group_algorithm_data_placement Placement>