Skip to content

Commit

Permalink
deprecate namespace dpcpp by sycl
Browse files Browse the repository at this point in the history
  • Loading branch information
yhmtsai committed Aug 22, 2023
1 parent 9b4779a commit 9eea078
Show file tree
Hide file tree
Showing 88 changed files with 200 additions and 173 deletions.
4 changes: 2 additions & 2 deletions common/unified/base/kernel_launch.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -105,7 +105,7 @@ GKO_INLINE GKO_ATTRIBUTES constexpr unpack_member_type<T> unpack_member(T value)

namespace gko {
namespace kernels {
namespace dpcpp {
namespace sycl {


template <typename T>
Expand All @@ -127,7 +127,7 @@ GKO_INLINE GKO_ATTRIBUTES constexpr unpack_member_type<T> unpack_member(T value)
return value;
}

} // namespace dpcpp
} // namespace sycl
} // namespace kernels
} // namespace gko

Expand Down
2 changes: 1 addition & 1 deletion core/base/kernel_declaration.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -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__; \
} \
Expand Down
4 changes: 2 additions & 2 deletions core/device_hooks/dpcpp_hooks.cpp
Original file line number Diff line number Diff line change
Expand Up @@ -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


Expand Down
4 changes: 2 additions & 2 deletions core/log/profiler_hook.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -155,7 +155,7 @@ using profiling_scope_guard = log::default_profiling_scope_guard;
} // namespace hip


namespace dpcpp {
namespace sycl {


class profiling_scope_guard {
Expand All @@ -174,7 +174,7 @@ class profiling_scope_guard {
};


} // namespace dpcpp
} // namespace sycl
} // namespace kernels
} // namespace gko

Expand Down
4 changes: 2 additions & 2 deletions core/matrix/fft_kernels.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -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
Expand Down
4 changes: 2 additions & 2 deletions core/stop/residual_norm_kernels.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -148,7 +148,7 @@ GKO_DECLARE_ALL_AS_TEMPLATES2;
} // namespace hip


namespace dpcpp {
namespace sycl {
namespace residual_norm {

GKO_DECLARE_ALL_AS_TEMPLATES;
Expand All @@ -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
Expand Down
4 changes: 2 additions & 2 deletions dpcpp/base/batch_multi_vector_kernels.dp.cpp
Original file line number Diff line number Diff line change
Expand Up @@ -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
Expand Down Expand Up @@ -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
4 changes: 2 additions & 2 deletions dpcpp/base/batch_struct.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -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
Expand Down Expand Up @@ -85,7 +85,7 @@ inline batch::multi_vector::uniform_batch<ValueType> get_batch_struct(
}


} // namespace dpcpp
} // namespace sycl
} // namespace kernels
} // namespace gko

Expand Down
4 changes: 2 additions & 2 deletions dpcpp/base/config.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -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 {
Expand Down Expand Up @@ -152,7 +152,7 @@ using dcfg_1sg_type_list_t =
using dcfg_1sg_list_t = encode_list<dcfg_1sg_type_list_t>::type;


} // namespace dpcpp
} // namespace sycl
} // namespace kernels
} // namespace gko

Expand Down
4 changes: 2 additions & 2 deletions dpcpp/base/device.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -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

Expand Down
4 changes: 2 additions & 2 deletions dpcpp/base/device_matrix_data_kernels.dp.cpp
Original file line number Diff line number Diff line change
Expand Up @@ -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 {


Expand Down Expand Up @@ -151,6 +151,6 @@ GKO_INSTANTIATE_FOR_EACH_VALUE_AND_INDEX_TYPE(


} // namespace components
} // namespace dpcpp
} // namespace sycl
} // namespace kernels
} // namespace gko
4 changes: 2 additions & 2 deletions dpcpp/base/dim3.dp.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -39,7 +39,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE.

namespace gko {
namespace kernels {
namespace dpcpp {
namespace sycl {


/**
Expand Down Expand Up @@ -88,7 +88,7 @@ inline sycl::nd_range<3> sycl_nd_range(dim3 grid, dim3 block)
}


} // namespace dpcpp
} // namespace sycl
} // namespace kernels
} // namespace gko

Expand Down
4 changes: 2 additions & 2 deletions dpcpp/base/executor.dp.cpp
Original file line number Diff line number Diff line change
Expand Up @@ -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
4 changes: 2 additions & 2 deletions dpcpp/base/helper.dp.cpp
Original file line number Diff line number Diff line change
Expand Up @@ -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,
Expand All @@ -57,6 +57,6 @@ bool validate(sycl::queue* queue, unsigned int workgroup_size,
}


} // namespace dpcpp
} // namespace sycl
} // namespace kernels
} // namespace gko
4 changes: 2 additions & 2 deletions dpcpp/base/helper.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -181,7 +181,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE.

namespace gko {
namespace kernels {
namespace dpcpp {
namespace sycl {


/**
Expand Down Expand Up @@ -223,7 +223,7 @@ std::uint32_t get_first_cfg(const IterArr& arr, Validate verify)
}


} // namespace dpcpp
} // namespace sycl
} // namespace kernels
} // namespace gko

Expand Down
4 changes: 2 additions & 2 deletions dpcpp/base/index_set_kernels.dp.cpp
Original file line number Diff line number Diff line change
Expand Up @@ -48,7 +48,7 @@ namespace kernels {
*
* @ingroup dpcpp
*/
namespace dpcpp {
namespace sycl {
/**
* @brief The index_set namespace.
*
Expand Down Expand Up @@ -108,6 +108,6 @@ GKO_INSTANTIATE_FOR_EACH_INDEX_TYPE(


} // namespace idx_set
} // namespace dpcpp
} // namespace sycl
} // namespace kernels
} // namespace gko
4 changes: 2 additions & 2 deletions dpcpp/base/kernel_launch.dp.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -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;
Expand Down Expand Up @@ -97,6 +97,6 @@ void run_kernel(std::shared_ptr<const DpcppExecutor> exec, KernelFunction fn,
}


} // namespace dpcpp
} // namespace sycl
} // namespace kernels
} // namespace gko
4 changes: 2 additions & 2 deletions dpcpp/base/kernel_launch_reduction.dp.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -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();
Expand Down Expand Up @@ -718,6 +718,6 @@ void run_kernel_col_reduction_cached(std::shared_ptr<const DpcppExecutor> exec,
}


} // namespace dpcpp
} // namespace sycl
} // namespace kernels
} // namespace gko
4 changes: 2 additions & 2 deletions dpcpp/base/kernel_launch_solver.dp.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -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 <typename KernelFunction, typename... KernelArgs>
Expand Down Expand Up @@ -71,6 +71,6 @@ void run_kernel_solver(std::shared_ptr<const DpcppExecutor> exec,
}


} // namespace dpcpp
} // namespace sycl
} // namespace kernels
} // namespace gko
4 changes: 2 additions & 2 deletions dpcpp/base/onedpl.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -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<const DpcppExecutor> exec)
Expand All @@ -53,7 +53,7 @@ inline auto onedpl_policy(std::shared_ptr<const DpcppExecutor> exec)
}


} // namespace dpcpp
} // namespace sycl
} // namespace kernels
} // namespace gko

Expand Down
4 changes: 2 additions & 2 deletions dpcpp/base/onemkl_bindings.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -56,7 +56,7 @@ namespace kernels {
*
* @ingroup dpcpp
*/
namespace dpcpp {
namespace sycl {
/**
* @brief The ONEMKL namespace.
*
Expand Down Expand Up @@ -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

Expand Down
4 changes: 2 additions & 2 deletions dpcpp/components/atomic.dp.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -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 {


Expand Down Expand Up @@ -283,7 +283,7 @@ __dpct_inline__ T atomic_max(T* __restrict__ addr, T val)
}


} // namespace dpcpp
} // namespace sycl
} // namespace kernels
} // namespace gko

Expand Down
4 changes: 2 additions & 2 deletions dpcpp/components/cooperative_groups.dp.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -46,7 +46,7 @@ OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE.

namespace gko {
namespace kernels {
namespace dpcpp {
namespace sycl {


/**
Expand Down Expand Up @@ -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

Expand Down
Loading

0 comments on commit 9eea078

Please sign in to comment.