1*f3782652STreehugger Robot /*
2*f3782652STreehugger Robot
3*f3782652STreehugger Robot Copyright (c) 2009, 2010, 2011 STMicroelectronics
4*f3782652STreehugger Robot Written by Christophe Lyon
5*f3782652STreehugger Robot
6*f3782652STreehugger Robot Permission is hereby granted, free of charge, to any person obtaining a copy
7*f3782652STreehugger Robot of this software and associated documentation files (the "Software"), to deal
8*f3782652STreehugger Robot in the Software without restriction, including without limitation the rights
9*f3782652STreehugger Robot to use, copy, modify, merge, publish, distribute, sublicense, and/or sell
10*f3782652STreehugger Robot copies of the Software, and to permit persons to whom the Software is
11*f3782652STreehugger Robot furnished to do so, subject to the following conditions:
12*f3782652STreehugger Robot
13*f3782652STreehugger Robot The above copyright notice and this permission notice shall be included in
14*f3782652STreehugger Robot all copies or substantial portions of the Software.
15*f3782652STreehugger Robot
16*f3782652STreehugger Robot THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR
17*f3782652STreehugger Robot IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,
18*f3782652STreehugger Robot FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. IN NO EVENT SHALL THE
19*f3782652STreehugger Robot AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER
20*f3782652STreehugger Robot LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING FROM,
21*f3782652STreehugger Robot OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN
22*f3782652STreehugger Robot THE SOFTWARE.
23*f3782652STreehugger Robot
24*f3782652STreehugger Robot */
25*f3782652STreehugger Robot
26*f3782652STreehugger Robot #if defined(__arm__) || defined(__aarch64__)
27*f3782652STreehugger Robot #include <arm_neon.h>
28*f3782652STreehugger Robot #else
29*f3782652STreehugger Robot #include "stm-arm-neon.h"
30*f3782652STreehugger Robot #endif
31*f3782652STreehugger Robot
32*f3782652STreehugger Robot #include "stm-arm-neon-ref.h"
33*f3782652STreehugger Robot
34*f3782652STreehugger Robot #define INSN vqshl
35*f3782652STreehugger Robot #define TEST_MSG "VQSHL/VQSHLQ"
36*f3782652STreehugger Robot
37*f3782652STreehugger Robot #define FNNAME1(NAME) void exec_ ## NAME (void)
38*f3782652STreehugger Robot #define FNNAME(NAME) FNNAME1(NAME)
39*f3782652STreehugger Robot
FNNAME(INSN)40*f3782652STreehugger Robot FNNAME (INSN)
41*f3782652STreehugger Robot {
42*f3782652STreehugger Robot /* Basic test: v3=vqshl(v1,v2), then store the result. */
43*f3782652STreehugger Robot #define TEST_VQSHL2(INSN, T3, Q, T1, T2, W, N) \
44*f3782652STreehugger Robot Set_Neon_Cumulative_Sat(0, VECT_VAR(vector_res, T1, W, N)); \
45*f3782652STreehugger Robot VECT_VAR(vector_res, T1, W, N) = \
46*f3782652STreehugger Robot INSN##Q##_##T2##W(VECT_VAR(vector, T1, W, N), \
47*f3782652STreehugger Robot VECT_VAR(vector_shift, T3, W, N)); \
48*f3782652STreehugger Robot vst1##Q##_##T2##W(VECT_VAR(result, T1, W, N), \
49*f3782652STreehugger Robot VECT_VAR(vector_res, T1, W, N)); \
50*f3782652STreehugger Robot dump_neon_cumulative_sat(TEST_MSG, xSTR(INSN##Q##_##T2##W), \
51*f3782652STreehugger Robot xSTR(T1), W, N)
52*f3782652STreehugger Robot
53*f3782652STreehugger Robot /* Two auxliary macros are necessary to expand INSN */
54*f3782652STreehugger Robot #define TEST_VQSHL1(INSN, T3, Q, T1, T2, W, N) \
55*f3782652STreehugger Robot TEST_VQSHL2(INSN, T3, Q, T1, T2, W, N)
56*f3782652STreehugger Robot
57*f3782652STreehugger Robot #define TEST_VQSHL(T3, Q, T1, T2, W, N) \
58*f3782652STreehugger Robot TEST_VQSHL1(INSN, T3, Q, T1, T2, W, N)
59*f3782652STreehugger Robot
60*f3782652STreehugger Robot
61*f3782652STreehugger Robot /* With ARM RVCT, we need to declare variables before any executable
62*f3782652STreehugger Robot statement */
63*f3782652STreehugger Robot DECL_VARIABLE_ALL_VARIANTS(vector);
64*f3782652STreehugger Robot DECL_VARIABLE_ALL_VARIANTS(vector_res);
65*f3782652STreehugger Robot
66*f3782652STreehugger Robot DECL_VARIABLE_SIGNED_VARIANTS(vector_shift);
67*f3782652STreehugger Robot
68*f3782652STreehugger Robot clean_results ();
69*f3782652STreehugger Robot
70*f3782652STreehugger Robot /* Fill input vector with 0, to check saturation on limits */
71*f3782652STreehugger Robot VDUP(vector, , int, s, 8, 8, 0);
72*f3782652STreehugger Robot VDUP(vector, , int, s, 16, 4, 0);
73*f3782652STreehugger Robot VDUP(vector, , int, s, 32, 2, 0);
74*f3782652STreehugger Robot VDUP(vector, , int, s, 64, 1, 0);
75*f3782652STreehugger Robot VDUP(vector, , uint, u, 8, 8, 0);
76*f3782652STreehugger Robot VDUP(vector, , uint, u, 16, 4, 0);
77*f3782652STreehugger Robot VDUP(vector, , uint, u, 32, 2, 0);
78*f3782652STreehugger Robot VDUP(vector, , uint, u, 64, 1, 0);
79*f3782652STreehugger Robot VDUP(vector, q, int, s, 8, 16, 0);
80*f3782652STreehugger Robot VDUP(vector, q, int, s, 16, 8, 0);
81*f3782652STreehugger Robot VDUP(vector, q, int, s, 32, 4, 0);
82*f3782652STreehugger Robot VDUP(vector, q, int, s, 64, 2, 0);
83*f3782652STreehugger Robot VDUP(vector, q, uint, u, 8, 16, 0);
84*f3782652STreehugger Robot VDUP(vector, q, uint, u, 16, 8, 0);
85*f3782652STreehugger Robot VDUP(vector, q, uint, u, 32, 4, 0);
86*f3782652STreehugger Robot VDUP(vector, q, uint, u, 64, 2, 0);
87*f3782652STreehugger Robot
88*f3782652STreehugger Robot /* Choose init value arbitrarily, will be used as shift amount */
89*f3782652STreehugger Robot /* Use values equal or one-less-than the type width to check
90*f3782652STreehugger Robot behaviour on limits */
91*f3782652STreehugger Robot /* Shift all lanes by 7 ... */
92*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 8, 8, 7);
93*f3782652STreehugger Robot /* except: lane 0 (by 6), lane 1 (by 8) and lane 2 (by 9) */
94*f3782652STreehugger Robot TEST_VSET_LANE(vector_shift, , int, s, 8, 8, 0, 6);
95*f3782652STreehugger Robot TEST_VSET_LANE(vector_shift, , int, s, 8, 8, 1, 8);
96*f3782652STreehugger Robot TEST_VSET_LANE(vector_shift, , int, s, 8, 8, 2, 9);
97*f3782652STreehugger Robot
98*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 16, 4, 15);
99*f3782652STreehugger Robot TEST_VSET_LANE(vector_shift, , int, s, 16, 4, 0, 14);
100*f3782652STreehugger Robot TEST_VSET_LANE(vector_shift, , int, s, 16, 4, 1, 16);
101*f3782652STreehugger Robot TEST_VSET_LANE(vector_shift, , int, s, 16, 4, 2, 17);
102*f3782652STreehugger Robot
103*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 32, 2, 31);
104*f3782652STreehugger Robot TEST_VSET_LANE(vector_shift, , int, s, 32, 2, 1, 30);
105*f3782652STreehugger Robot
106*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 64, 1, 63);
107*f3782652STreehugger Robot
108*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 8, 16, 8);
109*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 16, 8, 16);
110*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 32, 4, 32);
111*f3782652STreehugger Robot TEST_VSET_LANE(vector_shift, q, int, s, 32, 4, 1, 33);
112*f3782652STreehugger Robot
113*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 64, 2, 64);
114*f3782652STreehugger Robot TEST_VSET_LANE(vector_shift, q, int, s, 64, 2, 1, 62);
115*f3782652STreehugger Robot
116*f3782652STreehugger Robot fprintf(ref_file, "\n%s cumulative saturation output:\n",
117*f3782652STreehugger Robot TEST_MSG " (with input = 0)");
118*f3782652STreehugger Robot TEST_MACRO_ALL_VARIANTS_1_5(TEST_VQSHL, int);
119*f3782652STreehugger Robot dump_results_hex2 (TEST_MSG, " (with input = 0)");
120*f3782652STreehugger Robot
121*f3782652STreehugger Robot
122*f3782652STreehugger Robot /* Use negative shift amounts */
123*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 8, 8, -1);
124*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 16, 4, -2);
125*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 32, 2, -3);
126*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 64, 1, -4);
127*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 8, 16, -7);
128*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 16, 8, -11);
129*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 32, 4, -13);
130*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 64, 2, -20);
131*f3782652STreehugger Robot
132*f3782652STreehugger Robot fprintf(ref_file, "\n%s cumulative saturation output:\n",
133*f3782652STreehugger Robot TEST_MSG " (input 0 and negative shift amount)");
134*f3782652STreehugger Robot TEST_MACRO_ALL_VARIANTS_1_5(TEST_VQSHL, int);
135*f3782652STreehugger Robot dump_results_hex2 (TEST_MSG, " (input 0 and negative shift amount)");
136*f3782652STreehugger Robot
137*f3782652STreehugger Robot /* Test again, with predefined input values */
138*f3782652STreehugger Robot TEST_MACRO_ALL_VARIANTS_2_5(VLOAD, vector, buffer);
139*f3782652STreehugger Robot
140*f3782652STreehugger Robot /* Choose init value arbitrarily, will be used as shift amount */
141*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 8, 8, 1);
142*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 16, 4, 3);
143*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 32, 2, 8);
144*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 64, 1, -3);
145*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 8, 16, 10);
146*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 16, 8, 12);
147*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 32, 4, 32);
148*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 64, 2, 63);
149*f3782652STreehugger Robot
150*f3782652STreehugger Robot fprintf(ref_file, "\n%s cumulative saturation output:\n", TEST_MSG);
151*f3782652STreehugger Robot TEST_MACRO_ALL_VARIANTS_1_5(TEST_VQSHL, int);
152*f3782652STreehugger Robot dump_results_hex (TEST_MSG);
153*f3782652STreehugger Robot
154*f3782652STreehugger Robot /* Use negative shift amounts */
155*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 8, 8, -1);
156*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 16, 4, -2);
157*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 32, 2, -3);
158*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 64, 1, -4);
159*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 8, 16, -7);
160*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 16, 8, -11);
161*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 32, 4, -13);
162*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 64, 2, -20);
163*f3782652STreehugger Robot
164*f3782652STreehugger Robot fprintf(ref_file, "\n%s cumulative saturation output:\n",
165*f3782652STreehugger Robot TEST_MSG " (negative shift amount)");
166*f3782652STreehugger Robot TEST_MACRO_ALL_VARIANTS_1_5(TEST_VQSHL, int);
167*f3782652STreehugger Robot dump_results_hex2 (TEST_MSG, " (negative shift amount)");
168*f3782652STreehugger Robot
169*f3782652STreehugger Robot /* Use large shift amounts */
170*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 8, 8, 8);
171*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 16, 4, 16);
172*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 32, 2, 32);
173*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 64, 1, 64);
174*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 8, 16, 8);
175*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 16, 8, 16);
176*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 32, 4, 32);
177*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 64, 2, 64);
178*f3782652STreehugger Robot
179*f3782652STreehugger Robot fprintf(ref_file, "\n%s cumulative saturation output:\n",
180*f3782652STreehugger Robot TEST_MSG " (large shift amount, negative input)");
181*f3782652STreehugger Robot TEST_MACRO_ALL_VARIANTS_1_5(TEST_VQSHL, int);
182*f3782652STreehugger Robot dump_results_hex2 (TEST_MSG, " (large shift amount, negative input)");
183*f3782652STreehugger Robot
184*f3782652STreehugger Robot /* Fill input vector with max value, to check saturation on limits */
185*f3782652STreehugger Robot VDUP(vector, , int, s, 8, 8, 0x7F);
186*f3782652STreehugger Robot VDUP(vector, , int, s, 16, 4, 0x7FFF);
187*f3782652STreehugger Robot VDUP(vector, , int, s, 32, 2, 0x7FFFFFFF);
188*f3782652STreehugger Robot VDUP(vector, , int, s, 64, 1, 0x7FFFFFFFFFFFFFFFLL);
189*f3782652STreehugger Robot VDUP(vector, , uint, u, 8, 8, 0xFF);
190*f3782652STreehugger Robot VDUP(vector, , uint, u, 16, 4, 0xFFFF);
191*f3782652STreehugger Robot VDUP(vector, , uint, u, 32, 2, 0xFFFFFFFF);
192*f3782652STreehugger Robot VDUP(vector, , uint, u, 64, 1, 0xFFFFFFFFFFFFFFFFULL);
193*f3782652STreehugger Robot VDUP(vector, q, int, s, 8, 16, 0x7F);
194*f3782652STreehugger Robot VDUP(vector, q, int, s, 16, 8, 0x7FFF);
195*f3782652STreehugger Robot VDUP(vector, q, int, s, 32, 4, 0x7FFFFFFF);
196*f3782652STreehugger Robot VDUP(vector, q, int, s, 64, 2, 0x7FFFFFFFFFFFFFFFLL);
197*f3782652STreehugger Robot VDUP(vector, q, uint, u, 8, 16, 0xFF);
198*f3782652STreehugger Robot VDUP(vector, q, uint, u, 16, 8, 0xFFFF);
199*f3782652STreehugger Robot VDUP(vector, q, uint, u, 32, 4, 0xFFFFFFFF);
200*f3782652STreehugger Robot VDUP(vector, q, uint, u, 64, 2, 0xFFFFFFFFFFFFFFFFULL);
201*f3782652STreehugger Robot
202*f3782652STreehugger Robot /* Shift by -1 */
203*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 8, 8, -1);
204*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 16, 4, -1);
205*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 32, 2, -1);
206*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 64, 1, -1);
207*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 8, 16, -1);
208*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 16, 8, -1);
209*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 32, 4, -1);
210*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 64, 2, -1);
211*f3782652STreehugger Robot
212*f3782652STreehugger Robot fprintf(ref_file, "\n%s cumulative saturation output:\n",
213*f3782652STreehugger Robot TEST_MSG " (check cumulative saturation)");
214*f3782652STreehugger Robot TEST_MACRO_ALL_VARIANTS_1_5(TEST_VQSHL, int);
215*f3782652STreehugger Robot dump_results_hex2 (TEST_MSG, " (check cumulative saturation)");
216*f3782652STreehugger Robot
217*f3782652STreehugger Robot /* Use large shift amounts */
218*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 8, 8, 8);
219*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 16, 4, 16);
220*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 32, 2, 32);
221*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 64, 1, 64);
222*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 8, 16, 8);
223*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 16, 8, 16);
224*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 32, 4, 32);
225*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 64, 2, 64);
226*f3782652STreehugger Robot
227*f3782652STreehugger Robot fprintf(ref_file, "\n%s cumulative saturation output:\n",
228*f3782652STreehugger Robot TEST_MSG " (large shift amount, positive input)");
229*f3782652STreehugger Robot TEST_MACRO_ALL_VARIANTS_1_5(TEST_VQSHL, int);
230*f3782652STreehugger Robot dump_results_hex2 (TEST_MSG, " (large shift amount, positive input)");
231*f3782652STreehugger Robot
232*f3782652STreehugger Robot /* Check 64 bits saturation */
233*f3782652STreehugger Robot VDUP(vector, , int, s, 64, 1, -10);
234*f3782652STreehugger Robot VDUP(vector_shift, , int, s, 64, 1, 64);
235*f3782652STreehugger Robot VDUP(vector, q, int, s, 64, 2, 10);
236*f3782652STreehugger Robot VDUP(vector_shift, q, int, s, 64, 2, 64);
237*f3782652STreehugger Robot fprintf(ref_file, "\n%s cumulative saturation output:\n",
238*f3782652STreehugger Robot TEST_MSG " (check saturation on 64 bits)");
239*f3782652STreehugger Robot TEST_MACRO_ALL_VARIANTS_1_5(TEST_VQSHL, int);
240*f3782652STreehugger Robot dump_results_hex2 (TEST_MSG, " (check saturation on 64 bits)");
241*f3782652STreehugger Robot }
242