xref: /aosp_15_r20/external/ComputeLibrary/tests/validation/reference/ROIAlignLayer.cpp (revision c217d954acce2dbc11938adb493fc0abd69584f3)
1*c217d954SCole Faust /*
2*c217d954SCole Faust  * Copyright (c) 2018-2020 Arm Limited.
3*c217d954SCole Faust  *
4*c217d954SCole Faust  * SPDX-License-Identifier: MIT
5*c217d954SCole Faust  *
6*c217d954SCole Faust  * Permission is hereby granted, free of charge, to any person obtaining a copy
7*c217d954SCole Faust  * of this software and associated documentation files (the "Software"), to
8*c217d954SCole Faust  * deal in the Software without restriction, including without limitation the
9*c217d954SCole Faust  * rights to use, copy, modify, merge, publish, distribute, sublicense, and/or
10*c217d954SCole Faust  * sell copies of the Software, and to permit persons to whom the Software is
11*c217d954SCole Faust  * furnished to do so, subject to the following conditions:
12*c217d954SCole Faust  *
13*c217d954SCole Faust  * The above copyright notice and this permission notice shall be included in all
14*c217d954SCole Faust  * copies or substantial portions of the Software.
15*c217d954SCole Faust  *
16*c217d954SCole Faust  * THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR
17*c217d954SCole Faust  * IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,
18*c217d954SCole Faust  * FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. IN NO EVENT SHALL THE
19*c217d954SCole Faust  * AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER
20*c217d954SCole Faust  * LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING FROM,
21*c217d954SCole Faust  * OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN THE
22*c217d954SCole Faust  * SOFTWARE.
23*c217d954SCole Faust  */
24*c217d954SCole Faust #include "ROIAlignLayer.h"
25*c217d954SCole Faust 
26*c217d954SCole Faust #include "arm_compute/core/Types.h"
27*c217d954SCole Faust #include "arm_compute/core/utils/misc/ShapeCalculator.h"
28*c217d954SCole Faust #include "tests/validation/Helpers.h"
29*c217d954SCole Faust 
30*c217d954SCole Faust #include <algorithm>
31*c217d954SCole Faust 
32*c217d954SCole Faust namespace arm_compute
33*c217d954SCole Faust {
34*c217d954SCole Faust namespace test
35*c217d954SCole Faust {
36*c217d954SCole Faust namespace validation
37*c217d954SCole Faust {
38*c217d954SCole Faust namespace reference
39*c217d954SCole Faust {
40*c217d954SCole Faust namespace
41*c217d954SCole Faust {
42*c217d954SCole Faust /** Average pooling over an aligned window */
roi_align_1x1(const float * input,TensorShape input_shape,float region_start_x,float bin_size_x,int grid_size_x,float region_end_x,float region_start_y,float bin_size_y,int grid_size_y,float region_end_y,int pz)43*c217d954SCole Faust inline float roi_align_1x1(const float *input, TensorShape input_shape,
44*c217d954SCole Faust                            float region_start_x,
45*c217d954SCole Faust                            float bin_size_x,
46*c217d954SCole Faust                            int   grid_size_x,
47*c217d954SCole Faust                            float region_end_x,
48*c217d954SCole Faust                            float region_start_y,
49*c217d954SCole Faust                            float bin_size_y,
50*c217d954SCole Faust                            int   grid_size_y,
51*c217d954SCole Faust                            float region_end_y,
52*c217d954SCole Faust                            int   pz)
53*c217d954SCole Faust {
54*c217d954SCole Faust     if((region_end_x <= region_start_x) || (region_end_y <= region_start_y))
55*c217d954SCole Faust     {
56*c217d954SCole Faust         return 0;
57*c217d954SCole Faust     }
58*c217d954SCole Faust     else
59*c217d954SCole Faust     {
60*c217d954SCole Faust         float avg = 0;
61*c217d954SCole Faust         // Iterate through the aligned pooling region
62*c217d954SCole Faust         for(int iy = 0; iy < grid_size_y; ++iy)
63*c217d954SCole Faust         {
64*c217d954SCole Faust             for(int ix = 0; ix < grid_size_x; ++ix)
65*c217d954SCole Faust             {
66*c217d954SCole Faust                 // Align the window in the middle of every bin
67*c217d954SCole Faust                 float y = region_start_y + (iy + 0.5) * bin_size_y / float(grid_size_y);
68*c217d954SCole Faust                 float x = region_start_x + (ix + 0.5) * bin_size_x / float(grid_size_x);
69*c217d954SCole Faust 
70*c217d954SCole Faust                 // Interpolation in the [0,0] [0,1] [1,0] [1,1] square
71*c217d954SCole Faust                 const int y_low  = y;
72*c217d954SCole Faust                 const int x_low  = x;
73*c217d954SCole Faust                 const int y_high = y_low + 1;
74*c217d954SCole Faust                 const int x_high = x_low + 1;
75*c217d954SCole Faust 
76*c217d954SCole Faust                 const float ly = y - y_low;
77*c217d954SCole Faust                 const float lx = x - x_low;
78*c217d954SCole Faust                 const float hy = 1. - ly;
79*c217d954SCole Faust                 const float hx = 1. - lx;
80*c217d954SCole Faust 
81*c217d954SCole Faust                 const float w1 = hy * hx;
82*c217d954SCole Faust                 const float w2 = hy * lx;
83*c217d954SCole Faust                 const float w3 = ly * hx;
84*c217d954SCole Faust                 const float w4 = ly * lx;
85*c217d954SCole Faust 
86*c217d954SCole Faust                 const size_t idx1  = coord2index(input_shape, Coordinates(x_low, y_low, pz));
87*c217d954SCole Faust                 float        data1 = input[idx1];
88*c217d954SCole Faust 
89*c217d954SCole Faust                 const size_t idx2  = coord2index(input_shape, Coordinates(x_high, y_low, pz));
90*c217d954SCole Faust                 float        data2 = input[idx2];
91*c217d954SCole Faust 
92*c217d954SCole Faust                 const size_t idx3  = coord2index(input_shape, Coordinates(x_low, y_high, pz));
93*c217d954SCole Faust                 float        data3 = input[idx3];
94*c217d954SCole Faust 
95*c217d954SCole Faust                 const size_t idx4  = coord2index(input_shape, Coordinates(x_high, y_high, pz));
96*c217d954SCole Faust                 float        data4 = input[idx4];
97*c217d954SCole Faust 
98*c217d954SCole Faust                 avg += w1 * data1 + w2 * data2 + w3 * data3 + w4 * data4;
99*c217d954SCole Faust             }
100*c217d954SCole Faust         }
101*c217d954SCole Faust 
102*c217d954SCole Faust         avg /= grid_size_x * grid_size_y;
103*c217d954SCole Faust 
104*c217d954SCole Faust         return avg;
105*c217d954SCole Faust     }
106*c217d954SCole Faust }
107*c217d954SCole Faust 
108*c217d954SCole Faust template <typename TI, typename TO>
float_converter(const SimpleTensor<TI> & tensor,DataType dst_dt)109*c217d954SCole Faust SimpleTensor<TO> float_converter(const SimpleTensor<TI> &tensor, DataType dst_dt)
110*c217d954SCole Faust {
111*c217d954SCole Faust     SimpleTensor<TO> dst{ tensor.shape(), dst_dt, 1, QuantizationInfo(), tensor.data_layout() };
112*c217d954SCole Faust #if defined(_OPENMP)
113*c217d954SCole Faust     #pragma omp parallel for
114*c217d954SCole Faust #endif /* _OPENMP */
115*c217d954SCole Faust     for(int i = 0; i < tensor.num_elements(); ++i)
116*c217d954SCole Faust     {
117*c217d954SCole Faust         dst[i] = tensor[i];
118*c217d954SCole Faust     }
119*c217d954SCole Faust     return dst;
120*c217d954SCole Faust }
121*c217d954SCole Faust 
convert_rois_from_asymmetric(SimpleTensor<uint16_t> rois)122*c217d954SCole Faust SimpleTensor<float> convert_rois_from_asymmetric(SimpleTensor<uint16_t> rois)
123*c217d954SCole Faust {
124*c217d954SCole Faust     const UniformQuantizationInfo &quantization_info = rois.quantization_info().uniform();
125*c217d954SCole Faust     SimpleTensor<float>            dst{ rois.shape(), DataType::F32, 1, QuantizationInfo(), rois.data_layout() };
126*c217d954SCole Faust 
127*c217d954SCole Faust     for(int i = 0; i < rois.num_elements(); i += 5)
128*c217d954SCole Faust     {
129*c217d954SCole Faust         dst[i]     = static_cast<float>(rois[i]); // batch idx
130*c217d954SCole Faust         dst[i + 1] = dequantize_qasymm16(rois[i + 1], quantization_info);
131*c217d954SCole Faust         dst[i + 2] = dequantize_qasymm16(rois[i + 2], quantization_info);
132*c217d954SCole Faust         dst[i + 3] = dequantize_qasymm16(rois[i + 3], quantization_info);
133*c217d954SCole Faust         dst[i + 4] = dequantize_qasymm16(rois[i + 4], quantization_info);
134*c217d954SCole Faust     }
135*c217d954SCole Faust     return dst;
136*c217d954SCole Faust }
137*c217d954SCole Faust } // namespace
138*c217d954SCole Faust 
139*c217d954SCole Faust template <>
roi_align_layer(const SimpleTensor<float> & src,const SimpleTensor<float> & rois,const ROIPoolingLayerInfo & pool_info,const QuantizationInfo & output_qinfo)140*c217d954SCole Faust SimpleTensor<float> roi_align_layer(const SimpleTensor<float> &src, const SimpleTensor<float> &rois, const ROIPoolingLayerInfo &pool_info, const QuantizationInfo &output_qinfo)
141*c217d954SCole Faust {
142*c217d954SCole Faust     ARM_COMPUTE_UNUSED(output_qinfo);
143*c217d954SCole Faust 
144*c217d954SCole Faust     const size_t values_per_roi = rois.shape()[0];
145*c217d954SCole Faust     const size_t num_rois       = rois.shape()[1];
146*c217d954SCole Faust     DataType     dst_data_type  = src.data_type();
147*c217d954SCole Faust 
148*c217d954SCole Faust     const auto *rois_ptr = static_cast<const float *>(rois.data());
149*c217d954SCole Faust 
150*c217d954SCole Faust     TensorShape         input_shape = src.shape();
151*c217d954SCole Faust     TensorShape         output_shape(pool_info.pooled_width(), pool_info.pooled_height(), src.shape()[2], num_rois);
152*c217d954SCole Faust     SimpleTensor<float> dst(output_shape, dst_data_type);
153*c217d954SCole Faust 
154*c217d954SCole Faust     // Iterate over every pixel of the input image
155*c217d954SCole Faust     for(size_t px = 0; px < pool_info.pooled_width(); ++px)
156*c217d954SCole Faust     {
157*c217d954SCole Faust         for(size_t py = 0; py < pool_info.pooled_height(); ++py)
158*c217d954SCole Faust         {
159*c217d954SCole Faust             for(size_t pw = 0; pw < num_rois; ++pw)
160*c217d954SCole Faust             {
161*c217d954SCole Faust                 const unsigned int roi_batch = rois_ptr[values_per_roi * pw];
162*c217d954SCole Faust                 const auto         x1        = float(rois_ptr[values_per_roi * pw + 1]);
163*c217d954SCole Faust                 const auto         y1        = float(rois_ptr[values_per_roi * pw + 2]);
164*c217d954SCole Faust                 const auto         x2        = float(rois_ptr[values_per_roi * pw + 3]);
165*c217d954SCole Faust                 const auto         y2        = float(rois_ptr[values_per_roi * pw + 4]);
166*c217d954SCole Faust 
167*c217d954SCole Faust                 const float roi_anchor_x = x1 * pool_info.spatial_scale();
168*c217d954SCole Faust                 const float roi_anchor_y = y1 * pool_info.spatial_scale();
169*c217d954SCole Faust                 const float roi_dims_x   = std::max((x2 - x1) * pool_info.spatial_scale(), 1.0f);
170*c217d954SCole Faust                 const float roi_dims_y   = std::max((y2 - y1) * pool_info.spatial_scale(), 1.0f);
171*c217d954SCole Faust 
172*c217d954SCole Faust                 float bin_size_x     = roi_dims_x / pool_info.pooled_width();
173*c217d954SCole Faust                 float bin_size_y     = roi_dims_y / pool_info.pooled_height();
174*c217d954SCole Faust                 float region_start_x = px * bin_size_x + roi_anchor_x;
175*c217d954SCole Faust                 float region_start_y = py * bin_size_y + roi_anchor_y;
176*c217d954SCole Faust                 float region_end_x   = (px + 1) * bin_size_x + roi_anchor_x;
177*c217d954SCole Faust                 float region_end_y   = (py + 1) * bin_size_y + roi_anchor_y;
178*c217d954SCole Faust 
179*c217d954SCole Faust                 region_start_x = utility::clamp(region_start_x, 0.0f, float(input_shape[0]));
180*c217d954SCole Faust                 region_start_y = utility::clamp(region_start_y, 0.0f, float(input_shape[1]));
181*c217d954SCole Faust                 region_end_x   = utility::clamp(region_end_x, 0.0f, float(input_shape[0]));
182*c217d954SCole Faust                 region_end_y   = utility::clamp(region_end_y, 0.0f, float(input_shape[1]));
183*c217d954SCole Faust 
184*c217d954SCole Faust                 const int roi_bin_grid_x = (pool_info.sampling_ratio() > 0) ? pool_info.sampling_ratio() : int(ceil(bin_size_x));
185*c217d954SCole Faust                 const int roi_bin_grid_y = (pool_info.sampling_ratio() > 0) ? pool_info.sampling_ratio() : int(ceil(bin_size_y));
186*c217d954SCole Faust 
187*c217d954SCole Faust                 // Move input and output pointer across the fourth dimension
188*c217d954SCole Faust                 const size_t input_stride_w  = input_shape[0] * input_shape[1] * input_shape[2];
189*c217d954SCole Faust                 const size_t output_stride_w = output_shape[0] * output_shape[1] * output_shape[2];
190*c217d954SCole Faust                 const float *input_ptr       = src.data() + roi_batch * input_stride_w;
191*c217d954SCole Faust                 float       *output_ptr      = dst.data() + px + py * output_shape[0] + pw * output_stride_w;
192*c217d954SCole Faust 
193*c217d954SCole Faust                 for(int pz = 0; pz < int(input_shape[2]); ++pz)
194*c217d954SCole Faust                 {
195*c217d954SCole Faust                     // For every pixel pool over an aligned region
196*c217d954SCole Faust                     *(output_ptr + pz * output_shape[0] * output_shape[1]) = roi_align_1x1(input_ptr, input_shape,
197*c217d954SCole Faust                                                                                            region_start_x,
198*c217d954SCole Faust                                                                                            bin_size_x,
199*c217d954SCole Faust                                                                                            roi_bin_grid_x,
200*c217d954SCole Faust                                                                                            region_end_x,
201*c217d954SCole Faust                                                                                            region_start_y,
202*c217d954SCole Faust                                                                                            bin_size_y,
203*c217d954SCole Faust                                                                                            roi_bin_grid_y,
204*c217d954SCole Faust                                                                                            region_end_y, pz);
205*c217d954SCole Faust                 }
206*c217d954SCole Faust             }
207*c217d954SCole Faust         }
208*c217d954SCole Faust     }
209*c217d954SCole Faust     return dst;
210*c217d954SCole Faust }
211*c217d954SCole Faust 
212*c217d954SCole Faust template <>
roi_align_layer(const SimpleTensor<half> & src,const SimpleTensor<half> & rois,const ROIPoolingLayerInfo & pool_info,const QuantizationInfo & output_qinfo)213*c217d954SCole Faust SimpleTensor<half> roi_align_layer(const SimpleTensor<half> &src, const SimpleTensor<half> &rois, const ROIPoolingLayerInfo &pool_info, const QuantizationInfo &output_qinfo)
214*c217d954SCole Faust {
215*c217d954SCole Faust     SimpleTensor<float> src_tmp  = float_converter<half, float>(src, DataType::F32);
216*c217d954SCole Faust     SimpleTensor<float> rois_tmp = float_converter<half, float>(rois, DataType::F32);
217*c217d954SCole Faust     SimpleTensor<float> dst_tmp  = roi_align_layer<float, float>(src_tmp, rois_tmp, pool_info, output_qinfo);
218*c217d954SCole Faust     SimpleTensor<half>  dst      = float_converter<float, half>(dst_tmp, DataType::F16);
219*c217d954SCole Faust     return dst;
220*c217d954SCole Faust }
221*c217d954SCole Faust 
222*c217d954SCole Faust template <>
roi_align_layer(const SimpleTensor<uint8_t> & src,const SimpleTensor<uint16_t> & rois,const ROIPoolingLayerInfo & pool_info,const QuantizationInfo & output_qinfo)223*c217d954SCole Faust SimpleTensor<uint8_t> roi_align_layer(const SimpleTensor<uint8_t> &src, const SimpleTensor<uint16_t> &rois, const ROIPoolingLayerInfo &pool_info, const QuantizationInfo &output_qinfo)
224*c217d954SCole Faust {
225*c217d954SCole Faust     SimpleTensor<float>   src_tmp  = convert_from_asymmetric(src);
226*c217d954SCole Faust     SimpleTensor<float>   rois_tmp = convert_rois_from_asymmetric(rois);
227*c217d954SCole Faust     SimpleTensor<float>   dst_tmp  = roi_align_layer<float, float>(src_tmp, rois_tmp, pool_info, output_qinfo);
228*c217d954SCole Faust     SimpleTensor<uint8_t> dst      = convert_to_asymmetric<uint8_t>(dst_tmp, output_qinfo);
229*c217d954SCole Faust     return dst;
230*c217d954SCole Faust }
231*c217d954SCole Faust template <>
roi_align_layer(const SimpleTensor<int8_t> & src,const SimpleTensor<uint16_t> & rois,const ROIPoolingLayerInfo & pool_info,const QuantizationInfo & output_qinfo)232*c217d954SCole Faust SimpleTensor<int8_t> roi_align_layer(const SimpleTensor<int8_t> &src, const SimpleTensor<uint16_t> &rois, const ROIPoolingLayerInfo &pool_info, const QuantizationInfo &output_qinfo)
233*c217d954SCole Faust {
234*c217d954SCole Faust     SimpleTensor<float>  src_tmp  = convert_from_asymmetric(src);
235*c217d954SCole Faust     SimpleTensor<float>  rois_tmp = convert_rois_from_asymmetric(rois);
236*c217d954SCole Faust     SimpleTensor<float>  dst_tmp  = roi_align_layer<float, float>(src_tmp, rois_tmp, pool_info, output_qinfo);
237*c217d954SCole Faust     SimpleTensor<int8_t> dst      = convert_to_asymmetric<int8_t>(dst_tmp, output_qinfo);
238*c217d954SCole Faust     return dst;
239*c217d954SCole Faust }
240*c217d954SCole Faust } // namespace reference
241*c217d954SCole Faust } // namespace validation
242*c217d954SCole Faust } // namespace test
243*c217d954SCole Faust } // namespace arm_compute
244