1 /* { dg-final { check-function-bodies "**" "" "-DCHECK_ASM" { target { ! ilp32 } } } } */
2
3 #include "test_sve_acle.h"
4
5 /*
6 ** ldnt1_gather_f32_tied1:
7 ** ldnt1w z0\.s, p0/z, \[z0\.s\]
8 ** ret
9 */
10 TEST_LOAD_GATHER_ZS (ldnt1_gather_f32_tied1, svfloat32_t, svuint32_t,
11 z0_res = svldnt1_gather_u32base_f32 (p0, z0),
12 z0_res = svldnt1_gather_f32 (p0, z0))
13
14 /*
15 ** ldnt1_gather_f32_untied:
16 ** ldnt1w z0\.s, p0/z, \[z1\.s\]
17 ** ret
18 */
19 TEST_LOAD_GATHER_ZS (ldnt1_gather_f32_untied, svfloat32_t, svuint32_t,
20 z0_res = svldnt1_gather_u32base_f32 (p0, z1),
21 z0_res = svldnt1_gather_f32 (p0, z1))
22
23 /*
24 ** ldnt1_gather_x0_f32_offset:
25 ** ldnt1w z0\.s, p0/z, \[z0\.s, x0\]
26 ** ret
27 */
28 TEST_LOAD_GATHER_ZS (ldnt1_gather_x0_f32_offset, svfloat32_t, svuint32_t,
29 z0_res = svldnt1_gather_u32base_offset_f32 (p0, z0, x0),
30 z0_res = svldnt1_gather_offset_f32 (p0, z0, x0))
31
32 /*
33 ** ldnt1_gather_m4_f32_offset:
34 ** mov (x[0-9]+), #?-4
35 ** ldnt1w z0\.s, p0/z, \[z0\.s, \1\]
36 ** ret
37 */
38 TEST_LOAD_GATHER_ZS (ldnt1_gather_m4_f32_offset, svfloat32_t, svuint32_t,
39 z0_res = svldnt1_gather_u32base_offset_f32 (p0, z0, -4),
40 z0_res = svldnt1_gather_offset_f32 (p0, z0, -4))
41
42 /*
43 ** ldnt1_gather_0_f32_offset:
44 ** ldnt1w z0\.s, p0/z, \[z0\.s\]
45 ** ret
46 */
47 TEST_LOAD_GATHER_ZS (ldnt1_gather_0_f32_offset, svfloat32_t, svuint32_t,
48 z0_res = svldnt1_gather_u32base_offset_f32 (p0, z0, 0),
49 z0_res = svldnt1_gather_offset_f32 (p0, z0, 0))
50
51 /*
52 ** ldnt1_gather_5_f32_offset:
53 ** mov (x[0-9]+), #?5
54 ** ldnt1w z0\.s, p0/z, \[z0\.s, \1\]
55 ** ret
56 */
57 TEST_LOAD_GATHER_ZS (ldnt1_gather_5_f32_offset, svfloat32_t, svuint32_t,
58 z0_res = svldnt1_gather_u32base_offset_f32 (p0, z0, 5),
59 z0_res = svldnt1_gather_offset_f32 (p0, z0, 5))
60
61 /*
62 ** ldnt1_gather_6_f32_offset:
63 ** mov (x[0-9]+), #?6
64 ** ldnt1w z0\.s, p0/z, \[z0\.s, \1\]
65 ** ret
66 */
67 TEST_LOAD_GATHER_ZS (ldnt1_gather_6_f32_offset, svfloat32_t, svuint32_t,
68 z0_res = svldnt1_gather_u32base_offset_f32 (p0, z0, 6),
69 z0_res = svldnt1_gather_offset_f32 (p0, z0, 6))
70
71 /*
72 ** ldnt1_gather_7_f32_offset:
73 ** mov (x[0-9]+), #?7
74 ** ldnt1w z0\.s, p0/z, \[z0\.s, \1\]
75 ** ret
76 */
77 TEST_LOAD_GATHER_ZS (ldnt1_gather_7_f32_offset, svfloat32_t, svuint32_t,
78 z0_res = svldnt1_gather_u32base_offset_f32 (p0, z0, 7),
79 z0_res = svldnt1_gather_offset_f32 (p0, z0, 7))
80
81 /*
82 ** ldnt1_gather_8_f32_offset:
83 ** mov (x[0-9]+), #?8
84 ** ldnt1w z0\.s, p0/z, \[z0\.s, \1\]
85 ** ret
86 */
87 TEST_LOAD_GATHER_ZS (ldnt1_gather_8_f32_offset, svfloat32_t, svuint32_t,
88 z0_res = svldnt1_gather_u32base_offset_f32 (p0, z0, 8),
89 z0_res = svldnt1_gather_offset_f32 (p0, z0, 8))
90
91 /*
92 ** ldnt1_gather_124_f32_offset:
93 ** mov (x[0-9]+), #?124
94 ** ldnt1w z0\.s, p0/z, \[z0\.s, \1\]
95 ** ret
96 */
97 TEST_LOAD_GATHER_ZS (ldnt1_gather_124_f32_offset, svfloat32_t, svuint32_t,
98 z0_res = svldnt1_gather_u32base_offset_f32 (p0, z0, 124),
99 z0_res = svldnt1_gather_offset_f32 (p0, z0, 124))
100
101 /*
102 ** ldnt1_gather_128_f32_offset:
103 ** mov (x[0-9]+), #?128
104 ** ldnt1w z0\.s, p0/z, \[z0\.s, \1\]
105 ** ret
106 */
107 TEST_LOAD_GATHER_ZS (ldnt1_gather_128_f32_offset, svfloat32_t, svuint32_t,
108 z0_res = svldnt1_gather_u32base_offset_f32 (p0, z0, 128),
109 z0_res = svldnt1_gather_offset_f32 (p0, z0, 128))
110
111 /*
112 ** ldnt1_gather_x0_f32_index:
113 ** lsl (x[0-9]+), x0, #?2
114 ** ldnt1w z0\.s, p0/z, \[z0\.s, \1\]
115 ** ret
116 */
117 TEST_LOAD_GATHER_ZS (ldnt1_gather_x0_f32_index, svfloat32_t, svuint32_t,
118 z0_res = svldnt1_gather_u32base_index_f32 (p0, z0, x0),
119 z0_res = svldnt1_gather_index_f32 (p0, z0, x0))
120
121 /*
122 ** ldnt1_gather_m1_f32_index:
123 ** mov (x[0-9]+), #?-4
124 ** ldnt1w z0\.s, p0/z, \[z0\.s, \1\]
125 ** ret
126 */
127 TEST_LOAD_GATHER_ZS (ldnt1_gather_m1_f32_index, svfloat32_t, svuint32_t,
128 z0_res = svldnt1_gather_u32base_index_f32 (p0, z0, -1),
129 z0_res = svldnt1_gather_index_f32 (p0, z0, -1))
130
131 /*
132 ** ldnt1_gather_0_f32_index:
133 ** ldnt1w z0\.s, p0/z, \[z0\.s\]
134 ** ret
135 */
136 TEST_LOAD_GATHER_ZS (ldnt1_gather_0_f32_index, svfloat32_t, svuint32_t,
137 z0_res = svldnt1_gather_u32base_index_f32 (p0, z0, 0),
138 z0_res = svldnt1_gather_index_f32 (p0, z0, 0))
139
140 /*
141 ** ldnt1_gather_5_f32_index:
142 ** mov (x[0-9]+), #?20
143 ** ldnt1w z0\.s, p0/z, \[z0\.s, \1\]
144 ** ret
145 */
146 TEST_LOAD_GATHER_ZS (ldnt1_gather_5_f32_index, svfloat32_t, svuint32_t,
147 z0_res = svldnt1_gather_u32base_index_f32 (p0, z0, 5),
148 z0_res = svldnt1_gather_index_f32 (p0, z0, 5))
149
150 /*
151 ** ldnt1_gather_31_f32_index:
152 ** mov (x[0-9]+), #?124
153 ** ldnt1w z0\.s, p0/z, \[z0\.s, \1\]
154 ** ret
155 */
156 TEST_LOAD_GATHER_ZS (ldnt1_gather_31_f32_index, svfloat32_t, svuint32_t,
157 z0_res = svldnt1_gather_u32base_index_f32 (p0, z0, 31),
158 z0_res = svldnt1_gather_index_f32 (p0, z0, 31))
159
160 /*
161 ** ldnt1_gather_32_f32_index:
162 ** mov (x[0-9]+), #?128
163 ** ldnt1w z0\.s, p0/z, \[z0\.s, \1\]
164 ** ret
165 */
166 TEST_LOAD_GATHER_ZS (ldnt1_gather_32_f32_index, svfloat32_t, svuint32_t,
167 z0_res = svldnt1_gather_u32base_index_f32 (p0, z0, 32),
168 z0_res = svldnt1_gather_index_f32 (p0, z0, 32))
169
170 /*
171 ** ldnt1_gather_x0_f32_u32offset:
172 ** ldnt1w z0\.s, p0/z, \[z0\.s, x0\]
173 ** ret
174 */
175 TEST_LOAD_GATHER_SZ (ldnt1_gather_x0_f32_u32offset, svfloat32_t, float32_t, svuint32_t,
176 z0_res = svldnt1_gather_u32offset_f32 (p0, x0, z0),
177 z0_res = svldnt1_gather_offset (p0, x0, z0))
178
179 /*
180 ** ldnt1_gather_tied1_f32_u32offset:
181 ** ldnt1w z0\.s, p0/z, \[z0\.s, x0\]
182 ** ret
183 */
184 TEST_LOAD_GATHER_SZ (ldnt1_gather_tied1_f32_u32offset, svfloat32_t, float32_t, svuint32_t,
185 z0_res = svldnt1_gather_u32offset_f32 (p0, x0, z0),
186 z0_res = svldnt1_gather_offset (p0, x0, z0))
187
188 /*
189 ** ldnt1_gather_untied_f32_u32offset:
190 ** ldnt1w z0\.s, p0/z, \[z1\.s, x0\]
191 ** ret
192 */
193 TEST_LOAD_GATHER_SZ (ldnt1_gather_untied_f32_u32offset, svfloat32_t, float32_t, svuint32_t,
194 z0_res = svldnt1_gather_u32offset_f32 (p0, x0, z1),
195 z0_res = svldnt1_gather_offset (p0, x0, z1))