diff --git a/sycl/include/sycl/accessor.hpp b/sycl/include/sycl/accessor.hpp index 288cd82f9104f..672cb83d872e5 100644 --- a/sycl/include/sycl/accessor.hpp +++ b/sycl/include/sycl/accessor.hpp @@ -212,16 +212,10 @@ namespace sycl { __SYCL_INLINE_VER_NAMESPACE(_V1) { class stream; -namespace ext { -namespace intel { -namespace esimd { -namespace detail { +namespace ext::intel::esimd::detail { // Forward declare a "back-door" access class to support ESIMD. class AccessorPrivateProxy; -} // namespace detail -} // namespace esimd -} // namespace intel -} // namespace ext +} // namespace ext::intel::esimd::detail template class vec; -namespace detail { -namespace half_impl { +namespace detail::half_impl { class half; -} // namespace half_impl -} // namespace detail +} // namespace detail::half_impl } // __SYCL_INLINE_VER_NAMESPACE(_V1) } // namespace sycl diff --git a/sycl/include/sycl/buffer.hpp b/sycl/include/sycl/buffer.hpp index 868af8a4b7d7f..f968f40ac7a6f 100644 --- a/sycl/include/sycl/buffer.hpp +++ b/sycl/include/sycl/buffer.hpp @@ -36,11 +36,9 @@ class host_accessor; template class buffer; -namespace ext { -namespace oneapi { +namespace ext::oneapi { template class weak_object; -} // namespace oneapi -} // namespace ext +} // namespace ext::oneapi namespace detail { diff --git a/sycl/include/sycl/builtins.hpp b/sycl/include/sycl/builtins.hpp index 8f5a565005983..79eae8a82a0ca 100644 --- a/sycl/include/sycl/builtins.hpp +++ b/sycl/include/sycl/builtins.hpp @@ -889,16 +889,14 @@ std::enable_if_t::value, T> ctz(T x) __NOEXC { } // geninteger ctz (geninteger x) for calls with deprecated namespace -namespace ext { -namespace intel { +namespace ext::intel { template __SYCL_DEPRECATED( "'sycl::ext::intel::ctz' is deprecated, use 'sycl::ctz' instead") std::enable_if_t::value, T> ctz(T x) __NOEXC { return sycl::ctz(x); } -} // namespace intel -} // namespace ext +} // namespace ext::intel namespace __SYCL2020_DEPRECATED("use 'ext::intel' instead") intel { using namespace ext::intel; diff --git a/sycl/include/sycl/detail/generic_type_lists.hpp b/sycl/include/sycl/detail/generic_type_lists.hpp index 95bf664f3d87e..0238d273c0999 100644 --- a/sycl/include/sycl/detail/generic_type_lists.hpp +++ b/sycl/include/sycl/detail/generic_type_lists.hpp @@ -22,11 +22,9 @@ namespace sycl { __SYCL_INLINE_VER_NAMESPACE(_V1) { template class vec; template class marray; -namespace detail { -namespace half_impl { +namespace detail::half_impl { class half; -} -} // namespace detail +} // namespace detail::half_impl using half = detail::half_impl::half; } // __SYCL_INLINE_VER_NAMESPACE(_V1) } // namespace sycl diff --git a/sycl/include/sycl/detail/type_traits.hpp b/sycl/include/sycl/detail/type_traits.hpp index dde4c0c0b743d..1806882ae8637 100644 --- a/sycl/include/sycl/detail/type_traits.hpp +++ b/sycl/include/sycl/detail/type_traits.hpp @@ -20,8 +20,7 @@ namespace sycl { __SYCL_INLINE_VER_NAMESPACE(_V1) { template class group; -namespace ext { -namespace oneapi { +namespace ext::oneapi { struct sub_group; namespace experimental { @@ -35,8 +34,7 @@ struct is_group_helper> : std::true_type { }; } // namespace detail } // namespace experimental -} // namespace oneapi -} // namespace ext +} // namespace ext::oneapi namespace detail { diff --git a/sycl/include/sycl/detail/usm_impl.hpp b/sycl/include/sycl/detail/usm_impl.hpp index 5a737cce2b4dd..2eb39ba77575d 100644 --- a/sycl/include/sycl/detail/usm_impl.hpp +++ b/sycl/include/sycl/detail/usm_impl.hpp @@ -13,8 +13,7 @@ namespace sycl { __SYCL_INLINE_VER_NAMESPACE(_V1) { -namespace detail { -namespace usm { +namespace detail::usm { __SYCL_EXPORT void *alignedAlloc(size_t Alignment, size_t Bytes, const context &Ctxt, const device &Dev, @@ -28,7 +27,6 @@ __SYCL_EXPORT void *alignedAllocHost(size_t Alignment, size_t Bytes, __SYCL_EXPORT void free(void *Ptr, const context &Ctxt, const code_location &CL); -} // namespace usm -} // namespace detail +} // namespace detail::usm } // __SYCL_INLINE_VER_NAMESPACE(_V1) } // namespace sycl diff --git a/sycl/include/sycl/device.hpp b/sycl/include/sycl/device.hpp index cd61c722fbe93..e569714133a7c 100644 --- a/sycl/include/sycl/device.hpp +++ b/sycl/include/sycl/device.hpp @@ -35,12 +35,10 @@ class device_impl; auto getDeviceComparisonLambda(); } // namespace detail -namespace ext { -namespace oneapi { +namespace ext::oneapi { // Forward declaration class filter_selector; -} // namespace oneapi -} // namespace ext +} // namespace ext::oneapi /// The SYCL device class encapsulates a single SYCL device on which kernels /// may be executed. diff --git a/sycl/include/sycl/device_selector.hpp b/sycl/include/sycl/device_selector.hpp index 3a890bf5d0ef4..a3add35c3d415 100644 --- a/sycl/include/sycl/device_selector.hpp +++ b/sycl/include/sycl/device_selector.hpp @@ -21,11 +21,9 @@ __SYCL_INLINE_VER_NAMESPACE(_V1) { // Forward declarations class device; -namespace ext { -namespace oneapi { +namespace ext::oneapi { class filter_selector; -} -} // namespace ext +} // namespace ext::oneapi /// The SYCL 1.2.1 device_selector class provides ability to choose the /// best SYCL device based on heuristics specified by the user. diff --git a/sycl/include/sycl/ext/codeplay/experimental/fusion_properties.hpp b/sycl/include/sycl/ext/codeplay/experimental/fusion_properties.hpp index 5d820456f6e19..5ec2aef927a45 100644 --- a/sycl/include/sycl/ext/codeplay/experimental/fusion_properties.hpp +++ b/sycl/include/sycl/ext/codeplay/experimental/fusion_properties.hpp @@ -14,10 +14,7 @@ namespace sycl { __SYCL_INLINE_VER_NAMESPACE(_V1) { -namespace ext { -namespace codeplay { -namespace experimental { -namespace property { +namespace ext::codeplay::experimental::property { class promote_private : public detail::DataLessProperty {}; @@ -33,10 +30,7 @@ namespace queue { class enable_fusion : public detail::DataLessProperty {}; } // namespace queue -} // namespace property -} // namespace experimental -} // namespace codeplay -} // namespace ext +} // namespace ext::codeplay::experimental::property // Forward declarations template diff --git a/sycl/include/sycl/ext/codeplay/experimental/fusion_wrapper.hpp b/sycl/include/sycl/ext/codeplay/experimental/fusion_wrapper.hpp index c9fa33810da55..368aea65ed9fa 100644 --- a/sycl/include/sycl/ext/codeplay/experimental/fusion_wrapper.hpp +++ b/sycl/include/sycl/ext/codeplay/experimental/fusion_wrapper.hpp @@ -17,9 +17,7 @@ namespace detail { class fusion_wrapper_impl; } -namespace ext { -namespace codeplay { -namespace experimental { +namespace ext::codeplay::experimental { /// /// A wrapper wrapping a sycl::queue to provide access to the kernel fusion API, @@ -91,8 +89,6 @@ class __SYCL_EXPORT fusion_wrapper { private: std::shared_ptr MImpl; }; -} // namespace experimental -} // namespace codeplay -} // namespace ext +} // namespace ext::codeplay::experimental } // __SYCL_INLINE_VER_NAMESPACE(_V1) } // namespace sycl diff --git a/sycl/include/sycl/ext/intel/esimd/detail/host_util.hpp b/sycl/include/sycl/ext/intel/esimd/detail/host_util.hpp index cda0b020e6c56..d6123d5d2db36 100644 --- a/sycl/include/sycl/ext/intel/esimd/detail/host_util.hpp +++ b/sycl/include/sycl/ext/intel/esimd/detail/host_util.hpp @@ -23,11 +23,9 @@ namespace sycl { __SYCL_INLINE_VER_NAMESPACE(_V1) { -namespace detail { -namespace half_impl { +namespace detail::half_impl { class half; -} // namespace half_impl -} // namespace detail +} // namespace detail::half_impl } // __SYCL_INLINE_VER_NAMESPACE(_V1) } // namespace sycl diff --git a/sycl/include/sycl/ext/intel/esimd/detail/region.hpp b/sycl/include/sycl/ext/intel/esimd/detail/region.hpp index a158ec7ac611d..2cf6edb9f65e0 100644 --- a/sycl/include/sycl/ext/intel/esimd/detail/region.hpp +++ b/sycl/include/sycl/ext/intel/esimd/detail/region.hpp @@ -19,9 +19,7 @@ namespace sycl { __SYCL_INLINE_VER_NAMESPACE(_V1) { -namespace ext { -namespace intel { -namespace esimd { +namespace ext::intel::esimd { /// @cond ESIMD_DETAIL // TODO move to detail? @@ -135,9 +133,7 @@ template T getBaseRegion(std::pair Reg) { /// @endcond ESIMD_DETAIL -} // namespace esimd -} // namespace intel -} // namespace ext +} // namespace ext::intel::esimd } // __SYCL_INLINE_VER_NAMESPACE(_V1) } // namespace sycl diff --git a/sycl/include/sycl/ext/intel/esimd/detail/sycl_util.hpp b/sycl/include/sycl/ext/intel/esimd/detail/sycl_util.hpp index 51acefad05173..ad607c24e927e 100644 --- a/sycl/include/sycl/ext/intel/esimd/detail/sycl_util.hpp +++ b/sycl/include/sycl/ext/intel/esimd/detail/sycl_util.hpp @@ -17,10 +17,7 @@ namespace sycl { __SYCL_INLINE_VER_NAMESPACE(_V1) { -namespace ext { -namespace intel { -namespace esimd { -namespace detail { +namespace ext::intel::esimd::detail { // Checks that given type is a SYCL accessor type. Sets its static field // \c value accordingly. Also, if the check is succesful, sets \c mode and @@ -82,10 +79,7 @@ template ::value, RetT>; -} // namespace detail -} // namespace esimd -} // namespace intel -} // namespace ext +} // namespace ext::intel::esimd::detail } // __SYCL_INLINE_VER_NAMESPACE(_V1) } // namespace sycl diff --git a/sycl/include/sycl/ext/intel/esimd/native/common.hpp b/sycl/include/sycl/ext/intel/esimd/native/common.hpp index dab20a27515ec..0df73949a40b2 100644 --- a/sycl/include/sycl/ext/intel/esimd/native/common.hpp +++ b/sycl/include/sycl/ext/intel/esimd/native/common.hpp @@ -16,9 +16,7 @@ namespace sycl { __SYCL_INLINE_VER_NAMESPACE(_V1) { -namespace ext::intel::esimd { -namespace native { -namespace lsc { +namespace ext::intel::esimd::native::lsc { /// @addtogroup sycl_esimd_memory /// @{ @@ -62,8 +60,6 @@ enum class atomic_op : uint8_t { /// @} sycl_esimd_memory_lsc -} // namespace lsc -} // namespace native -} // namespace ext::intel::esimd +} // namespace ext::intel::esimd::native::lsc } // __SYCL_INLINE_VER_NAMESPACE(_V1) } // namespace sycl diff --git a/sycl/include/sycl/ext/intel/experimental/esimd/memory.hpp b/sycl/include/sycl/ext/intel/experimental/esimd/memory.hpp index 880fa2ceb7e7a..705eba5818f11 100644 --- a/sycl/include/sycl/ext/intel/experimental/esimd/memory.hpp +++ b/sycl/include/sycl/ext/intel/experimental/esimd/memory.hpp @@ -17,10 +17,8 @@ namespace sycl { __SYCL_INLINE_VER_NAMESPACE(_V1) { -namespace ext { -namespace intel { -namespace experimental { -namespace esimd { +namespace ext::intel { +namespace experimental::esimd { /// @addtogroup sycl_esimd_memory /// @{ @@ -1723,8 +1721,7 @@ __ESIMD_API void lsc_fence(__ESIMD_NS::simd_mask pred = 1) { /// @} sycl_esimd_memory_lsc -} // namespace esimd -} // namespace experimental +} // namespace experimental::esimd namespace esimd { @@ -1759,7 +1756,6 @@ __ESIMD_API simd atomic_update(T *p, simd offset, } } // namespace esimd -} // namespace intel -} // namespace ext +} // namespace ext::intel } // __SYCL_INLINE_VER_NAMESPACE(_V1) } // namespace sycl diff --git a/sycl/include/sycl/ext/intel/experimental/fpga_lsu.hpp b/sycl/include/sycl/ext/intel/experimental/fpga_lsu.hpp index 6701dfedb9d41..275157cea5b4b 100644 --- a/sycl/include/sycl/ext/intel/experimental/fpga_lsu.hpp +++ b/sycl/include/sycl/ext/intel/experimental/fpga_lsu.hpp @@ -14,9 +14,7 @@ namespace sycl { __SYCL_INLINE_VER_NAMESPACE(_V1) { -namespace ext { -namespace intel { -namespace experimental { +namespace ext::intel::experimental { constexpr uint8_t BURST_COALESCE = 0x1; constexpr uint8_t CACHE = 0x2; @@ -201,8 +199,6 @@ template class lsu final { #endif }; -} // namespace experimental -} // namespace intel -} // namespace ext +} // namespace ext::intel::experimental } // __SYCL_INLINE_VER_NAMESPACE(_V1) } // namespace sycl diff --git a/sycl/include/sycl/ext/intel/experimental/online_compiler.hpp b/sycl/include/sycl/ext/intel/experimental/online_compiler.hpp index 8c118250c826c..7767dbdce941e 100644 --- a/sycl/include/sycl/ext/intel/experimental/online_compiler.hpp +++ b/sycl/include/sycl/ext/intel/experimental/online_compiler.hpp @@ -17,9 +17,7 @@ namespace sycl { __SYCL_INLINE_VER_NAMESPACE(_V1) { -namespace ext { -namespace intel { -namespace experimental { +namespace ext::intel::experimental { using byte = unsigned char; @@ -222,8 +220,6 @@ online_compiler::compile(const std::string &src) { return compile(src, std::vector{}); } -} // namespace experimental -} // namespace intel -} // namespace ext +} // namespace ext::intel::experimental } // __SYCL_INLINE_VER_NAMESPACE(_V1) } // namespace sycl diff --git a/sycl/include/sycl/ext/intel/experimental/pipes.hpp b/sycl/include/sycl/ext/intel/experimental/pipes.hpp index 7c3db4d0777b7..b327e1fdd167d 100644 --- a/sycl/include/sycl/ext/intel/experimental/pipes.hpp +++ b/sycl/include/sycl/ext/intel/experimental/pipes.hpp @@ -17,9 +17,7 @@ namespace sycl { __SYCL_INLINE_VER_NAMESPACE(_V1) { -namespace ext { -namespace intel { -namespace experimental { +namespace ext::intel::experimental { template { public: device_read_only() = default; }; -} // namespace usm -} // namespace property -} // namespace oneapi +} // namespace oneapi::property::usm -namespace intel { -namespace experimental { -namespace property { -namespace usm { +namespace intel::experimental::property::usm { class buffer_location : public sycl::detail::PropertyWithData< @@ -36,10 +29,7 @@ class buffer_location uint64_t MLocation; }; -} // namespace usm -} // namespace property -} // namespace experimental -} // namespace intel +} // namespace intel::experimental::property::usm } // namespace ext template <> diff --git a/sycl/include/sycl/ext/intel/fpga_device_selector.hpp b/sycl/include/sycl/ext/intel/fpga_device_selector.hpp index b2170e4f6f25b..8cf3e920045c3 100644 --- a/sycl/include/sycl/ext/intel/fpga_device_selector.hpp +++ b/sycl/include/sycl/ext/intel/fpga_device_selector.hpp @@ -20,8 +20,7 @@ __SYCL_INLINE_VER_NAMESPACE(_V1) { // Forward declaration class platform; -namespace ext { -namespace intel { +namespace ext::intel { namespace detail { // Scores a device by platform name. @@ -102,8 +101,7 @@ class __SYCL2020_DEPRECATED( } }; -} // namespace intel -} // namespace ext +} // namespace ext::intel } // __SYCL_INLINE_VER_NAMESPACE(_V1) } // namespace sycl diff --git a/sycl/include/sycl/ext/intel/fpga_lsu.hpp b/sycl/include/sycl/ext/intel/fpga_lsu.hpp index f5428d57bfe48..da331ce51cb1f 100644 --- a/sycl/include/sycl/ext/intel/fpga_lsu.hpp +++ b/sycl/include/sycl/ext/intel/fpga_lsu.hpp @@ -13,8 +13,7 @@ namespace sycl { __SYCL_INLINE_VER_NAMESPACE(_V1) { -namespace ext { -namespace intel { +namespace ext::intel { constexpr uint8_t BURST_COALESCE = 0x1; constexpr uint8_t CACHE = 0x2; constexpr uint8_t STATICALLY_COALESCE = 0x4; @@ -124,8 +123,7 @@ template class lsu final { "unable to implement a store LSU with a prefetcher."); } }; -} // namespace intel -} // namespace ext +} // namespace ext::intel } // __SYCL_INLINE_VER_NAMESPACE(_V1) } // namespace sycl diff --git a/sycl/include/sycl/ext/intel/fpga_reg.hpp b/sycl/include/sycl/ext/intel/fpga_reg.hpp index 2c527c8f5ec36..b9f486c347689 100644 --- a/sycl/include/sycl/ext/intel/fpga_reg.hpp +++ b/sycl/include/sycl/ext/intel/fpga_reg.hpp @@ -13,8 +13,7 @@ namespace sycl { __SYCL_INLINE_VER_NAMESPACE(_V1) { -namespace ext { -namespace intel { +namespace ext::intel { // Returns a registered copy of the input // This function is intended for FPGA users to instruct the compiler to insert @@ -43,8 +42,7 @@ fpga_reg(_T t) { #endif } -} // namespace intel -} // namespace ext +} // namespace ext::intel } // __SYCL_INLINE_VER_NAMESPACE(_V1) } // namespace sycl diff --git a/sycl/include/sycl/ext/intel/fpga_utils.hpp b/sycl/include/sycl/ext/intel/fpga_utils.hpp index 289f9edbc7d79..a6954fac357ba 100644 --- a/sycl/include/sycl/ext/intel/fpga_utils.hpp +++ b/sycl/include/sycl/ext/intel/fpga_utils.hpp @@ -14,8 +14,7 @@ namespace sycl { __SYCL_INLINE_VER_NAMESPACE(_V1) { -namespace ext { -namespace intel { +namespace ext::intel { template