1/*
2
3Copyright (c) 2009, 2010, 2011 STMicroelectronics
4Written by Christophe Lyon
5
6Permission is hereby granted, free of charge, to any person obtaining a copy
7of this software and associated documentation files (the "Software"), to deal
8in the Software without restriction, including without limitation the rights
9to use, copy, modify, merge, publish, distribute, sublicense, and/or sell
10copies of the Software, and to permit persons to whom the Software is
11furnished to do so, subject to the following conditions:
12
13The above copyright notice and this permission notice shall be included in
14all copies or substantial portions of the Software.
15
16THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR
17IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,
18FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. IN NO EVENT SHALL THE
19AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER
20LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING FROM,
21OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN
22THE SOFTWARE.
23
24*/
25
26#if defined(__arm__) || defined(__aarch64__)
27#include <arm_neon.h>
28#else
29#include "stm-arm-neon.h"
30#endif
31
32#include "stm-arm-neon-ref.h"
33
34#define INSN vqrshrun_n
35#define TEST_MSG "VQRSHRUN_N"
36
37#define FNNAME1(NAME) void exec_ ## NAME (void)
38#define FNNAME(NAME) FNNAME1(NAME)
39
40FNNAME (INSN)
41{
42  /* Basic test: y=vqrshrun_n(x,v), then store the result.  */
43#define TEST_VQRSHRUN_N2(INSN, T1, T2, W, W2, N, V)			\
44  Set_Neon_Cumulative_Sat(0, VECT_VAR(vector_res, uint, W2, N));	\
45  VECT_VAR(vector_res, uint, W2, N) =					\
46    INSN##_##T2##W(VECT_VAR(vector, T1, W, N),				\
47		   V);							\
48  vst1_u##W2(VECT_VAR(result, uint, W2, N),				\
49	     VECT_VAR(vector_res, uint, W2, N));			\
50  dump_neon_cumulative_sat(TEST_MSG, xSTR(INSN##_##T2##W),		\
51			   xSTR(T1), W, N)
52
53  /* Two auxliary macros are necessary to expand INSN */
54#define TEST_VQRSHRUN_N1(INSN, T1, T2, W, W2, N, V)	\
55  TEST_VQRSHRUN_N2(INSN, T1, T2, W, W2, N, V)
56
57#define TEST_VQRSHRUN_N(T1, T2, W, W2, N, V)	\
58  TEST_VQRSHRUN_N1(INSN, T1, T2, W, W2, N, V)
59
60
61  /* With ARM RVCT, we need to declare variables before any executable
62     statement */
63
64  /* vector is twice as large as vector_res */
65  DECL_VARIABLE(vector, int, 16, 8);
66  DECL_VARIABLE(vector, int, 32, 4);
67  DECL_VARIABLE(vector, int, 64, 2);
68
69  DECL_VARIABLE(vector_res, uint, 8, 8);
70  DECL_VARIABLE(vector_res, uint, 16, 4);
71  DECL_VARIABLE(vector_res, uint, 32, 2);
72
73  clean_results ();
74
75  /* Fill input vector with negative values, to check saturation on limits */
76  VDUP(vector, q, int, s, 16, 8, -2);
77  VDUP(vector, q, int, s, 32, 4, -3);
78  VDUP(vector, q, int, s, 64, 2, -4);
79
80  /* Choose shift amount arbitrarily  */
81  fprintf(ref_file, "\n%s cumulative saturation output:\n",
82	  TEST_MSG " (negative input)");
83  TEST_VQRSHRUN_N(int, s, 16, 8, 8, 3);
84  TEST_VQRSHRUN_N(int, s, 32, 16, 4, 4);
85  TEST_VQRSHRUN_N(int, s, 64, 32, 2, 2);
86
87  /* FIXME: only a few result buffers are used, but we output all of them */
88  dump_results_hex2 (TEST_MSG, " (negative input)");
89
90  /* Fill input vector with max value, to check saturation on limits */
91  VDUP(vector, q, int, s, 16, 8, 0x7FFF);
92  VDUP(vector, q, int, s, 32, 4, 0x7FFFFFFF);
93  VDUP(vector, q, int, s, 64, 2, 0x7FFFFFFFFFFFFFFFLL);
94
95  /* shift by 1  */
96  fprintf(ref_file, "\n%s cumulative saturation output:\n",
97	  TEST_MSG " (check cumulative saturation: shift by 1)");
98  TEST_VQRSHRUN_N(int, s, 16, 8, 8, 1);
99  TEST_VQRSHRUN_N(int, s, 32, 16, 4, 1);
100  TEST_VQRSHRUN_N(int, s, 64, 32, 2, 1);
101
102  dump_results_hex2 (TEST_MSG, " (check cumulative saturation: shift by 1)");
103
104  /* shift by max  */
105  fprintf(ref_file, "\n%s cumulative saturation output:\n",
106	  TEST_MSG " (check cumulative saturation: shift by max, positive input)");
107  TEST_VQRSHRUN_N(int, s, 16, 8, 8, 8);
108  TEST_VQRSHRUN_N(int, s, 32, 16, 4, 16);
109  TEST_VQRSHRUN_N(int, s, 64, 32, 2, 32);
110
111  dump_results_hex2 (TEST_MSG,
112		     " (check cumulative saturation: shift by max, positive input)");
113
114
115  /* Fill input vector with min value, to check saturation on limits */
116  VDUP(vector, q, int, s, 16, 8, 0x8000);
117  VDUP(vector, q, int, s, 32, 4, 0x80000000);
118  VDUP(vector, q, int, s, 64, 2, 0x8000000000000000LL);
119
120  /* shift by max  */
121  fprintf(ref_file, "\n%s cumulative saturation output:\n",
122	  TEST_MSG " (check cumulative saturation: shift by max, negative input)");
123  TEST_VQRSHRUN_N(int, s, 16, 8, 8, 8);
124  TEST_VQRSHRUN_N(int, s, 32, 16, 4, 16);
125  TEST_VQRSHRUN_N(int, s, 64, 32, 2, 32);
126
127  dump_results_hex2 (TEST_MSG,
128		     " (check cumulative saturation: shift by max, negative input)");
129
130  /* Fill input vector with positive values, to check normal case */
131  VDUP(vector, q, int, s, 16, 8, 0x1234);
132  VDUP(vector, q, int, s, 32, 4, 0x87654321);
133  VDUP(vector, q, int, s, 64, 2, 0xDEADBEEF);
134
135  /* shift arbitrary amount  */
136  fprintf(ref_file, "\n%s cumulative saturation output:\n", TEST_MSG);
137  TEST_VQRSHRUN_N(int, s, 16, 8, 8, 6);
138  TEST_VQRSHRUN_N(int, s, 32, 16, 4, 7);
139  TEST_VQRSHRUN_N(int, s, 64, 32, 2, 8);
140
141  dump_results_hex (TEST_MSG);
142}
143