Compute Library
 23.11
Public Member Functions | Static Public Member Functions
CLPriorBoxLayerKernel Class Reference

Interface for the PriorBox layer kernel. More...

#include <CLPriorBoxLayerKernel.h>

Collaboration diagram for CLPriorBoxLayerKernel:
[legend]

Public Member Functions

 CLPriorBoxLayerKernel ()
 Constructor. More...
 
 CLPriorBoxLayerKernel (const CLPriorBoxLayerKernel &)=delete
 Prevent instances of this class from being copied (As this class contains pointers) More...
 
CLPriorBoxLayerKernel & operator= (const CLPriorBoxLayerKernel &)=delete
 Prevent instances of this class from being copied (As this class contains pointers) More...
 
 CLPriorBoxLayerKernel (CLPriorBoxLayerKernel &&)=default
 Default Move Constructor. More...
 
CLPriorBoxLayerKernel & operator= (CLPriorBoxLayerKernel &&)=default
 Default move assignment operator. More...
 
 ~CLPriorBoxLayerKernel ()=default
 Default destructor. More...
 
void configure (const ICLTensor *input1, const ICLTensor *input2, ICLTensor *output, const PriorBoxLayerInfo &info, cl::Buffer *min, cl::Buffer *max, cl::Buffer *aspect_ratios)
 Set the input and output tensors. More...
 
void configure (const CLCompileContext &compile_context, const ICLTensor *input1, const ICLTensor *input2, ICLTensor *output, const PriorBoxLayerInfo &info, cl::Buffer *min, cl::Buffer *max, cl::Buffer *aspect_ratios)
 Set the input and output tensors. More...
 
void run (const Window &window, cl::CommandQueue &queue) override
 Enqueue the OpenCL kernel to process the given window on the passed OpenCL command queue. More...
 
- Public Member Functions inherited from ICLKernel
 ICLKernel ()
 Constructor. More...
 
cl::Kernel & kernel ()
 Returns a reference to the OpenCL kernel of this object. More...
 
CLKernelType type () const
 Returns the CL kernel type. More...
 
template<typename T >
void add_1D_array_argument (unsigned int &idx, const ICLArray< T > *array, const Strides &strides, unsigned int num_dimensions, const Window &window)
 Add the passed 1D array's parameters to the object's kernel's arguments starting from the index idx. More...
 
void add_1D_tensor_argument (unsigned int &idx, const ICLTensor *tensor, const Window &window)
 Add the passed 1D tensor's parameters to the object's kernel's arguments starting from the index idx. More...
 
void add_1D_tensor_argument_if (bool cond, unsigned int &idx, const ICLTensor *tensor, const Window &window)
 Add the passed 1D tensor's parameters to the object's kernel's arguments starting from the index idx if the condition is true. More...
 
void add_2D_tensor_argument (unsigned int &idx, const ICLTensor *tensor, const Window &window)
 Add the passed 2D tensor's parameters to the object's kernel's arguments starting from the index idx. More...
 
void add_2D_tensor_argument_if (bool cond, unsigned int &idx, const ICLTensor *tensor, const Window &window)
 Add the passed 2D tensor's parameters to the object's kernel's arguments starting from the index idx if the condition is true. More...
 
void add_3D_tensor_argument (unsigned int &idx, const ICLTensor *tensor, const Window &window)
 Add the passed 3D tensor's parameters to the object's kernel's arguments starting from the index idx. More...
 
void add_4D_tensor_argument (unsigned int &idx, const ICLTensor *tensor, const Window &window)
 Add the passed 4D tensor's parameters to the object's kernel's arguments starting from the index idx. More...
 
void add_5D_tensor_argument (unsigned int &idx, const ICLTensor *tensor, const Window &window)
 Add the passed 5D tensor's parameters to the object's kernel's arguments starting from the index idx. More...
 
void add_3d_tensor_nhw_argument (unsigned int &idx, const ICLTensor *tensor)
 Add the passed NHW 3D tensor's parameters to the object's kernel's arguments by passing strides, dimensions and the offset to the first valid element in bytes. More...
 
void add_4d_tensor_nhwc_argument (unsigned int &idx, const ICLTensor *tensor)
 Add the passed NHWC 4D tensor's parameters to the object's kernel's arguments by passing strides, dimensions and the offset to the first valid element in bytes. More...
 
virtual void run_op (ITensorPack &tensors, const Window &window, cl::CommandQueue &queue)
 Enqueue the OpenCL kernel to process the given window on the passed OpenCL command queue. More...
 
template<typename T >
void add_argument (unsigned int &idx, T value)
 Add the passed parameters to the object's kernel's arguments starting from the index idx. More...
 
void set_lws_hint (const cl::NDRange &lws_hint)
 Set the Local-Workgroup-Size hint. More...
 
cl::NDRange lws_hint () const
 Return the Local-Workgroup-Size hint. More...
 
void set_wbsm_hint (const cl_int &wbsm_hint)
 Set the workgroup batch size modifier hint. More...
 
cl_int wbsm_hint () const
 Return the workgroup batch size modifier hint. More...
 
const std::string & config_id () const
 Get the configuration ID. More...
 
void set_target (GPUTarget target)
 Set the targeted GPU architecture. More...
 
void set_target (cl::Device &device)
 Set the targeted GPU architecture according to the CL device. More...
 
GPUTarget get_target () const
 Get the targeted GPU architecture. More...
 
size_t get_max_workgroup_size ()
 Get the maximum workgroup size for the device the CLKernelLibrary uses. More...
 
cl::NDRange get_cached_gws () const
 Get the cached gws used to enqueue this kernel. More...
 
void cache_gws (const cl::NDRange &gws)
 Cache the latest gws used to enqueue this kernel. More...
 
template<unsigned int dimension_size>
void add_tensor_argument (unsigned &idx, const ICLTensor *tensor, const Window &window)
 
template<typename T , unsigned int dimension_size>
void add_array_argument (unsigned &idx, const ICLArray< T > *array, const Strides &strides, unsigned int num_dimensions, const Window &window)
 Add the passed array's parameters to the object's kernel's arguments starting from the index idx. More...
 
- Public Member Functions inherited from IKernel
 IKernel ()
 Constructor. More...
 
virtual ~IKernel ()=default
 Destructor. More...
 
virtual bool is_parallelisable () const
 Indicates whether or not the kernel is parallelisable. More...
 
virtual BorderSize border_size () const
 The size of the border for that kernel. More...
 
const Window & window () const
 The maximum window the kernel can be executed on. More...
 
bool is_window_configured () const
 Function to check if the embedded window of this kernel has been configured. More...
 

Static Public Member Functions

static Status validate (const ITensorInfo *input1, const ITensorInfo *input2, const ITensorInfo *output, const PriorBoxLayerInfo &info)
 Static function to check if given info will lead to a valid configuration of CLPriorBoxLayerKernel. More...
 
- Static Public Member Functions inherited from ICLKernel
constexpr static unsigned int num_arguments_per_3d_tensor_nhw ()
 Returns the number of arguments enqueued per NHW 3D Tensor object. More...
 
constexpr static unsigned int num_arguments_per_4d_tensor_nhwc ()
 Returns the number of arguments enqueued per NHWC 4D Tensor object. More...
 
constexpr static unsigned int num_arguments_per_1D_array ()
 Returns the number of arguments enqueued per 1D array object. More...
 
constexpr static unsigned int num_arguments_per_1D_tensor ()
 Returns the number of arguments enqueued per 1D tensor object. More...
 
constexpr static unsigned int num_arguments_per_2D_tensor ()
 Returns the number of arguments enqueued per 2D tensor object. More...
 
constexpr static unsigned int num_arguments_per_3D_tensor ()
 Returns the number of arguments enqueued per 3D tensor object. More...
 
constexpr static unsigned int num_arguments_per_4D_tensor ()
 Returns the number of arguments enqueued per 4D tensor object. More...
 
static cl::NDRange gws_from_window (const Window &window, bool use_dummy_work_items)
 Get the global work size given an execution window. More...
 

Detailed Description

Interface for the PriorBox layer kernel.

Definition at line 34 of file CLPriorBoxLayerKernel.h.

Constructor & Destructor Documentation

◆ CLPriorBoxLayerKernel() [1/3]

CLPriorBoxLayerKernel ( )

Constructor.

Definition at line 109 of file CLPriorBoxLayerKernel.cpp.

110  : _input1(nullptr), _input2(nullptr), _output(nullptr), _info(), _num_priors(), _min(), _max(), _aspect_ratios()
111 {
112  _type = CLKernelType::ELEMENTWISE;
113 }

◆ CLPriorBoxLayerKernel() [2/3]

CLPriorBoxLayerKernel ( const CLPriorBoxLayerKernel &  )
delete

Prevent instances of this class from being copied (As this class contains pointers)

◆ CLPriorBoxLayerKernel() [3/3]

CLPriorBoxLayerKernel ( CLPriorBoxLayerKernel &&  )
default

Default Move Constructor.

◆ ~CLPriorBoxLayerKernel()

~CLPriorBoxLayerKernel ( )
default

Default destructor.

Member Function Documentation

◆ configure() [1/2]

void configure ( const CLCompileContext &  compile_context,
const ICLTensor *  input1,
const ICLTensor *  input2,
ICLTensor *  output,
const PriorBoxLayerInfo &  info,
cl::Buffer *  min,
cl::Buffer *  max,
cl::Buffer *  aspect_ratios 
)

Set the input and output tensors.

Parameters
[in]compile_contextThe compile context to be used.
[in]input1First source tensor. Data types supported: F32. Data layouts supported: NCHW/NHWC.
[in]input2Second source tensor. Data types and layouts supported: same as input1
[out]outputDestination tensor. Output dimensions are [W * H * num_priors * 4, 2]. Data types and layouts supported: same as input1
[in]infoPrior box layer info.
[in]minMinimum prior box values
[in]maxMaximum prior box values
[in]aspect_ratiosAspect ratio values

Definition at line 126 of file CLPriorBoxLayerKernel.cpp.

134 {
135  ARM_COMPUTE_ERROR_ON_NULLPTR(input1, input2, output);
136 
137  _input1 = input1;
138  _input2 = input2;
139  _output = output;
140  _info = info;
141  _min = min;
142  _max = max;
143  _aspect_ratios = aspect_ratios;
144 
145  ARM_COMPUTE_ERROR_THROW_ON(validate_arguments(input1->info(), input2->info(), output->info(), info));
146 
147  // Calculate number of aspect ratios
148  _num_priors = info.aspect_ratios().size() * info.min_sizes().size() + info.max_sizes().size();
149 
150  const DataLayout data_layout = input1->info()->data_layout();
151 
152  const int width_idx = get_data_layout_dimension_index(data_layout, DataLayoutDimension::WIDTH);
153  const int height_idx = get_data_layout_dimension_index(data_layout, DataLayoutDimension::HEIGHT);
154 
155  const int layer_width = input1->info()->dimension(width_idx);
156  const int layer_height = input1->info()->dimension(height_idx);
157 
158  int img_width = info.img_size().x;
159  int img_height = info.img_size().y;
160  if (img_width == 0 || img_height == 0)
161  {
162  img_width = input2->info()->dimension(width_idx);
163  img_height = input2->info()->dimension(height_idx);
164  }
165 
166  float step_x = info.steps()[0];
167  float step_y = info.steps()[0];
168  if (step_x == 0.f || step_y == 0.f)
169  {
170  step_x = static_cast<float>(img_width) / layer_width;
171  step_y = static_cast<float>(img_height) / layer_height;
172  }
173 
174  // Set build options
175  CLBuildOptions build_opts;
176  build_opts.add_option("-DDATA_TYPE=" + get_cl_type_from_data_type(input1->info()->data_type()));
177  build_opts.add_option("-DWIDTH=" + support::cpp11::to_string(img_width));
178  build_opts.add_option("-DHEIGHT=" + support::cpp11::to_string(img_height));
179  build_opts.add_option("-DLAYER_WIDTH=" + support::cpp11::to_string(layer_width));
180  build_opts.add_option("-DLAYER_HEIGHT=" + support::cpp11::to_string(layer_height));
181  build_opts.add_option("-DSTEP_X=" + support::cpp11::to_string(step_x));
182  build_opts.add_option("-DSTEP_Y=" + support::cpp11::to_string(step_y));
183  build_opts.add_option("-DNUM_PRIORS=" + support::cpp11::to_string(_num_priors));
184  build_opts.add_option("-DOFFSET=" + support::cpp11::to_string(info.offset()));
185  build_opts.add_option_if(info.clip(), "-DIN_PLACE");
186 
187  if (info.variances().size() > 1)
188  {
189  for (unsigned int i = 0; i < info.variances().size(); ++i)
190  {
191  build_opts.add_option("-DVARIANCE_" + support::cpp11::to_string(i) + "=" +
192  support::cpp11::to_string(info.variances().at(i)));
193  }
194  }
195  else
196  {
197  for (unsigned int i = 0; i < 4; ++i)
198  {
199  build_opts.add_option("-DVARIANCE_" + support::cpp11::to_string(i) + "=" +
200  support::cpp11::to_string(info.variances().at(0)));
201  }
202  }
203 
204  unsigned int idx = num_arguments_per_2D_tensor();
205  _kernel = create_kernel(compile_context, "prior_box_layer_nchw", build_opts.options());
206 
207  _kernel.setArg(idx++, *_min);
208  _kernel.setArg(idx++, *_max);
209  _kernel.setArg(idx++, *_aspect_ratios);
210  _kernel.setArg<unsigned int>(idx++, info.min_sizes().size());
211  _kernel.setArg<unsigned int>(idx++, info.max_sizes().size());
212  _kernel.setArg<unsigned int>(idx++, info.aspect_ratios().size());
213 
214  // Configure kernel window
215  auto win_config = validate_and_configure_window(input1->info(), input2->info(), output->info(), info, _num_priors);
216 
217  ARM_COMPUTE_ERROR_THROW_ON(win_config.first);
218  ICLKernel::configure_internal(win_config.second);
219 }

References CLBuildOptions::add_option(), CLBuildOptions::add_option_if(), ARM_COMPUTE_ERROR_ON_NULLPTR, ARM_COMPUTE_ERROR_THROW_ON, arm_compute::create_kernel(), arm_compute::cpu::data_layout, ITensorInfo::data_layout(), ITensorInfo::data_type(), ITensorInfo::dimension(), arm_compute::get_cl_type_from_data_type(), arm_compute::get_data_layout_dimension_index(), arm_compute::HEIGHT, arm_compute::cpu::height_idx, ITensor::info(), arm_compute::test::validation::info, ICLKernel::num_arguments_per_2D_tensor(), CLBuildOptions::options(), arm_compute::support::cpp11::to_string(), arm_compute::cpu::kernels::validate_and_configure_window(), arm_compute::cpu::kernels::validate_arguments(), arm_compute::WIDTH, and arm_compute::cpu::width_idx.

◆ configure() [2/2]

void configure ( const ICLTensor *  input1,
const ICLTensor *  input2,
ICLTensor *  output,
const PriorBoxLayerInfo &  info,
cl::Buffer *  min,
cl::Buffer *  max,
cl::Buffer *  aspect_ratios 
)

Set the input and output tensors.

Parameters
[in]input1First source tensor. Data types supported: F32. Data layouts supported: NCHW/NHWC.
[in]input2Second source tensor. Data types and layouts supported: same as input1
[out]outputDestination tensor. Output dimensions are [W * H * num_priors * 4, 2]. Data types and layouts supported: same as input1
[in]infoPrior box layer info.
[in]minMinimum prior box values
[in]maxMaximum prior box values
[in]aspect_ratiosAspect ratio values

Definition at line 115 of file CLPriorBoxLayerKernel.cpp.

122 {
123  configure(CLKernelLibrary::get().get_compile_context(), input1, input2, output, info, min, max, aspect_ratios);
124 }

References CLKernelLibrary::get(), and arm_compute::test::validation::info.

◆ operator=() [1/2]

CLPriorBoxLayerKernel& operator= ( CLPriorBoxLayerKernel &&  )
default

Default move assignment operator.

◆ operator=() [2/2]

CLPriorBoxLayerKernel& operator= ( const CLPriorBoxLayerKernel &  )
delete

Prevent instances of this class from being copied (As this class contains pointers)

◆ run()

void run ( const Window &  window,
cl::CommandQueue &  queue 
)
overridevirtual

Enqueue the OpenCL kernel to process the given window on the passed OpenCL command queue.

Note
The queue is not flushed by this method, and therefore the kernel will not have been executed by the time this method returns.
Parameters
[in]windowRegion on which to execute the kernel. (Must be a valid region of the window returned by window()).
[in,out]queueCommand queue on which to enqueue the kernel.

Reimplemented from ICLKernel.

Definition at line 236 of file CLPriorBoxLayerKernel.cpp.

237 {
238  ARM_COMPUTE_ERROR_ON_UNCONFIGURED_KERNEL(this);
239  ARM_COMPUTE_ERROR_ON_INVALID_SUBWINDOW(IKernel::window(), window);
240 
241  queue.enqueueWriteBuffer(*_min, CL_TRUE, 0, _info.min_sizes().size() * sizeof(float), _info.min_sizes().data());
242  queue.enqueueWriteBuffer(*_aspect_ratios, CL_TRUE, 0, _info.aspect_ratios().size() * sizeof(float),
243  _info.aspect_ratios().data());
244  if (!_info.max_sizes().empty())
245  {
246  queue.enqueueWriteBuffer(*_max, CL_TRUE, 0, _info.max_sizes().size() * sizeof(float), _info.max_sizes().data());
247  }
248 
249  Window slice = window.first_slice_window_2D();
250  slice.set(Window::DimY, Window::Dimension(0, _output->info()->dimension(1), 2));
251 
252  unsigned int idx = 0;
253  add_2D_tensor_argument(idx, _output, slice);
254  enqueue(queue, *this, slice, lws_hint());
255 }

References ICLKernel::add_2D_tensor_argument(), ARM_COMPUTE_ERROR_ON_INVALID_SUBWINDOW, ARM_COMPUTE_ERROR_ON_UNCONFIGURED_KERNEL, PriorBoxLayerInfo::aspect_ratios(), ITensorInfo::dimension(), Window::DimY, arm_compute::enqueue(), Window::first_slice_window_2D(), ITensor::info(), ICLKernel::lws_hint(), PriorBoxLayerInfo::max_sizes(), PriorBoxLayerInfo::min_sizes(), arm_compute::test::validation::reference::slice(), and IKernel::window().

◆ validate()

Status validate ( const ITensorInfo *  input1,
const ITensorInfo *  input2,
const ITensorInfo *  output,
const PriorBoxLayerInfo &  info 
)
static

Static function to check if given info will lead to a valid configuration of CLPriorBoxLayerKernel.

Parameters
[in]input1First source tensor info. Data types supported: F32. Data layouts supported: NCHW/NHWC.
[in]input2Second source tensor info. Data types and layouts supported: same as input1
[in]outputDestination tensor info. Output dimensions are [W * H * num_priors * 4, 2]. Data type supported: same as input1
[in]infoPrior box layer info.
Returns
a status

Definition at line 221 of file CLPriorBoxLayerKernel.cpp.

225 {
226  ARM_COMPUTE_ERROR_ON_NULLPTR(input1, input2, output);
227  ARM_COMPUTE_RETURN_ON_ERROR(validate_arguments(input1, input2, output, info));
228  const int num_priors = info.aspect_ratios().size() * info.min_sizes().size() + info.max_sizes().size();
229  ARM_COMPUTE_RETURN_ON_ERROR(validate_and_configure_window(input1->clone().get(), input2->clone().get(),
230  output->clone().get(), info, num_priors)
231  .first);
232 
233  return Status{};
234 }

References ARM_COMPUTE_ERROR_ON_NULLPTR, ARM_COMPUTE_RETURN_ON_ERROR, ICloneable< T >::clone(), arm_compute::test::validation::info, arm_compute::cpu::kernels::validate_and_configure_window(), and arm_compute::cpu::kernels::validate_arguments().

Referenced by CLPriorBoxLayer::validate().

The documentation for this class was generated from the following files:
arm_compute::support::cpp11::to_string
std::string to_string(T &&value)
Convert integer and float values to string.
Definition: StringSupport.h:168
arm_compute::PriorBoxLayerInfo::max_sizes
std::vector< float > max_sizes() const
Get max sizes.
Definition: Types.h:753
arm_compute::PriorBoxLayerInfo::min_sizes
std::vector< float > min_sizes() const
Get min sizes.
Definition: Types.h:718
arm_compute::PriorBoxLayerInfo::aspect_ratios
std::vector< float > aspect_ratios() const
Get aspect ratios.
Definition: Types.h:758
arm_compute::DataLayout
DataLayout
[DataLayout enum definition]
Definition: CoreTypes.h:110
arm_compute::cpu::kernels::validate_arguments
Status validate_arguments(const ITensorInfo *src, const ITensorInfo *weights, const ITensorInfo *dst, const PadStrideInfo &conv_info)
Definition: CpuDirectConv2dKernel.cpp:57
arm_compute::ICLKernel::num_arguments_per_2D_tensor
constexpr static unsigned int num_arguments_per_2D_tensor()
Returns the number of arguments enqueued per 2D tensor object.
Definition: ICLKernel.h:313
ARM_COMPUTE_ERROR_ON_UNCONFIGURED_KERNEL
#define ARM_COMPUTE_ERROR_ON_UNCONFIGURED_KERNEL(k)
Definition: Validate.h:1079
arm_compute::CLPriorBoxLayerKernel::configure
void configure(const ICLTensor *input1, const ICLTensor *input2, ICLTensor *output, const PriorBoxLayerInfo &info, cl::Buffer *min, cl::Buffer *max, cl::Buffer *aspect_ratios)
Set the input and output tensors.
Definition: CLPriorBoxLayerKernel.cpp:115
arm_compute::CLKernelLibrary::get
static CLKernelLibrary & get()
Access the KernelLibrary singleton.
Definition: CLKernelLibrary.cpp:41
arm_compute::DataLayoutDimension::WIDTH
@ WIDTH
width
arm_compute::cpu::data_layout
constexpr auto data_layout
Definition: impl.h:36
arm_compute::ICLKernel::add_2D_tensor_argument
void add_2D_tensor_argument(unsigned int &idx, const ICLTensor *tensor, const Window &window)
Add the passed 2D tensor's parameters to the object's kernel's arguments starting from the index idx.
Definition: ICLKernel.h:210
ARM_COMPUTE_RETURN_ON_ERROR
#define ARM_COMPUTE_RETURN_ON_ERROR(status)
Checks if a status contains an error and returns it.
Definition: Error.h:205
arm_compute::ITensorInfo::dimension
virtual size_t dimension(size_t index) const =0
Return the size of the requested dimension.
ARM_COMPUTE_ERROR_ON_NULLPTR
#define ARM_COMPUTE_ERROR_ON_NULLPTR(...)
Definition: Validate.h:159
arm_compute::ITensor::info
virtual ITensorInfo * info() const =0
Interface to be implemented by the child class to return the tensor's metadata.
ARM_COMPUTE_ERROR_THROW_ON
#define ARM_COMPUTE_ERROR_THROW_ON(status)
Definition: Error.h:455
arm_compute::DataLayoutDimension::HEIGHT
@ HEIGHT
height
arm_compute::create_kernel
cl::Kernel create_kernel(const CLCompileContext &ctx, const std::string &kernel_name, const std::set< std::string > &build_opts=std::set< std::string >())
Creates an opencl kernel using a compile context.
Definition: CLHelpers.cpp:409
ARM_COMPUTE_ERROR_ON_INVALID_SUBWINDOW
#define ARM_COMPUTE_ERROR_ON_INVALID_SUBWINDOW(f, s)
Definition: Validate.h:203
arm_compute::cpu::kernels::validate_and_configure_window
std::pair< Status, Window > validate_and_configure_window(ITensorInfo *src, ITensorInfo *dst)
Definition: CpuDirectConv2dKernel.cpp:92
arm_compute::Window::DimY
static constexpr size_t DimY
Alias for dimension 1 also known as Y dimension.
Definition: Window.h:45
arm_compute::IKernel::window
const Window & window() const
The maximum window the kernel can be executed on.
Definition: IKernel.cpp:28
arm_compute::get_cl_type_from_data_type
std::string get_cl_type_from_data_type(const DataType &dt)
Translates a tensor data type to the appropriate OpenCL type.
Definition: CLHelpers.cpp:41
arm_compute::get_data_layout_dimension_index
size_t get_data_layout_dimension_index(const DataLayout &data_layout, const DataLayoutDimension &data_layout_dimension)
Get the index of the given dimension.
Definition: Helpers.inl:201
arm_compute::ELEMENTWISE
@ ELEMENTWISE
Elementwise CL kernel type.
Definition: CLTypes.h:83
arm_compute::ICLKernel::lws_hint
cl::NDRange lws_hint() const
Return the Local-Workgroup-Size hint.
Definition: ICLKernel.h:383
arm_compute::cpu::width_idx
const size_t width_idx
Definition: impl.h:37
arm_compute::test::validation::info
ScaleKernelInfo info(interpolation_policy, default_border_mode, PixelValue(), sampling_policy, false)
arm_compute::test::validation::reference::slice
SimpleTensor< T > slice(const SimpleTensor< T > &src, Coordinates starts, Coordinates ends)
Definition: SliceOperations.cpp:38
arm_compute::Window::first_slice_window_2D
Window first_slice_window_2D() const
First 2D slice of the window.
Definition: Window.h:298
arm_compute::cpu::height_idx
const size_t height_idx
Definition: impl.h:38
arm_compute::enqueue
void enqueue(cl::CommandQueue &queue, ICLKernel &kernel, const Window &window, const cl::NDRange &lws_hint=CLKernelLibrary::get().default_ndrange(), bool use_dummy_work_items=false)
Add the kernel to the command queue with the given window.
Definition: ICLKernel.cpp:33