ContinuousConvSYCLKernels.cpp File Reference

(d32b4fc (Mon Sep 14 15:46:25 2026 -0700))

#include "open3d/ml/impl/continuous_conv/ContinuousConvSYCLKernels.h"
#include "open3d/ml/impl/continuous_conv/CoordinateTransformationSYCL.h"

Namespaces
namespace	open3d
namespace	open3d::ml
namespace	open3d::ml::impl

Macros
#define	FN_PARAMETERS
#define	CALL_TEMPLATE(INTERPOLATION, MAPPING, ALIGN_CORNERS)
#define	CALL_TEMPLATE2(INTERPOLATION, MAPPING)
#define	CALL_TEMPLATE3(INTERPOLATION)
#define	CALL_TEMPLATE4
#define	FN_PARAMETERS
#define	CALL_TEMPLATE(INTERPOLATION, MAPPING, ALIGN_CORNERS)
#define	CALL_TEMPLATE2(INTERPOLATION, MAPPING)
#define	CALL_TEMPLATE3(INTERPOLATION)
#define	CALL_TEMPLATE4

Functions
template<class T >
sycl::event	open3d::ml::impl::MultiplyColumnsSYCL (sycl::queue &queue, size_t rows, size_t cols, T *col_major_matrix, const T *const vector, const std::vector< sycl::event > &deps)
template<class T >
sycl::event	open3d::ml::impl::MultiplyAndCopyColumnsSYCL (sycl::queue &queue, size_t rows, size_t cols, T *out_ptr, const T *const col_major_matrix, const T *const vector, const std::vector< sycl::event > &deps)
template sycl::event	open3d::ml::impl::MultiplyColumnsSYCL< float > (sycl::queue &queue, size_t rows, size_t cols, float *col_major_matrix, const float *const vector, const std::vector< sycl::event > &deps)
template sycl::event	open3d::ml::impl::MultiplyAndCopyColumnsSYCL< float > (sycl::queue &queue, size_t rows, size_t cols, float *out_ptr, const float *const col_major_matrix, const float *const vector, const std::vector< sycl::event > &deps)
template<class TFeat , class TReal , class TIndex >
sycl::event	open3d::ml::impl::FillColumnSYCL (sycl::queue &queue, TFeat *columns, int in_channels, TIndex begin_idx, TIndex end_idx, TIndex num_out, const TReal *const out_positions, TIndex num_inp, const TReal *const inp_positions, const TFeat *const inp_features, const TFeat *const inp_importance, size_t neighbors_index_size, const TIndex *const neighbors_index, const TFeat *const neighbors_importance, const int64_t *const neighbors_row_splits, const TReal *const extents, const TReal *const offsets, const std::vector< int > &filter_dims, InterpolationMode interpolation, CoordinateMapping coordinate_mapping, bool align_corners, bool individual_extent, bool isotropic_extent, bool normalize, const std::vector< sycl::event > &deps)
template<class TFeat , class TReal , class TIndex >
sycl::event	open3d::ml::impl::FillColumnTransposeSYCL (sycl::queue &queue, TFeat *columns, int in_channels, TIndex begin_idx, TIndex end_idx, TIndex num_out, const TReal *const out_positions, TIndex num_inp, const TReal *const inp_positions, const TFeat *const inp_features, const TFeat *const inp_neighbors_importance_sum, const int64_t *const inp_neighbors_prefix_sum, size_t neighbors_index_size, const TIndex *const neighbors_index, const TFeat *const neighbors_importance, const int64_t *const neighbors_row_splits, const TReal *const extents, const TReal *const offsets, const std::vector< int > &filter_dims, InterpolationMode interpolation, CoordinateMapping coordinate_mapping, bool align_corners, bool individual_extent, bool isotropic_extent, bool normalize, const std::vector< sycl::event > &deps)
template sycl::event	open3d::ml::impl::FillColumnSYCL< float, float, int32_t > (sycl::queue &queue, float *columns, int in_channels, int32_t begin_idx, int32_t end_idx, int32_t num_out, const float *const out_positions, int32_t num_inp, const float *const inp_positions, const float *const inp_features, const float *const inp_importance, size_t neighbors_index_size, const int32_t *const neighbors_index, const float *const neighbors_importance, const int64_t *const neighbors_row_splits, const float *const extents, const float *const offsets, const std::vector< int > &filter_dims, InterpolationMode interpolation, CoordinateMapping coordinate_mapping, bool align_corners, bool individual_extent, bool isotropic_extent, bool normalize, const std::vector< sycl::event > &deps)
template sycl::event	open3d::ml::impl::FillColumnTransposeSYCL< float, float, int32_t > (sycl::queue &queue, float *columns, int in_channels, int32_t begin_idx, int32_t end_idx, int32_t num_out, const float *const out_positions, int32_t num_inp, const float *const inp_positions, const float *const inp_features, const float *const inp_neighbors_importance_sum, const int64_t *const inp_neighbors_prefix_sum, size_t neighbors_index_size, const int32_t *const neighbors_index, const float *const neighbors_importance, const int64_t *const neighbors_row_splits, const float *const extents, const float *const offsets, const std::vector< int > &filter_dims, InterpolationMode interpolation, CoordinateMapping coordinate_mapping, bool align_corners, bool individual_extent, bool isotropic_extent, bool normalize, const std::vector< sycl::event > &deps)

Macro Definition Documentation

CALL_TEMPLATE [1/2]

#define CALL_TEMPLATE	(		INTERPOLATION,
			MAPPING,
			ALIGN_CORNERS
	)

Value:

    if (INTERPOLATION == interpolation && MAPPING == coordinate_mapping && \
        ALIGN_CORNERS == align_corners)                                    \
        result_event =                                                     \
                FillColumnKernelSYCL<TFeat, TReal, TIndex, ALIGN_CORNERS,  \
                                     MAPPING, INTERPOLATION>(FN_PARAMETERS);

CALL_TEMPLATE [2/2]

#define CALL_TEMPLATE	(		INTERPOLATION,
			MAPPING,
			ALIGN_CORNERS
	)

Value:

    if (INTERPOLATION == interpolation && MAPPING == coordinate_mapping &&    \
        ALIGN_CORNERS == align_corners)                                       \
        result_event = FillColumnTransposeKernelSYCL<                         \
                TFeat, TReal, TIndex, ALIGN_CORNERS, MAPPING, INTERPOLATION>( \
                FN_PARAMETERS);

CALL_TEMPLATE2 [1/2]

#define CALL_TEMPLATE2	(		INTERPOLATION,
			MAPPING
	)

Value:

    CALL_TEMPLATE(INTERPOLATION, MAPPING, true) \
    CALL_TEMPLATE(INTERPOLATION, MAPPING, false)

CALL_TEMPLATE2 [2/2]

#define CALL_TEMPLATE2	(		INTERPOLATION,
			MAPPING
	)

Value:

    CALL_TEMPLATE(INTERPOLATION, MAPPING, true) \
    CALL_TEMPLATE(INTERPOLATION, MAPPING, false)

CALL_TEMPLATE3 [1/2]

#define CALL_TEMPLATE3

(

INTERPOLATION

)

Value:

    CALL_TEMPLATE2(INTERPOLATION, CoordinateMapping::BALL_TO_CUBE_RADIAL) \
    CALL_TEMPLATE2(INTERPOLATION,                                         \
                   CoordinateMapping::BALL_TO_CUBE_VOLUME_PRESERVING)     \
    CALL_TEMPLATE2(INTERPOLATION, CoordinateMapping::IDENTITY)

CALL_TEMPLATE3 [2/2]

#define CALL_TEMPLATE3

(

INTERPOLATION

)

Value:

    CALL_TEMPLATE2(INTERPOLATION, CoordinateMapping::BALL_TO_CUBE_RADIAL) \
    CALL_TEMPLATE2(INTERPOLATION,                                         \
                   CoordinateMapping::BALL_TO_CUBE_VOLUME_PRESERVING)     \
    CALL_TEMPLATE2(INTERPOLATION, CoordinateMapping::IDENTITY)

CALL_TEMPLATE4 [1/2]

#define CALL_TEMPLATE4

Value:

    CALL_TEMPLATE3(InterpolationMode::LINEAR)        \
    CALL_TEMPLATE3(InterpolationMode::LINEAR_BORDER) \
    CALL_TEMPLATE3(InterpolationMode::NEAREST_NEIGHBOR)

CALL_TEMPLATE4 [2/2]

#define CALL_TEMPLATE4

Value:

    CALL_TEMPLATE3(InterpolationMode::LINEAR)        \
    CALL_TEMPLATE3(InterpolationMode::LINEAR_BORDER) \
    CALL_TEMPLATE3(InterpolationMode::NEAREST_NEIGHBOR)

FN_PARAMETERS [1/2]

#define FN_PARAMETERS

Value:

    queue, columns, in_channels, begin_idx, end_idx, num_out, out_positions,   \
            num_inp, inp_positions, inp_features, inp_importance,              \
            neighbors_index_size, neighbors_index, neighbors_importance,       \
            neighbors_row_splits, extents, offsets, filter_size_x,             \
            filter_size_y, filter_size_z, individual_extent, isotropic_extent, \
            normalize, deps

FN_PARAMETERS [2/2]

#define FN_PARAMETERS

Value:

    queue, columns, in_channels, begin_idx, end_idx, num_out, out_positions,   \
            num_inp, inp_positions, inp_features,                              \
            inp_neighbors_importance_sum, inp_neighbors_prefix_sum,            \
            neighbors_index_size, neighbors_index, neighbors_importance,       \
            neighbors_row_splits, extents, offsets, filter_size_x,             \
            filter_size_y, filter_size_z, individual_extent, isotropic_extent, \
            normalize, deps