1 // RUN: %clang_cc1 -triple aarch64-none-linux-gnu -target-feature +sve2 -fallow-half-arguments-and-returns -S -O1 -Werror -Wall -emit-llvm -o - %s | FileCheck %s
2 // RUN: %clang_cc1 -triple aarch64-none-linux-gnu -target-feature +sve2 -fallow-half-arguments-and-returns -S -O1 -Werror -Wall -emit-llvm -o - -x c++ %s | FileCheck %s
3 // RUN: %clang_cc1 -DSVE_OVERLOADED_FORMS -triple aarch64-none-linux-gnu -target-feature +sve2 -fallow-half-arguments-and-returns -S -O1 -Werror -Wall -emit-llvm -o - %s | FileCheck %s
4 // RUN: %clang_cc1 -DSVE_OVERLOADED_FORMS -triple aarch64-none-linux-gnu -target-feature +sve2 -fallow-half-arguments-and-returns -S -O1 -Werror -Wall -emit-llvm -o - -x c++ %s | FileCheck %s
5 // RUN: %clang_cc1 -triple aarch64-none-linux-gnu -target-feature +sve -fallow-half-arguments-and-returns -fsyntax-only -verify -verify-ignore-unexpected=error %s
6 // RUN: %clang_cc1 -DSVE_OVERLOADED_FORMS -triple aarch64-none-linux-gnu -target-feature +sve -fallow-half-arguments-and-returns -fsyntax-only -verify=overload -verify-ignore-unexpected=error %s
7
8 #include <arm_sve.h>
9
10 #ifdef SVE_OVERLOADED_FORMS
11 // A simple used,unused... macro, long enough to represent any SVE builtin.
12 #define SVE_ACLE_FUNC(A1, A2_UNUSED, A3, A4_UNUSED) A1##A3
13 #else
14 #define SVE_ACLE_FUNC(A1, A2, A3, A4) A1##A2##A3##A4
15 #endif
16
test_svstnt1_scatter_u32base_s32(svbool_t pg,svuint32_t bases,svint32_t data)17 void test_svstnt1_scatter_u32base_s32(svbool_t pg, svuint32_t bases, svint32_t data) {
18 // CHECK-LABEL: test_svstnt1_scatter_u32base_s32
19 // CHECK: [[PG:%.*]] = call <vscale x 4 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv4i1(<vscale x 16 x i1> %pg)
20 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.scalar.offset.nxv4i32.nxv4i32(<vscale x 4 x i32> %data, <vscale x 4 x i1> [[PG]], <vscale x 4 x i32> %bases, i64 0)
21 // CHECK: ret void
22 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter'}}
23 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u32base_s32'}}
24 return SVE_ACLE_FUNC(svstnt1_scatter, _u32base, , _s32)(pg, bases, data);
25 }
26
test_svstnt1_scatter_u64base_s64(svbool_t pg,svuint64_t bases,svint64_t data)27 void test_svstnt1_scatter_u64base_s64(svbool_t pg, svuint64_t bases, svint64_t data) {
28 // CHECK-LABEL: test_svstnt1_scatter_u64base_s64
29 // CHECK: [[PG:%.*]] = call <vscale x 2 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv2i1(<vscale x 16 x i1> %pg)
30 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.scalar.offset.nxv2i64.nxv2i64(<vscale x 2 x i64> %data, <vscale x 2 x i1> [[PG]], <vscale x 2 x i64> %bases, i64 0)
31 // CHECK: ret void
32 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter'}}
33 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u64base_s64'}}
34 return SVE_ACLE_FUNC(svstnt1_scatter, _u64base, , _s64)(pg, bases, data);
35 }
36
test_svstnt1_scatter_u32base_u32(svbool_t pg,svuint32_t bases,svuint32_t data)37 void test_svstnt1_scatter_u32base_u32(svbool_t pg, svuint32_t bases, svuint32_t data) {
38 // CHECK-LABEL: test_svstnt1_scatter_u32base_u32
39 // CHECK: [[PG:%.*]] = call <vscale x 4 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv4i1(<vscale x 16 x i1> %pg)
40 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.scalar.offset.nxv4i32.nxv4i32(<vscale x 4 x i32> %data, <vscale x 4 x i1> [[PG]], <vscale x 4 x i32> %bases, i64 0)
41 // CHECK: ret void
42 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter'}}
43 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u32base_u32'}}
44 return SVE_ACLE_FUNC(svstnt1_scatter, _u32base, , _u32)(pg, bases, data);
45 }
46
test_svstnt1_scatter_u64base_u64(svbool_t pg,svuint64_t bases,svuint64_t data)47 void test_svstnt1_scatter_u64base_u64(svbool_t pg, svuint64_t bases, svuint64_t data) {
48 // CHECK-LABEL: test_svstnt1_scatter_u64base_u64
49 // CHECK: [[PG:%.*]] = call <vscale x 2 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv2i1(<vscale x 16 x i1> %pg)
50 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.scalar.offset.nxv2i64.nxv2i64(<vscale x 2 x i64> %data, <vscale x 2 x i1> [[PG]], <vscale x 2 x i64> %bases, i64 0)
51 // CHECK: ret void
52 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter'}}
53 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u64base_u64'}}
54 return SVE_ACLE_FUNC(svstnt1_scatter, _u64base, , _u64)(pg, bases, data);
55 }
56
test_svstnt1_scatter_u32base_f32(svbool_t pg,svuint32_t bases,svfloat32_t data)57 void test_svstnt1_scatter_u32base_f32(svbool_t pg, svuint32_t bases, svfloat32_t data) {
58 // CHECK-LABEL: test_svstnt1_scatter_u32base_f32
59 // CHECK: [[PG:%.*]] = call <vscale x 4 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv4i1(<vscale x 16 x i1> %pg)
60 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.scalar.offset.nxv4f32.nxv4i32(<vscale x 4 x float> %data, <vscale x 4 x i1> [[PG]], <vscale x 4 x i32> %bases, i64 0)
61 // CHECK: ret void
62 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter'}}
63 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u32base_f32'}}
64 return SVE_ACLE_FUNC(svstnt1_scatter, _u32base, , _f32)(pg, bases, data);
65 }
66
test_svstnt1_scatter_u64base_f64(svbool_t pg,svuint64_t bases,svfloat64_t data)67 void test_svstnt1_scatter_u64base_f64(svbool_t pg, svuint64_t bases, svfloat64_t data) {
68 // CHECK-LABEL: test_svstnt1_scatter_u64base_f64
69 // CHECK: [[PG:%.*]] = call <vscale x 2 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv2i1(<vscale x 16 x i1> %pg)
70 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.scalar.offset.nxv2f64.nxv2i64(<vscale x 2 x double> %data, <vscale x 2 x i1> [[PG]], <vscale x 2 x i64> %bases, i64 0)
71 // CHECK: ret void
72 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter'}}
73 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u64base_f64'}}
74 return SVE_ACLE_FUNC(svstnt1_scatter, _u64base, , _f64)(pg, bases, data);
75 }
76
test_svstnt1_scatter_s64offset_s64(svbool_t pg,int64_t * base,svint64_t offsets,svint64_t data)77 void test_svstnt1_scatter_s64offset_s64(svbool_t pg, int64_t *base, svint64_t offsets, svint64_t data) {
78 // CHECK-LABEL: test_svstnt1_scatter_s64offset_s64
79 // CHECK: [[PG:%.*]] = call <vscale x 2 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv2i1(<vscale x 16 x i1> %pg)
80 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.nxv2i64(<vscale x 2 x i64> %data, <vscale x 2 x i1> [[PG]], i64* %base, <vscale x 2 x i64> %offsets)
81 // CHECK: ret void
82 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_offset'}}
83 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_s64offset_s64'}}
84 return SVE_ACLE_FUNC(svstnt1_scatter_, s64, offset, _s64)(pg, base, offsets, data);
85 }
86
test_svstnt1_scatter_s64offset_u64(svbool_t pg,uint64_t * base,svint64_t offsets,svuint64_t data)87 void test_svstnt1_scatter_s64offset_u64(svbool_t pg, uint64_t *base, svint64_t offsets, svuint64_t data) {
88 // CHECK-LABEL: test_svstnt1_scatter_s64offset_u64
89 // CHECK: [[PG:%.*]] = call <vscale x 2 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv2i1(<vscale x 16 x i1> %pg)
90 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.nxv2i64(<vscale x 2 x i64> %data, <vscale x 2 x i1> [[PG]], i64* %base, <vscale x 2 x i64> %offsets)
91 // CHECK: ret void
92 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_offset'}}
93 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_s64offset_u64'}}
94 return SVE_ACLE_FUNC(svstnt1_scatter_, s64, offset, _u64)(pg, base, offsets, data);
95 }
96
test_svstnt1_scatter_s64offset_f64(svbool_t pg,float64_t * base,svint64_t offsets,svfloat64_t data)97 void test_svstnt1_scatter_s64offset_f64(svbool_t pg, float64_t *base, svint64_t offsets, svfloat64_t data) {
98 // CHECK-LABEL: test_svstnt1_scatter_s64offset_f64
99 // CHECK: [[PG:%.*]] = call <vscale x 2 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv2i1(<vscale x 16 x i1> %pg)
100 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.nxv2f64(<vscale x 2 x double> %data, <vscale x 2 x i1> [[PG]], double* %base, <vscale x 2 x i64> %offsets)
101 // CHECK: ret void
102 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_offset'}}
103 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_s64offset_f64'}}
104 return SVE_ACLE_FUNC(svstnt1_scatter_, s64, offset, _f64)(pg, base, offsets, data);
105 }
106
test_svstnt1_scatter_u32offset_s32(svbool_t pg,int32_t * base,svuint32_t offsets,svint32_t data)107 void test_svstnt1_scatter_u32offset_s32(svbool_t pg, int32_t *base, svuint32_t offsets, svint32_t data) {
108 // CHECK-LABEL: test_svstnt1_scatter_u32offset_s32
109 // CHECK: [[PG:%.*]] = call <vscale x 4 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv4i1(<vscale x 16 x i1> %pg)
110 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.uxtw.nxv4i32(<vscale x 4 x i32> %data, <vscale x 4 x i1> [[PG]], i32* %base, <vscale x 4 x i32> %offsets)
111 // CHECK: ret void
112 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_offset'}}
113 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u32offset_s32'}}
114 return SVE_ACLE_FUNC(svstnt1_scatter_, u32, offset, _s32)(pg, base, offsets, data);
115 }
116
test_svstnt1_scatter_u64offset_s64(svbool_t pg,int64_t * base,svuint64_t offsets,svint64_t data)117 void test_svstnt1_scatter_u64offset_s64(svbool_t pg, int64_t *base, svuint64_t offsets, svint64_t data) {
118 // CHECK-LABEL: test_svstnt1_scatter_u64offset_s64
119 // CHECK: [[PG:%.*]] = call <vscale x 2 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv2i1(<vscale x 16 x i1> %pg)
120 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.nxv2i64(<vscale x 2 x i64> %data, <vscale x 2 x i1> [[PG]], i64* %base, <vscale x 2 x i64> %offsets)
121 // CHECK: ret void
122 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_offset'}}
123 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u64offset_s64'}}
124 return SVE_ACLE_FUNC(svstnt1_scatter_, u64, offset, _s64)(pg, base, offsets, data);
125 }
126
test_svstnt1_scatter_u32offset_u32(svbool_t pg,uint32_t * base,svuint32_t offsets,svuint32_t data)127 void test_svstnt1_scatter_u32offset_u32(svbool_t pg, uint32_t *base, svuint32_t offsets, svuint32_t data) {
128 // CHECK-LABEL: test_svstnt1_scatter_u32offset_u32
129 // CHECK: [[PG:%.*]] = call <vscale x 4 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv4i1(<vscale x 16 x i1> %pg)
130 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.uxtw.nxv4i32(<vscale x 4 x i32> %data, <vscale x 4 x i1> [[PG]], i32* %base, <vscale x 4 x i32> %offsets)
131 // CHECK: ret void
132 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_offset'}}
133 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u32offset_u32'}}
134 return SVE_ACLE_FUNC(svstnt1_scatter_, u32, offset, _u32)(pg, base, offsets, data);
135 }
136
test_svstnt1_scatter_u64offset_u64(svbool_t pg,uint64_t * base,svuint64_t offsets,svuint64_t data)137 void test_svstnt1_scatter_u64offset_u64(svbool_t pg, uint64_t *base, svuint64_t offsets, svuint64_t data) {
138 // CHECK-LABEL: test_svstnt1_scatter_u64offset_u64
139 // CHECK: [[PG:%.*]] = call <vscale x 2 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv2i1(<vscale x 16 x i1> %pg)
140 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.nxv2i64(<vscale x 2 x i64> %data, <vscale x 2 x i1> [[PG]], i64* %base, <vscale x 2 x i64> %offsets)
141 // CHECK: ret void
142 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_offset'}}
143 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u64offset_u64'}}
144 return SVE_ACLE_FUNC(svstnt1_scatter_, u64, offset, _u64)(pg, base, offsets, data);
145 }
146
test_svstnt1_scatter_u32offset_f32(svbool_t pg,float32_t * base,svuint32_t offsets,svfloat32_t data)147 void test_svstnt1_scatter_u32offset_f32(svbool_t pg, float32_t *base, svuint32_t offsets, svfloat32_t data) {
148 // CHECK-LABEL: test_svstnt1_scatter_u32offset_f32
149 // CHECK: [[PG:%.*]] = call <vscale x 4 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv4i1(<vscale x 16 x i1> %pg)
150 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.uxtw.nxv4f32(<vscale x 4 x float> %data, <vscale x 4 x i1> [[PG]], float* %base, <vscale x 4 x i32> %offsets)
151 // CHECK: ret void
152 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_offset'}}
153 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u32offset_f32'}}
154 return SVE_ACLE_FUNC(svstnt1_scatter_, u32, offset, _f32)(pg, base, offsets, data);
155 }
156
test_svstnt1_scatter_u64offset_f64(svbool_t pg,float64_t * base,svuint64_t offsets,svfloat64_t data)157 void test_svstnt1_scatter_u64offset_f64(svbool_t pg, float64_t *base, svuint64_t offsets, svfloat64_t data) {
158 // CHECK-LABEL: test_svstnt1_scatter_u64offset_f64
159 // CHECK: [[PG:%.*]] = call <vscale x 2 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv2i1(<vscale x 16 x i1> %pg)
160 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.nxv2f64(<vscale x 2 x double> %data, <vscale x 2 x i1> [[PG]], double* %base, <vscale x 2 x i64> %offsets)
161 // CHECK: ret void
162 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_offset'}}
163 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u64offset_f64'}}
164 return SVE_ACLE_FUNC(svstnt1_scatter_, u64, offset, _f64)(pg, base, offsets, data);
165 }
166
test_svstnt1_scatter_u32base_offset_s32(svbool_t pg,svuint32_t bases,int64_t offset,svint32_t data)167 void test_svstnt1_scatter_u32base_offset_s32(svbool_t pg, svuint32_t bases, int64_t offset, svint32_t data) {
168 // CHECK-LABEL: test_svstnt1_scatter_u32base_offset_s32
169 // CHECK: [[PG:%.*]] = call <vscale x 4 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv4i1(<vscale x 16 x i1> %pg)
170 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.scalar.offset.nxv4i32.nxv4i32(<vscale x 4 x i32> %data, <vscale x 4 x i1> [[PG]], <vscale x 4 x i32> %bases, i64 %offset)
171 // CHECK: ret void
172 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_offset'}}
173 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u32base_offset_s32'}}
174 return SVE_ACLE_FUNC(svstnt1_scatter, _u32base, _offset, _s32)(pg, bases, offset, data);
175 }
176
test_svstnt1_scatter_u64base_offset_s64(svbool_t pg,svuint64_t bases,int64_t offset,svint64_t data)177 void test_svstnt1_scatter_u64base_offset_s64(svbool_t pg, svuint64_t bases, int64_t offset, svint64_t data) {
178 // CHECK-LABEL: test_svstnt1_scatter_u64base_offset_s64
179 // CHECK: [[PG:%.*]] = call <vscale x 2 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv2i1(<vscale x 16 x i1> %pg)
180 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.scalar.offset.nxv2i64.nxv2i64(<vscale x 2 x i64> %data, <vscale x 2 x i1> [[PG]], <vscale x 2 x i64> %bases, i64 %offset)
181 // CHECK: ret void
182 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_offset'}}
183 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u64base_offset_s64'}}
184 return SVE_ACLE_FUNC(svstnt1_scatter, _u64base, _offset, _s64)(pg, bases, offset, data);
185 }
186
test_svstnt1_scatter_u32base_offset_u32(svbool_t pg,svuint32_t bases,int64_t offset,svuint32_t data)187 void test_svstnt1_scatter_u32base_offset_u32(svbool_t pg, svuint32_t bases, int64_t offset, svuint32_t data) {
188 // CHECK-LABEL: test_svstnt1_scatter_u32base_offset_u32
189 // CHECK: [[PG:%.*]] = call <vscale x 4 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv4i1(<vscale x 16 x i1> %pg)
190 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.scalar.offset.nxv4i32.nxv4i32(<vscale x 4 x i32> %data, <vscale x 4 x i1> [[PG]], <vscale x 4 x i32> %bases, i64 %offset)
191 // CHECK: ret void
192 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_offset'}}
193 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u32base_offset_u32'}}
194 return SVE_ACLE_FUNC(svstnt1_scatter, _u32base, _offset, _u32)(pg, bases, offset, data);
195 }
196
test_svstnt1_scatter_u64base_offset_u64(svbool_t pg,svuint64_t bases,int64_t offset,svuint64_t data)197 void test_svstnt1_scatter_u64base_offset_u64(svbool_t pg, svuint64_t bases, int64_t offset, svuint64_t data) {
198 // CHECK-LABEL: test_svstnt1_scatter_u64base_offset_u64
199 // CHECK: [[PG:%.*]] = call <vscale x 2 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv2i1(<vscale x 16 x i1> %pg)
200 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.scalar.offset.nxv2i64.nxv2i64(<vscale x 2 x i64> %data, <vscale x 2 x i1> [[PG]], <vscale x 2 x i64> %bases, i64 %offset)
201 // CHECK: ret void
202 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_offset'}}
203 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u64base_offset_u64'}}
204 return SVE_ACLE_FUNC(svstnt1_scatter, _u64base, _offset, _u64)(pg, bases, offset, data);
205 }
206
test_svstnt1_scatter_u32base_offset_f32(svbool_t pg,svuint32_t bases,int64_t offset,svfloat32_t data)207 void test_svstnt1_scatter_u32base_offset_f32(svbool_t pg, svuint32_t bases, int64_t offset, svfloat32_t data) {
208 // CHECK-LABEL: test_svstnt1_scatter_u32base_offset_f32
209 // CHECK: [[PG:%.*]] = call <vscale x 4 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv4i1(<vscale x 16 x i1> %pg)
210 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.scalar.offset.nxv4f32.nxv4i32(<vscale x 4 x float> %data, <vscale x 4 x i1> [[PG]], <vscale x 4 x i32> %bases, i64 %offset)
211 // CHECK: ret void
212 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_offset'}}
213 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u32base_offset_f32'}}
214 return SVE_ACLE_FUNC(svstnt1_scatter, _u32base, _offset, _f32)(pg, bases, offset, data);
215 }
216
test_svstnt1_scatter_u64base_offset_f64(svbool_t pg,svuint64_t bases,int64_t offset,svfloat64_t data)217 void test_svstnt1_scatter_u64base_offset_f64(svbool_t pg, svuint64_t bases, int64_t offset, svfloat64_t data) {
218 // CHECK-LABEL: test_svstnt1_scatter_u64base_offset_f64
219 // CHECK: [[PG:%.*]] = call <vscale x 2 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv2i1(<vscale x 16 x i1> %pg)
220 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.scalar.offset.nxv2f64.nxv2i64(<vscale x 2 x double> %data, <vscale x 2 x i1> [[PG]], <vscale x 2 x i64> %bases, i64 %offset)
221 // CHECK: ret void
222 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_offset'}}
223 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u64base_offset_f64'}}
224 return SVE_ACLE_FUNC(svstnt1_scatter, _u64base, _offset, _f64)(pg, bases, offset, data);
225 }
226
test_svstnt1_scatter_s64index_s64(svbool_t pg,int64_t * base,svint64_t indices,svint64_t data)227 void test_svstnt1_scatter_s64index_s64(svbool_t pg, int64_t *base, svint64_t indices, svint64_t data) {
228 // CHECK-LABEL: test_svstnt1_scatter_s64index_s64
229 // CHECK: [[PG:%.*]] = call <vscale x 2 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv2i1(<vscale x 16 x i1> %pg)
230 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.index.nxv2i64(<vscale x 2 x i64> %data, <vscale x 2 x i1> [[PG]], i64* %base, <vscale x 2 x i64> %indices)
231 // CHECK: ret void
232 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_index'}}
233 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_s64index_s64'}}
234 return SVE_ACLE_FUNC(svstnt1_scatter_, s64, index, _s64)(pg, base, indices, data);
235 }
236
test_svstnt1_scatter_s64index_u64(svbool_t pg,uint64_t * base,svint64_t indices,svuint64_t data)237 void test_svstnt1_scatter_s64index_u64(svbool_t pg, uint64_t *base, svint64_t indices, svuint64_t data) {
238 // CHECK-LABEL: test_svstnt1_scatter_s64index_u64
239 // CHECK: [[PG:%.*]] = call <vscale x 2 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv2i1(<vscale x 16 x i1> %pg)
240 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.index.nxv2i64(<vscale x 2 x i64> %data, <vscale x 2 x i1> [[PG]], i64* %base, <vscale x 2 x i64> %indices)
241 // CHECK: ret void
242 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_index'}}
243 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_s64index_u64'}}
244 return SVE_ACLE_FUNC(svstnt1_scatter_, s64, index, _u64)(pg, base, indices, data);
245 }
246
test_svstnt1_scatter_s64index_f64(svbool_t pg,float64_t * base,svint64_t indices,svfloat64_t data)247 void test_svstnt1_scatter_s64index_f64(svbool_t pg, float64_t *base, svint64_t indices, svfloat64_t data) {
248 // CHECK-LABEL: test_svstnt1_scatter_s64index_f64
249 // CHECK: [[PG:%.*]] = call <vscale x 2 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv2i1(<vscale x 16 x i1> %pg)
250 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.index.nxv2f64(<vscale x 2 x double> %data, <vscale x 2 x i1> [[PG]], double* %base, <vscale x 2 x i64> %indices)
251 // CHECK: ret void
252 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_index'}}
253 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_s64index_f64'}}
254 return SVE_ACLE_FUNC(svstnt1_scatter_, s64, index, _f64)(pg, base, indices, data);
255 }
256
test_svstnt1_scatter_u64index_s64(svbool_t pg,int64_t * base,svuint64_t indices,svint64_t data)257 void test_svstnt1_scatter_u64index_s64(svbool_t pg, int64_t *base, svuint64_t indices, svint64_t data) {
258 // CHECK-LABEL: test_svstnt1_scatter_u64index_s64
259 // CHECK: [[PG:%.*]] = call <vscale x 2 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv2i1(<vscale x 16 x i1> %pg)
260 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.index.nxv2i64(<vscale x 2 x i64> %data, <vscale x 2 x i1> [[PG]], i64* %base, <vscale x 2 x i64> %indices)
261 // CHECK: ret void
262 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_index'}}
263 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u64index_s64'}}
264 return SVE_ACLE_FUNC(svstnt1_scatter_, u64, index, _s64)(pg, base, indices, data);
265 }
266
test_svstnt1_scatter_u64index_u64(svbool_t pg,uint64_t * base,svuint64_t indices,svuint64_t data)267 void test_svstnt1_scatter_u64index_u64(svbool_t pg, uint64_t *base, svuint64_t indices, svuint64_t data) {
268 // CHECK-LABEL: test_svstnt1_scatter_u64index_u64
269 // CHECK: [[PG:%.*]] = call <vscale x 2 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv2i1(<vscale x 16 x i1> %pg)
270 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.index.nxv2i64(<vscale x 2 x i64> %data, <vscale x 2 x i1> [[PG]], i64* %base, <vscale x 2 x i64> %indices)
271 // CHECK: ret void
272 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_index'}}
273 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u64index_u64'}}
274 return SVE_ACLE_FUNC(svstnt1_scatter_, u64, index, _u64)(pg, base, indices, data);
275 }
276
test_svstnt1_scatter_u64index_f64(svbool_t pg,float64_t * base,svuint64_t indices,svfloat64_t data)277 void test_svstnt1_scatter_u64index_f64(svbool_t pg, float64_t *base, svuint64_t indices, svfloat64_t data) {
278 // CHECK-LABEL: test_svstnt1_scatter_u64index_f64
279 // CHECK: [[PG:%.*]] = call <vscale x 2 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv2i1(<vscale x 16 x i1> %pg)
280 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.index.nxv2f64(<vscale x 2 x double> %data, <vscale x 2 x i1> [[PG]], double* %base, <vscale x 2 x i64> %indices)
281 // CHECK: ret void
282 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_index'}}
283 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u64index_f64'}}
284 return SVE_ACLE_FUNC(svstnt1_scatter_, u64, index, _f64)(pg, base, indices, data);
285 }
286
test_svstnt1_scatter_u32base_index_s32(svbool_t pg,svuint32_t bases,int64_t index,svint32_t data)287 void test_svstnt1_scatter_u32base_index_s32(svbool_t pg, svuint32_t bases, int64_t index, svint32_t data) {
288 // CHECK-LABEL: test_svstnt1_scatter_u32base_index_s32
289 // CHECK-DAG: [[PG:%.*]] = call <vscale x 4 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv4i1(<vscale x 16 x i1> %pg)
290 // CHECK-DAG: [[SHL:%.*]] = shl i64 %index, 2
291 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.scalar.offset.nxv4i32.nxv4i32(<vscale x 4 x i32> %data, <vscale x 4 x i1> [[PG]], <vscale x 4 x i32> %bases, i64 [[SHL]])
292 // CHECK: ret void
293 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_index'}}
294 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u32base_index_s32'}}
295 return SVE_ACLE_FUNC(svstnt1_scatter, _u32base, _index, _s32)(pg, bases, index, data);
296 }
297
test_svstnt1_scatter_u64base_index_s64(svbool_t pg,svuint64_t bases,int64_t index,svint64_t data)298 void test_svstnt1_scatter_u64base_index_s64(svbool_t pg, svuint64_t bases, int64_t index, svint64_t data) {
299 // CHECK-LABEL: test_svstnt1_scatter_u64base_index_s64
300 // CHECK-DAG: [[PG:%.*]] = call <vscale x 2 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv2i1(<vscale x 16 x i1> %pg)
301 // CHECK-DAG: [[SHL:%.*]] = shl i64 %index, 3
302 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.scalar.offset.nxv2i64.nxv2i64(<vscale x 2 x i64> %data, <vscale x 2 x i1> [[PG]], <vscale x 2 x i64> %bases, i64 [[SHL]])
303 // CHECK: ret void
304 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_index'}}
305 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u64base_index_s64'}}
306 return SVE_ACLE_FUNC(svstnt1_scatter, _u64base, _index, _s64)(pg, bases, index, data);
307 }
308
test_svstnt1_scatter_u32base_index_u32(svbool_t pg,svuint32_t bases,int64_t index,svuint32_t data)309 void test_svstnt1_scatter_u32base_index_u32(svbool_t pg, svuint32_t bases, int64_t index, svuint32_t data) {
310 // CHECK-LABEL: test_svstnt1_scatter_u32base_index_u32
311 // CHECK-DAG: [[PG:%.*]] = call <vscale x 4 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv4i1(<vscale x 16 x i1> %pg)
312 // CHECK-DAG: [[SHL:%.*]] = shl i64 %index, 2
313 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.scalar.offset.nxv4i32.nxv4i32(<vscale x 4 x i32> %data, <vscale x 4 x i1> [[PG]], <vscale x 4 x i32> %bases, i64 [[SHL]])
314 // CHECK: ret void
315 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_index'}}
316 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u32base_index_u32'}}
317 return SVE_ACLE_FUNC(svstnt1_scatter, _u32base, _index, _u32)(pg, bases, index, data);
318 }
319
test_svstnt1_scatter_u64base_index_u64(svbool_t pg,svuint64_t bases,int64_t index,svuint64_t data)320 void test_svstnt1_scatter_u64base_index_u64(svbool_t pg, svuint64_t bases, int64_t index, svuint64_t data) {
321 // CHECK-LABEL: test_svstnt1_scatter_u64base_index_u64
322 // CHECK-DAG: [[PG:%.*]] = call <vscale x 2 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv2i1(<vscale x 16 x i1> %pg)
323 // CHECK-DAG: [[SHL:%.*]] = shl i64 %index, 3
324 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.scalar.offset.nxv2i64.nxv2i64(<vscale x 2 x i64> %data, <vscale x 2 x i1> [[PG]], <vscale x 2 x i64> %bases, i64 [[SHL]])
325 // CHECK: ret void
326 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_index'}}
327 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u64base_index_u64'}}
328 return SVE_ACLE_FUNC(svstnt1_scatter, _u64base, _index, _u64)(pg, bases, index, data);
329 }
330
test_svstnt1_scatter_u32base_index_f32(svbool_t pg,svuint32_t bases,int64_t index,svfloat32_t data)331 void test_svstnt1_scatter_u32base_index_f32(svbool_t pg, svuint32_t bases, int64_t index, svfloat32_t data) {
332 // CHECK-LABEL: test_svstnt1_scatter_u32base_index_f32
333 // CHECK-DAG: [[PG:%.*]] = call <vscale x 4 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv4i1(<vscale x 16 x i1> %pg)
334 // CHECK-DAG: [[SHL:%.*]] = shl i64 %index, 2
335 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.scalar.offset.nxv4f32.nxv4i32(<vscale x 4 x float> %data, <vscale x 4 x i1> [[PG]], <vscale x 4 x i32> %bases, i64 [[SHL]])
336 // CHECK: ret void
337 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_index'}}
338 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u32base_index_f32'}}
339 return SVE_ACLE_FUNC(svstnt1_scatter, _u32base, _index, _f32)(pg, bases, index, data);
340 }
341
test_svstnt1_scatter_u64base_index_f64(svbool_t pg,svuint64_t bases,int64_t index,svfloat64_t data)342 void test_svstnt1_scatter_u64base_index_f64(svbool_t pg, svuint64_t bases, int64_t index, svfloat64_t data) {
343 // CHECK-LABEL: test_svstnt1_scatter_u64base_index_f64
344 // CHECK-DAG: [[PG:%.*]] = call <vscale x 2 x i1> @llvm.aarch64.sve.convert.from.svbool.nxv2i1(<vscale x 16 x i1> %pg)
345 // CHECK-DAG: [[SHL:%.*]] = shl i64 %index, 3
346 // CHECK: call void @llvm.aarch64.sve.stnt1.scatter.scalar.offset.nxv2f64.nxv2i64(<vscale x 2 x double> %data, <vscale x 2 x i1> [[PG]], <vscale x 2 x i64> %bases, i64 [[SHL]])
347 // CHECK: ret void
348 // overload-warning@+2 {{implicit declaration of function 'svstnt1_scatter_index'}}
349 // expected-warning@+1 {{implicit declaration of function 'svstnt1_scatter_u64base_index_f64'}}
350 return SVE_ACLE_FUNC(svstnt1_scatter, _u64base, _index, _f64)(pg, bases, index, data);
351 }
352