1073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon/*
2073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon
3c94d4c1e27bb7e2b2869cc230872669df1459533Christophe LyonCopyright (c) 2009, 2010, 2011, 2012 STMicroelectronics
4073831adf9442c019e8d34b18b0c04b1d780a19Christophe LyonWritten by Christophe Lyon
5073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon
6073831adf9442c019e8d34b18b0c04b1d780a19Christophe LyonPermission is hereby granted, free of charge, to any person obtaining a copy
7073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyonof this software and associated documentation files (the "Software"), to deal
8073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyonin the Software without restriction, including without limitation the rights
9073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyonto use, copy, modify, merge, publish, distribute, sublicense, and/or sell
10073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyoncopies of the Software, and to permit persons to whom the Software is
11073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyonfurnished to do so, subject to the following conditions:
12073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon
13073831adf9442c019e8d34b18b0c04b1d780a19Christophe LyonThe above copyright notice and this permission notice shall be included in
14073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyonall copies or substantial portions of the Software.
15073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon
16073831adf9442c019e8d34b18b0c04b1d780a19Christophe LyonTHE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR
17073831adf9442c019e8d34b18b0c04b1d780a19Christophe LyonIMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,
18073831adf9442c019e8d34b18b0c04b1d780a19Christophe LyonFITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. IN NO EVENT SHALL THE
19073831adf9442c019e8d34b18b0c04b1d780a19Christophe LyonAUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER
20073831adf9442c019e8d34b18b0c04b1d780a19Christophe LyonLIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING FROM,
21073831adf9442c019e8d34b18b0c04b1d780a19Christophe LyonOUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN
22073831adf9442c019e8d34b18b0c04b1d780a19Christophe LyonTHE SOFTWARE.
23073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon
24073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon*/
25073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon
26073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon/* Template file for unary saturating operator validation */
27073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon
281775be0bcaa673c19bb1f60f0c1bce1b91cdb414Christophe Lyon#if defined(__arm__) || defined(__aarch64__)
29073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon#include <arm_neon.h>
30073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon#else
310dab5f72da4b2434882b51b44ac377af9e3160feChristophe Lyon#include "stm-arm-neon.h"
32073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon#endif
33073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon
34073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon#include "stm-arm-neon-ref.h"
35073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon
36073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon#define FNNAME1(NAME) void exec_ ## NAME (void)
37073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon#define FNNAME(NAME) FNNAME1(NAME)
38073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon
39073831adf9442c019e8d34b18b0c04b1d780a19Christophe LyonFNNAME (INSN_NAME)
40073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon{
41073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  /* Basic test: y=OP(x), then store the result.  */
424a6e5cc95176769664bc9e56d4e7c92b7a2fc816Christophe Lyon#define TEST_UNARY_SAT_OP1(INSN, Q, T1, T2, W, N)		\
43c1cc7826d74587e0dc1c855810633a219b161ab3Christophe Lyon  Set_Neon_Cumulative_Sat(0, VECT_VAR(vector_res, T1, W, N));	\
444a6e5cc95176769664bc9e56d4e7c92b7a2fc816Christophe Lyon  VECT_VAR(vector_res, T1, W, N) =				\
454a6e5cc95176769664bc9e56d4e7c92b7a2fc816Christophe Lyon    INSN##Q##_##T2##W(VECT_VAR(vector, T1, W, N));		\
464a6e5cc95176769664bc9e56d4e7c92b7a2fc816Christophe Lyon  vst1##Q##_##T2##W(VECT_VAR(result, T1, W, N),			\
474a6e5cc95176769664bc9e56d4e7c92b7a2fc816Christophe Lyon		    VECT_VAR(vector_res, T1, W, N));		\
484a6e5cc95176769664bc9e56d4e7c92b7a2fc816Christophe Lyon  dump_neon_cumulative_sat(TEST_MSG, xSTR(INSN##Q##_##T2##W),	\
494a6e5cc95176769664bc9e56d4e7c92b7a2fc816Christophe Lyon			   xSTR(T1), W, N)
50073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon
51073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon#define TEST_UNARY_SAT_OP(INSN, Q, T1, T2, W, N)	\
52073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  TEST_UNARY_SAT_OP1(INSN, Q, T1, T2, W, N)
53073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon
54073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon    /* With ARM RVCT, we need to declare variables before any executable
55073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon       statement  */
56073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon
57073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  /* No need for 64 bits variants */
58073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  DECL_VARIABLE(vector, int, 8, 8);
59073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  DECL_VARIABLE(vector, int, 16, 4);
60073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  DECL_VARIABLE(vector, int, 32, 2);
61073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  DECL_VARIABLE(vector, int, 8, 16);
62073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  DECL_VARIABLE(vector, int, 16, 8);
63073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  DECL_VARIABLE(vector, int, 32, 4);
64073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon
65073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  DECL_VARIABLE(vector_res, int, 8, 8);
66073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  DECL_VARIABLE(vector_res, int, 16, 4);
67073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  DECL_VARIABLE(vector_res, int, 32, 2);
68073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  DECL_VARIABLE(vector_res, int, 8, 16);
69073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  DECL_VARIABLE(vector_res, int, 16, 8);
70073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  DECL_VARIABLE(vector_res, int, 32, 4);
71073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon
72073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  clean_results ();
73073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon
74073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  /* Initialize input "vector" from "buffer"  */
75f20536724d4cc8432d5b804082415c8391f88f9bChristophe Lyon  VLOAD(vector, buffer, , int, s, 8, 8);
76f20536724d4cc8432d5b804082415c8391f88f9bChristophe Lyon  VLOAD(vector, buffer, , int, s, 16, 4);
77f20536724d4cc8432d5b804082415c8391f88f9bChristophe Lyon  VLOAD(vector, buffer, , int, s, 32, 2);
78f20536724d4cc8432d5b804082415c8391f88f9bChristophe Lyon  VLOAD(vector, buffer, q, int, s, 8, 16);
79f20536724d4cc8432d5b804082415c8391f88f9bChristophe Lyon  VLOAD(vector, buffer, q, int, s, 16, 8);
80f20536724d4cc8432d5b804082415c8391f88f9bChristophe Lyon  VLOAD(vector, buffer, q, int, s, 32, 4);
81073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon
82073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  /* Apply a unary operator named INSN_NAME  */
834a6e5cc95176769664bc9e56d4e7c92b7a2fc816Christophe Lyon  fprintf(ref_file, "\n%s cumulative saturation output:\n", TEST_MSG);
84073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  TEST_UNARY_SAT_OP(INSN_NAME, , int, s, 8, 8);
85073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  TEST_UNARY_SAT_OP(INSN_NAME, , int, s, 16, 4);
86073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  TEST_UNARY_SAT_OP(INSN_NAME, , int, s, 32, 2);
87073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  TEST_UNARY_SAT_OP(INSN_NAME, q, int, s, 8, 16);
88073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  TEST_UNARY_SAT_OP(INSN_NAME, q, int, s, 16, 8);
89073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  TEST_UNARY_SAT_OP(INSN_NAME, q, int, s, 32, 4);
90073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon
91073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  dump_results_hex (TEST_MSG);
92073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon
93073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon#ifdef EXTRA_TESTS
94073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon  EXTRA_TESTS();
95073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon#endif
96073831adf9442c019e8d34b18b0c04b1d780a19Christophe Lyon}
97