clang/test/CodeGen/aarch64-sve-intrinsics/acle_sve_reinterpret.c

   1 // NOTE: Assertions have been autogenerated by utils/update_cc_test_checks.py
   2 // REQUIRES: aarch64-registered-target
   3 // RUN: %clang_cc1 -triple aarch64-none-linux-gnu -target-feature +sve -S -disable-O0-optnone -Werror -Wall -emit-llvm -o - %s | opt -S -passes=mem2reg,tailcallelim | FileCheck %s
   4 // RUN: %clang_cc1 -triple aarch64-none-linux-gnu -target-feature +sve -S -disable-O0-optnone -Werror -Wall -emit-llvm -o - -x c++ %s | opt -S -passes=mem2reg,tailcallelim | FileCheck %s -check-prefix=CPP-CHECK
   5 // RUN: %clang_cc1 -DSVE_OVERLOADED_FORMS -triple aarch64-none-linux-gnu -target-feature +sve -S -disable-O0-optnone -Werror -Wall -emit-llvm -o - %s | opt -S -passes=mem2reg,tailcallelim | FileCheck %s
   6 // RUN: %clang_cc1 -DSVE_OVERLOADED_FORMS -triple aarch64-none-linux-gnu -target-feature +sve -S -disable-O0-optnone -Werror -Wall -emit-llvm -o - -x c++ %s | opt -S -passes=mem2reg,tailcallelim | FileCheck %s -check-prefix=CPP-CHECK
   7 // RUN: %clang_cc1 -triple aarch64-none-linux-gnu -target-feature +sve -S -disable-O0-optnone -Werror -Wall -o /dev/null %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_svreinterpret_s8_s8(
  19 // CHECK-NEXT:  entry:
  20 // CHECK-NEXT:    ret <vscale x 16 x i8> [[OP:%.*]]
  21 //
  22 // CPP-CHECK-LABEL: @_Z24test_svreinterpret_s8_s8u10__SVInt8_t(
  23 // CPP-CHECK-NEXT:  entry:
  24 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[OP:%.*]]
  25 //
  26 svint8_t test_svreinterpret_s8_s8(svint8_t op)
  27 {
  28   return SVE_ACLE_FUNC(svreinterpret_s8,_s8,,)(op);
  29 }
  30
  31 // CHECK-LABEL: @test_svreinterpret_s8_s16(
  32 // CHECK-NEXT:  entry:
  33 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 16 x i8>
  34 // CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
  35 //
  36 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_s8_s16u11__SVInt16_t(
  37 // CPP-CHECK-NEXT:  entry:
  38 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 16 x i8>
  39 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
  40 //
  41 svint8_t test_svreinterpret_s8_s16(svint16_t op)
  42 {
  43   return SVE_ACLE_FUNC(svreinterpret_s8,_s16,,)(op);
  44 }
  45
  46 // CHECK-LABEL: @test_svreinterpret_s8_s32(
  47 // CHECK-NEXT:  entry:
  48 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 16 x i8>
  49 // CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
  50 //
  51 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_s8_s32u11__SVInt32_t(
  52 // CPP-CHECK-NEXT:  entry:
  53 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 16 x i8>
  54 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
  55 //
  56 svint8_t test_svreinterpret_s8_s32(svint32_t op)
  57 {
  58   return SVE_ACLE_FUNC(svreinterpret_s8,_s32,,)(op);
  59 }
  60
  61 // CHECK-LABEL: @test_svreinterpret_s8_s64(
  62 // CHECK-NEXT:  entry:
  63 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 16 x i8>
  64 // CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
  65 //
  66 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_s8_s64u11__SVInt64_t(
  67 // CPP-CHECK-NEXT:  entry:
  68 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 16 x i8>
  69 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
  70 //
  71 svint8_t test_svreinterpret_s8_s64(svint64_t op)
  72 {
  73   return SVE_ACLE_FUNC(svreinterpret_s8,_s64,,)(op);
  74 }
  75
  76 // CHECK-LABEL: @test_svreinterpret_s8_u8(
  77 // CHECK-NEXT:  entry:
  78 // CHECK-NEXT:    ret <vscale x 16 x i8> [[OP:%.*]]
  79 //
  80 // CPP-CHECK-LABEL: @_Z24test_svreinterpret_s8_u8u11__SVUint8_t(
  81 // CPP-CHECK-NEXT:  entry:
  82 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[OP:%.*]]
  83 //
  84 svint8_t test_svreinterpret_s8_u8(svuint8_t op)
  85 {
  86   return SVE_ACLE_FUNC(svreinterpret_s8,_u8,,)(op);
  87 }
  88
  89 // CHECK-LABEL: @test_svreinterpret_s8_u16(
  90 // CHECK-NEXT:  entry:
  91 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 16 x i8>
  92 // CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
  93 //
  94 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_s8_u16u12__SVUint16_t(
  95 // CPP-CHECK-NEXT:  entry:
  96 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 16 x i8>
  97 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
  98 //
  99 svint8_t test_svreinterpret_s8_u16(svuint16_t op)
 100 {
 101   return SVE_ACLE_FUNC(svreinterpret_s8,_u16,,)(op);
 102 }
 103
 104 // CHECK-LABEL: @test_svreinterpret_s8_u32(
 105 // CHECK-NEXT:  entry:
 106 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 16 x i8>
 107 // CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 108 //
 109 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_s8_u32u12__SVUint32_t(
 110 // CPP-CHECK-NEXT:  entry:
 111 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 16 x i8>
 112 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 113 //
 114 svint8_t test_svreinterpret_s8_u32(svuint32_t op)
 115 {
 116   return SVE_ACLE_FUNC(svreinterpret_s8,_u32,,)(op);
 117 }
 118
 119 // CHECK-LABEL: @test_svreinterpret_s8_u64(
 120 // CHECK-NEXT:  entry:
 121 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 16 x i8>
 122 // CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 123 //
 124 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_s8_u64u12__SVUint64_t(
 125 // CPP-CHECK-NEXT:  entry:
 126 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 16 x i8>
 127 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 128 //
 129 svint8_t test_svreinterpret_s8_u64(svuint64_t op)
 130 {
 131   return SVE_ACLE_FUNC(svreinterpret_s8,_u64,,)(op);
 132 }
 133
 134 // CHECK-LABEL: @test_svreinterpret_s8_f16(
 135 // CHECK-NEXT:  entry:
 136 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x half> [[OP:%.*]] to <vscale x 16 x i8>
 137 // CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 138 //
 139 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_s8_f16u13__SVFloat16_t(
 140 // CPP-CHECK-NEXT:  entry:
 141 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x half> [[OP:%.*]] to <vscale x 16 x i8>
 142 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 143 //
 144 svint8_t test_svreinterpret_s8_f16(svfloat16_t op)
 145 {
 146   return SVE_ACLE_FUNC(svreinterpret_s8,_f16,,)(op);
 147 }
 148
 149 // CHECK-LABEL: @test_svreinterpret_s8_f32(
 150 // CHECK-NEXT:  entry:
 151 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x float> [[OP:%.*]] to <vscale x 16 x i8>
 152 // CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 153 //
 154 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_s8_f32u13__SVFloat32_t(
 155 // CPP-CHECK-NEXT:  entry:
 156 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x float> [[OP:%.*]] to <vscale x 16 x i8>
 157 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 158 //
 159 svint8_t test_svreinterpret_s8_f32(svfloat32_t op)
 160 {
 161   return SVE_ACLE_FUNC(svreinterpret_s8,_f32,,)(op);
 162 }
 163
 164 // CHECK-LABEL: @test_svreinterpret_s8_f64(
 165 // CHECK-NEXT:  entry:
 166 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x double> [[OP:%.*]] to <vscale x 16 x i8>
 167 // CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 168 //
 169 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_s8_f64u13__SVFloat64_t(
 170 // CPP-CHECK-NEXT:  entry:
 171 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x double> [[OP:%.*]] to <vscale x 16 x i8>
 172 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 173 //
 174 svint8_t test_svreinterpret_s8_f64(svfloat64_t op)
 175 {
 176   return SVE_ACLE_FUNC(svreinterpret_s8,_f64,,)(op);
 177 }
 178
 179 // CHECK-LABEL: @test_svreinterpret_s16_s8(
 180 // CHECK-NEXT:  entry:
 181 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 8 x i16>
 182 // CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 183 //
 184 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_s16_s8u10__SVInt8_t(
 185 // CPP-CHECK-NEXT:  entry:
 186 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 8 x i16>
 187 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 188 //
 189 svint16_t test_svreinterpret_s16_s8(svint8_t op)
 190 {
 191   return SVE_ACLE_FUNC(svreinterpret_s16,_s8,,)(op);
 192 }
 193
 194 // CHECK-LABEL: @test_svreinterpret_s16_s16(
 195 // CHECK-NEXT:  entry:
 196 // CHECK-NEXT:    ret <vscale x 8 x i16> [[OP:%.*]]
 197 //
 198 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s16_s16u11__SVInt16_t(
 199 // CPP-CHECK-NEXT:  entry:
 200 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[OP:%.*]]
 201 //
 202 svint16_t test_svreinterpret_s16_s16(svint16_t op)
 203 {
 204   return SVE_ACLE_FUNC(svreinterpret_s16,_s16,,)(op);
 205 }
 206
 207 // CHECK-LABEL: @test_svreinterpret_s16_s32(
 208 // CHECK-NEXT:  entry:
 209 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 8 x i16>
 210 // CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 211 //
 212 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s16_s32u11__SVInt32_t(
 213 // CPP-CHECK-NEXT:  entry:
 214 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 8 x i16>
 215 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 216 //
 217 svint16_t test_svreinterpret_s16_s32(svint32_t op)
 218 {
 219   return SVE_ACLE_FUNC(svreinterpret_s16,_s32,,)(op);
 220 }
 221
 222 // CHECK-LABEL: @test_svreinterpret_s16_s64(
 223 // CHECK-NEXT:  entry:
 224 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 8 x i16>
 225 // CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 226 //
 227 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s16_s64u11__SVInt64_t(
 228 // CPP-CHECK-NEXT:  entry:
 229 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 8 x i16>
 230 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 231 //
 232 svint16_t test_svreinterpret_s16_s64(svint64_t op)
 233 {
 234   return SVE_ACLE_FUNC(svreinterpret_s16,_s64,,)(op);
 235 }
 236
 237 // CHECK-LABEL: @test_svreinterpret_s16_u8(
 238 // CHECK-NEXT:  entry:
 239 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 8 x i16>
 240 // CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 241 //
 242 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_s16_u8u11__SVUint8_t(
 243 // CPP-CHECK-NEXT:  entry:
 244 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 8 x i16>
 245 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 246 //
 247 svint16_t test_svreinterpret_s16_u8(svuint8_t op)
 248 {
 249   return SVE_ACLE_FUNC(svreinterpret_s16,_u8,,)(op);
 250 }
 251
 252 // CHECK-LABEL: @test_svreinterpret_s16_u16(
 253 // CHECK-NEXT:  entry:
 254 // CHECK-NEXT:    ret <vscale x 8 x i16> [[OP:%.*]]
 255 //
 256 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s16_u16u12__SVUint16_t(
 257 // CPP-CHECK-NEXT:  entry:
 258 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[OP:%.*]]
 259 //
 260 svint16_t test_svreinterpret_s16_u16(svuint16_t op)
 261 {
 262   return SVE_ACLE_FUNC(svreinterpret_s16,_u16,,)(op);
 263 }
 264
 265 // CHECK-LABEL: @test_svreinterpret_s16_u32(
 266 // CHECK-NEXT:  entry:
 267 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 8 x i16>
 268 // CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 269 //
 270 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s16_u32u12__SVUint32_t(
 271 // CPP-CHECK-NEXT:  entry:
 272 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 8 x i16>
 273 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 274 //
 275 svint16_t test_svreinterpret_s16_u32(svuint32_t op)
 276 {
 277   return SVE_ACLE_FUNC(svreinterpret_s16,_u32,,)(op);
 278 }
 279
 280 // CHECK-LABEL: @test_svreinterpret_s16_u64(
 281 // CHECK-NEXT:  entry:
 282 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 8 x i16>
 283 // CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 284 //
 285 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s16_u64u12__SVUint64_t(
 286 // CPP-CHECK-NEXT:  entry:
 287 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 8 x i16>
 288 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 289 //
 290 svint16_t test_svreinterpret_s16_u64(svuint64_t op)
 291 {
 292   return SVE_ACLE_FUNC(svreinterpret_s16,_u64,,)(op);
 293 }
 294
 295 // CHECK-LABEL: @test_svreinterpret_s16_f16(
 296 // CHECK-NEXT:  entry:
 297 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x half> [[OP:%.*]] to <vscale x 8 x i16>
 298 // CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 299 //
 300 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s16_f16u13__SVFloat16_t(
 301 // CPP-CHECK-NEXT:  entry:
 302 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x half> [[OP:%.*]] to <vscale x 8 x i16>
 303 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 304 //
 305 svint16_t test_svreinterpret_s16_f16(svfloat16_t op)
 306 {
 307   return SVE_ACLE_FUNC(svreinterpret_s16,_f16,,)(op);
 308 }
 309
 310 // CHECK-LABEL: @test_svreinterpret_s16_f32(
 311 // CHECK-NEXT:  entry:
 312 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x float> [[OP:%.*]] to <vscale x 8 x i16>
 313 // CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 314 //
 315 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s16_f32u13__SVFloat32_t(
 316 // CPP-CHECK-NEXT:  entry:
 317 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x float> [[OP:%.*]] to <vscale x 8 x i16>
 318 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 319 //
 320 svint16_t test_svreinterpret_s16_f32(svfloat32_t op)
 321 {
 322   return SVE_ACLE_FUNC(svreinterpret_s16,_f32,,)(op);
 323 }
 324
 325 // CHECK-LABEL: @test_svreinterpret_s16_f64(
 326 // CHECK-NEXT:  entry:
 327 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x double> [[OP:%.*]] to <vscale x 8 x i16>
 328 // CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 329 //
 330 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s16_f64u13__SVFloat64_t(
 331 // CPP-CHECK-NEXT:  entry:
 332 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x double> [[OP:%.*]] to <vscale x 8 x i16>
 333 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 334 //
 335 svint16_t test_svreinterpret_s16_f64(svfloat64_t op)
 336 {
 337   return SVE_ACLE_FUNC(svreinterpret_s16,_f64,,)(op);
 338 }
 339
 340 // CHECK-LABEL: @test_svreinterpret_s32_s8(
 341 // CHECK-NEXT:  entry:
 342 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 4 x i32>
 343 // CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 344 //
 345 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_s32_s8u10__SVInt8_t(
 346 // CPP-CHECK-NEXT:  entry:
 347 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 4 x i32>
 348 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 349 //
 350 svint32_t test_svreinterpret_s32_s8(svint8_t op)
 351 {
 352   return SVE_ACLE_FUNC(svreinterpret_s32,_s8,,)(op);
 353 }
 354
 355 // CHECK-LABEL: @test_svreinterpret_s32_s16(
 356 // CHECK-NEXT:  entry:
 357 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 4 x i32>
 358 // CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 359 //
 360 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s32_s16u11__SVInt16_t(
 361 // CPP-CHECK-NEXT:  entry:
 362 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 4 x i32>
 363 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 364 //
 365 svint32_t test_svreinterpret_s32_s16(svint16_t op)
 366 {
 367   return SVE_ACLE_FUNC(svreinterpret_s32,_s16,,)(op);
 368 }
 369
 370 //
 371 // CHECK-LABEL: @test_svreinterpret_s32_s32(
 372 // CHECK-NEXT:  entry:
 373 // CHECK-NEXT:    ret <vscale x 4 x i32> [[OP:%.*]]
 374 //
 375 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s32_s32u11__SVInt32_t(
 376 // CPP-CHECK-NEXT:  entry:
 377 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[OP:%.*]]
 378 //
 379 svint32_t test_svreinterpret_s32_s32(svint32_t op)
 380 {
 381   return SVE_ACLE_FUNC(svreinterpret_s32,_s32,,)(op);
 382 }
 383
 384 // CHECK-LABEL: @test_svreinterpret_s32_s64(
 385 // CHECK-NEXT:  entry:
 386 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 4 x i32>
 387 // CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 388 //
 389 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s32_s64u11__SVInt64_t(
 390 // CPP-CHECK-NEXT:  entry:
 391 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 4 x i32>
 392 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 393 //
 394 svint32_t test_svreinterpret_s32_s64(svint64_t op)
 395 {
 396   return SVE_ACLE_FUNC(svreinterpret_s32,_s64,,)(op);
 397 }
 398
 399 // CHECK-LABEL: @test_svreinterpret_s32_u8(
 400 // CHECK-NEXT:  entry:
 401 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 4 x i32>
 402 // CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 403 //
 404 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_s32_u8u11__SVUint8_t(
 405 // CPP-CHECK-NEXT:  entry:
 406 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 4 x i32>
 407 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 408 //
 409 svint32_t test_svreinterpret_s32_u8(svuint8_t op)
 410 {
 411   return SVE_ACLE_FUNC(svreinterpret_s32,_u8,,)(op);
 412 }
 413
 414 // CHECK-LABEL: @test_svreinterpret_s32_u16(
 415 // CHECK-NEXT:  entry:
 416 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 4 x i32>
 417 // CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 418 //
 419 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s32_u16u12__SVUint16_t(
 420 // CPP-CHECK-NEXT:  entry:
 421 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 4 x i32>
 422 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 423 //
 424 svint32_t test_svreinterpret_s32_u16(svuint16_t op)
 425 {
 426   return SVE_ACLE_FUNC(svreinterpret_s32,_u16,,)(op);
 427 }
 428
 429 // CHECK-LABEL: @test_svreinterpret_s32_u32(
 430 // CHECK-NEXT:  entry:
 431 // CHECK-NEXT:    ret <vscale x 4 x i32> [[OP:%.*]]
 432 //
 433 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s32_u32u12__SVUint32_t(
 434 // CPP-CHECK-NEXT:  entry:
 435 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[OP:%.*]]
 436 //
 437 svint32_t test_svreinterpret_s32_u32(svuint32_t op)
 438 {
 439   return SVE_ACLE_FUNC(svreinterpret_s32,_u32,,)(op);
 440 }
 441
 442 // CHECK-LABEL: @test_svreinterpret_s32_u64(
 443 // CHECK-NEXT:  entry:
 444 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 4 x i32>
 445 // CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 446 //
 447 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s32_u64u12__SVUint64_t(
 448 // CPP-CHECK-NEXT:  entry:
 449 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 4 x i32>
 450 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 451 //
 452 svint32_t test_svreinterpret_s32_u64(svuint64_t op)
 453 {
 454   return SVE_ACLE_FUNC(svreinterpret_s32,_u64,,)(op);
 455 }
 456
 457 // CHECK-LABEL: @test_svreinterpret_s32_f16(
 458 // CHECK-NEXT:  entry:
 459 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x half> [[OP:%.*]] to <vscale x 4 x i32>
 460 // CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 461 //
 462 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s32_f16u13__SVFloat16_t(
 463 // CPP-CHECK-NEXT:  entry:
 464 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x half> [[OP:%.*]] to <vscale x 4 x i32>
 465 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 466 //
 467 svint32_t test_svreinterpret_s32_f16(svfloat16_t op)
 468 {
 469   return SVE_ACLE_FUNC(svreinterpret_s32,_f16,,)(op);
 470 }
 471
 472 // CHECK-LABEL: @test_svreinterpret_s32_f32(
 473 // CHECK-NEXT:  entry:
 474 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x float> [[OP:%.*]] to <vscale x 4 x i32>
 475 // CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 476 //
 477 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s32_f32u13__SVFloat32_t(
 478 // CPP-CHECK-NEXT:  entry:
 479 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x float> [[OP:%.*]] to <vscale x 4 x i32>
 480 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 481 //
 482 svint32_t test_svreinterpret_s32_f32(svfloat32_t op)
 483 {
 484   return SVE_ACLE_FUNC(svreinterpret_s32,_f32,,)(op);
 485 }
 486
 487 // CHECK-LABEL: @test_svreinterpret_s32_f64(
 488 // CHECK-NEXT:  entry:
 489 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x double> [[OP:%.*]] to <vscale x 4 x i32>
 490 // CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 491 //
 492 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s32_f64u13__SVFloat64_t(
 493 // CPP-CHECK-NEXT:  entry:
 494 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x double> [[OP:%.*]] to <vscale x 4 x i32>
 495 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 496 //
 497 svint32_t test_svreinterpret_s32_f64(svfloat64_t op)
 498 {
 499   return SVE_ACLE_FUNC(svreinterpret_s32,_f64,,)(op);
 500 }
 501
 502 // CHECK-LABEL: @test_svreinterpret_s64_s8(
 503 // CHECK-NEXT:  entry:
 504 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 2 x i64>
 505 // CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
 506 //
 507 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_s64_s8u10__SVInt8_t(
 508 // CPP-CHECK-NEXT:  entry:
 509 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 2 x i64>
 510 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
 511 //
 512 svint64_t test_svreinterpret_s64_s8(svint8_t op)
 513 {
 514   return SVE_ACLE_FUNC(svreinterpret_s64,_s8,,)(op);
 515 }
 516
 517 // CHECK-LABEL: @test_svreinterpret_s64_s16(
 518 // CHECK-NEXT:  entry:
 519 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 2 x i64>
 520 // CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
 521 //
 522 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s64_s16u11__SVInt16_t(
 523 // CPP-CHECK-NEXT:  entry:
 524 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 2 x i64>
 525 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
 526 //
 527 svint64_t test_svreinterpret_s64_s16(svint16_t op)
 528 {
 529   return SVE_ACLE_FUNC(svreinterpret_s64,_s16,,)(op);
 530 }
 531
 532 // CHECK-LABEL: @test_svreinterpret_s64_s32(
 533 // CHECK-NEXT:  entry:
 534 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 2 x i64>
 535 // CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
 536 //
 537 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s64_s32u11__SVInt32_t(
 538 // CPP-CHECK-NEXT:  entry:
 539 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 2 x i64>
 540 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
 541 //
 542 svint64_t test_svreinterpret_s64_s32(svint32_t op)
 543 {
 544   return SVE_ACLE_FUNC(svreinterpret_s64,_s32,,)(op);
 545 }
 546
 547 // CHECK-LABEL: @test_svreinterpret_s64_s64(
 548 // CHECK-NEXT:  entry:
 549 // CHECK-NEXT:    ret <vscale x 2 x i64> [[OP:%.*]]
 550 //
 551 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s64_s64u11__SVInt64_t(
 552 // CPP-CHECK-NEXT:  entry:
 553 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[OP:%.*]]
 554 //
 555 svint64_t test_svreinterpret_s64_s64(svint64_t op)
 556 {
 557   return SVE_ACLE_FUNC(svreinterpret_s64,_s64,,)(op);
 558 }
 559
 560 // CHECK-LABEL: @test_svreinterpret_s64_u8(
 561 // CHECK-NEXT:  entry:
 562 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 2 x i64>
 563 // CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
 564 //
 565 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_s64_u8u11__SVUint8_t(
 566 // CPP-CHECK-NEXT:  entry:
 567 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 2 x i64>
 568 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
 569 //
 570 svint64_t test_svreinterpret_s64_u8(svuint8_t op)
 571 {
 572   return SVE_ACLE_FUNC(svreinterpret_s64,_u8,,)(op);
 573 }
 574
 575 // CHECK-LABEL: @test_svreinterpret_s64_u16(
 576 // CHECK-NEXT:  entry:
 577 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 2 x i64>
 578 // CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
 579 //
 580 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s64_u16u12__SVUint16_t(
 581 // CPP-CHECK-NEXT:  entry:
 582 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 2 x i64>
 583 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
 584 //
 585 svint64_t test_svreinterpret_s64_u16(svuint16_t op)
 586 {
 587   return SVE_ACLE_FUNC(svreinterpret_s64,_u16,,)(op);
 588 }
 589
 590 // CHECK-LABEL: @test_svreinterpret_s64_u32(
 591 // CHECK-NEXT:  entry:
 592 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 2 x i64>
 593 // CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
 594 //
 595 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s64_u32u12__SVUint32_t(
 596 // CPP-CHECK-NEXT:  entry:
 597 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 2 x i64>
 598 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
 599 //
 600 svint64_t test_svreinterpret_s64_u32(svuint32_t op)
 601 {
 602   return SVE_ACLE_FUNC(svreinterpret_s64,_u32,,)(op);
 603 }
 604
 605 // CHECK-LABEL: @test_svreinterpret_s64_u64(
 606 // CHECK-NEXT:  entry:
 607 // CHECK-NEXT:    ret <vscale x 2 x i64> [[OP:%.*]]
 608 //
 609 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s64_u64u12__SVUint64_t(
 610 // CPP-CHECK-NEXT:  entry:
 611 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[OP:%.*]]
 612 //
 613 svint64_t test_svreinterpret_s64_u64(svuint64_t op)
 614 {
 615   return SVE_ACLE_FUNC(svreinterpret_s64,_u64,,)(op);
 616 }
 617
 618 // CHECK-LABEL: @test_svreinterpret_s64_f16(
 619 // CHECK-NEXT:  entry:
 620 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x half> [[OP:%.*]] to <vscale x 2 x i64>
 621 // CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
 622 //
 623 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s64_f16u13__SVFloat16_t(
 624 // CPP-CHECK-NEXT:  entry:
 625 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x half> [[OP:%.*]] to <vscale x 2 x i64>
 626 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
 627 //
 628 svint64_t test_svreinterpret_s64_f16(svfloat16_t op)
 629 {
 630   return SVE_ACLE_FUNC(svreinterpret_s64,_f16,,)(op);
 631 }
 632
 633 // CHECK-LABEL: @test_svreinterpret_s64_f32(
 634 // CHECK-NEXT:  entry:
 635 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x float> [[OP:%.*]] to <vscale x 2 x i64>
 636 // CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
 637 //
 638 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s64_f32u13__SVFloat32_t(
 639 // CPP-CHECK-NEXT:  entry:
 640 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x float> [[OP:%.*]] to <vscale x 2 x i64>
 641 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
 642 //
 643 svint64_t test_svreinterpret_s64_f32(svfloat32_t op)
 644 {
 645   return SVE_ACLE_FUNC(svreinterpret_s64,_f32,,)(op);
 646 }
 647
 648 // CHECK-LABEL: @test_svreinterpret_s64_f64(
 649 // CHECK-NEXT:  entry:
 650 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x double> [[OP:%.*]] to <vscale x 2 x i64>
 651 // CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
 652 //
 653 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s64_f64u13__SVFloat64_t(
 654 // CPP-CHECK-NEXT:  entry:
 655 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x double> [[OP:%.*]] to <vscale x 2 x i64>
 656 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
 657 //
 658 svint64_t test_svreinterpret_s64_f64(svfloat64_t op)
 659 {
 660   return SVE_ACLE_FUNC(svreinterpret_s64,_f64,,)(op);
 661 }
 662
 663 // CHECK-LABEL: @test_svreinterpret_u8_s8(
 664 // CHECK-NEXT:  entry:
 665 // CHECK-NEXT:    ret <vscale x 16 x i8> [[OP:%.*]]
 666 //
 667 // CPP-CHECK-LABEL: @_Z24test_svreinterpret_u8_s8u10__SVInt8_t(
 668 // CPP-CHECK-NEXT:  entry:
 669 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[OP:%.*]]
 670 //
 671 svuint8_t test_svreinterpret_u8_s8(svint8_t op)
 672 {
 673   return SVE_ACLE_FUNC(svreinterpret_u8,_s8,,)(op);
 674 }
 675
 676 // CHECK-LABEL: @test_svreinterpret_u8_s16(
 677 // CHECK-NEXT:  entry:
 678 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 16 x i8>
 679 // CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 680 //
 681 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_u8_s16u11__SVInt16_t(
 682 // CPP-CHECK-NEXT:  entry:
 683 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 16 x i8>
 684 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 685 //
 686 svuint8_t test_svreinterpret_u8_s16(svint16_t op)
 687 {
 688   return SVE_ACLE_FUNC(svreinterpret_u8,_s16,,)(op);
 689 }
 690
 691 // CHECK-LABEL: @test_svreinterpret_u8_s32(
 692 // CHECK-NEXT:  entry:
 693 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 16 x i8>
 694 // CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 695 //
 696 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_u8_s32u11__SVInt32_t(
 697 // CPP-CHECK-NEXT:  entry:
 698 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 16 x i8>
 699 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 700 //
 701 svuint8_t test_svreinterpret_u8_s32(svint32_t op)
 702 {
 703   return SVE_ACLE_FUNC(svreinterpret_u8,_s32,,)(op);
 704 }
 705
 706 // CHECK-LABEL: @test_svreinterpret_u8_s64(
 707 // CHECK-NEXT:  entry:
 708 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 16 x i8>
 709 // CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 710 //
 711 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_u8_s64u11__SVInt64_t(
 712 // CPP-CHECK-NEXT:  entry:
 713 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 16 x i8>
 714 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 715 //
 716 svuint8_t test_svreinterpret_u8_s64(svint64_t op)
 717 {
 718   return SVE_ACLE_FUNC(svreinterpret_u8,_s64,,)(op);
 719 }
 720
 721 // CHECK-LABEL: @test_svreinterpret_u8_u8(
 722 // CHECK-NEXT:  entry:
 723 // CHECK-NEXT:    ret <vscale x 16 x i8> [[OP:%.*]]
 724 //
 725 // CPP-CHECK-LABEL: @_Z24test_svreinterpret_u8_u8u11__SVUint8_t(
 726 // CPP-CHECK-NEXT:  entry:
 727 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[OP:%.*]]
 728 //
 729 svuint8_t test_svreinterpret_u8_u8(svuint8_t op)
 730 {
 731   return SVE_ACLE_FUNC(svreinterpret_u8,_u8,,)(op);
 732 }
 733
 734 // CHECK-LABEL: @test_svreinterpret_u8_u16(
 735 // CHECK-NEXT:  entry:
 736 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 16 x i8>
 737 // CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 738 //
 739 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_u8_u16u12__SVUint16_t(
 740 // CPP-CHECK-NEXT:  entry:
 741 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 16 x i8>
 742 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 743 //
 744 svuint8_t test_svreinterpret_u8_u16(svuint16_t op)
 745 {
 746   return SVE_ACLE_FUNC(svreinterpret_u8,_u16,,)(op);
 747 }
 748
 749 // CHECK-LABEL: @test_svreinterpret_u8_u32(
 750 // CHECK-NEXT:  entry:
 751 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 16 x i8>
 752 // CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 753 //
 754 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_u8_u32u12__SVUint32_t(
 755 // CPP-CHECK-NEXT:  entry:
 756 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 16 x i8>
 757 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 758 //
 759 svuint8_t test_svreinterpret_u8_u32(svuint32_t op)
 760 {
 761   return SVE_ACLE_FUNC(svreinterpret_u8,_u32,,)(op);
 762 }
 763
 764 // CHECK-LABEL: @test_svreinterpret_u8_u64(
 765 // CHECK-NEXT:  entry:
 766 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 16 x i8>
 767 // CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 768 //
 769 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_u8_u64u12__SVUint64_t(
 770 // CPP-CHECK-NEXT:  entry:
 771 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 16 x i8>
 772 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 773 //
 774 svuint8_t test_svreinterpret_u8_u64(svuint64_t op)
 775 {
 776   return SVE_ACLE_FUNC(svreinterpret_u8,_u64,,)(op);
 777 }
 778
 779 // CHECK-LABEL: @test_svreinterpret_u8_f16(
 780 // CHECK-NEXT:  entry:
 781 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x half> [[OP:%.*]] to <vscale x 16 x i8>
 782 // CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 783 //
 784 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_u8_f16u13__SVFloat16_t(
 785 // CPP-CHECK-NEXT:  entry:
 786 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x half> [[OP:%.*]] to <vscale x 16 x i8>
 787 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 788 //
 789 svuint8_t test_svreinterpret_u8_f16(svfloat16_t op)
 790 {
 791   return SVE_ACLE_FUNC(svreinterpret_u8,_f16,,)(op);
 792 }
 793
 794 // CHECK-LABEL: @test_svreinterpret_u8_f32(
 795 // CHECK-NEXT:  entry:
 796 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x float> [[OP:%.*]] to <vscale x 16 x i8>
 797 // CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 798 //
 799 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_u8_f32u13__SVFloat32_t(
 800 // CPP-CHECK-NEXT:  entry:
 801 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x float> [[OP:%.*]] to <vscale x 16 x i8>
 802 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 803 //
 804 svuint8_t test_svreinterpret_u8_f32(svfloat32_t op)
 805 {
 806   return SVE_ACLE_FUNC(svreinterpret_u8,_f32,,)(op);
 807 }
 808
 809 // CHECK-LABEL: @test_svreinterpret_u8_f64(
 810 // CHECK-NEXT:  entry:
 811 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x double> [[OP:%.*]] to <vscale x 16 x i8>
 812 // CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 813 //
 814 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_u8_f64u13__SVFloat64_t(
 815 // CPP-CHECK-NEXT:  entry:
 816 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x double> [[OP:%.*]] to <vscale x 16 x i8>
 817 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
 818 //
 819 svuint8_t test_svreinterpret_u8_f64(svfloat64_t op)
 820 {
 821   return SVE_ACLE_FUNC(svreinterpret_u8,_f64,,)(op);
 822 }
 823
 824 // CHECK-LABEL: @test_svreinterpret_u16_s8(
 825 // CHECK-NEXT:  entry:
 826 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 8 x i16>
 827 // CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 828 //
 829 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_u16_s8u10__SVInt8_t(
 830 // CPP-CHECK-NEXT:  entry:
 831 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 8 x i16>
 832 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 833 //
 834 svuint16_t test_svreinterpret_u16_s8(svint8_t op)
 835 {
 836   return SVE_ACLE_FUNC(svreinterpret_u16,_s8,,)(op);
 837 }
 838
 839 // CHECK-LABEL: @test_svreinterpret_u16_s16(
 840 // CHECK-NEXT:  entry:
 841 // CHECK-NEXT:    ret <vscale x 8 x i16> [[OP:%.*]]
 842 //
 843 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u16_s16u11__SVInt16_t(
 844 // CPP-CHECK-NEXT:  entry:
 845 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[OP:%.*]]
 846 //
 847 svuint16_t test_svreinterpret_u16_s16(svint16_t op)
 848 {
 849   return SVE_ACLE_FUNC(svreinterpret_u16,_s16,,)(op);
 850 }
 851
 852 // CHECK-LABEL: @test_svreinterpret_u16_s32(
 853 // CHECK-NEXT:  entry:
 854 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 8 x i16>
 855 // CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 856 //
 857 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u16_s32u11__SVInt32_t(
 858 // CPP-CHECK-NEXT:  entry:
 859 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 8 x i16>
 860 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 861 //
 862 svuint16_t test_svreinterpret_u16_s32(svint32_t op)
 863 {
 864   return SVE_ACLE_FUNC(svreinterpret_u16,_s32,,)(op);
 865 }
 866
 867 // CHECK-LABEL: @test_svreinterpret_u16_s64(
 868 // CHECK-NEXT:  entry:
 869 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 8 x i16>
 870 // CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 871 //
 872 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u16_s64u11__SVInt64_t(
 873 // CPP-CHECK-NEXT:  entry:
 874 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 8 x i16>
 875 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 876 //
 877 svuint16_t test_svreinterpret_u16_s64(svint64_t op)
 878 {
 879   return SVE_ACLE_FUNC(svreinterpret_u16,_s64,,)(op);
 880 }
 881
 882 // CHECK-LABEL: @test_svreinterpret_u16_u8(
 883 // CHECK-NEXT:  entry:
 884 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 8 x i16>
 885 // CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 886 //
 887 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_u16_u8u11__SVUint8_t(
 888 // CPP-CHECK-NEXT:  entry:
 889 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 8 x i16>
 890 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 891 //
 892 svuint16_t test_svreinterpret_u16_u8(svuint8_t op)
 893 {
 894   return SVE_ACLE_FUNC(svreinterpret_u16,_u8,,)(op);
 895 }
 896
 897 // CHECK-LABEL: @test_svreinterpret_u16_u16(
 898 // CHECK-NEXT:  entry:
 899 // CHECK-NEXT:    ret <vscale x 8 x i16> [[OP:%.*]]
 900 //
 901 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u16_u16u12__SVUint16_t(
 902 // CPP-CHECK-NEXT:  entry:
 903 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[OP:%.*]]
 904 //
 905 svuint16_t test_svreinterpret_u16_u16(svuint16_t op)
 906 {
 907   return SVE_ACLE_FUNC(svreinterpret_u16,_u16,,)(op);
 908 }
 909
 910 // CHECK-LABEL: @test_svreinterpret_u16_u32(
 911 // CHECK-NEXT:  entry:
 912 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 8 x i16>
 913 // CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 914 //
 915 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u16_u32u12__SVUint32_t(
 916 // CPP-CHECK-NEXT:  entry:
 917 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 8 x i16>
 918 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 919 //
 920 svuint16_t test_svreinterpret_u16_u32(svuint32_t op)
 921 {
 922   return SVE_ACLE_FUNC(svreinterpret_u16,_u32,,)(op);
 923 }
 924
 925 // CHECK-LABEL: @test_svreinterpret_u16_u64(
 926 // CHECK-NEXT:  entry:
 927 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 8 x i16>
 928 // CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 929 //
 930 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u16_u64u12__SVUint64_t(
 931 // CPP-CHECK-NEXT:  entry:
 932 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 8 x i16>
 933 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 934 //
 935 svuint16_t test_svreinterpret_u16_u64(svuint64_t op)
 936 {
 937   return SVE_ACLE_FUNC(svreinterpret_u16,_u64,,)(op);
 938 }
 939
 940 // CHECK-LABEL: @test_svreinterpret_u16_f16(
 941 // CHECK-NEXT:  entry:
 942 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x half> [[OP:%.*]] to <vscale x 8 x i16>
 943 // CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 944 //
 945 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u16_f16u13__SVFloat16_t(
 946 // CPP-CHECK-NEXT:  entry:
 947 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x half> [[OP:%.*]] to <vscale x 8 x i16>
 948 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 949 //
 950 svuint16_t test_svreinterpret_u16_f16(svfloat16_t op)
 951 {
 952   return SVE_ACLE_FUNC(svreinterpret_u16,_f16,,)(op);
 953 }
 954
 955 // CHECK-LABEL: @test_svreinterpret_u16_f32(
 956 // CHECK-NEXT:  entry:
 957 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x float> [[OP:%.*]] to <vscale x 8 x i16>
 958 // CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 959 //
 960 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u16_f32u13__SVFloat32_t(
 961 // CPP-CHECK-NEXT:  entry:
 962 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x float> [[OP:%.*]] to <vscale x 8 x i16>
 963 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 964 //
 965 svuint16_t test_svreinterpret_u16_f32(svfloat32_t op)
 966 {
 967   return SVE_ACLE_FUNC(svreinterpret_u16,_f32,,)(op);
 968 }
 969
 970 // CHECK-LABEL: @test_svreinterpret_u16_f64(
 971 // CHECK-NEXT:  entry:
 972 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x double> [[OP:%.*]] to <vscale x 8 x i16>
 973 // CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 974 //
 975 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u16_f64u13__SVFloat64_t(
 976 // CPP-CHECK-NEXT:  entry:
 977 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x double> [[OP:%.*]] to <vscale x 8 x i16>
 978 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 979 //
 980 svuint16_t test_svreinterpret_u16_f64(svfloat64_t op)
 981 {
 982   return SVE_ACLE_FUNC(svreinterpret_u16,_f64,,)(op);
 983 }
 984
 985 // CHECK-LABEL: @test_svreinterpret_u32_s8(
 986 // CHECK-NEXT:  entry:
 987 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 4 x i32>
 988 // CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 989 //
 990 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_u32_s8u10__SVInt8_t(
 991 // CPP-CHECK-NEXT:  entry:
 992 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 4 x i32>
 993 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 994 //
 995 svuint32_t test_svreinterpret_u32_s8(svint8_t op)
 996 {
 997   return SVE_ACLE_FUNC(svreinterpret_u32,_s8,,)(op);
 998 }
 999
1000 // CHECK-LABEL: @test_svreinterpret_u32_s16(
1001 // CHECK-NEXT:  entry:
1002 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 4 x i32>
1003 // CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
1004 //
1005 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u32_s16u11__SVInt16_t(
1006 // CPP-CHECK-NEXT:  entry:
1007 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 4 x i32>
1008 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
1009 //
1010 svuint32_t test_svreinterpret_u32_s16(svint16_t op)
1011 {
1012   return SVE_ACLE_FUNC(svreinterpret_u32,_s16,,)(op);
1013 }
1014
1015 // CHECK-LABEL: @test_svreinterpret_u32_s32(
1016 // CHECK-NEXT:  entry:
1017 // CHECK-NEXT:    ret <vscale x 4 x i32> [[OP:%.*]]
1018 //
1019 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u32_s32u11__SVInt32_t(
1020 // CPP-CHECK-NEXT:  entry:
1021 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[OP:%.*]]
1022 //
1023 svuint32_t test_svreinterpret_u32_s32(svint32_t op)
1024 {
1025   return SVE_ACLE_FUNC(svreinterpret_u32,_s32,,)(op);
1026 }
1027
1028 // CHECK-LABEL: @test_svreinterpret_u32_s64(
1029 // CHECK-NEXT:  entry:
1030 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 4 x i32>
1031 // CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
1032 //
1033 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u32_s64u11__SVInt64_t(
1034 // CPP-CHECK-NEXT:  entry:
1035 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 4 x i32>
1036 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
1037 //
1038 svuint32_t test_svreinterpret_u32_s64(svint64_t op)
1039 {
1040   return SVE_ACLE_FUNC(svreinterpret_u32,_s64,,)(op);
1041 }
1042
1043 // CHECK-LABEL: @test_svreinterpret_u32_u8(
1044 // CHECK-NEXT:  entry:
1045 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 4 x i32>
1046 // CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
1047 //
1048 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_u32_u8u11__SVUint8_t(
1049 // CPP-CHECK-NEXT:  entry:
1050 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 4 x i32>
1051 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
1052 //
1053 svuint32_t test_svreinterpret_u32_u8(svuint8_t op)
1054 {
1055   return SVE_ACLE_FUNC(svreinterpret_u32,_u8,,)(op);
1056 }
1057
1058 // CHECK-LABEL: @test_svreinterpret_u32_u16(
1059 // CHECK-NEXT:  entry:
1060 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 4 x i32>
1061 // CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
1062 //
1063 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u32_u16u12__SVUint16_t(
1064 // CPP-CHECK-NEXT:  entry:
1065 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 4 x i32>
1066 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
1067 //
1068 svuint32_t test_svreinterpret_u32_u16(svuint16_t op)
1069 {
1070   return SVE_ACLE_FUNC(svreinterpret_u32,_u16,,)(op);
1071 }
1072
1073 // CHECK-LABEL: @test_svreinterpret_u32_u32(
1074 // CHECK-NEXT:  entry:
1075 // CHECK-NEXT:    ret <vscale x 4 x i32> [[OP:%.*]]
1076 //
1077 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u32_u32u12__SVUint32_t(
1078 // CPP-CHECK-NEXT:  entry:
1079 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[OP:%.*]]
1080 //
1081 svuint32_t test_svreinterpret_u32_u32(svuint32_t op)
1082 {
1083   return SVE_ACLE_FUNC(svreinterpret_u32,_u32,,)(op);
1084 }
1085
1086 // CHECK-LABEL: @test_svreinterpret_u32_u64(
1087 // CHECK-NEXT:  entry:
1088 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 4 x i32>
1089 // CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
1090 //
1091 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u32_u64u12__SVUint64_t(
1092 // CPP-CHECK-NEXT:  entry:
1093 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 4 x i32>
1094 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
1095 //
1096 svuint32_t test_svreinterpret_u32_u64(svuint64_t op)
1097 {
1098   return SVE_ACLE_FUNC(svreinterpret_u32,_u64,,)(op);
1099 }
1100
1101 // CHECK-LABEL: @test_svreinterpret_u32_f16(
1102 // CHECK-NEXT:  entry:
1103 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x half> [[OP:%.*]] to <vscale x 4 x i32>
1104 // CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
1105 //
1106 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u32_f16u13__SVFloat16_t(
1107 // CPP-CHECK-NEXT:  entry:
1108 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x half> [[OP:%.*]] to <vscale x 4 x i32>
1109 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
1110 //
1111 svuint32_t test_svreinterpret_u32_f16(svfloat16_t op)
1112 {
1113   return SVE_ACLE_FUNC(svreinterpret_u32,_f16,,)(op);
1114 }
1115
1116 // CHECK-LABEL: @test_svreinterpret_u32_f32(
1117 // CHECK-NEXT:  entry:
1118 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x float> [[OP:%.*]] to <vscale x 4 x i32>
1119 // CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
1120 //
1121 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u32_f32u13__SVFloat32_t(
1122 // CPP-CHECK-NEXT:  entry:
1123 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x float> [[OP:%.*]] to <vscale x 4 x i32>
1124 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
1125 //
1126 svuint32_t test_svreinterpret_u32_f32(svfloat32_t op)
1127 {
1128   return SVE_ACLE_FUNC(svreinterpret_u32,_f32,,)(op);
1129 }
1130
1131 // CHECK-LABEL: @test_svreinterpret_u32_f64(
1132 // CHECK-NEXT:  entry:
1133 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x double> [[OP:%.*]] to <vscale x 4 x i32>
1134 // CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
1135 //
1136 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u32_f64u13__SVFloat64_t(
1137 // CPP-CHECK-NEXT:  entry:
1138 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x double> [[OP:%.*]] to <vscale x 4 x i32>
1139 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
1140 //
1141 svuint32_t test_svreinterpret_u32_f64(svfloat64_t op)
1142 {
1143   return SVE_ACLE_FUNC(svreinterpret_u32,_f64,,)(op);
1144 }
1145
1146 // CHECK-LABEL: @test_svreinterpret_u64_s8(
1147 // CHECK-NEXT:  entry:
1148 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 2 x i64>
1149 // CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
1150 //
1151 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_u64_s8u10__SVInt8_t(
1152 // CPP-CHECK-NEXT:  entry:
1153 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 2 x i64>
1154 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
1155 //
1156 svuint64_t test_svreinterpret_u64_s8(svint8_t op)
1157 {
1158   return SVE_ACLE_FUNC(svreinterpret_u64,_s8,,)(op);
1159 }
1160
1161 // CHECK-LABEL: @test_svreinterpret_u64_s16(
1162 // CHECK-NEXT:  entry:
1163 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 2 x i64>
1164 // CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
1165 //
1166 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u64_s16u11__SVInt16_t(
1167 // CPP-CHECK-NEXT:  entry:
1168 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 2 x i64>
1169 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
1170 //
1171 svuint64_t test_svreinterpret_u64_s16(svint16_t op)
1172 {
1173   return SVE_ACLE_FUNC(svreinterpret_u64,_s16,,)(op);
1174 }
1175
1176 // CHECK-LABEL: @test_svreinterpret_u64_s32(
1177 // CHECK-NEXT:  entry:
1178 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 2 x i64>
1179 // CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
1180 //
1181 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u64_s32u11__SVInt32_t(
1182 // CPP-CHECK-NEXT:  entry:
1183 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 2 x i64>
1184 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
1185 //
1186 svuint64_t test_svreinterpret_u64_s32(svint32_t op)
1187 {
1188   return SVE_ACLE_FUNC(svreinterpret_u64,_s32,,)(op);
1189 }
1190
1191 // CHECK-LABEL: @test_svreinterpret_u64_s64(
1192 // CHECK-NEXT:  entry:
1193 // CHECK-NEXT:    ret <vscale x 2 x i64> [[OP:%.*]]
1194 //
1195 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u64_s64u11__SVInt64_t(
1196 // CPP-CHECK-NEXT:  entry:
1197 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[OP:%.*]]
1198 //
1199 svuint64_t test_svreinterpret_u64_s64(svint64_t op)
1200 {
1201   return SVE_ACLE_FUNC(svreinterpret_u64,_s64,,)(op);
1202 }
1203
1204 // CHECK-LABEL: @test_svreinterpret_u64_u8(
1205 // CHECK-NEXT:  entry:
1206 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 2 x i64>
1207 // CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
1208 //
1209 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_u64_u8u11__SVUint8_t(
1210 // CPP-CHECK-NEXT:  entry:
1211 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 2 x i64>
1212 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
1213 //
1214 svuint64_t test_svreinterpret_u64_u8(svuint8_t op)
1215 {
1216   return SVE_ACLE_FUNC(svreinterpret_u64,_u8,,)(op);
1217 }
1218
1219 // CHECK-LABEL: @test_svreinterpret_u64_u16(
1220 // CHECK-NEXT:  entry:
1221 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 2 x i64>
1222 // CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
1223 //
1224 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u64_u16u12__SVUint16_t(
1225 // CPP-CHECK-NEXT:  entry:
1226 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 2 x i64>
1227 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
1228 //
1229 svuint64_t test_svreinterpret_u64_u16(svuint16_t op)
1230 {
1231   return SVE_ACLE_FUNC(svreinterpret_u64,_u16,,)(op);
1232 }
1233
1234 // CHECK-LABEL: @test_svreinterpret_u64_u32(
1235 // CHECK-NEXT:  entry:
1236 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 2 x i64>
1237 // CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
1238 //
1239 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u64_u32u12__SVUint32_t(
1240 // CPP-CHECK-NEXT:  entry:
1241 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 2 x i64>
1242 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
1243 //
1244 svuint64_t test_svreinterpret_u64_u32(svuint32_t op)
1245 {
1246   return SVE_ACLE_FUNC(svreinterpret_u64,_u32,,)(op);
1247 }
1248
1249 // CHECK-LABEL: @test_svreinterpret_u64_u64(
1250 // CHECK-NEXT:  entry:
1251 // CHECK-NEXT:    ret <vscale x 2 x i64> [[OP:%.*]]
1252 //
1253 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u64_u64u12__SVUint64_t(
1254 // CPP-CHECK-NEXT:  entry:
1255 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[OP:%.*]]
1256 //
1257 svuint64_t test_svreinterpret_u64_u64(svuint64_t op)
1258 {
1259   return SVE_ACLE_FUNC(svreinterpret_u64,_u64,,)(op);
1260 }
1261
1262 // CHECK-LABEL: @test_svreinterpret_u64_f16(
1263 // CHECK-NEXT:  entry:
1264 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x half> [[OP:%.*]] to <vscale x 2 x i64>
1265 // CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
1266 //
1267 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u64_f16u13__SVFloat16_t(
1268 // CPP-CHECK-NEXT:  entry:
1269 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x half> [[OP:%.*]] to <vscale x 2 x i64>
1270 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
1271 //
1272 svuint64_t test_svreinterpret_u64_f16(svfloat16_t op)
1273 {
1274   return SVE_ACLE_FUNC(svreinterpret_u64,_f16,,)(op);
1275 }
1276
1277 // CHECK-LABEL: @test_svreinterpret_u64_f32(
1278 // CHECK-NEXT:  entry:
1279 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x float> [[OP:%.*]] to <vscale x 2 x i64>
1280 // CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
1281 //
1282 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u64_f32u13__SVFloat32_t(
1283 // CPP-CHECK-NEXT:  entry:
1284 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x float> [[OP:%.*]] to <vscale x 2 x i64>
1285 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
1286 //
1287 svuint64_t test_svreinterpret_u64_f32(svfloat32_t op)
1288 {
1289   return SVE_ACLE_FUNC(svreinterpret_u64,_f32,,)(op);
1290 }
1291
1292 // CHECK-LABEL: @test_svreinterpret_u64_f64(
1293 // CHECK-NEXT:  entry:
1294 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x double> [[OP:%.*]] to <vscale x 2 x i64>
1295 // CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
1296 //
1297 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u64_f64u13__SVFloat64_t(
1298 // CPP-CHECK-NEXT:  entry:
1299 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x double> [[OP:%.*]] to <vscale x 2 x i64>
1300 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
1301 //
1302 svuint64_t test_svreinterpret_u64_f64(svfloat64_t op)
1303 {
1304   return SVE_ACLE_FUNC(svreinterpret_u64,_f64,,)(op);
1305 }
1306
1307 // CHECK-LABEL: @test_svreinterpret_f16_s8(
1308 // CHECK-NEXT:  entry:
1309 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 8 x half>
1310 // CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
1311 //
1312 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_f16_s8u10__SVInt8_t(
1313 // CPP-CHECK-NEXT:  entry:
1314 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 8 x half>
1315 // CPP-CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
1316 //
1317 svfloat16_t test_svreinterpret_f16_s8(svint8_t op)
1318 {
1319   return SVE_ACLE_FUNC(svreinterpret_f16,_s8,,)(op);
1320 }
1321
1322 // CHECK-LABEL: @test_svreinterpret_f16_s16(
1323 // CHECK-NEXT:  entry:
1324 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 8 x half>
1325 // CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
1326 //
1327 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f16_s16u11__SVInt16_t(
1328 // CPP-CHECK-NEXT:  entry:
1329 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 8 x half>
1330 // CPP-CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
1331 //
1332 svfloat16_t test_svreinterpret_f16_s16(svint16_t op)
1333 {
1334   return SVE_ACLE_FUNC(svreinterpret_f16,_s16,,)(op);
1335 }
1336
1337 // CHECK-LABEL: @test_svreinterpret_f16_s32(
1338 // CHECK-NEXT:  entry:
1339 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 8 x half>
1340 // CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
1341 //
1342 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f16_s32u11__SVInt32_t(
1343 // CPP-CHECK-NEXT:  entry:
1344 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 8 x half>
1345 // CPP-CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
1346 //
1347 svfloat16_t test_svreinterpret_f16_s32(svint32_t op)
1348 {
1349   return SVE_ACLE_FUNC(svreinterpret_f16,_s32,,)(op);
1350 }
1351
1352 // CHECK-LABEL: @test_svreinterpret_f16_s64(
1353 // CHECK-NEXT:  entry:
1354 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 8 x half>
1355 // CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
1356 //
1357 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f16_s64u11__SVInt64_t(
1358 // CPP-CHECK-NEXT:  entry:
1359 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 8 x half>
1360 // CPP-CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
1361 //
1362 svfloat16_t test_svreinterpret_f16_s64(svint64_t op)
1363 {
1364   return SVE_ACLE_FUNC(svreinterpret_f16,_s64,,)(op);
1365 }
1366
1367 // CHECK-LABEL: @test_svreinterpret_f16_u8(
1368 // CHECK-NEXT:  entry:
1369 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 8 x half>
1370 // CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
1371 //
1372 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_f16_u8u11__SVUint8_t(
1373 // CPP-CHECK-NEXT:  entry:
1374 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 8 x half>
1375 // CPP-CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
1376 //
1377 svfloat16_t test_svreinterpret_f16_u8(svuint8_t op)
1378 {
1379   return SVE_ACLE_FUNC(svreinterpret_f16,_u8,,)(op);
1380 }
1381
1382 // CHECK-LABEL: @test_svreinterpret_f16_u16(
1383 // CHECK-NEXT:  entry:
1384 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 8 x half>
1385 // CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
1386 //
1387 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f16_u16u12__SVUint16_t(
1388 // CPP-CHECK-NEXT:  entry:
1389 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 8 x half>
1390 // CPP-CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
1391 //
1392 svfloat16_t test_svreinterpret_f16_u16(svuint16_t op)
1393 {
1394   return SVE_ACLE_FUNC(svreinterpret_f16,_u16,,)(op);
1395 }
1396
1397 // CHECK-LABEL: @test_svreinterpret_f16_u32(
1398 // CHECK-NEXT:  entry:
1399 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 8 x half>
1400 // CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
1401 //
1402 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f16_u32u12__SVUint32_t(
1403 // CPP-CHECK-NEXT:  entry:
1404 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 8 x half>
1405 // CPP-CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
1406 //
1407 svfloat16_t test_svreinterpret_f16_u32(svuint32_t op)
1408 {
1409   return SVE_ACLE_FUNC(svreinterpret_f16,_u32,,)(op);
1410 }
1411
1412 // CHECK-LABEL: @test_svreinterpret_f16_u64(
1413 // CHECK-NEXT:  entry:
1414 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 8 x half>
1415 // CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
1416 //
1417 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f16_u64u12__SVUint64_t(
1418 // CPP-CHECK-NEXT:  entry:
1419 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 8 x half>
1420 // CPP-CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
1421 //
1422 svfloat16_t test_svreinterpret_f16_u64(svuint64_t op)
1423 {
1424   return SVE_ACLE_FUNC(svreinterpret_f16,_u64,,)(op);
1425 }
1426
1427 // CHECK-LABEL: @test_svreinterpret_f16_f16(
1428 // CHECK-NEXT:  entry:
1429 // CHECK-NEXT:    ret <vscale x 8 x half> [[OP:%.*]]
1430 //
1431 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f16_f16u13__SVFloat16_t(
1432 // CPP-CHECK-NEXT:  entry:
1433 // CPP-CHECK-NEXT:    ret <vscale x 8 x half> [[OP:%.*]]
1434 //
1435 svfloat16_t test_svreinterpret_f16_f16(svfloat16_t op)
1436 {
1437   return SVE_ACLE_FUNC(svreinterpret_f16,_f16,,)(op);
1438 }
1439
1440 // CHECK-LABEL: @test_svreinterpret_f16_f32(
1441 // CHECK-NEXT:  entry:
1442 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x float> [[OP:%.*]] to <vscale x 8 x half>
1443 // CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
1444 //
1445 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f16_f32u13__SVFloat32_t(
1446 // CPP-CHECK-NEXT:  entry:
1447 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x float> [[OP:%.*]] to <vscale x 8 x half>
1448 // CPP-CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
1449 //
1450 svfloat16_t test_svreinterpret_f16_f32(svfloat32_t op)
1451 {
1452   return SVE_ACLE_FUNC(svreinterpret_f16,_f32,,)(op);
1453 }
1454
1455 // CHECK-LABEL: @test_svreinterpret_f16_f64(
1456 // CHECK-NEXT:  entry:
1457 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x double> [[OP:%.*]] to <vscale x 8 x half>
1458 // CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
1459 //
1460 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f16_f64u13__SVFloat64_t(
1461 // CPP-CHECK-NEXT:  entry:
1462 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x double> [[OP:%.*]] to <vscale x 8 x half>
1463 // CPP-CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
1464 //
1465 svfloat16_t test_svreinterpret_f16_f64(svfloat64_t op)
1466 {
1467   return SVE_ACLE_FUNC(svreinterpret_f16,_f64,,)(op);
1468 }
1469
1470 // CHECK-LABEL: @test_svreinterpret_f32_s8(
1471 // CHECK-NEXT:  entry:
1472 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 4 x float>
1473 // CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
1474 //
1475 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_f32_s8u10__SVInt8_t(
1476 // CPP-CHECK-NEXT:  entry:
1477 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 4 x float>
1478 // CPP-CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
1479 //
1480 svfloat32_t test_svreinterpret_f32_s8(svint8_t op)
1481 {
1482   return SVE_ACLE_FUNC(svreinterpret_f32,_s8,,)(op);
1483 }
1484
1485 // CHECK-LABEL: @test_svreinterpret_f32_s16(
1486 // CHECK-NEXT:  entry:
1487 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 4 x float>
1488 // CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
1489 //
1490 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f32_s16u11__SVInt16_t(
1491 // CPP-CHECK-NEXT:  entry:
1492 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 4 x float>
1493 // CPP-CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
1494 //
1495 svfloat32_t test_svreinterpret_f32_s16(svint16_t op)
1496 {
1497   return SVE_ACLE_FUNC(svreinterpret_f32,_s16,,)(op);
1498 }
1499
1500 // CHECK-LABEL: @test_svreinterpret_f32_s32(
1501 // CHECK-NEXT:  entry:
1502 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 4 x float>
1503 // CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
1504 //
1505 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f32_s32u11__SVInt32_t(
1506 // CPP-CHECK-NEXT:  entry:
1507 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 4 x float>
1508 // CPP-CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
1509 //
1510 svfloat32_t test_svreinterpret_f32_s32(svint32_t op)
1511 {
1512   return SVE_ACLE_FUNC(svreinterpret_f32,_s32,,)(op);
1513 }
1514
1515 // CHECK-LABEL: @test_svreinterpret_f32_s64(
1516 // CHECK-NEXT:  entry:
1517 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 4 x float>
1518 // CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
1519 //
1520 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f32_s64u11__SVInt64_t(
1521 // CPP-CHECK-NEXT:  entry:
1522 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 4 x float>
1523 // CPP-CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
1524 //
1525 svfloat32_t test_svreinterpret_f32_s64(svint64_t op)
1526 {
1527   return SVE_ACLE_FUNC(svreinterpret_f32,_s64,,)(op);
1528 }
1529
1530 // CHECK-LABEL: @test_svreinterpret_f32_u8(
1531 // CHECK-NEXT:  entry:
1532 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 4 x float>
1533 // CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
1534 //
1535 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_f32_u8u11__SVUint8_t(
1536 // CPP-CHECK-NEXT:  entry:
1537 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 4 x float>
1538 // CPP-CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
1539 //
1540 svfloat32_t test_svreinterpret_f32_u8(svuint8_t op)
1541 {
1542   return SVE_ACLE_FUNC(svreinterpret_f32,_u8,,)(op);
1543 }
1544
1545 // CHECK-LABEL: @test_svreinterpret_f32_u16(
1546 // CHECK-NEXT:  entry:
1547 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 4 x float>
1548 // CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
1549 //
1550 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f32_u16u12__SVUint16_t(
1551 // CPP-CHECK-NEXT:  entry:
1552 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 4 x float>
1553 // CPP-CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
1554 //
1555 svfloat32_t test_svreinterpret_f32_u16(svuint16_t op)
1556 {
1557   return SVE_ACLE_FUNC(svreinterpret_f32,_u16,,)(op);
1558 }
1559
1560 // CHECK-LABEL: @test_svreinterpret_f32_u32(
1561 // CHECK-NEXT:  entry:
1562 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 4 x float>
1563 // CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
1564 //
1565 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f32_u32u12__SVUint32_t(
1566 // CPP-CHECK-NEXT:  entry:
1567 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 4 x float>
1568 // CPP-CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
1569 //
1570 svfloat32_t test_svreinterpret_f32_u32(svuint32_t op)
1571 {
1572   return SVE_ACLE_FUNC(svreinterpret_f32,_u32,,)(op);
1573 }
1574
1575 // CHECK-LABEL: @test_svreinterpret_f32_u64(
1576 // CHECK-NEXT:  entry:
1577 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 4 x float>
1578 // CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
1579 //
1580 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f32_u64u12__SVUint64_t(
1581 // CPP-CHECK-NEXT:  entry:
1582 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 4 x float>
1583 // CPP-CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
1584 //
1585 svfloat32_t test_svreinterpret_f32_u64(svuint64_t op)
1586 {
1587   return SVE_ACLE_FUNC(svreinterpret_f32,_u64,,)(op);
1588 }
1589
1590 // CHECK-LABEL: @test_svreinterpret_f32_f16(
1591 // CHECK-NEXT:  entry:
1592 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x half> [[OP:%.*]] to <vscale x 4 x float>
1593 // CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
1594 //
1595 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f32_f16u13__SVFloat16_t(
1596 // CPP-CHECK-NEXT:  entry:
1597 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x half> [[OP:%.*]] to <vscale x 4 x float>
1598 // CPP-CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
1599 //
1600 svfloat32_t test_svreinterpret_f32_f16(svfloat16_t op)
1601 {
1602   return SVE_ACLE_FUNC(svreinterpret_f32,_f16,,)(op);
1603 }
1604
1605 // CHECK-LABEL: @test_svreinterpret_f32_f32(
1606 // CHECK-NEXT:  entry:
1607 // CHECK-NEXT:    ret <vscale x 4 x float> [[OP:%.*]]
1608 //
1609 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f32_f32u13__SVFloat32_t(
1610 // CPP-CHECK-NEXT:  entry:
1611 // CPP-CHECK-NEXT:    ret <vscale x 4 x float> [[OP:%.*]]
1612 //
1613 svfloat32_t test_svreinterpret_f32_f32(svfloat32_t op)
1614 {
1615   return SVE_ACLE_FUNC(svreinterpret_f32,_f32,,)(op);
1616 }
1617
1618 // CHECK-LABEL: @test_svreinterpret_f32_f64(
1619 // CHECK-NEXT:  entry:
1620 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x double> [[OP:%.*]] to <vscale x 4 x float>
1621 // CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
1622 //
1623 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f32_f64u13__SVFloat64_t(
1624 // CPP-CHECK-NEXT:  entry:
1625 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x double> [[OP:%.*]] to <vscale x 4 x float>
1626 // CPP-CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
1627 //
1628 svfloat32_t test_svreinterpret_f32_f64(svfloat64_t op)
1629 {
1630   return SVE_ACLE_FUNC(svreinterpret_f32,_f64,,)(op);
1631 }
1632
1633 // CHECK-LABEL: @test_svreinterpret_f64_s8(
1634 // CHECK-NEXT:  entry:
1635 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 2 x double>
1636 // CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
1637 //
1638 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_f64_s8u10__SVInt8_t(
1639 // CPP-CHECK-NEXT:  entry:
1640 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 2 x double>
1641 // CPP-CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
1642 //
1643 svfloat64_t test_svreinterpret_f64_s8(svint8_t op)
1644 {
1645   return SVE_ACLE_FUNC(svreinterpret_f64,_s8,,)(op);
1646 }
1647
1648 // CHECK-LABEL: @test_svreinterpret_f64_s16(
1649 // CHECK-NEXT:  entry:
1650 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 2 x double>
1651 // CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
1652 //
1653 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f64_s16u11__SVInt16_t(
1654 // CPP-CHECK-NEXT:  entry:
1655 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 2 x double>
1656 // CPP-CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
1657 //
1658 svfloat64_t test_svreinterpret_f64_s16(svint16_t op)
1659 {
1660   return SVE_ACLE_FUNC(svreinterpret_f64,_s16,,)(op);
1661 }
1662
1663 // CHECK-LABEL: @test_svreinterpret_f64_s32(
1664 // CHECK-NEXT:  entry:
1665 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 2 x double>
1666 // CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
1667 //
1668 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f64_s32u11__SVInt32_t(
1669 // CPP-CHECK-NEXT:  entry:
1670 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 2 x double>
1671 // CPP-CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
1672 //
1673 svfloat64_t test_svreinterpret_f64_s32(svint32_t op)
1674 {
1675   return SVE_ACLE_FUNC(svreinterpret_f64,_s32,,)(op);
1676 }
1677
1678 // CHECK-LABEL: @test_svreinterpret_f64_s64(
1679 // CHECK-NEXT:  entry:
1680 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 2 x double>
1681 // CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
1682 //
1683 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f64_s64u11__SVInt64_t(
1684 // CPP-CHECK-NEXT:  entry:
1685 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 2 x double>
1686 // CPP-CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
1687 //
1688 svfloat64_t test_svreinterpret_f64_s64(svint64_t op)
1689 {
1690   return SVE_ACLE_FUNC(svreinterpret_f64,_s64,,)(op);
1691 }
1692
1693 // CHECK-LABEL: @test_svreinterpret_f64_u8(
1694 // CHECK-NEXT:  entry:
1695 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 2 x double>
1696 // CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
1697 //
1698 // CPP-CHECK-LABEL: @_Z25test_svreinterpret_f64_u8u11__SVUint8_t(
1699 // CPP-CHECK-NEXT:  entry:
1700 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 2 x double>
1701 // CPP-CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
1702 //
1703 svfloat64_t test_svreinterpret_f64_u8(svuint8_t op)
1704 {
1705   return SVE_ACLE_FUNC(svreinterpret_f64,_u8,,)(op);
1706 }
1707
1708 // CHECK-LABEL: @test_svreinterpret_f64_u16(
1709 // CHECK-NEXT:  entry:
1710 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 2 x double>
1711 // CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
1712 //
1713 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f64_u16u12__SVUint16_t(
1714 // CPP-CHECK-NEXT:  entry:
1715 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 2 x double>
1716 // CPP-CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
1717 //
1718 svfloat64_t test_svreinterpret_f64_u16(svuint16_t op)
1719 {
1720   return SVE_ACLE_FUNC(svreinterpret_f64,_u16,,)(op);
1721 }
1722
1723 // CHECK-LABEL: @test_svreinterpret_f64_u32(
1724 // CHECK-NEXT:  entry:
1725 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 2 x double>
1726 // CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
1727 //
1728 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f64_u32u12__SVUint32_t(
1729 // CPP-CHECK-NEXT:  entry:
1730 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 2 x double>
1731 // CPP-CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
1732 //
1733 svfloat64_t test_svreinterpret_f64_u32(svuint32_t op)
1734 {
1735   return SVE_ACLE_FUNC(svreinterpret_f64,_u32,,)(op);
1736 }
1737
1738 // CHECK-LABEL: @test_svreinterpret_f64_u64(
1739 // CHECK-NEXT:  entry:
1740 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 2 x double>
1741 // CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
1742 //
1743 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f64_u64u12__SVUint64_t(
1744 // CPP-CHECK-NEXT:  entry:
1745 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 2 x double>
1746 // CPP-CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
1747 //
1748 svfloat64_t test_svreinterpret_f64_u64(svuint64_t op)
1749 {
1750   return SVE_ACLE_FUNC(svreinterpret_f64,_u64,,)(op);
1751 }
1752
1753 // CHECK-LABEL: @test_svreinterpret_f64_f16(
1754 // CHECK-NEXT:  entry:
1755 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x half> [[OP:%.*]] to <vscale x 2 x double>
1756 // CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
1757 //
1758 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f64_f16u13__SVFloat16_t(
1759 // CPP-CHECK-NEXT:  entry:
1760 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x half> [[OP:%.*]] to <vscale x 2 x double>
1761 // CPP-CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
1762 //
1763 svfloat64_t test_svreinterpret_f64_f16(svfloat16_t op)
1764 {
1765   return SVE_ACLE_FUNC(svreinterpret_f64,_f16,,)(op);
1766 }
1767
1768 // CHECK-LABEL: @test_svreinterpret_f64_f32(
1769 // CHECK-NEXT:  entry:
1770 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x float> [[OP:%.*]] to <vscale x 2 x double>
1771 // CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
1772 //
1773 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f64_f32u13__SVFloat32_t(
1774 // CPP-CHECK-NEXT:  entry:
1775 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x float> [[OP:%.*]] to <vscale x 2 x double>
1776 // CPP-CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
1777 //
1778 svfloat64_t test_svreinterpret_f64_f32(svfloat32_t op)
1779 {
1780   return SVE_ACLE_FUNC(svreinterpret_f64,_f32,,)(op);
1781 }
1782
1783 // CHECK-LABEL: @test_svreinterpret_f64_f64(
1784 // CHECK-NEXT:  entry:
1785 // CHECK-NEXT:    ret <vscale x 2 x double> [[OP:%.*]]
1786 //
1787 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_f64_f64u13__SVFloat64_t(
1788 // CPP-CHECK-NEXT:  entry:
1789 // CPP-CHECK-NEXT:    ret <vscale x 2 x double> [[OP:%.*]]
1790 //
1791 svfloat64_t test_svreinterpret_f64_f64(svfloat64_t op)
1792 {
1793   return SVE_ACLE_FUNC(svreinterpret_f64,_f64,,)(op);
1794 }