1*c217d954SCole Faust /*
2*c217d954SCole Faust * Copyright (c) 2017-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 "DepthConcatenateLayer.h"
25*c217d954SCole Faust
26*c217d954SCole Faust #include "tests/validation/Helpers.h"
27*c217d954SCole Faust
28*c217d954SCole Faust namespace arm_compute
29*c217d954SCole Faust {
30*c217d954SCole Faust namespace test
31*c217d954SCole Faust {
32*c217d954SCole Faust namespace validation
33*c217d954SCole Faust {
34*c217d954SCole Faust namespace reference
35*c217d954SCole Faust {
36*c217d954SCole Faust template <typename T>
depthconcatenate_layer(const std::vector<SimpleTensor<T>> & srcs,SimpleTensor<T> & dst)37*c217d954SCole Faust SimpleTensor<T> depthconcatenate_layer(const std::vector<SimpleTensor<T>> &srcs, SimpleTensor<T> &dst)
38*c217d954SCole Faust {
39*c217d954SCole Faust // Create reference
40*c217d954SCole Faust std::vector<TensorShape> shapes;
41*c217d954SCole Faust shapes.reserve(srcs.size());
42*c217d954SCole Faust for(const auto &src : srcs)
43*c217d954SCole Faust {
44*c217d954SCole Faust shapes.emplace_back(src.shape());
45*c217d954SCole Faust }
46*c217d954SCole Faust
47*c217d954SCole Faust // Compute reference
48*c217d954SCole Faust int depth_offset = 0;
49*c217d954SCole Faust const int width_out = dst.shape().x();
50*c217d954SCole Faust const int height_out = dst.shape().y();
51*c217d954SCole Faust const int depth_out = dst.shape().z();
52*c217d954SCole Faust const int out_stride_z = width_out * height_out;
53*c217d954SCole Faust const int batches = dst.shape().total_size_upper(3);
54*c217d954SCole Faust auto have_different_quantization_info = [&](const SimpleTensor<T> &tensor)
55*c217d954SCole Faust {
56*c217d954SCole Faust return tensor.quantization_info() != dst.quantization_info();
57*c217d954SCole Faust };
58*c217d954SCole Faust
59*c217d954SCole Faust if(srcs[0].data_type() == DataType::QASYMM8 && std::any_of(srcs.cbegin(), srcs.cend(), have_different_quantization_info))
60*c217d954SCole Faust {
61*c217d954SCole Faust #if defined(_OPENMP)
62*c217d954SCole Faust #pragma omp parallel for
63*c217d954SCole Faust #endif /* _OPENMP */
64*c217d954SCole Faust for(int b = 0; b < batches; ++b)
65*c217d954SCole Faust {
66*c217d954SCole Faust // input tensors can have smaller width and height than the output, so for each output's slice we need to requantize 0 (as this is the value
67*c217d954SCole Faust // used in NEFillBorderKernel by NEDepthConcatenateLayer) using the corresponding quantization info for that particular slice/input tensor.
68*c217d954SCole Faust int slice = 0;
69*c217d954SCole Faust for(const auto &src : srcs)
70*c217d954SCole Faust {
71*c217d954SCole Faust auto ptr_slice = static_cast<T *>(dst(Coordinates(0, 0, slice, b)));
72*c217d954SCole Faust const auto num_elems_in_slice((dst.num_elements() / depth_out) * src.shape().z());
73*c217d954SCole Faust const UniformQuantizationInfo iq_info = src.quantization_info().uniform();
74*c217d954SCole Faust const UniformQuantizationInfo oq_info = dst.quantization_info().uniform();
75*c217d954SCole Faust
76*c217d954SCole Faust std::transform(ptr_slice, ptr_slice + num_elems_in_slice, ptr_slice, [&](T)
77*c217d954SCole Faust {
78*c217d954SCole Faust return quantize_qasymm8(dequantize_qasymm8(0, iq_info), oq_info);
79*c217d954SCole Faust });
80*c217d954SCole Faust slice += src.shape().z();
81*c217d954SCole Faust }
82*c217d954SCole Faust }
83*c217d954SCole Faust }
84*c217d954SCole Faust else
85*c217d954SCole Faust {
86*c217d954SCole Faust std::fill_n(dst.data(), dst.num_elements(), 0);
87*c217d954SCole Faust }
88*c217d954SCole Faust
89*c217d954SCole Faust for(const auto &src : srcs)
90*c217d954SCole Faust {
91*c217d954SCole Faust ARM_COMPUTE_ERROR_ON(depth_offset >= depth_out);
92*c217d954SCole Faust ARM_COMPUTE_ERROR_ON(batches != static_cast<int>(src.shape().total_size_upper(3)));
93*c217d954SCole Faust
94*c217d954SCole Faust const int width = src.shape().x();
95*c217d954SCole Faust const int height = src.shape().y();
96*c217d954SCole Faust const int depth = src.shape().z();
97*c217d954SCole Faust const int x_diff = (width_out - width) / 2;
98*c217d954SCole Faust const int y_diff = (height_out - height) / 2;
99*c217d954SCole Faust
100*c217d954SCole Faust const T *src_ptr = src.data();
101*c217d954SCole Faust
102*c217d954SCole Faust for(int b = 0; b < batches; ++b)
103*c217d954SCole Faust {
104*c217d954SCole Faust const size_t offset_to_first_element = b * out_stride_z * depth_out + depth_offset * out_stride_z + y_diff * width_out + x_diff;
105*c217d954SCole Faust
106*c217d954SCole Faust for(int d = 0; d < depth; ++d)
107*c217d954SCole Faust {
108*c217d954SCole Faust for(int r = 0; r < height; ++r)
109*c217d954SCole Faust {
110*c217d954SCole Faust if(src.data_type() == DataType::QASYMM8 && src.quantization_info() != dst.quantization_info())
111*c217d954SCole Faust {
112*c217d954SCole Faust const UniformQuantizationInfo iq_info = src.quantization_info().uniform();
113*c217d954SCole Faust const UniformQuantizationInfo oq_info = dst.quantization_info().uniform();
114*c217d954SCole Faust std::transform(src_ptr, src_ptr + width, dst.data() + offset_to_first_element + d * out_stride_z + r * width_out, [&](T t)
115*c217d954SCole Faust {
116*c217d954SCole Faust const float dequantized_input = dequantize_qasymm8(t, iq_info);
117*c217d954SCole Faust return quantize_qasymm8(dequantized_input, oq_info);
118*c217d954SCole Faust });
119*c217d954SCole Faust src_ptr += width;
120*c217d954SCole Faust }
121*c217d954SCole Faust else
122*c217d954SCole Faust {
123*c217d954SCole Faust std::copy(src_ptr, src_ptr + width, dst.data() + offset_to_first_element + d * out_stride_z + r * width_out);
124*c217d954SCole Faust src_ptr += width;
125*c217d954SCole Faust }
126*c217d954SCole Faust }
127*c217d954SCole Faust }
128*c217d954SCole Faust }
129*c217d954SCole Faust
130*c217d954SCole Faust depth_offset += depth;
131*c217d954SCole Faust }
132*c217d954SCole Faust
133*c217d954SCole Faust return dst;
134*c217d954SCole Faust }
135*c217d954SCole Faust
136*c217d954SCole Faust template SimpleTensor<uint8_t> depthconcatenate_layer(const std::vector<SimpleTensor<uint8_t>> &srcs, SimpleTensor<uint8_t> &dst);
137*c217d954SCole Faust template SimpleTensor<float> depthconcatenate_layer(const std::vector<SimpleTensor<float>> &srcs, SimpleTensor<float> &dst);
138*c217d954SCole Faust template SimpleTensor<half> depthconcatenate_layer(const std::vector<SimpleTensor<half>> &srcs, SimpleTensor<half> &dst);
139*c217d954SCole Faust } // namespace reference
140*c217d954SCole Faust } // namespace validation
141*c217d954SCole Faust } // namespace test
142*c217d954SCole Faust } // namespace arm_compute
143