mirror of
git://gcc.gnu.org/git/gcc.git
synced 2025-04-10 16:00:55 +08:00
vqrdmulh_n.c: New file.
2015-05-19 Christophe Lyon <christophe.lyon@linaro.org> * gcc.target/aarch64/advsimd-intrinsics/vqrdmulh_n.c: New file. From-SVN: r223376
This commit is contained in:
Christophe Lyon
Christophe Lyon
parent
4f24fac171
commit
396fa23a27
@ -1,3 +1,7 @@
|
||||
2015-05-19 Christophe Lyon <christophe.lyon@linaro.org>
|
||||
|
||||
* gcc.target/aarch64/advsimd-intrinsics/vqrdmulh_n.c: New file.
|
||||
|
||||
2015-05-19 Christophe Lyon <christophe.lyon@linaro.org>
|
||||
|
||||
* gcc.target/aarch64/advsimd-intrinsics/vqrdmulh_lane.c: New file.
|
||||
|
||||
155
gcc/testsuite/gcc.target/aarch64/advsimd-intrinsics/vqrdmulh_n.c
Normal file
155
gcc/testsuite/gcc.target/aarch64/advsimd-intrinsics/vqrdmulh_n.c
Normal file
@ -0,0 +1,155 @@
|
||||
#include <arm_neon.h>
|
||||
#include "arm-neon-ref.h"
|
||||
#include "compute-ref-data.h"
|
||||
|
||||
/* Expected values of cumulative_saturation flag. */
|
||||
int VECT_VAR(expected_cumulative_sat,int,16,4) = 0;
|
||||
int VECT_VAR(expected_cumulative_sat,int,32,2) = 0;
|
||||
int VECT_VAR(expected_cumulative_sat,int,16,8) = 0;
|
||||
int VECT_VAR(expected_cumulative_sat,int,32,4) = 0;
|
||||
|
||||
/* Expected results. */
|
||||
VECT_VAR_DECL(expected,int,16,4) [] = { 0xfffc, 0xfffc, 0xfffc, 0xfffd };
|
||||
VECT_VAR_DECL(expected,int,32,2) [] = { 0xfffffffe, 0xfffffffe };
|
||||
VECT_VAR_DECL(expected,int,16,8) [] = { 0x6, 0x6, 0x6, 0x5,
|
||||
0x5, 0x4, 0x4, 0x4 };
|
||||
VECT_VAR_DECL(expected,int,32,4) [] = { 0xfffffffe, 0xfffffffe,
|
||||
0xfffffffe, 0xfffffffe };
|
||||
|
||||
/* Expected values of cumulative_saturation flag when multiplication
|
||||
saturates. */
|
||||
int VECT_VAR(expected_cumulative_sat_mul,int,16,4) = 1;
|
||||
int VECT_VAR(expected_cumulative_sat_mul,int,32,2) = 1;
|
||||
int VECT_VAR(expected_cumulative_sat_mul,int,16,8) = 1;
|
||||
int VECT_VAR(expected_cumulative_sat_mul,int,32,4) = 1;
|
||||
|
||||
/* Expected results when multiplication saturates. */
|
||||
VECT_VAR_DECL(expected_mul,int,16,4) [] = { 0x7fff, 0x7fff, 0x7fff, 0x7fff };
|
||||
VECT_VAR_DECL(expected_mul,int,32,2) [] = { 0x7fffffff, 0x7fffffff };
|
||||
VECT_VAR_DECL(expected_mul,int,16,8) [] = { 0x7fff, 0x7fff, 0x7fff, 0x7fff,
|
||||
0x7fff, 0x7fff, 0x7fff, 0x7fff };
|
||||
VECT_VAR_DECL(expected_mul,int,32,4) [] = { 0x7fffffff, 0x7fffffff,
|
||||
0x7fffffff, 0x7fffffff };
|
||||
|
||||
/* Expected values of cumulative_saturation flag when rounding
|
||||
should not cause saturation. */
|
||||
int VECT_VAR(expected_cumulative_sat_round,int,16,4) = 0;
|
||||
int VECT_VAR(expected_cumulative_sat_round,int,32,2) = 0;
|
||||
int VECT_VAR(expected_cumulative_sat_round,int,16,8) = 0;
|
||||
int VECT_VAR(expected_cumulative_sat_round,int,32,4) = 0;
|
||||
|
||||
/* Expected results when rounding should not cause saturation. */
|
||||
VECT_VAR_DECL(expected_round,int,16,4) [] = { 0x7fff, 0x7fff, 0x7fff, 0x7fff };
|
||||
VECT_VAR_DECL(expected_round,int,32,2) [] = { 0x7fffffff, 0x7fffffff };
|
||||
VECT_VAR_DECL(expected_round,int,16,8) [] = { 0x7fff, 0x7fff, 0x7fff, 0x7fff,
|
||||
0x7fff, 0x7fff, 0x7fff, 0x7fff };
|
||||
VECT_VAR_DECL(expected_round,int,32,4) [] = { 0x7fffffff, 0x7fffffff,
|
||||
0x7fffffff, 0x7fffffff };
|
||||
|
||||
#define INSN vqrdmulh
|
||||
#define TEST_MSG "VQRDMULH_N"
|
||||
|
||||
#define FNNAME1(NAME) void exec_ ## NAME ## _n (void)
|
||||
#define FNNAME(NAME) FNNAME1(NAME)
|
||||
|
||||
FNNAME (INSN)
|
||||
{
|
||||
int i;
|
||||
|
||||
/* vector_res = vqrdmulh_n(vector,val), then store the result. */
|
||||
#define TEST_VQRDMULH_N2(INSN, Q, T1, T2, W, N, L, EXPECTED_CUMULATIVE_SAT, CMT) \
|
||||
Set_Neon_Cumulative_Sat(0, VECT_VAR(vector_res, T1, W, N)); \
|
||||
VECT_VAR(vector_res, T1, W, N) = \
|
||||
INSN##Q##_n_##T2##W(VECT_VAR(vector, T1, W, N), \
|
||||
L); \
|
||||
vst1##Q##_##T2##W(VECT_VAR(result, T1, W, N), \
|
||||
VECT_VAR(vector_res, T1, W, N)); \
|
||||
CHECK_CUMULATIVE_SAT(TEST_MSG, T1, W, N, EXPECTED_CUMULATIVE_SAT, CMT)
|
||||
|
||||
/* Two auxliary macros are necessary to expand INSN */
|
||||
#define TEST_VQRDMULH_N1(INSN, Q, T1, T2, W, N, L, EXPECTED_CUMULATIVE_SAT, CMT) \
|
||||
TEST_VQRDMULH_N2(INSN, Q, T1, T2, W, N, L, EXPECTED_CUMULATIVE_SAT, CMT)
|
||||
|
||||
#define TEST_VQRDMULH_N(Q, T1, T2, W, N, L, EXPECTED_CUMULATIVE_SAT, CMT) \
|
||||
TEST_VQRDMULH_N1(INSN, Q, T1, T2, W, N, L, EXPECTED_CUMULATIVE_SAT, CMT)
|
||||
|
||||
|
||||
DECL_VARIABLE(vector, int, 16, 4);
|
||||
DECL_VARIABLE(vector, int, 32, 2);
|
||||
DECL_VARIABLE(vector, int, 16, 8);
|
||||
DECL_VARIABLE(vector, int, 32, 4);
|
||||
|
||||
DECL_VARIABLE(vector_res, int, 16, 4);
|
||||
DECL_VARIABLE(vector_res, int, 32, 2);
|
||||
DECL_VARIABLE(vector_res, int, 16, 8);
|
||||
DECL_VARIABLE(vector_res, int, 32, 4);
|
||||
|
||||
clean_results ();
|
||||
|
||||
VLOAD(vector, buffer, , int, s, 16, 4);
|
||||
VLOAD(vector, buffer, , int, s, 32, 2);
|
||||
VLOAD(vector, buffer, q, int, s, 16, 8);
|
||||
VLOAD(vector, buffer, q, int, s, 32, 4);
|
||||
|
||||
/* Choose multiplier arbitrarily. */
|
||||
#define CMT ""
|
||||
TEST_VQRDMULH_N(, int, s, 16, 4, 0x2233, expected_cumulative_sat, CMT);
|
||||
TEST_VQRDMULH_N(, int, s, 32, 2, 0x12345678, expected_cumulative_sat, CMT);
|
||||
TEST_VQRDMULH_N(q, int, s, 16, 8, 0xCD12, expected_cumulative_sat, CMT);
|
||||
TEST_VQRDMULH_N(q, int, s, 32, 4, 0xFA23456, expected_cumulative_sat, CMT);
|
||||
|
||||
CHECK(TEST_MSG, int, 16, 4, PRIx16, expected, CMT);
|
||||
CHECK(TEST_MSG, int, 32, 2, PRIx32, expected, CMT);
|
||||
CHECK(TEST_MSG, int, 16, 8, PRIx16, expected, CMT);
|
||||
CHECK(TEST_MSG, int, 32, 4, PRIx32, expected, CMT);
|
||||
|
||||
/* Now use input values such that the multiplication causes
|
||||
saturation. */
|
||||
#define TEST_MSG_MUL " (check mul cumulative saturation)"
|
||||
VDUP(vector, , int, s, 16, 4, 0x8000);
|
||||
VDUP(vector, , int, s, 32, 2, 0x80000000);
|
||||
VDUP(vector, q, int, s, 16, 8, 0x8000);
|
||||
VDUP(vector, q, int, s, 32, 4, 0x80000000);
|
||||
|
||||
TEST_VQRDMULH_N(, int, s, 16, 4, 0x8000, expected_cumulative_sat_mul,
|
||||
TEST_MSG_MUL);
|
||||
TEST_VQRDMULH_N(, int, s, 32, 2, 0x80000000, expected_cumulative_sat_mul,
|
||||
TEST_MSG_MUL);
|
||||
TEST_VQRDMULH_N(q, int, s, 16, 8, 0x8000, expected_cumulative_sat_mul,
|
||||
TEST_MSG_MUL);
|
||||
TEST_VQRDMULH_N(q, int, s, 32, 4, 0x80000000, expected_cumulative_sat_mul,
|
||||
TEST_MSG_MUL);
|
||||
|
||||
CHECK(TEST_MSG, int, 16, 4, PRIx16, expected_mul, TEST_MSG_MUL);
|
||||
CHECK(TEST_MSG, int, 32, 2, PRIx32, expected_mul, TEST_MSG_MUL);
|
||||
CHECK(TEST_MSG, int, 16, 8, PRIx16, expected_mul, TEST_MSG_MUL);
|
||||
CHECK(TEST_MSG, int, 32, 4, PRIx32, expected_mul, TEST_MSG_MUL);
|
||||
|
||||
/* Use input values where rounding produces a result equal to the
|
||||
saturation value, but does not set the saturation flag. */
|
||||
#define TEST_MSG_ROUND " (check rounding)"
|
||||
VDUP(vector, , int, s, 16, 4, 0x8000);
|
||||
VDUP(vector, , int, s, 32, 2, 0x80000000);
|
||||
VDUP(vector, q, int, s, 16, 8, 0x8000);
|
||||
VDUP(vector, q, int, s, 32, 4, 0x80000000);
|
||||
|
||||
TEST_VQRDMULH_N(, int, s, 16, 4, 0x8001, expected_cumulative_sat_round,
|
||||
TEST_MSG_ROUND);
|
||||
TEST_VQRDMULH_N(, int, s, 32, 2, 0x80000001, expected_cumulative_sat_round,
|
||||
TEST_MSG_ROUND);
|
||||
TEST_VQRDMULH_N(q, int, s, 16, 8, 0x8001, expected_cumulative_sat_round,
|
||||
TEST_MSG_ROUND);
|
||||
TEST_VQRDMULH_N(q, int, s, 32, 4, 0x80000001, expected_cumulative_sat_round,
|
||||
TEST_MSG_ROUND);
|
||||
|
||||
CHECK(TEST_MSG, int, 16, 4, PRIx16, expected_round, TEST_MSG_ROUND);
|
||||
CHECK(TEST_MSG, int, 32, 2, PRIx32, expected_round, TEST_MSG_ROUND);
|
||||
CHECK(TEST_MSG, int, 16, 8, PRIx16, expected_round, TEST_MSG_ROUND);
|
||||
CHECK(TEST_MSG, int, 32, 4, PRIx32, expected_round, TEST_MSG_ROUND);
|
||||
}
|
||||
|
||||
int main (void)
|
||||
{
|
||||
exec_vqrdmulh_n ();
|
||||
return 0;
|
||||
}
|
||||
Loading…
x
Reference in New Issue
Block a user