1*f3782652STreehugger Robot /*
2*f3782652STreehugger Robot
3*f3782652STreehugger Robot Copyright (c) 2009, 2010, 2011, 2013 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
exec_vtbX(void)34*f3782652STreehugger Robot void exec_vtbX (void)
35*f3782652STreehugger Robot {
36*f3782652STreehugger Robot int i;
37*f3782652STreehugger Robot
38*f3782652STreehugger Robot /* In this case, input variables are arrays of vectors */
39*f3782652STreehugger Robot #define DECL_VTBX(T1, W, N, X) \
40*f3782652STreehugger Robot VECT_ARRAY_TYPE(T1, W, N, X) VECT_ARRAY_VAR(table_vector, T1, W, N, X)
41*f3782652STreehugger Robot
42*f3782652STreehugger Robot /* The vtbl1 variant is different from vtbl{2,3,4} because it takes a
43*f3782652STreehugger Robot vector as 1st param, instead of an array of vectors */
44*f3782652STreehugger Robot #define TEST_VTBL1(T1, T2, T3, W, N) \
45*f3782652STreehugger Robot VECT_VAR(table_vector, T1, W, N) = \
46*f3782652STreehugger Robot vld1##_##T2##W((T1##W##_t *)lookup_table); \
47*f3782652STreehugger Robot \
48*f3782652STreehugger Robot VECT_VAR(vector_res, T1, W, N) = \
49*f3782652STreehugger Robot vtbl1_##T2##W(VECT_VAR(table_vector, T1, W, N), \
50*f3782652STreehugger Robot VECT_VAR(vector, T3, W, N)); \
51*f3782652STreehugger Robot vst1_##T2##W(VECT_VAR(result, T1, W, N), \
52*f3782652STreehugger Robot VECT_VAR(vector_res, T1, W, N));
53*f3782652STreehugger Robot
54*f3782652STreehugger Robot #define TEST_VTBLX(T1, T2, T3, W, N, X) \
55*f3782652STreehugger Robot VECT_ARRAY_VAR(table_vector, T1, W, N, X) = \
56*f3782652STreehugger Robot vld##X##_##T2##W((T1##W##_t *)lookup_table); \
57*f3782652STreehugger Robot \
58*f3782652STreehugger Robot VECT_VAR(vector_res, T1, W, N) = \
59*f3782652STreehugger Robot vtbl##X##_##T2##W(VECT_ARRAY_VAR(table_vector, T1, W, N, X), \
60*f3782652STreehugger Robot VECT_VAR(vector, T3, W, N)); \
61*f3782652STreehugger Robot vst1_##T2##W(VECT_VAR(result, T1, W, N), \
62*f3782652STreehugger Robot VECT_VAR(vector_res, T1, W, N));
63*f3782652STreehugger Robot
64*f3782652STreehugger Robot /* With ARM RVCT, we need to declare variables before any executable
65*f3782652STreehugger Robot statement */
66*f3782652STreehugger Robot
67*f3782652STreehugger Robot /* We need to define a lookup table */
68*f3782652STreehugger Robot uint8_t lookup_table[32];
69*f3782652STreehugger Robot
70*f3782652STreehugger Robot DECL_VARIABLE(vector, int, 8, 8);
71*f3782652STreehugger Robot DECL_VARIABLE(vector, uint, 8, 8);
72*f3782652STreehugger Robot DECL_VARIABLE(vector, poly, 8, 8);
73*f3782652STreehugger Robot DECL_VARIABLE(vector_res, int, 8, 8);
74*f3782652STreehugger Robot DECL_VARIABLE(vector_res, uint, 8, 8);
75*f3782652STreehugger Robot DECL_VARIABLE(vector_res, poly, 8, 8);
76*f3782652STreehugger Robot
77*f3782652STreehugger Robot /* For vtbl1 */
78*f3782652STreehugger Robot DECL_VARIABLE(table_vector, int, 8, 8);
79*f3782652STreehugger Robot DECL_VARIABLE(table_vector, uint, 8, 8);
80*f3782652STreehugger Robot DECL_VARIABLE(table_vector, poly, 8, 8);
81*f3782652STreehugger Robot
82*f3782652STreehugger Robot /* For vtbx* */
83*f3782652STreehugger Robot DECL_VARIABLE(default_vector, int, 8, 8);
84*f3782652STreehugger Robot DECL_VARIABLE(default_vector, uint, 8, 8);
85*f3782652STreehugger Robot DECL_VARIABLE(default_vector, poly, 8, 8);
86*f3782652STreehugger Robot
87*f3782652STreehugger Robot /* We need only 8 bits variants */
88*f3782652STreehugger Robot #define DECL_ALL_VTBLX(X) \
89*f3782652STreehugger Robot DECL_VTBX(int, 8, 8, X); \
90*f3782652STreehugger Robot DECL_VTBX(uint, 8, 8, X); \
91*f3782652STreehugger Robot DECL_VTBX(poly, 8, 8, X)
92*f3782652STreehugger Robot
93*f3782652STreehugger Robot #define TEST_ALL_VTBL1() \
94*f3782652STreehugger Robot TEST_VTBL1(int, s, int, 8, 8); \
95*f3782652STreehugger Robot TEST_VTBL1(uint, u, uint, 8, 8); \
96*f3782652STreehugger Robot TEST_VTBL1(poly, p, uint, 8, 8)
97*f3782652STreehugger Robot
98*f3782652STreehugger Robot #define TEST_ALL_VTBLX(X) \
99*f3782652STreehugger Robot TEST_VTBLX(int, s, int, 8, 8, X); \
100*f3782652STreehugger Robot TEST_VTBLX(uint, u, uint, 8, 8, X); \
101*f3782652STreehugger Robot TEST_VTBLX(poly, p, uint, 8, 8, X)
102*f3782652STreehugger Robot
103*f3782652STreehugger Robot /* Declare the temporary buffers / variables */
104*f3782652STreehugger Robot DECL_ALL_VTBLX(2);
105*f3782652STreehugger Robot DECL_ALL_VTBLX(3);
106*f3782652STreehugger Robot DECL_ALL_VTBLX(4);
107*f3782652STreehugger Robot
108*f3782652STreehugger Robot /* Fill the lookup table */
109*f3782652STreehugger Robot for (i=0; i<32; i++) {
110*f3782652STreehugger Robot lookup_table[i] = i-15;
111*f3782652STreehugger Robot }
112*f3782652STreehugger Robot
113*f3782652STreehugger Robot /* Choose init value arbitrarily, will be used as table index */
114*f3782652STreehugger Robot VDUP(vector, , int, s, 8, 8, 1);
115*f3782652STreehugger Robot VDUP(vector, , uint, u, 8, 8, 2);
116*f3782652STreehugger Robot VDUP(vector, , poly, p, 8, 8, 2);
117*f3782652STreehugger Robot
118*f3782652STreehugger Robot /* To ensure code coverage of lib, add some indexes larger than 8,16 and 32 */
119*f3782652STreehugger Robot /* except: lane 0 (by 6), lane 1 (by 8) and lane 2 (by 9) */
120*f3782652STreehugger Robot TEST_VSET_LANE(vector, , int, s, 8, 8, 0, 10);
121*f3782652STreehugger Robot TEST_VSET_LANE(vector, , int, s, 8, 8, 4, 20);
122*f3782652STreehugger Robot TEST_VSET_LANE(vector, , int, s, 8, 8, 5, 40);
123*f3782652STreehugger Robot TEST_VSET_LANE(vector, , uint, u, 8, 8, 0, 10);
124*f3782652STreehugger Robot TEST_VSET_LANE(vector, , uint, u, 8, 8, 4, 20);
125*f3782652STreehugger Robot TEST_VSET_LANE(vector, , uint, u, 8, 8, 5, 40);
126*f3782652STreehugger Robot TEST_VSET_LANE(vector, , poly, p, 8, 8, 0, 10);
127*f3782652STreehugger Robot TEST_VSET_LANE(vector, , poly, p, 8, 8, 4, 20);
128*f3782652STreehugger Robot TEST_VSET_LANE(vector, , poly, p, 8, 8, 5, 40);
129*f3782652STreehugger Robot
130*f3782652STreehugger Robot
131*f3782652STreehugger Robot /* Check vtbl1 */
132*f3782652STreehugger Robot clean_results ();
133*f3782652STreehugger Robot #define TEST_MSG "VTBL1"
134*f3782652STreehugger Robot TEST_ALL_VTBL1();
135*f3782652STreehugger Robot dump_results_hex (TEST_MSG);
136*f3782652STreehugger Robot
137*f3782652STreehugger Robot /* Check vtbl2 */
138*f3782652STreehugger Robot clean_results ();
139*f3782652STreehugger Robot #undef TEST_MSG
140*f3782652STreehugger Robot #define TEST_MSG "VTBL2"
141*f3782652STreehugger Robot TEST_ALL_VTBLX(2);
142*f3782652STreehugger Robot dump_results_hex (TEST_MSG);
143*f3782652STreehugger Robot
144*f3782652STreehugger Robot /* Check vtbl3 */
145*f3782652STreehugger Robot clean_results ();
146*f3782652STreehugger Robot #undef TEST_MSG
147*f3782652STreehugger Robot #define TEST_MSG "VTBL3"
148*f3782652STreehugger Robot TEST_ALL_VTBLX(3);
149*f3782652STreehugger Robot dump_results_hex (TEST_MSG);
150*f3782652STreehugger Robot
151*f3782652STreehugger Robot /* Check vtbl4 */
152*f3782652STreehugger Robot clean_results ();
153*f3782652STreehugger Robot #undef TEST_MSG
154*f3782652STreehugger Robot #define TEST_MSG "VTBL4"
155*f3782652STreehugger Robot TEST_ALL_VTBLX(4);
156*f3782652STreehugger Robot dump_results_hex (TEST_MSG);
157*f3782652STreehugger Robot
158*f3782652STreehugger Robot
159*f3782652STreehugger Robot /* Now test VTBX */
160*f3782652STreehugger Robot
161*f3782652STreehugger Robot /* The vtbx1 variant is different from vtbx{2,3,4} because it takes a
162*f3782652STreehugger Robot vector as 1st param, instead of an array of vectors */
163*f3782652STreehugger Robot #define TEST_VTBX1(T1, T2, T3, W, N) \
164*f3782652STreehugger Robot VECT_VAR(table_vector, T1, W, N) = \
165*f3782652STreehugger Robot vld1##_##T2##W((T1##W##_t *)lookup_table); \
166*f3782652STreehugger Robot \
167*f3782652STreehugger Robot VECT_VAR(vector_res, T1, W, N) = \
168*f3782652STreehugger Robot vtbx1_##T2##W(VECT_VAR(default_vector, T1, W, N), \
169*f3782652STreehugger Robot VECT_VAR(table_vector, T1, W, N), \
170*f3782652STreehugger Robot VECT_VAR(vector, T3, W, N)); \
171*f3782652STreehugger Robot vst1_##T2##W(VECT_VAR(result, T1, W, N), \
172*f3782652STreehugger Robot VECT_VAR(vector_res, T1, W, N));
173*f3782652STreehugger Robot
174*f3782652STreehugger Robot #define TEST_VTBXX(T1, T2, T3, W, N, X) \
175*f3782652STreehugger Robot VECT_ARRAY_VAR(table_vector, T1, W, N, X) = \
176*f3782652STreehugger Robot vld##X##_##T2##W((T1##W##_t *)lookup_table); \
177*f3782652STreehugger Robot \
178*f3782652STreehugger Robot VECT_VAR(vector_res, T1, W, N) = \
179*f3782652STreehugger Robot vtbx##X##_##T2##W(VECT_VAR(default_vector, T1, W, N), \
180*f3782652STreehugger Robot VECT_ARRAY_VAR(table_vector, T1, W, N, X), \
181*f3782652STreehugger Robot VECT_VAR(vector, T3, W, N)); \
182*f3782652STreehugger Robot vst1_##T2##W(VECT_VAR(result, T1, W, N), \
183*f3782652STreehugger Robot VECT_VAR(vector_res, T1, W, N));
184*f3782652STreehugger Robot
185*f3782652STreehugger Robot #define TEST_ALL_VTBX1() \
186*f3782652STreehugger Robot TEST_VTBX1(int, s, int, 8, 8); \
187*f3782652STreehugger Robot TEST_VTBX1(uint, u, uint, 8, 8); \
188*f3782652STreehugger Robot TEST_VTBX1(poly, p, uint, 8, 8)
189*f3782652STreehugger Robot
190*f3782652STreehugger Robot #define TEST_ALL_VTBXX(X) \
191*f3782652STreehugger Robot TEST_VTBXX(int, s, int, 8, 8, X); \
192*f3782652STreehugger Robot TEST_VTBXX(uint, u, uint, 8, 8, X); \
193*f3782652STreehugger Robot TEST_VTBXX(poly, p, uint, 8, 8, X)
194*f3782652STreehugger Robot
195*f3782652STreehugger Robot /* Choose init value arbitrarily, will be used as default value */
196*f3782652STreehugger Robot VDUP(default_vector, , int, s, 8, 8, 0x33);
197*f3782652STreehugger Robot VDUP(default_vector, , uint, u, 8, 8, 0xCC);
198*f3782652STreehugger Robot VDUP(default_vector, , poly, p, 8, 8, 0xCC);
199*f3782652STreehugger Robot
200*f3782652STreehugger Robot /* Check vtbx1 */
201*f3782652STreehugger Robot clean_results ();
202*f3782652STreehugger Robot #undef TEST_MSG
203*f3782652STreehugger Robot #define TEST_MSG "VTBX1"
204*f3782652STreehugger Robot TEST_ALL_VTBX1();
205*f3782652STreehugger Robot dump_results_hex (TEST_MSG);
206*f3782652STreehugger Robot
207*f3782652STreehugger Robot /* Check vtbx2 */
208*f3782652STreehugger Robot clean_results ();
209*f3782652STreehugger Robot #undef TEST_MSG
210*f3782652STreehugger Robot #define TEST_MSG "VTBX2"
211*f3782652STreehugger Robot TEST_ALL_VTBXX(2);
212*f3782652STreehugger Robot dump_results_hex (TEST_MSG);
213*f3782652STreehugger Robot
214*f3782652STreehugger Robot /* Check vtbx3 */
215*f3782652STreehugger Robot clean_results ();
216*f3782652STreehugger Robot #undef TEST_MSG
217*f3782652STreehugger Robot #define TEST_MSG "VTBX3"
218*f3782652STreehugger Robot TEST_ALL_VTBXX(3);
219*f3782652STreehugger Robot dump_results_hex (TEST_MSG);
220*f3782652STreehugger Robot
221*f3782652STreehugger Robot /* Check vtbx4 */
222*f3782652STreehugger Robot clean_results ();
223*f3782652STreehugger Robot #undef TEST_MSG
224*f3782652STreehugger Robot #define TEST_MSG "VTBX4"
225*f3782652STreehugger Robot TEST_ALL_VTBXX(4);
226*f3782652STreehugger Robot dump_results_hex (TEST_MSG);
227*f3782652STreehugger Robot }
228