clang/test/CodeGen/aarch64-sve-intrinsics/acle_sve_reinterpret-bfloat.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 -target-feature +bf16 -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 -target-feature +bf16 -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 -target-feature +bf16 -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 -target-feature +bf16 -S -disable-O0-optnone -Werror -Wall -emit-llvm -o - -x c++ %s | opt -S -passes=mem2reg,tailcallelim | FileCheck %s -check-prefix=CPP-CHECK
   7
   8 // RUN: %clang_cc1 -triple aarch64-none-linux-gnu -target-feature +sve -target-feature +bf16 -S -disable-O0-optnone -Werror -Wall -o /dev/null %s
   9
  10 #include <arm_sve.h>
  11
  12 #ifdef SVE_OVERLOADED_FORMS
  13 // A simple used,unused... macro, long enough to represent any SVE builtin.
  14 #define SVE_ACLE_FUNC(A1, A2_UNUSED, A3, A4_UNUSED) A1##A3
  15 #else
  16 #define SVE_ACLE_FUNC(A1, A2, A3, A4) A1##A2##A3##A4
  17 #endif
  18
  19 // CHECK-LABEL: @test_svreinterpret_s8_bf16(
  20 // CHECK-NEXT:  entry:
  21 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x bfloat> [[OP:%.*]] to <vscale x 16 x i8>
  22 // CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
  23 //
  24 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_s8_bf16u14__SVBfloat16_t(
  25 // CPP-CHECK-NEXT:  entry:
  26 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x bfloat> [[OP:%.*]] to <vscale x 16 x i8>
  27 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
  28 //
  29 svint8_t test_svreinterpret_s8_bf16(svbfloat16_t op) {
  30   return SVE_ACLE_FUNC(svreinterpret_s8, _bf16, , )(op);
  31 }
  32
  33 // CHECK-LABEL: @test_svreinterpret_s16_bf16(
  34 // CHECK-NEXT:  entry:
  35 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x bfloat> [[OP:%.*]] to <vscale x 8 x i16>
  36 // CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
  37 //
  38 // CPP-CHECK-LABEL: @_Z27test_svreinterpret_s16_bf16u14__SVBfloat16_t(
  39 // CPP-CHECK-NEXT:  entry:
  40 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x bfloat> [[OP:%.*]] to <vscale x 8 x i16>
  41 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
  42 //
  43 svint16_t test_svreinterpret_s16_bf16(svbfloat16_t op) {
  44   return SVE_ACLE_FUNC(svreinterpret_s16, _bf16, , )(op);
  45 }
  46
  47 // CHECK-LABEL: @test_svreinterpret_s32_bf16(
  48 // CHECK-NEXT:  entry:
  49 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x bfloat> [[OP:%.*]] to <vscale x 4 x i32>
  50 // CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
  51 //
  52 // CPP-CHECK-LABEL: @_Z27test_svreinterpret_s32_bf16u14__SVBfloat16_t(
  53 // CPP-CHECK-NEXT:  entry:
  54 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x bfloat> [[OP:%.*]] to <vscale x 4 x i32>
  55 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
  56 //
  57 svint32_t test_svreinterpret_s32_bf16(svbfloat16_t op) {
  58   return SVE_ACLE_FUNC(svreinterpret_s32, _bf16, , )(op);
  59 }
  60 // CHECK-LABEL: @test_svreinterpret_s64_bf16(
  61 // CHECK-NEXT:  entry:
  62 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x bfloat> [[OP:%.*]] to <vscale x 2 x i64>
  63 // CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
  64 //
  65 // CPP-CHECK-LABEL: @_Z27test_svreinterpret_s64_bf16u14__SVBfloat16_t(
  66 // CPP-CHECK-NEXT:  entry:
  67 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x bfloat> [[OP:%.*]] to <vscale x 2 x i64>
  68 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
  69 //
  70 svint64_t test_svreinterpret_s64_bf16(svbfloat16_t op) {
  71   return SVE_ACLE_FUNC(svreinterpret_s64, _bf16, , )(op);
  72 }
  73
  74 // CHECK-LABEL: @test_svreinterpret_u8_bf16(
  75 // CHECK-NEXT:  entry:
  76 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x bfloat> [[OP:%.*]] to <vscale x 16 x i8>
  77 // CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
  78 //
  79 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_u8_bf16u14__SVBfloat16_t(
  80 // CPP-CHECK-NEXT:  entry:
  81 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x bfloat> [[OP:%.*]] to <vscale x 16 x i8>
  82 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
  83 //
  84 svuint8_t test_svreinterpret_u8_bf16(svbfloat16_t op) {
  85   return SVE_ACLE_FUNC(svreinterpret_u8, _bf16, , )(op);
  86 }
  87
  88 // CHECK-LABEL: @test_svreinterpret_u16_bf16(
  89 // CHECK-NEXT:  entry:
  90 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x bfloat> [[OP:%.*]] to <vscale x 8 x i16>
  91 // CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
  92 //
  93 // CPP-CHECK-LABEL: @_Z27test_svreinterpret_u16_bf16u14__SVBfloat16_t(
  94 // CPP-CHECK-NEXT:  entry:
  95 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x bfloat> [[OP:%.*]] to <vscale x 8 x i16>
  96 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
  97 //
  98 svuint16_t test_svreinterpret_u16_bf16(svbfloat16_t op) {
  99   return SVE_ACLE_FUNC(svreinterpret_u16, _bf16, , )(op);
 100 }
 101
 102 // CHECK-LABEL: @test_svreinterpret_u32_bf16(
 103 // CHECK-NEXT:  entry:
 104 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x bfloat> [[OP:%.*]] to <vscale x 4 x i32>
 105 // CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 106 //
 107 // CPP-CHECK-LABEL: @_Z27test_svreinterpret_u32_bf16u14__SVBfloat16_t(
 108 // CPP-CHECK-NEXT:  entry:
 109 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x bfloat> [[OP:%.*]] to <vscale x 4 x i32>
 110 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 111 //
 112 svuint32_t test_svreinterpret_u32_bf16(svbfloat16_t op) {
 113   return SVE_ACLE_FUNC(svreinterpret_u32, _bf16, , )(op);
 114 }
 115
 116 // CHECK-LABEL: @test_svreinterpret_u64_bf16(
 117 // CHECK-NEXT:  entry:
 118 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x bfloat> [[OP:%.*]] to <vscale x 2 x i64>
 119 // CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
 120 //
 121 // CPP-CHECK-LABEL: @_Z27test_svreinterpret_u64_bf16u14__SVBfloat16_t(
 122 // CPP-CHECK-NEXT:  entry:
 123 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x bfloat> [[OP:%.*]] to <vscale x 2 x i64>
 124 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
 125 //
 126 svuint64_t test_svreinterpret_u64_bf16(svbfloat16_t op) {
 127   return SVE_ACLE_FUNC(svreinterpret_u64, _bf16, , )(op);
 128 }
 129
 130 // CHECK-LABEL: @test_svreinterpret_bf16_s8(
 131 // CHECK-NEXT:  entry:
 132 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 8 x bfloat>
 133 // CHECK-NEXT:    ret <vscale x 8 x bfloat> [[TMP0]]
 134 //
 135 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_bf16_s8u10__SVInt8_t(
 136 // CPP-CHECK-NEXT:  entry:
 137 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 8 x bfloat>
 138 // CPP-CHECK-NEXT:    ret <vscale x 8 x bfloat> [[TMP0]]
 139 //
 140 svbfloat16_t test_svreinterpret_bf16_s8(svint8_t op) {
 141   return SVE_ACLE_FUNC(svreinterpret_bf16, _s8, , )(op);
 142 }
 143
 144 // CHECK-LABEL: @test_svreinterpret_bf16_s16(
 145 // CHECK-NEXT:  entry:
 146 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 8 x bfloat>
 147 // CHECK-NEXT:    ret <vscale x 8 x bfloat> [[TMP0]]
 148 //
 149 // CPP-CHECK-LABEL: @_Z27test_svreinterpret_bf16_s16u11__SVInt16_t(
 150 // CPP-CHECK-NEXT:  entry:
 151 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 8 x bfloat>
 152 // CPP-CHECK-NEXT:    ret <vscale x 8 x bfloat> [[TMP0]]
 153 //
 154 svbfloat16_t test_svreinterpret_bf16_s16(svint16_t op) {
 155   return SVE_ACLE_FUNC(svreinterpret_bf16, _s16, , )(op);
 156 }
 157
 158 // CHECK-LABEL: @test_svreinterpret_bf16_s32(
 159 // CHECK-NEXT:  entry:
 160 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 8 x bfloat>
 161 // CHECK-NEXT:    ret <vscale x 8 x bfloat> [[TMP0]]
 162 //
 163 // CPP-CHECK-LABEL: @_Z27test_svreinterpret_bf16_s32u11__SVInt32_t(
 164 // CPP-CHECK-NEXT:  entry:
 165 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 8 x bfloat>
 166 // CPP-CHECK-NEXT:    ret <vscale x 8 x bfloat> [[TMP0]]
 167 //
 168 svbfloat16_t test_svreinterpret_bf16_s32(svint32_t op) {
 169   return SVE_ACLE_FUNC(svreinterpret_bf16, _s32, , )(op);
 170 }
 171
 172 // CHECK-LABEL: @test_svreinterpret_bf16_s64(
 173 // CHECK-NEXT:  entry:
 174 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 8 x bfloat>
 175 // CHECK-NEXT:    ret <vscale x 8 x bfloat> [[TMP0]]
 176 //
 177 // CPP-CHECK-LABEL: @_Z27test_svreinterpret_bf16_s64u11__SVInt64_t(
 178 // CPP-CHECK-NEXT:  entry:
 179 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 8 x bfloat>
 180 // CPP-CHECK-NEXT:    ret <vscale x 8 x bfloat> [[TMP0]]
 181 //
 182 svbfloat16_t test_svreinterpret_bf16_s64(svint64_t op) {
 183   return SVE_ACLE_FUNC(svreinterpret_bf16, _s64, , )(op);
 184 }
 185
 186 // CHECK-LABEL: @test_svreinterpret_bf16_u8(
 187 // CHECK-NEXT:  entry:
 188 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 8 x bfloat>
 189 // CHECK-NEXT:    ret <vscale x 8 x bfloat> [[TMP0]]
 190 //
 191 // CPP-CHECK-LABEL: @_Z26test_svreinterpret_bf16_u8u11__SVUint8_t(
 192 // CPP-CHECK-NEXT:  entry:
 193 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 16 x i8> [[OP:%.*]] to <vscale x 8 x bfloat>
 194 // CPP-CHECK-NEXT:    ret <vscale x 8 x bfloat> [[TMP0]]
 195 //
 196 svbfloat16_t test_svreinterpret_bf16_u8(svuint8_t op) {
 197   return SVE_ACLE_FUNC(svreinterpret_bf16, _u8, , )(op);
 198 }
 199
 200 // CHECK-LABEL: @test_svreinterpret_bf16_u16(
 201 // CHECK-NEXT:  entry:
 202 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 8 x bfloat>
 203 // CHECK-NEXT:    ret <vscale x 8 x bfloat> [[TMP0]]
 204 //
 205 // CPP-CHECK-LABEL: @_Z27test_svreinterpret_bf16_u16u12__SVUint16_t(
 206 // CPP-CHECK-NEXT:  entry:
 207 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x i16> [[OP:%.*]] to <vscale x 8 x bfloat>
 208 // CPP-CHECK-NEXT:    ret <vscale x 8 x bfloat> [[TMP0]]
 209 //
 210 svbfloat16_t test_svreinterpret_bf16_u16(svuint16_t op) {
 211   return SVE_ACLE_FUNC(svreinterpret_bf16, _u16, , )(op);
 212 }
 213
 214 // CHECK-LABEL: @test_svreinterpret_bf16_u32(
 215 // CHECK-NEXT:  entry:
 216 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 8 x bfloat>
 217 // CHECK-NEXT:    ret <vscale x 8 x bfloat> [[TMP0]]
 218 //
 219 // CPP-CHECK-LABEL: @_Z27test_svreinterpret_bf16_u32u12__SVUint32_t(
 220 // CPP-CHECK-NEXT:  entry:
 221 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x i32> [[OP:%.*]] to <vscale x 8 x bfloat>
 222 // CPP-CHECK-NEXT:    ret <vscale x 8 x bfloat> [[TMP0]]
 223 //
 224 svbfloat16_t test_svreinterpret_bf16_u32(svuint32_t op) {
 225   return SVE_ACLE_FUNC(svreinterpret_bf16, _u32, , )(op);
 226 }
 227
 228 // CHECK-LABEL: @test_svreinterpret_bf16_u64(
 229 // CHECK-NEXT:  entry:
 230 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 8 x bfloat>
 231 // CHECK-NEXT:    ret <vscale x 8 x bfloat> [[TMP0]]
 232 //
 233 // CPP-CHECK-LABEL: @_Z27test_svreinterpret_bf16_u64u12__SVUint64_t(
 234 // CPP-CHECK-NEXT:  entry:
 235 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x i64> [[OP:%.*]] to <vscale x 8 x bfloat>
 236 // CPP-CHECK-NEXT:    ret <vscale x 8 x bfloat> [[TMP0]]
 237 //
 238 svbfloat16_t test_svreinterpret_bf16_u64(svuint64_t op) {
 239   return SVE_ACLE_FUNC(svreinterpret_bf16, _u64, , )(op);
 240 }
 241
 242 // CHECK-LABEL: @test_svreinterpret_bf16_bf16(
 243 // CHECK-NEXT:  entry:
 244 // CHECK-NEXT:    ret <vscale x 8 x bfloat> [[OP:%.*]]
 245 //
 246 // CPP-CHECK-LABEL: @_Z28test_svreinterpret_bf16_bf16u14__SVBfloat16_t(
 247 // CPP-CHECK-NEXT:  entry:
 248 // CPP-CHECK-NEXT:    ret <vscale x 8 x bfloat> [[OP:%.*]]
 249 //
 250 svbfloat16_t test_svreinterpret_bf16_bf16(svbfloat16_t op) {
 251   return SVE_ACLE_FUNC(svreinterpret_bf16, _bf16, , )(op);
 252 }
 253
 254 // CHECK-LABEL: @test_svreinterpret_bf16_f16(
 255 // CHECK-NEXT:  entry:
 256 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x half> [[OP:%.*]] to <vscale x 8 x bfloat>
 257 // CHECK-NEXT:    ret <vscale x 8 x bfloat> [[TMP0]]
 258 //
 259 // CPP-CHECK-LABEL: @_Z27test_svreinterpret_bf16_f16u13__SVFloat16_t(
 260 // CPP-CHECK-NEXT:  entry:
 261 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x half> [[OP:%.*]] to <vscale x 8 x bfloat>
 262 // CPP-CHECK-NEXT:    ret <vscale x 8 x bfloat> [[TMP0]]
 263 //
 264 svbfloat16_t test_svreinterpret_bf16_f16(svfloat16_t op) {
 265   return SVE_ACLE_FUNC(svreinterpret_bf16, _f16, , )(op);
 266 }
 267
 268 // CHECK-LABEL: @test_svreinterpret_bf16_f32(
 269 // CHECK-NEXT:  entry:
 270 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x float> [[OP:%.*]] to <vscale x 8 x bfloat>
 271 // CHECK-NEXT:    ret <vscale x 8 x bfloat> [[TMP0]]
 272 //
 273 // CPP-CHECK-LABEL: @_Z27test_svreinterpret_bf16_f32u13__SVFloat32_t(
 274 // CPP-CHECK-NEXT:  entry:
 275 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 4 x float> [[OP:%.*]] to <vscale x 8 x bfloat>
 276 // CPP-CHECK-NEXT:    ret <vscale x 8 x bfloat> [[TMP0]]
 277 //
 278 svbfloat16_t test_svreinterpret_bf16_f32(svfloat32_t op) {
 279   return SVE_ACLE_FUNC(svreinterpret_bf16, _f32, , )(op);
 280 }
 281
 282 // CHECK-LABEL: @test_svreinterpret_bf16_f64(
 283 // CHECK-NEXT:  entry:
 284 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x double> [[OP:%.*]] to <vscale x 8 x bfloat>
 285 // CHECK-NEXT:    ret <vscale x 8 x bfloat> [[TMP0]]
 286 //
 287 // CPP-CHECK-LABEL: @_Z27test_svreinterpret_bf16_f64u13__SVFloat64_t(
 288 // CPP-CHECK-NEXT:  entry:
 289 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 2 x double> [[OP:%.*]] to <vscale x 8 x bfloat>
 290 // CPP-CHECK-NEXT:    ret <vscale x 8 x bfloat> [[TMP0]]
 291 //
 292 svbfloat16_t test_svreinterpret_bf16_f64(svfloat64_t op) {
 293   return SVE_ACLE_FUNC(svreinterpret_bf16, _f64, , )(op);
 294 }
 295
 296 // CHECK-LABEL: @test_svreinterpret_f32_bf16(
 297 // CHECK-NEXT:  entry:
 298 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x bfloat> [[OP:%.*]] to <vscale x 4 x float>
 299 // CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
 300 //
 301 // CPP-CHECK-LABEL: @_Z27test_svreinterpret_f32_bf16u14__SVBfloat16_t(
 302 // CPP-CHECK-NEXT:  entry:
 303 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x bfloat> [[OP:%.*]] to <vscale x 4 x float>
 304 // CPP-CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
 305 //
 306 svfloat32_t test_svreinterpret_f32_bf16(svbfloat16_t op) {
 307   return SVE_ACLE_FUNC(svreinterpret_f32, _bf16, , )(op);
 308 }
 309
 310 // CHECK-LABEL: @test_svreinterpret_f16_bf16(
 311 // CHECK-NEXT:  entry:
 312 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x bfloat> [[OP:%.*]] to <vscale x 8 x half>
 313 // CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
 314 //
 315 // CPP-CHECK-LABEL: @_Z27test_svreinterpret_f16_bf16u14__SVBfloat16_t(
 316 // CPP-CHECK-NEXT:  entry:
 317 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x bfloat> [[OP:%.*]] to <vscale x 8 x half>
 318 // CPP-CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
 319 //
 320 svfloat16_t test_svreinterpret_f16_bf16(svbfloat16_t op) {
 321   return SVE_ACLE_FUNC(svreinterpret_f16, _bf16, , )(op);
 322 }
 323
 324 // CHECK-LABEL: @test_svreinterpret_f64_bf16(
 325 // CHECK-NEXT:  entry:
 326 // CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x bfloat> [[OP:%.*]] to <vscale x 2 x double>
 327 // CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
 328 //
 329 // CPP-CHECK-LABEL: @_Z27test_svreinterpret_f64_bf16u14__SVBfloat16_t(
 330 // CPP-CHECK-NEXT:  entry:
 331 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = bitcast <vscale x 8 x bfloat> [[OP:%.*]] to <vscale x 2 x double>
 332 // CPP-CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
 333 //
 334 svfloat64_t test_svreinterpret_f64_bf16(svbfloat16_t op) {
 335   return SVE_ACLE_FUNC(svreinterpret_f64, _bf16, , )(op);
 336 }