1 // NOTE: Assertions have been autogenerated by utils/update_cc_test_checks.py
2 // 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
3 // 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 -check-prefix=CPP-CHECK
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 - %s | FileCheck %s
5 // 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 -check-prefix=CPP-CHECK
6 // RUN: %clang_cc1 -triple aarch64-none-linux-gnu -target-feature +sve -fallow-half-arguments-and-returns -fsyntax-only -verify -verify-ignore-unexpected=error %s
7 // 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
8
9 #include <arm_sve.h>
10
11 #ifdef SVE_OVERLOADED_FORMS
12 // A simple used,unused... macro, long enough to represent any SVE builtin.
13 #define SVE_ACLE_FUNC(A1,A2_UNUSED,A3,A4_UNUSED) A1##A3
14 #else
15 #define SVE_ACLE_FUNC(A1,A2,A3,A4) A1##A2##A3##A4
16 #endif
17
18 // CHECK-LABEL: @test_svtbx_s8(
19 // CHECK-NEXT: entry:
20 // CHECK-NEXT: [[TMP0:%.*]] = call <vscale x 16 x i8> @llvm.aarch64.sve.tbx.nxv16i8(<vscale x 16 x i8> [[FALLBACK:%.*]], <vscale x 16 x i8> [[DATA:%.*]], <vscale x 16 x i8> [[INDICES:%.*]])
21 // CHECK-NEXT: ret <vscale x 16 x i8> [[TMP0]]
22 //
23 // CPP-CHECK-LABEL: @_Z13test_svtbx_s8u10__SVInt8_tu10__SVInt8_tu11__SVUint8_t(
24 // CPP-CHECK-NEXT: entry:
25 // CPP-CHECK-NEXT: [[TMP0:%.*]] = call <vscale x 16 x i8> @llvm.aarch64.sve.tbx.nxv16i8(<vscale x 16 x i8> [[FALLBACK:%.*]], <vscale x 16 x i8> [[DATA:%.*]], <vscale x 16 x i8> [[INDICES:%.*]])
26 // CPP-CHECK-NEXT: ret <vscale x 16 x i8> [[TMP0]]
27 //
test_svtbx_s8(svint8_t fallback,svint8_t data,svuint8_t indices)28 svint8_t test_svtbx_s8(svint8_t fallback, svint8_t data, svuint8_t indices)
29 {
30 // overload-warning@+2 {{implicit declaration of function 'svtbx'}}
31 // expected-warning@+1 {{implicit declaration of function 'svtbx_s8'}}
32 return SVE_ACLE_FUNC(svtbx,_s8,,)(fallback, data, indices);
33 }
34
35 // CHECK-LABEL: @test_svtbx_s16(
36 // CHECK-NEXT: entry:
37 // CHECK-NEXT: [[TMP0:%.*]] = call <vscale x 8 x i16> @llvm.aarch64.sve.tbx.nxv8i16(<vscale x 8 x i16> [[FALLBACK:%.*]], <vscale x 8 x i16> [[DATA:%.*]], <vscale x 8 x i16> [[INDICES:%.*]])
38 // CHECK-NEXT: ret <vscale x 8 x i16> [[TMP0]]
39 //
40 // CPP-CHECK-LABEL: @_Z14test_svtbx_s16u11__SVInt16_tu11__SVInt16_tu12__SVUint16_t(
41 // CPP-CHECK-NEXT: entry:
42 // CPP-CHECK-NEXT: [[TMP0:%.*]] = call <vscale x 8 x i16> @llvm.aarch64.sve.tbx.nxv8i16(<vscale x 8 x i16> [[FALLBACK:%.*]], <vscale x 8 x i16> [[DATA:%.*]], <vscale x 8 x i16> [[INDICES:%.*]])
43 // CPP-CHECK-NEXT: ret <vscale x 8 x i16> [[TMP0]]
44 //
test_svtbx_s16(svint16_t fallback,svint16_t data,svuint16_t indices)45 svint16_t test_svtbx_s16(svint16_t fallback, svint16_t data, svuint16_t indices)
46 {
47 // overload-warning@+2 {{implicit declaration of function 'svtbx'}}
48 // expected-warning@+1 {{implicit declaration of function 'svtbx_s16'}}
49 return SVE_ACLE_FUNC(svtbx,_s16,,)(fallback, data, indices);
50 }
51
52 // CHECK-LABEL: @test_svtbx_s32(
53 // CHECK-NEXT: entry:
54 // CHECK-NEXT: [[TMP0:%.*]] = call <vscale x 4 x i32> @llvm.aarch64.sve.tbx.nxv4i32(<vscale x 4 x i32> [[FALLBACK:%.*]], <vscale x 4 x i32> [[DATA:%.*]], <vscale x 4 x i32> [[INDICES:%.*]])
55 // CHECK-NEXT: ret <vscale x 4 x i32> [[TMP0]]
56 //
57 // CPP-CHECK-LABEL: @_Z14test_svtbx_s32u11__SVInt32_tu11__SVInt32_tu12__SVUint32_t(
58 // CPP-CHECK-NEXT: entry:
59 // CPP-CHECK-NEXT: [[TMP0:%.*]] = call <vscale x 4 x i32> @llvm.aarch64.sve.tbx.nxv4i32(<vscale x 4 x i32> [[FALLBACK:%.*]], <vscale x 4 x i32> [[DATA:%.*]], <vscale x 4 x i32> [[INDICES:%.*]])
60 // CPP-CHECK-NEXT: ret <vscale x 4 x i32> [[TMP0]]
61 //
test_svtbx_s32(svint32_t fallback,svint32_t data,svuint32_t indices)62 svint32_t test_svtbx_s32(svint32_t fallback, svint32_t data, svuint32_t indices)
63 {
64 // overload-warning@+2 {{implicit declaration of function 'svtbx'}}
65 // expected-warning@+1 {{implicit declaration of function 'svtbx_s32'}}
66 return SVE_ACLE_FUNC(svtbx,_s32,,)(fallback, data, indices);
67 }
68
69 // CHECK-LABEL: @test_svtbx_s64(
70 // CHECK-NEXT: entry:
71 // CHECK-NEXT: [[TMP0:%.*]] = call <vscale x 2 x i64> @llvm.aarch64.sve.tbx.nxv2i64(<vscale x 2 x i64> [[FALLBACK:%.*]], <vscale x 2 x i64> [[DATA:%.*]], <vscale x 2 x i64> [[INDICES:%.*]])
72 // CHECK-NEXT: ret <vscale x 2 x i64> [[TMP0]]
73 //
74 // CPP-CHECK-LABEL: @_Z14test_svtbx_s64u11__SVInt64_tu11__SVInt64_tu12__SVUint64_t(
75 // CPP-CHECK-NEXT: entry:
76 // CPP-CHECK-NEXT: [[TMP0:%.*]] = call <vscale x 2 x i64> @llvm.aarch64.sve.tbx.nxv2i64(<vscale x 2 x i64> [[FALLBACK:%.*]], <vscale x 2 x i64> [[DATA:%.*]], <vscale x 2 x i64> [[INDICES:%.*]])
77 // CPP-CHECK-NEXT: ret <vscale x 2 x i64> [[TMP0]]
78 //
test_svtbx_s64(svint64_t fallback,svint64_t data,svuint64_t indices)79 svint64_t test_svtbx_s64(svint64_t fallback, svint64_t data, svuint64_t indices)
80 {
81 // overload-warning@+2 {{implicit declaration of function 'svtbx'}}
82 // expected-warning@+1 {{implicit declaration of function 'svtbx_s64'}}
83 return SVE_ACLE_FUNC(svtbx,_s64,,)(fallback, data, indices);
84 }
85
86 // CHECK-LABEL: @test_svtbx_u8(
87 // CHECK-NEXT: entry:
88 // CHECK-NEXT: [[TMP0:%.*]] = call <vscale x 16 x i8> @llvm.aarch64.sve.tbx.nxv16i8(<vscale x 16 x i8> [[FALLBACK:%.*]], <vscale x 16 x i8> [[DATA:%.*]], <vscale x 16 x i8> [[INDICES:%.*]])
89 // CHECK-NEXT: ret <vscale x 16 x i8> [[TMP0]]
90 //
91 // CPP-CHECK-LABEL: @_Z13test_svtbx_u8u11__SVUint8_tu11__SVUint8_tu11__SVUint8_t(
92 // CPP-CHECK-NEXT: entry:
93 // CPP-CHECK-NEXT: [[TMP0:%.*]] = call <vscale x 16 x i8> @llvm.aarch64.sve.tbx.nxv16i8(<vscale x 16 x i8> [[FALLBACK:%.*]], <vscale x 16 x i8> [[DATA:%.*]], <vscale x 16 x i8> [[INDICES:%.*]])
94 // CPP-CHECK-NEXT: ret <vscale x 16 x i8> [[TMP0]]
95 //
test_svtbx_u8(svuint8_t fallback,svuint8_t data,svuint8_t indices)96 svuint8_t test_svtbx_u8(svuint8_t fallback, svuint8_t data, svuint8_t indices)
97 {
98 // overload-warning@+2 {{implicit declaration of function 'svtbx'}}
99 // expected-warning@+1 {{implicit declaration of function 'svtbx_u8'}}
100 return SVE_ACLE_FUNC(svtbx,_u8,,)(fallback, data, indices);
101 }
102
103 // CHECK-LABEL: @test_svtbx_u16(
104 // CHECK-NEXT: entry:
105 // CHECK-NEXT: [[TMP0:%.*]] = call <vscale x 8 x i16> @llvm.aarch64.sve.tbx.nxv8i16(<vscale x 8 x i16> [[FALLBACK:%.*]], <vscale x 8 x i16> [[DATA:%.*]], <vscale x 8 x i16> [[INDICES:%.*]])
106 // CHECK-NEXT: ret <vscale x 8 x i16> [[TMP0]]
107 //
108 // CPP-CHECK-LABEL: @_Z14test_svtbx_u16u12__SVUint16_tu12__SVUint16_tu12__SVUint16_t(
109 // CPP-CHECK-NEXT: entry:
110 // CPP-CHECK-NEXT: [[TMP0:%.*]] = call <vscale x 8 x i16> @llvm.aarch64.sve.tbx.nxv8i16(<vscale x 8 x i16> [[FALLBACK:%.*]], <vscale x 8 x i16> [[DATA:%.*]], <vscale x 8 x i16> [[INDICES:%.*]])
111 // CPP-CHECK-NEXT: ret <vscale x 8 x i16> [[TMP0]]
112 //
test_svtbx_u16(svuint16_t fallback,svuint16_t data,svuint16_t indices)113 svuint16_t test_svtbx_u16(svuint16_t fallback, svuint16_t data, svuint16_t indices)
114 {
115 // overload-warning@+2 {{implicit declaration of function 'svtbx'}}
116 // expected-warning@+1 {{implicit declaration of function 'svtbx_u16'}}
117 return SVE_ACLE_FUNC(svtbx,_u16,,)(fallback, data, indices);
118 }
119
120 // CHECK-LABEL: @test_svtbx_u32(
121 // CHECK-NEXT: entry:
122 // CHECK-NEXT: [[TMP0:%.*]] = call <vscale x 4 x i32> @llvm.aarch64.sve.tbx.nxv4i32(<vscale x 4 x i32> [[FALLBACK:%.*]], <vscale x 4 x i32> [[DATA:%.*]], <vscale x 4 x i32> [[INDICES:%.*]])
123 // CHECK-NEXT: ret <vscale x 4 x i32> [[TMP0]]
124 //
125 // CPP-CHECK-LABEL: @_Z14test_svtbx_u32u12__SVUint32_tu12__SVUint32_tu12__SVUint32_t(
126 // CPP-CHECK-NEXT: entry:
127 // CPP-CHECK-NEXT: [[TMP0:%.*]] = call <vscale x 4 x i32> @llvm.aarch64.sve.tbx.nxv4i32(<vscale x 4 x i32> [[FALLBACK:%.*]], <vscale x 4 x i32> [[DATA:%.*]], <vscale x 4 x i32> [[INDICES:%.*]])
128 // CPP-CHECK-NEXT: ret <vscale x 4 x i32> [[TMP0]]
129 //
test_svtbx_u32(svuint32_t fallback,svuint32_t data,svuint32_t indices)130 svuint32_t test_svtbx_u32(svuint32_t fallback, svuint32_t data, svuint32_t indices)
131 {
132 // overload-warning@+2 {{implicit declaration of function 'svtbx'}}
133 // expected-warning@+1 {{implicit declaration of function 'svtbx_u32'}}
134 return SVE_ACLE_FUNC(svtbx,_u32,,)(fallback, data, indices);
135 }
136
137 // CHECK-LABEL: @test_svtbx_u64(
138 // CHECK-NEXT: entry:
139 // CHECK-NEXT: [[TMP0:%.*]] = call <vscale x 2 x i64> @llvm.aarch64.sve.tbx.nxv2i64(<vscale x 2 x i64> [[FALLBACK:%.*]], <vscale x 2 x i64> [[DATA:%.*]], <vscale x 2 x i64> [[INDICES:%.*]])
140 // CHECK-NEXT: ret <vscale x 2 x i64> [[TMP0]]
141 //
142 // CPP-CHECK-LABEL: @_Z14test_svtbx_u64u12__SVUint64_tu12__SVUint64_tu12__SVUint64_t(
143 // CPP-CHECK-NEXT: entry:
144 // CPP-CHECK-NEXT: [[TMP0:%.*]] = call <vscale x 2 x i64> @llvm.aarch64.sve.tbx.nxv2i64(<vscale x 2 x i64> [[FALLBACK:%.*]], <vscale x 2 x i64> [[DATA:%.*]], <vscale x 2 x i64> [[INDICES:%.*]])
145 // CPP-CHECK-NEXT: ret <vscale x 2 x i64> [[TMP0]]
146 //
test_svtbx_u64(svuint64_t fallback,svuint64_t data,svuint64_t indices)147 svuint64_t test_svtbx_u64(svuint64_t fallback, svuint64_t data, svuint64_t indices)
148 {
149 // overload-warning@+2 {{implicit declaration of function 'svtbx'}}
150 // expected-warning@+1 {{implicit declaration of function 'svtbx_u64'}}
151 return SVE_ACLE_FUNC(svtbx,_u64,,)(fallback, data, indices);
152 }
153
154 // CHECK-LABEL: @test_svtbx_f16(
155 // CHECK-NEXT: entry:
156 // CHECK-NEXT: [[TMP0:%.*]] = call <vscale x 8 x half> @llvm.aarch64.sve.tbx.nxv8f16(<vscale x 8 x half> [[FALLBACK:%.*]], <vscale x 8 x half> [[DATA:%.*]], <vscale x 8 x i16> [[INDICES:%.*]])
157 // CHECK-NEXT: ret <vscale x 8 x half> [[TMP0]]
158 //
159 // CPP-CHECK-LABEL: @_Z14test_svtbx_f16u13__SVFloat16_tu13__SVFloat16_tu12__SVUint16_t(
160 // CPP-CHECK-NEXT: entry:
161 // CPP-CHECK-NEXT: [[TMP0:%.*]] = call <vscale x 8 x half> @llvm.aarch64.sve.tbx.nxv8f16(<vscale x 8 x half> [[FALLBACK:%.*]], <vscale x 8 x half> [[DATA:%.*]], <vscale x 8 x i16> [[INDICES:%.*]])
162 // CPP-CHECK-NEXT: ret <vscale x 8 x half> [[TMP0]]
163 //
test_svtbx_f16(svfloat16_t fallback,svfloat16_t data,svuint16_t indices)164 svfloat16_t test_svtbx_f16(svfloat16_t fallback, svfloat16_t data, svuint16_t indices)
165 {
166 // overload-warning@+2 {{implicit declaration of function 'svtbx'}}
167 // expected-warning@+1 {{implicit declaration of function 'svtbx_f16'}}
168 return SVE_ACLE_FUNC(svtbx,_f16,,)(fallback, data, indices);
169 }
170
171 // CHECK-LABEL: @test_svtbx_f32(
172 // CHECK-NEXT: entry:
173 // CHECK-NEXT: [[TMP0:%.*]] = call <vscale x 4 x float> @llvm.aarch64.sve.tbx.nxv4f32(<vscale x 4 x float> [[FALLBACK:%.*]], <vscale x 4 x float> [[DATA:%.*]], <vscale x 4 x i32> [[INDICES:%.*]])
174 // CHECK-NEXT: ret <vscale x 4 x float> [[TMP0]]
175 //
176 // CPP-CHECK-LABEL: @_Z14test_svtbx_f32u13__SVFloat32_tu13__SVFloat32_tu12__SVUint32_t(
177 // CPP-CHECK-NEXT: entry:
178 // CPP-CHECK-NEXT: [[TMP0:%.*]] = call <vscale x 4 x float> @llvm.aarch64.sve.tbx.nxv4f32(<vscale x 4 x float> [[FALLBACK:%.*]], <vscale x 4 x float> [[DATA:%.*]], <vscale x 4 x i32> [[INDICES:%.*]])
179 // CPP-CHECK-NEXT: ret <vscale x 4 x float> [[TMP0]]
180 //
test_svtbx_f32(svfloat32_t fallback,svfloat32_t data,svuint32_t indices)181 svfloat32_t test_svtbx_f32(svfloat32_t fallback, svfloat32_t data, svuint32_t indices)
182 {
183 // overload-warning@+2 {{implicit declaration of function 'svtbx'}}
184 // expected-warning@+1 {{implicit declaration of function 'svtbx_f32'}}
185 return SVE_ACLE_FUNC(svtbx,_f32,,)(fallback, data, indices);
186 }
187
188 // CHECK-LABEL: @test_svtbx_f64(
189 // CHECK-NEXT: entry:
190 // CHECK-NEXT: [[TMP0:%.*]] = call <vscale x 2 x double> @llvm.aarch64.sve.tbx.nxv2f64(<vscale x 2 x double> [[FALLBACK:%.*]], <vscale x 2 x double> [[DATA:%.*]], <vscale x 2 x i64> [[INDICES:%.*]])
191 // CHECK-NEXT: ret <vscale x 2 x double> [[TMP0]]
192 //
193 // CPP-CHECK-LABEL: @_Z14test_svtbx_f64u13__SVFloat64_tu13__SVFloat64_tu12__SVUint64_t(
194 // CPP-CHECK-NEXT: entry:
195 // CPP-CHECK-NEXT: [[TMP0:%.*]] = call <vscale x 2 x double> @llvm.aarch64.sve.tbx.nxv2f64(<vscale x 2 x double> [[FALLBACK:%.*]], <vscale x 2 x double> [[DATA:%.*]], <vscale x 2 x i64> [[INDICES:%.*]])
196 // CPP-CHECK-NEXT: ret <vscale x 2 x double> [[TMP0]]
197 //
test_svtbx_f64(svfloat64_t fallback,svfloat64_t data,svuint64_t indices)198 svfloat64_t test_svtbx_f64(svfloat64_t fallback, svfloat64_t data, svuint64_t indices)
199 {
200 // overload-warning@+2 {{implicit declaration of function 'svtbx'}}
201 // expected-warning@+1 {{implicit declaration of function 'svtbx_f64'}}
202 return SVE_ACLE_FUNC(svtbx,_f64,,)(fallback, data, indices);
203 }
204