1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
66
67
68
69
70
71
72
73
74
75
76
77
78
79
80
81
82
83
84
85
86
87
88
89
90
91
92
93
94
95
96
97
98
99
100
101
|
/* { dg-do run } */
/* { dg-options "-O3 --save-temps" } */
#include <arm_neon.h>
extern void abort (void);
#define ETYPE(size) int##size##_t
#define VTYPE(size, lanes) int##size##x##lanes##_t
#define TEST_VABS(q, size, lanes) \
static void \
test_vabs##q##_##size (ETYPE (size) * res, \
const ETYPE (size) *in1) \
{ \
VTYPE (size, lanes) a = vld1##q##_s##size (res); \
VTYPE (size, lanes) b = vld1##q##_s##size (in1); \
a = vabs##q##_s##size (b); \
vst1##q##_s##size (res, a); \
}
#define BUILD_VARS(width, n_lanes, n_half_lanes) \
TEST_VABS (, width, n_half_lanes) \
TEST_VABS (q, width, n_lanes) \
BUILD_VARS (64, 2, 1)
BUILD_VARS (32, 4, 2)
BUILD_VARS (16, 8, 4)
BUILD_VARS (8, 16, 8)
#define POOL1 {-10}
#define POOL2 {2, -10}
#define POOL4 {0, -10, 2, -3}
#define POOL8 {0, -10, 2, -3, 4, -50, 6, -70}
#define POOL16 {0, -10, 2, -3, 4, -50, 6, -70, \
-5, 10, -2, 3, -4, 50, -6, 70}
#define EXPECTED1 {10}
#define EXPECTED2 {2, 10}
#define EXPECTED4 {0, 10, 2, 3}
#define EXPECTED8 {0, 10, 2, 3, 4, 50, 6, 70}
#define EXPECTED16 {0, 10, 2, 3, 4, 50, 6, 70, \
5, 10, 2, 3, 4, 50, 6, 70}
#define BUILD_TEST(size, lanes_64, lanes_128) \
static void \
test_##size (void) \
{ \
int i; \
ETYPE (size) pool1[lanes_64] = POOL##lanes_64; \
ETYPE (size) res1[lanes_64] = {0}; \
ETYPE (size) expected1[lanes_64] = EXPECTED##lanes_64; \
ETYPE (size) pool2[lanes_128] = POOL##lanes_128; \
ETYPE (size) res2[lanes_128] = {0}; \
ETYPE (size) expected2[lanes_128] = EXPECTED##lanes_128; \
\
/* Forcefully avoid optimization. */ \
asm volatile ("" : : : "memory"); \
test_vabs_##size (res1, pool1); \
for (i = 0; i < lanes_64; i++) \
if (res1[i] != expected1[i]) \
abort (); \
\
/* Forcefully avoid optimization. */ \
asm volatile ("" : : : "memory"); \
test_vabsq_##size (res2, pool2); \
for (i = 0; i < lanes_128; i++) \
if (res2[i] != expected2[i]) \
abort (); \
}
/* { dg-final { scan-assembler-times "abs\\tv\[0-9\]+\.8b, v\[0-9\]+\.8b" 1 } } */
/* { dg-final { scan-assembler-times "abs\\tv\[0-9\]+\.16b, v\[0-9\]+\.16b" 1 } } */
BUILD_TEST (8 , 8, 16)
/* { dg-final { scan-assembler-times "abs\\tv\[0-9\]+\.4h, v\[0-9\]+\.4h" 1 } } */
/* { dg-final { scan-assembler-times "abs\\tv\[0-9\]+\.8h, v\[0-9\]+\.8h" 1 } } */
BUILD_TEST (16, 4, 8)
/* { dg-final { scan-assembler-times "abs\\tv\[0-9\]+\.2s, v\[0-9\]+\.2s" 1 } } */
/* { dg-final { scan-assembler-times "abs\\tv\[0-9\]+\.4s, v\[0-9\]+\.4s" 1 } } */
BUILD_TEST (32, 2, 4)
/* { dg-final { scan-assembler-times "abs\\tv\[0-9\]+\.2d, v\[0-9\]+\.2d" 1 } } */
BUILD_TEST (64, 1, 2)
#undef BUILD_TEST
#define BUILD_TEST(size) test_##size ()
int
main (int argc, char **argv)
{
BUILD_TEST (8);
BUILD_TEST (16);
BUILD_TEST (32);
BUILD_TEST (64);
return 0;
}
/* { dg-final { cleanup-saved-temps } } */
|
