ArangeSYCL.cpp

Go to the documentation of this file.

// ----------------------------------------------------------------------------
// -                        CloudViewer: www.cloudViewer.org                  -
// ----------------------------------------------------------------------------
// Copyright (c) 2018-2024 www.cloudViewer.org
// SPDX-License-Identifier: MIT
// ----------------------------------------------------------------------------
 
#include "cloudViewer/core/Dispatch.h"
#include "cloudViewer/core/SYCLContext.h"
#include "cloudViewer/core/Tensor.h"
#include "cloudViewer/core/kernel/Arange.h"
 
namespace cloudViewer {
namespace core {
namespace kernel {
 
void ArangeSYCL(const Tensor& start,
                const Tensor& stop,
                const Tensor& step,
                Tensor& dst) {
    Dtype dtype = start.GetDtype();
    sycl::queue queue =
            sy::SYCLContext::GetInstance().GetDefaultQueue(start.GetDevice());
    DISPATCH_DTYPE_TO_TEMPLATE(dtype, [&]() {
        scalar_t sstart = start.Item<scalar_t>();
        scalar_t sstep = step.Item<scalar_t>();
        scalar_t* dst_ptr = dst.GetDataPtr<scalar_t>();
        int64_t n = dst.GetLength();
        queue.parallel_for(n, [=](int64_t i) {
                 dst_ptr[i] = sstart + static_cast<scalar_t>(sstep * i);
             }).wait_and_throw();
    });
}
 
}  // namespace kernel
}  // namespace core
}  // namespace cloudViewer