diff --git a/common/unified/base/kernel_launch.hpp b/common/unified/base/kernel_launch.hpp index 99f8f151c17..0f4ddf594b5 100644 --- a/common/unified/base/kernel_launch.hpp +++ b/common/unified/base/kernel_launch.hpp @@ -105,7 +105,7 @@ GKO_INLINE GKO_ATTRIBUTES constexpr unpack_member_type unpack_member(T value) namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { template @@ -127,7 +127,7 @@ GKO_INLINE GKO_ATTRIBUTES constexpr unpack_member_type unpack_member(T value) return value; } -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/core/base/kernel_declaration.hpp b/core/base/kernel_declaration.hpp index 2a726128e2b..32089466cf8 100644 --- a/core/base/kernel_declaration.hpp +++ b/core/base/kernel_declaration.hpp @@ -57,7 +57,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. __VA_ARGS__; \ } \ } \ - namespace dpcpp { \ + namespace sycl { \ namespace _kernel_namespace { \ __VA_ARGS__; \ } \ diff --git a/core/device_hooks/dpcpp_hooks.cpp b/core/device_hooks/dpcpp_hooks.cpp index 532e9c55bbe..efca9737725 100644 --- a/core/device_hooks/dpcpp_hooks.cpp +++ b/core/device_hooks/dpcpp_hooks.cpp @@ -147,13 +147,13 @@ scoped_device_id_guard::scoped_device_id_guard(const DpcppExecutor* exec, namespace kernels { -namespace dpcpp { +namespace sycl { void destroy_event(sycl::event* event) GKO_NOT_COMPILED(dpcpp); -} // namespace dpcpp +} // namespace sycl } // namespace kernels diff --git a/core/log/profiler_hook.hpp b/core/log/profiler_hook.hpp index edff8480489..d0e5bc9c04c 100644 --- a/core/log/profiler_hook.hpp +++ b/core/log/profiler_hook.hpp @@ -155,7 +155,7 @@ using profiling_scope_guard = log::default_profiling_scope_guard; } // namespace hip -namespace dpcpp { +namespace sycl { class profiling_scope_guard { @@ -174,7 +174,7 @@ class profiling_scope_guard { }; -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/core/matrix/fft_kernels.hpp b/core/matrix/fft_kernels.hpp index 09e16dc8a1a..0bac39c06bd 100644 --- a/core/matrix/fft_kernels.hpp +++ b/core/matrix/fft_kernels.hpp @@ -108,13 +108,13 @@ GKO_DECLARE_ALL_AS_TEMPLATES; } // namespace hip -namespace dpcpp { +namespace sycl { namespace fft { GKO_DECLARE_ALL_AS_TEMPLATES; } // namespace fft -} // namespace dpcpp +} // namespace sycl #undef GKO_DECLARE_ALL_AS_TEMPLATES diff --git a/core/stop/residual_norm_kernels.hpp b/core/stop/residual_norm_kernels.hpp index f9c2ce89f93..6fcd2fc6aea 100644 --- a/core/stop/residual_norm_kernels.hpp +++ b/core/stop/residual_norm_kernels.hpp @@ -148,7 +148,7 @@ GKO_DECLARE_ALL_AS_TEMPLATES2; } // namespace hip -namespace dpcpp { +namespace sycl { namespace residual_norm { GKO_DECLARE_ALL_AS_TEMPLATES; @@ -161,7 +161,7 @@ namespace implicit_residual_norm { GKO_DECLARE_ALL_AS_TEMPLATES2; } // namespace implicit_residual_norm -} // namespace dpcpp +} // namespace sycl #undef GKO_DECLARE_ALL_AS_TEMPLATES diff --git a/dpcpp/base/batch_multi_vector_kernels.dp.cpp b/dpcpp/base/batch_multi_vector_kernels.dp.cpp index 10e47ba080e..42c6263651d 100644 --- a/dpcpp/base/batch_multi_vector_kernels.dp.cpp +++ b/dpcpp/base/batch_multi_vector_kernels.dp.cpp @@ -56,7 +56,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The MultiVector matrix format namespace. * @ref MultiVector @@ -319,6 +319,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_TYPE(GKO_DECLARE_BATCH_MULTI_VECTOR_COPY_KERNEL); } // namespace batch_multi_vector -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/base/batch_struct.hpp b/dpcpp/base/batch_struct.hpp index 9c752a94b4f..6637cef6930 100644 --- a/dpcpp/base/batch_struct.hpp +++ b/dpcpp/base/batch_struct.hpp @@ -44,7 +44,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** @file batch_struct.hpp @@ -85,7 +85,7 @@ inline batch::multi_vector::uniform_batch get_batch_struct( } -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/base/config.hpp b/dpcpp/base/config.hpp index a11910ee92e..466ae9b1027 100644 --- a/dpcpp/base/config.hpp +++ b/dpcpp/base/config.hpp @@ -44,7 +44,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { struct config { @@ -152,7 +152,7 @@ using dcfg_1sg_type_list_t = using dcfg_1sg_list_t = encode_list::type; -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/base/device.hpp b/dpcpp/base/device.hpp index 6047fbed615..a603bf4a395 100644 --- a/dpcpp/base/device.hpp +++ b/dpcpp/base/device.hpp @@ -39,14 +39,14 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** calls delete on the given event. */ void destroy_event(sycl::event* event); -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/base/device_matrix_data_kernels.dp.cpp b/dpcpp/base/device_matrix_data_kernels.dp.cpp index f8185d884c1..949be778dd4 100644 --- a/dpcpp/base/device_matrix_data_kernels.dp.cpp +++ b/dpcpp/base/device_matrix_data_kernels.dp.cpp @@ -47,7 +47,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { namespace components { @@ -151,6 +151,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace components -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/base/dim3.dp.hpp b/dpcpp/base/dim3.dp.hpp index 4f586700575..525fd8a3b90 100644 --- a/dpcpp/base/dim3.dp.hpp +++ b/dpcpp/base/dim3.dp.hpp @@ -39,7 +39,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** @@ -88,7 +88,7 @@ inline sycl::nd_range<3> sycl_nd_range(dim3 grid, dim3 block) } -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/base/executor.dp.cpp b/dpcpp/base/executor.dp.cpp index 3d01e271f15..6c1ff739de9 100644 --- a/dpcpp/base/executor.dp.cpp +++ b/dpcpp/base/executor.dp.cpp @@ -317,12 +317,12 @@ void DpcppExecutor::set_device_property(dpcpp_queue_property property) namespace kernels { -namespace dpcpp { +namespace sycl { void destroy_event(sycl::event* event) { delete event; } -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/base/helper.dp.cpp b/dpcpp/base/helper.dp.cpp index 26ee0c3cbd2..e43fe3fd6b4 100644 --- a/dpcpp/base/helper.dp.cpp +++ b/dpcpp/base/helper.dp.cpp @@ -38,7 +38,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { bool validate(sycl::queue* queue, unsigned int workgroup_size, @@ -57,6 +57,6 @@ bool validate(sycl::queue* queue, unsigned int workgroup_size, } -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/base/helper.hpp b/dpcpp/base/helper.hpp index b38b6c1ef8b..edc7695c296 100644 --- a/dpcpp/base/helper.hpp +++ b/dpcpp/base/helper.hpp @@ -181,7 +181,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** @@ -223,7 +223,7 @@ std::uint32_t get_first_cfg(const IterArr& arr, Validate verify) } -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/base/index_set_kernels.dp.cpp b/dpcpp/base/index_set_kernels.dp.cpp index ee90e435d63..c9dd46a7824 100644 --- a/dpcpp/base/index_set_kernels.dp.cpp +++ b/dpcpp/base/index_set_kernels.dp.cpp @@ -48,7 +48,7 @@ namespace kernels { * * @ingroup dpcpp */ -namespace dpcpp { +namespace sycl { /** * @brief The index_set namespace. * @@ -108,6 +108,6 @@ GKO_INSTANTIATE_FOR_EACH_INDEX_TYPE( } // namespace idx_set -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/base/kernel_launch.dp.hpp b/dpcpp/base/kernel_launch.dp.hpp index b6d5c7342ae..0a179c0b382 100644 --- a/dpcpp/base/kernel_launch.dp.hpp +++ b/dpcpp/base/kernel_launch.dp.hpp @@ -44,7 +44,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { namespace device_std = std; @@ -97,6 +97,6 @@ void run_kernel(std::shared_ptr exec, KernelFunction fn, } -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/base/kernel_launch_reduction.dp.hpp b/dpcpp/base/kernel_launch_reduction.dp.hpp index 1cf7c1f774a..f9fa63f1ac2 100644 --- a/dpcpp/base/kernel_launch_reduction.dp.hpp +++ b/dpcpp/base/kernel_launch_reduction.dp.hpp @@ -51,7 +51,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { static constexpr auto dcfg_1d_list_simple_reduction = dcfg_1d_list_t(); @@ -718,6 +718,6 @@ void run_kernel_col_reduction_cached(std::shared_ptr exec, } -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/base/kernel_launch_solver.dp.hpp b/dpcpp/base/kernel_launch_solver.dp.hpp index 5b2e583c3c6..95bf7eb5da5 100644 --- a/dpcpp/base/kernel_launch_solver.dp.hpp +++ b/dpcpp/base/kernel_launch_solver.dp.hpp @@ -38,7 +38,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { template @@ -71,6 +71,6 @@ void run_kernel_solver(std::shared_ptr exec, } -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/base/onedpl.hpp b/dpcpp/base/onedpl.hpp index 4af31d3e115..db4052ee9b0 100644 --- a/dpcpp/base/onedpl.hpp +++ b/dpcpp/base/onedpl.hpp @@ -44,7 +44,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { inline auto onedpl_policy(std::shared_ptr exec) @@ -53,7 +53,7 @@ inline auto onedpl_policy(std::shared_ptr exec) } -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/base/onemkl_bindings.hpp b/dpcpp/base/onemkl_bindings.hpp index 73a77132ab9..0d0e9e70827 100644 --- a/dpcpp/base/onemkl_bindings.hpp +++ b/dpcpp/base/onemkl_bindings.hpp @@ -56,7 +56,7 @@ namespace kernels { * * @ingroup dpcpp */ -namespace dpcpp { +namespace sycl { /** * @brief The ONEMKL namespace. * @@ -125,7 +125,7 @@ GKO_BIND_DOT(ValueType, conj_dot, detail::not_implemented); #undef GKO_BIND_DOT } // namespace onemkl -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/components/atomic.dp.hpp b/dpcpp/components/atomic.dp.hpp index d936f78aa94..6fb793cf6a8 100644 --- a/dpcpp/components/atomic.dp.hpp +++ b/dpcpp/components/atomic.dp.hpp @@ -45,7 +45,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { namespace atomic { @@ -283,7 +283,7 @@ __dpct_inline__ T atomic_max(T* __restrict__ addr, T val) } -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/components/cooperative_groups.dp.hpp b/dpcpp/components/cooperative_groups.dp.hpp index e2212285954..f8ae4039e00 100644 --- a/dpcpp/components/cooperative_groups.dp.hpp +++ b/dpcpp/components/cooperative_groups.dp.hpp @@ -46,7 +46,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** @@ -474,7 +474,7 @@ __dpct_inline__ grid_group this_grid(sycl::nd_item<3>& group) } // namespace group -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/components/diagonal_block_manipulation.dp.hpp b/dpcpp/components/diagonal_block_manipulation.dp.hpp index 34b524acfd7..900e669ee72 100644 --- a/dpcpp/components/diagonal_block_manipulation.dp.hpp +++ b/dpcpp/components/diagonal_block_manipulation.dp.hpp @@ -47,7 +47,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { namespace csr { @@ -120,7 +120,7 @@ __dpct_inline__ void extract_transposed_diag_blocks( } // namespace csr -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/components/format_conversion.dp.hpp b/dpcpp/components/format_conversion.dp.hpp index 215c436c9b7..31f17ead068 100644 --- a/dpcpp/components/format_conversion.dp.hpp +++ b/dpcpp/components/format_conversion.dp.hpp @@ -56,7 +56,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { namespace coo { namespace host_kernel { @@ -90,7 +90,7 @@ size_type calculate_nwarps(std::shared_ptr exec, } // namespace host_kernel } // namespace coo -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/components/intrinsics.dp.hpp b/dpcpp/components/intrinsics.dp.hpp index d166f6d4cba..fd2778adcee 100644 --- a/dpcpp/components/intrinsics.dp.hpp +++ b/dpcpp/components/intrinsics.dp.hpp @@ -45,7 +45,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** @@ -88,7 +88,7 @@ __dpct_inline__ int clz(uint32 mask) { return sycl::clz(mask); } __dpct_inline__ int clz(uint64 mask) { return sycl::clz(mask); } -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/components/matrix_operations.dp.hpp b/dpcpp/components/matrix_operations.dp.hpp index 16c6f2da663..e7639c67263 100644 --- a/dpcpp/components/matrix_operations.dp.hpp +++ b/dpcpp/components/matrix_operations.dp.hpp @@ -39,7 +39,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** @@ -53,7 +53,7 @@ remove_complex compute_inf_norm( size_type stride) GKO_NOT_IMPLEMENTED; -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/components/merging.dp.hpp b/dpcpp/components/merging.dp.hpp index 85de4698bb6..f772a1a567f 100644 --- a/dpcpp/components/merging.dp.hpp +++ b/dpcpp/components/merging.dp.hpp @@ -48,7 +48,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { namespace detail { @@ -328,7 +328,7 @@ __dpct_inline__ void sequential_match(const ValueType* a, IndexType a_size, }); } -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/components/prefix_sum.dp.hpp b/dpcpp/components/prefix_sum.dp.hpp index 10897550801..7d4cf21f22d 100644 --- a/dpcpp/components/prefix_sum.dp.hpp +++ b/dpcpp/components/prefix_sum.dp.hpp @@ -50,7 +50,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { // TODO: porting - some functions name still use subwarp @@ -250,7 +250,7 @@ void finalize_prefix_sum(dim3 grid, dim3 block, size_type dynamic_shared_memory, } -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/components/prefix_sum_kernels.dp.cpp b/dpcpp/components/prefix_sum_kernels.dp.cpp index 8a36f2658d6..01f6e62c283 100644 --- a/dpcpp/components/prefix_sum_kernels.dp.cpp +++ b/dpcpp/components/prefix_sum_kernels.dp.cpp @@ -47,7 +47,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { namespace components { @@ -102,6 +102,6 @@ template GKO_DECLARE_PREFIX_SUM_NONNEGATIVE_KERNEL(size_type); } // namespace components -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/components/reduction.dp.hpp b/dpcpp/components/reduction.dp.hpp index cbd7b250c73..1b25f77186f 100644 --- a/dpcpp/components/reduction.dp.hpp +++ b/dpcpp/components/reduction.dp.hpp @@ -59,7 +59,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { static constexpr int default_block_size = 256; @@ -290,7 +290,7 @@ ValueType reduce_add_array(std::shared_ptr exec, } -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/components/searching.dp.hpp b/dpcpp/components/searching.dp.hpp index 589676a6095..5a5e18c2034 100644 --- a/dpcpp/components/searching.dp.hpp +++ b/dpcpp/components/searching.dp.hpp @@ -44,7 +44,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** @@ -252,7 +252,7 @@ __dpct_inline__ IndexType group_ary_search(IndexType offset, IndexType length, } -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/components/segment_scan.dp.hpp b/dpcpp/components/segment_scan.dp.hpp index b73ae12e9b3..765039f9751 100644 --- a/dpcpp/components/segment_scan.dp.hpp +++ b/dpcpp/components/segment_scan.dp.hpp @@ -44,7 +44,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** @@ -79,7 +79,7 @@ __dpct_inline__ bool segment_scan( } -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/components/sorting.dp.hpp b/dpcpp/components/sorting.dp.hpp index 7a1a42743e1..a7ec4f26eb6 100644 --- a/dpcpp/components/sorting.dp.hpp +++ b/dpcpp/components/sorting.dp.hpp @@ -44,7 +44,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { namespace detail { @@ -341,7 +341,7 @@ __dpct_inline__ void bitonic_sort(ValueType* local_elements, } -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/components/thread_ids.dp.hpp b/dpcpp/components/thread_ids.dp.hpp index e689e9f14ba..358b7b495f8 100644 --- a/dpcpp/components/thread_ids.dp.hpp +++ b/dpcpp/components/thread_ids.dp.hpp @@ -43,7 +43,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The DPCPP thread namespace. * @@ -319,7 +319,7 @@ __dpct_inline__ IndexType get_subwarp_num_flat(sycl::nd_item<3> item_ct1) } // namespace thread -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/components/uninitialized_array.hpp b/dpcpp/components/uninitialized_array.hpp index 205754232cf..a44d61e275b 100644 --- a/dpcpp/components/uninitialized_array.hpp +++ b/dpcpp/components/uninitialized_array.hpp @@ -42,7 +42,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { // TODO: porting - consider directly use the array as shared memory @@ -113,7 +113,7 @@ class uninitialized_array { }; -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/components/warp_blas.dp.hpp b/dpcpp/components/warp_blas.dp.hpp index c61f47bb95c..cbe2ba8623b 100644 --- a/dpcpp/components/warp_blas.dp.hpp +++ b/dpcpp/components/warp_blas.dp.hpp @@ -51,7 +51,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** @@ -465,7 +465,7 @@ __dpct_inline__ remove_complex compute_infinity_norm( } -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/distributed/matrix_kernels.dp.cpp b/dpcpp/distributed/matrix_kernels.dp.cpp index e75eee91501..a15340e23ab 100644 --- a/dpcpp/distributed/matrix_kernels.dp.cpp +++ b/dpcpp/distributed/matrix_kernels.dp.cpp @@ -38,7 +38,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { namespace distributed_matrix { @@ -64,6 +64,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_LOCAL_GLOBAL_INDEX_TYPE( } // namespace distributed_matrix -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/distributed/partition_helpers_kernels.dp.cpp b/dpcpp/distributed/partition_helpers_kernels.dp.cpp index 8b0171cd349..938efc5d909 100644 --- a/dpcpp/distributed/partition_helpers_kernels.dp.cpp +++ b/dpcpp/distributed/partition_helpers_kernels.dp.cpp @@ -42,7 +42,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { namespace partition_helpers { struct stride { @@ -114,6 +114,6 @@ GKO_INSTANTIATE_FOR_EACH_INDEX_TYPE( } // namespace partition_helpers -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/distributed/partition_kernels.dp.cpp b/dpcpp/distributed/partition_kernels.dp.cpp index 04b7ff215ed..34ec5880b0c 100644 --- a/dpcpp/distributed/partition_kernels.dp.cpp +++ b/dpcpp/distributed/partition_kernels.dp.cpp @@ -46,7 +46,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { namespace partition { namespace kernel { @@ -163,6 +163,6 @@ GKO_INSTANTIATE_FOR_EACH_LOCAL_GLOBAL_INDEX_TYPE( } // namespace partition -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/distributed/vector_kernels.dp.cpp b/dpcpp/distributed/vector_kernels.dp.cpp index c8569cc2396..e8d33ff7149 100644 --- a/dpcpp/distributed/vector_kernels.dp.cpp +++ b/dpcpp/distributed/vector_kernels.dp.cpp @@ -38,7 +38,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { namespace distributed_vector { @@ -56,6 +56,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_LOCAL_GLOBAL_INDEX_TYPE( } // namespace distributed_vector -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/factorization/cholesky_kernels.dp.cpp b/dpcpp/factorization/cholesky_kernels.dp.cpp index ef3b25b1e2e..b23673bfff2 100644 --- a/dpcpp/factorization/cholesky_kernels.dp.cpp +++ b/dpcpp/factorization/cholesky_kernels.dp.cpp @@ -48,7 +48,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The Cholesky namespace. * @@ -209,6 +209,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE(GKO_DECLARE_CHOLESKY_FACTORIZE); } // namespace cholesky -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/factorization/factorization_kernels.dp.cpp b/dpcpp/factorization/factorization_kernels.dp.cpp index cdc58db929e..292cf13917a 100644 --- a/dpcpp/factorization/factorization_kernels.dp.cpp +++ b/dpcpp/factorization/factorization_kernels.dp.cpp @@ -52,7 +52,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The factorization namespace. * @@ -686,6 +686,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace factorization -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/factorization/ic_kernels.dp.cpp b/dpcpp/factorization/ic_kernels.dp.cpp index 93026e78545..6a4ea1b169b 100644 --- a/dpcpp/factorization/ic_kernels.dp.cpp +++ b/dpcpp/factorization/ic_kernels.dp.cpp @@ -35,7 +35,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The ic factorization namespace. * @@ -52,6 +52,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE(GKO_DECLARE_IC_COMPUTE_KERNEL); } // namespace ic_factorization -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/factorization/ilu_kernels.dp.cpp b/dpcpp/factorization/ilu_kernels.dp.cpp index 99aa4e5f94f..120ebe52a91 100644 --- a/dpcpp/factorization/ilu_kernels.dp.cpp +++ b/dpcpp/factorization/ilu_kernels.dp.cpp @@ -35,7 +35,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The ilu factorization namespace. * @@ -53,6 +53,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace ilu_factorization -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/factorization/lu_kernels.dp.cpp b/dpcpp/factorization/lu_kernels.dp.cpp index caa555d6203..978a78e523c 100644 --- a/dpcpp/factorization/lu_kernels.dp.cpp +++ b/dpcpp/factorization/lu_kernels.dp.cpp @@ -46,7 +46,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The LU namespace. * @@ -77,6 +77,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE(GKO_DECLARE_LU_FACTORIZE); } // namespace lu_factorization -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/factorization/par_ic_kernels.dp.cpp b/dpcpp/factorization/par_ic_kernels.dp.cpp index ba9dba201ff..bf954e3c374 100644 --- a/dpcpp/factorization/par_ic_kernels.dp.cpp +++ b/dpcpp/factorization/par_ic_kernels.dp.cpp @@ -47,7 +47,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The parallel ic factorization namespace. * @@ -188,6 +188,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace par_ic_factorization -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/factorization/par_ict_kernels.dp.cpp b/dpcpp/factorization/par_ict_kernels.dp.cpp index bf4da3e0354..31aef75edde 100644 --- a/dpcpp/factorization/par_ict_kernels.dp.cpp +++ b/dpcpp/factorization/par_ict_kernels.dp.cpp @@ -63,7 +63,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The parallel ICT factorization namespace. * @@ -542,6 +542,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace par_ict_factorization -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/factorization/par_ilu_kernels.dp.cpp b/dpcpp/factorization/par_ilu_kernels.dp.cpp index e74cc155fe3..351f2129216 100644 --- a/dpcpp/factorization/par_ilu_kernels.dp.cpp +++ b/dpcpp/factorization/par_ilu_kernels.dp.cpp @@ -45,7 +45,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The parallel ilu factorization namespace. * @@ -162,6 +162,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace par_ilu_factorization -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/factorization/par_ilut_approx_filter_kernel.dp.cpp b/dpcpp/factorization/par_ilut_approx_filter_kernel.dp.cpp index 69047038414..a6469ef83ae 100644 --- a/dpcpp/factorization/par_ilut_approx_filter_kernel.dp.cpp +++ b/dpcpp/factorization/par_ilut_approx_filter_kernel.dp.cpp @@ -65,7 +65,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The parallel ILUT factorization namespace. * @@ -203,6 +203,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace par_ilut_factorization -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/factorization/par_ilut_filter_kernel.dp.cpp b/dpcpp/factorization/par_ilut_filter_kernel.dp.cpp index 428c52f2f70..43a91766ebb 100644 --- a/dpcpp/factorization/par_ilut_filter_kernel.dp.cpp +++ b/dpcpp/factorization/par_ilut_filter_kernel.dp.cpp @@ -57,7 +57,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The parallel ILUT factorization namespace. * @@ -157,6 +157,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace par_ilut_factorization -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/factorization/par_ilut_kernels.dp.cpp b/dpcpp/factorization/par_ilut_kernels.dp.cpp index 12280118430..becd871bbf7 100644 --- a/dpcpp/factorization/par_ilut_kernels.dp.cpp +++ b/dpcpp/factorization/par_ilut_kernels.dp.cpp @@ -56,7 +56,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The parallel ILUT factorization namespace. * @@ -147,6 +147,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace par_ilut_factorization -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/factorization/par_ilut_select_common.dp.cpp b/dpcpp/factorization/par_ilut_select_common.dp.cpp index c7287cf6001..2489912f017 100644 --- a/dpcpp/factorization/par_ilut_select_common.dp.cpp +++ b/dpcpp/factorization/par_ilut_select_common.dp.cpp @@ -53,7 +53,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The parallel ILUT factorization namespace. * @@ -123,6 +123,6 @@ GKO_INSTANTIATE_FOR_EACH_INDEX_TYPE(DECLARE_SSSS_FIND_BUCKET); } // namespace par_ilut_factorization -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/factorization/par_ilut_select_common.dp.hpp b/dpcpp/factorization/par_ilut_select_common.dp.hpp index f0b819c9929..5b37b9b50d6 100644 --- a/dpcpp/factorization/par_ilut_select_common.dp.hpp +++ b/dpcpp/factorization/par_ilut_select_common.dp.hpp @@ -41,7 +41,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { namespace par_ilut_factorization { @@ -71,7 +71,7 @@ sampleselect_bucket sampleselect_find_bucket( } // namespace par_ilut_factorization -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/factorization/par_ilut_select_kernel.dp.cpp b/dpcpp/factorization/par_ilut_select_kernel.dp.cpp index 0027ee0ab56..f5515a59b72 100644 --- a/dpcpp/factorization/par_ilut_select_kernel.dp.cpp +++ b/dpcpp/factorization/par_ilut_select_kernel.dp.cpp @@ -59,7 +59,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The parallel ILUT factorization namespace. * @@ -186,6 +186,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace par_ilut_factorization -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/factorization/par_ilut_spgeam_kernel.dp.cpp b/dpcpp/factorization/par_ilut_spgeam_kernel.dp.cpp index a4b23a4084d..e0fe8caaf85 100644 --- a/dpcpp/factorization/par_ilut_spgeam_kernel.dp.cpp +++ b/dpcpp/factorization/par_ilut_spgeam_kernel.dp.cpp @@ -62,7 +62,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The parallel ILUT factorization namespace. * @@ -468,6 +468,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace par_ilut_factorization -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/factorization/par_ilut_sweep_kernel.dp.cpp b/dpcpp/factorization/par_ilut_sweep_kernel.dp.cpp index 9862ae43b67..0373d77bbe5 100644 --- a/dpcpp/factorization/par_ilut_sweep_kernel.dp.cpp +++ b/dpcpp/factorization/par_ilut_sweep_kernel.dp.cpp @@ -60,7 +60,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The parallel ILUT factorization namespace. * @@ -253,6 +253,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace par_ilut_factorization -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/matrix/coo_kernels.dp.cpp b/dpcpp/matrix/coo_kernels.dp.cpp index 24fd97433af..6168491ee97 100644 --- a/dpcpp/matrix/coo_kernels.dp.cpp +++ b/dpcpp/matrix/coo_kernels.dp.cpp @@ -61,7 +61,7 @@ namespace kernels { * * @ingroup dpcpp */ -namespace dpcpp { +namespace sycl { /** * @brief The Coordinate matrix format namespace. * @@ -386,6 +386,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace coo -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/matrix/csr_kernels.dp.cpp b/dpcpp/matrix/csr_kernels.dp.cpp index 11309b67b9b..39b78e6c639 100644 --- a/dpcpp/matrix/csr_kernels.dp.cpp +++ b/dpcpp/matrix/csr_kernels.dp.cpp @@ -72,7 +72,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The Compressed sparse row matrix format namespace. * @@ -2505,6 +2505,6 @@ GKO_INSTANTIATE_FOR_EACH_INDEX_TYPE(GKO_DECLARE_CSR_BUILD_LOOKUP_KERNEL); } // namespace csr -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/matrix/dense_kernels.dp.cpp b/dpcpp/matrix/dense_kernels.dp.cpp index fba518f387b..565c25e82de 100644 --- a/dpcpp/matrix/dense_kernels.dp.cpp +++ b/dpcpp/matrix/dense_kernels.dp.cpp @@ -62,7 +62,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The Dense matrix format namespace. * @@ -602,6 +602,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_TYPE(GKO_DECLARE_DENSE_CONJ_TRANSPOSE_KERNEL); } // namespace dense -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/matrix/diagonal_kernels.dp.cpp b/dpcpp/matrix/diagonal_kernels.dp.cpp index 99c94b58c83..acb1f138bf7 100644 --- a/dpcpp/matrix/diagonal_kernels.dp.cpp +++ b/dpcpp/matrix/diagonal_kernels.dp.cpp @@ -49,7 +49,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The Diagonal matrix format namespace. * @@ -118,6 +118,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace diagonal -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/matrix/ell_kernels.dp.cpp b/dpcpp/matrix/ell_kernels.dp.cpp index 65fad771140..32d167c6de2 100644 --- a/dpcpp/matrix/ell_kernels.dp.cpp +++ b/dpcpp/matrix/ell_kernels.dp.cpp @@ -64,7 +64,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The ELL matrix format namespace. * @@ -482,6 +482,6 @@ GKO_INSTANTIATE_FOR_EACH_MIXED_VALUE_AND_INDEX_TYPE( } // namespace ell -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/matrix/fbcsr_kernels.dp.cpp b/dpcpp/matrix/fbcsr_kernels.dp.cpp index 0f789c1c27e..977bfec653f 100644 --- a/dpcpp/matrix/fbcsr_kernels.dp.cpp +++ b/dpcpp/matrix/fbcsr_kernels.dp.cpp @@ -48,7 +48,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The fixed-size block compressed sparse row matrix format namespace. * @@ -156,6 +156,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace fbcsr -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/matrix/fft_kernels.dp.cpp b/dpcpp/matrix/fft_kernels.dp.cpp index e7f049d4edc..f15e589a84f 100644 --- a/dpcpp/matrix/fft_kernels.dp.cpp +++ b/dpcpp/matrix/fft_kernels.dp.cpp @@ -40,7 +40,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The FFT matrix format namespace. * @ref Fft @@ -79,6 +79,6 @@ GKO_INSTANTIATE_FOR_EACH_NON_COMPLEX_VALUE_TYPE(GKO_DECLARE_FFT3_KERNEL); } // namespace fft -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/matrix/sellp_kernels.dp.cpp b/dpcpp/matrix/sellp_kernels.dp.cpp index 2633c6e823e..aefb958323a 100644 --- a/dpcpp/matrix/sellp_kernels.dp.cpp +++ b/dpcpp/matrix/sellp_kernels.dp.cpp @@ -54,7 +54,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The SELL-P matrix format namespace. * @@ -178,6 +178,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace sellp -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/matrix/sparsity_csr_kernels.dp.cpp b/dpcpp/matrix/sparsity_csr_kernels.dp.cpp index 1acc16d7026..8e7fd4a7ee9 100644 --- a/dpcpp/matrix/sparsity_csr_kernels.dp.cpp +++ b/dpcpp/matrix/sparsity_csr_kernels.dp.cpp @@ -52,7 +52,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The Compressed sparse row matrix format namespace. * @@ -360,6 +360,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace sparsity_csr -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/multigrid/pgm_kernels.dp.cpp b/dpcpp/multigrid/pgm_kernels.dp.cpp index b404b1c10ab..6ee2fae4a10 100644 --- a/dpcpp/multigrid/pgm_kernels.dp.cpp +++ b/dpcpp/multigrid/pgm_kernels.dp.cpp @@ -52,7 +52,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The PGM solver namespace. * @@ -130,6 +130,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace pgm -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/preconditioner/isai_kernels.dp.cpp b/dpcpp/preconditioner/isai_kernels.dp.cpp index 918b7784285..f3e1c2c58ac 100644 --- a/dpcpp/preconditioner/isai_kernels.dp.cpp +++ b/dpcpp/preconditioner/isai_kernels.dp.cpp @@ -56,7 +56,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The Isai preconditioner namespace. * @ref Isai @@ -778,6 +778,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace isai -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/preconditioner/jacobi_advanced_apply_instantiate.inc.dp.cpp b/dpcpp/preconditioner/jacobi_advanced_apply_instantiate.inc.dp.cpp index 40acfd67d73..2f5b4c70991 100644 --- a/dpcpp/preconditioner/jacobi_advanced_apply_instantiate.inc.dp.cpp +++ b/dpcpp/preconditioner/jacobi_advanced_apply_instantiate.inc.dp.cpp @@ -53,7 +53,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The Jacobi preconditioner namespace. * @ref Jacobi @@ -234,6 +234,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace jacobi -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/preconditioner/jacobi_advanced_apply_kernel.dp.cpp b/dpcpp/preconditioner/jacobi_advanced_apply_kernel.dp.cpp index dfb8e251426..b0c82a273c3 100644 --- a/dpcpp/preconditioner/jacobi_advanced_apply_kernel.dp.cpp +++ b/dpcpp/preconditioner/jacobi_advanced_apply_kernel.dp.cpp @@ -43,7 +43,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The Jacobi preconditioner namespace. * @ref Jacobi @@ -100,6 +100,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE(GKO_DECLARE_JACOBI_APPLY_KERNEL); } // namespace jacobi -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/preconditioner/jacobi_common.hpp.in b/dpcpp/preconditioner/jacobi_common.hpp.in index dc93bd26666..63009bde0df 100644 --- a/dpcpp/preconditioner/jacobi_common.hpp.in +++ b/dpcpp/preconditioner/jacobi_common.hpp.in @@ -38,7 +38,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { namespace jacobi { @@ -66,6 +66,6 @@ constexpr int get_larger_power(int value, int guess = 1) } // namespace jacobi -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/preconditioner/jacobi_generate_instantiate.inc.dp.cpp b/dpcpp/preconditioner/jacobi_generate_instantiate.inc.dp.cpp index f70974256d2..31c8693abb7 100644 --- a/dpcpp/preconditioner/jacobi_generate_instantiate.inc.dp.cpp +++ b/dpcpp/preconditioner/jacobi_generate_instantiate.inc.dp.cpp @@ -57,7 +57,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The Jacobi preconditioner namespace. * @ref Jacobi @@ -427,6 +427,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace jacobi -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/preconditioner/jacobi_generate_kernel.dp.cpp b/dpcpp/preconditioner/jacobi_generate_kernel.dp.cpp index 9479dfd997a..7ed6b16a6ec 100644 --- a/dpcpp/preconditioner/jacobi_generate_kernel.dp.cpp +++ b/dpcpp/preconditioner/jacobi_generate_kernel.dp.cpp @@ -44,7 +44,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The Jacobi preconditioner namespace. * @ref Jacobi @@ -97,6 +97,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace jacobi -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/preconditioner/jacobi_kernels.dp.cpp b/dpcpp/preconditioner/jacobi_kernels.dp.cpp index 24692e6d04e..52128c6bda1 100644 --- a/dpcpp/preconditioner/jacobi_kernels.dp.cpp +++ b/dpcpp/preconditioner/jacobi_kernels.dp.cpp @@ -51,7 +51,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The Jacobi preconditioner namespace. * @ref Jacobi @@ -525,6 +525,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace jacobi -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/preconditioner/jacobi_simple_apply_instantiate.inc.dp.cpp b/dpcpp/preconditioner/jacobi_simple_apply_instantiate.inc.dp.cpp index e96bf883fee..39e78f37d1c 100644 --- a/dpcpp/preconditioner/jacobi_simple_apply_instantiate.inc.dp.cpp +++ b/dpcpp/preconditioner/jacobi_simple_apply_instantiate.inc.dp.cpp @@ -53,7 +53,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The Jacobi preconditioner namespace. * @ref Jacobi @@ -227,6 +227,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace jacobi -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/preconditioner/jacobi_simple_apply_kernel.dp.cpp b/dpcpp/preconditioner/jacobi_simple_apply_kernel.dp.cpp index a815db95e7a..0303e430fac 100644 --- a/dpcpp/preconditioner/jacobi_simple_apply_kernel.dp.cpp +++ b/dpcpp/preconditioner/jacobi_simple_apply_kernel.dp.cpp @@ -43,7 +43,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The Jacobi preconditioner namespace. * @ref Jacobi @@ -97,6 +97,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace jacobi -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/reorder/rcm_kernels.dp.cpp b/dpcpp/reorder/rcm_kernels.dp.cpp index 3d5e33a6ce8..f773cf7b1be 100644 --- a/dpcpp/reorder/rcm_kernels.dp.cpp +++ b/dpcpp/reorder/rcm_kernels.dp.cpp @@ -46,7 +46,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The reordering namespace. * @@ -76,6 +76,6 @@ GKO_INSTANTIATE_FOR_EACH_INDEX_TYPE(GKO_DECLARE_RCM_GET_PERMUTATION_KERNEL); } // namespace rcm -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/solver/cb_gmres_kernels.dp.cpp b/dpcpp/solver/cb_gmres_kernels.dp.cpp index 9630b8dcb91..618159151ca 100644 --- a/dpcpp/solver/cb_gmres_kernels.dp.cpp +++ b/dpcpp/solver/cb_gmres_kernels.dp.cpp @@ -62,7 +62,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The CB_GMRES solver namespace. * @@ -1353,6 +1353,6 @@ GKO_INSTANTIATE_FOR_EACH_CB_GMRES_CONST_TYPE( } // namespace cb_gmres -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/solver/idr_kernels.dp.cpp b/dpcpp/solver/idr_kernels.dp.cpp index 3e7b5737f0f..00e36972c86 100644 --- a/dpcpp/solver/idr_kernels.dp.cpp +++ b/dpcpp/solver/idr_kernels.dp.cpp @@ -57,7 +57,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The IDR solver namespace. * @@ -883,6 +883,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_TYPE(GKO_DECLARE_IDR_COMPUTE_OMEGA_KERNEL); } // namespace idr -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/solver/lower_trs_kernels.dp.cpp b/dpcpp/solver/lower_trs_kernels.dp.cpp index 5d507517c20..ce09c3ac0e3 100644 --- a/dpcpp/solver/lower_trs_kernels.dp.cpp +++ b/dpcpp/solver/lower_trs_kernels.dp.cpp @@ -50,7 +50,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The LOWER_TRS solver namespace. * @@ -95,6 +95,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace lower_trs -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/solver/multigrid_kernels.dp.cpp b/dpcpp/solver/multigrid_kernels.dp.cpp index 110b1df0d3d..efea39da0d3 100644 --- a/dpcpp/solver/multigrid_kernels.dp.cpp +++ b/dpcpp/solver/multigrid_kernels.dp.cpp @@ -44,7 +44,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The MULTIGRID solver namespace. * @@ -89,6 +89,6 @@ GKO_INSTANTIATE_FOR_EACH_NON_COMPLEX_VALUE_TYPE( } // namespace multigrid -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/solver/upper_trs_kernels.dp.cpp b/dpcpp/solver/upper_trs_kernels.dp.cpp index 255e088fef5..12cdcc72183 100644 --- a/dpcpp/solver/upper_trs_kernels.dp.cpp +++ b/dpcpp/solver/upper_trs_kernels.dp.cpp @@ -50,7 +50,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The UPPER_TRS solver namespace. * @@ -95,6 +95,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE( } // namespace upper_trs -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/stop/criterion_kernels.dp.cpp b/dpcpp/stop/criterion_kernels.dp.cpp index aa4b542c2cc..5fd78cc2115 100644 --- a/dpcpp/stop/criterion_kernels.dp.cpp +++ b/dpcpp/stop/criterion_kernels.dp.cpp @@ -41,7 +41,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The Setting of all statuses namespace. * @ref set_status @@ -66,6 +66,6 @@ void set_all_statuses(std::shared_ptr exec, } // namespace set_all_statuses -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/stop/residual_norm_kernels.dp.cpp b/dpcpp/stop/residual_norm_kernels.dp.cpp index 6d47c5bdcb2..6b351e8a421 100644 --- a/dpcpp/stop/residual_norm_kernels.dp.cpp +++ b/dpcpp/stop/residual_norm_kernels.dp.cpp @@ -47,7 +47,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { /** * @brief The Residual norm stopping criterion namespace. * @ref resnorm @@ -160,6 +160,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_TYPE(GKO_DECLARE_IMPLICIT_RESIDUAL_NORM_KERNEL); } // namespace implicit_residual_norm -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/dpcpp/test/base/kernel_launch.dp.cpp b/dpcpp/test/base/kernel_launch.dp.cpp index 01b4e6a22e1..4bf383eeed3 100644 --- a/dpcpp/test/base/kernel_launch.dp.cpp +++ b/dpcpp/test/base/kernel_launch.dp.cpp @@ -71,7 +71,7 @@ move_only_type move_only_val{}; namespace gko { namespace kernels { -namespace dpcpp { +namespace sycl { template <> @@ -82,7 +82,7 @@ struct to_device_type_impl { }; -} // namespace dpcpp +} // namespace sycl } // namespace kernels } // namespace gko diff --git a/include/ginkgo/core/base/executor.hpp b/include/ginkgo/core/base/executor.hpp index 456b69d3d7e..01b15e2c5ef 100644 --- a/include/ginkgo/core/base/executor.hpp +++ b/include/ginkgo/core/base/executor.hpp @@ -410,7 +410,7 @@ RegisteredOperation make_register_operation(const char* name, * // hip code * } * } - * namespace dpcpp { + * namespace sycl { * void my_kernel(int x) { * // dpcpp code * } @@ -2084,8 +2084,15 @@ class DpcppExecutor : public detail::ExecutorBase, namespace kernels { -namespace dpcpp { +namespace sycl { using DefaultExecutor = DpcppExecutor; +} // namespace sycl +} // namespace kernels + + +namespace kernels { +namespace dpcpp { +using DefaultExecutor [[deprecated("using sycl namespace")]] = DpcppExecutor; } // namespace dpcpp } // namespace kernels diff --git a/include/ginkgo/core/base/math.hpp b/include/ginkgo/core/base/math.hpp index 70e4db5bb2d..f66c3e7bb8e 100644 --- a/include/ginkgo/core/base/math.hpp +++ b/include/ginkgo/core/base/math.hpp @@ -95,7 +95,7 @@ using std::sqrt; namespace kernels { -namespace dpcpp { +namespace sycl { using std::abs; @@ -104,6 +104,26 @@ using std::abs; using std::sqrt; +} // namespace sycl + + +namespace dpcpp { + + +template +[[deprecated("using sycl namespace")]] inline auto abs(T val) +{ + return std::abs(val); +} + + +template +[[deprecated("using sycl namespace")]] inline auto sqrt(T val) +{ + return std::sqrt(val); +} + + } // namespace dpcpp } // namespace kernels diff --git a/test/base/executor.cpp b/test/base/executor.cpp index 97814de4756..c51fcb8c1f1 100644 --- a/test/base/executor.cpp +++ b/test/base/executor.cpp @@ -59,7 +59,7 @@ namespace hip { int value = 3; } -namespace dpcpp { +namespace sycl { int value = 4; }