clang/test/CodeGen/aarch64-sve2-intrinsics/acle_sve2_tbx.c

   1 // NOTE: Assertions have been autogenerated by utils/update_cc_test_checks.py
   2 // RUN: %clang_cc1 -triple aarch64-none-linux-gnu -target-feature +sve2 -S -O1 -Werror -Wall -emit-llvm -o - %s | FileCheck %s
   3 // RUN: %clang_cc1 -triple aarch64-none-linux-gnu -target-feature +sve2 -S -O1 -Werror -Wall -emit-llvm -o - -x c++ %s | FileCheck %s -check-prefix=CPP-CHECK
   4 // RUN: %clang_cc1 -DSVE_OVERLOADED_FORMS -triple aarch64-none-linux-gnu -target-feature +sve2 -S -O1 -Werror -Wall -emit-llvm -o - %s | FileCheck %s
   5 // RUN: %clang_cc1 -DSVE_OVERLOADED_FORMS -triple aarch64-none-linux-gnu -target-feature +sve2 -S -O1 -Werror -Wall -emit-llvm -o - -x c++ %s | FileCheck %s -check-prefix=CPP-CHECK
   6
   7 // REQUIRES: aarch64-registered-target
   8
   9 #include <arm_sve.h>
  10
  11 #ifdef SVE_OVERLOADED_FORMS
  12 // A simple used,unused... macro, long enough to represent any SVE builtin.
  13 #define SVE_ACLE_FUNC(A1,A2_UNUSED,A3,A4_UNUSED) A1##A3
  14 #else
  15 #define SVE_ACLE_FUNC(A1,A2,A3,A4) A1##A2##A3##A4
  16 #endif
  17
  18 // CHECK-LABEL: @test_svtbx_s8(
  19 // CHECK-NEXT:  entry:
  20 // CHECK-NEXT:    [[TMP0:%.*]] = tail call <vscale x 16 x i8> @llvm.aarch64.sve.tbx.nxv16i8(<vscale x 16 x i8> [[FALLBACK:%.*]], <vscale x 16 x i8> [[DATA:%.*]], <vscale x 16 x i8> [[INDICES:%.*]])
  21 // CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
  22 //
  23 // CPP-CHECK-LABEL: @_Z13test_svtbx_s8u10__SVInt8_tS_u11__SVUint8_t(
  24 // CPP-CHECK-NEXT:  entry:
  25 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = tail call <vscale x 16 x i8> @llvm.aarch64.sve.tbx.nxv16i8(<vscale x 16 x i8> [[FALLBACK:%.*]], <vscale x 16 x i8> [[DATA:%.*]], <vscale x 16 x i8> [[INDICES:%.*]])
  26 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
  27 //
  28 svint8_t test_svtbx_s8(svint8_t fallback, svint8_t data, svuint8_t indices)
  29 {
  30   return SVE_ACLE_FUNC(svtbx,_s8,,)(fallback, data, indices);
  31 }
  32
  33 // CHECK-LABEL: @test_svtbx_s16(
  34 // CHECK-NEXT:  entry:
  35 // CHECK-NEXT:    [[TMP0:%.*]] = tail call <vscale x 8 x i16> @llvm.aarch64.sve.tbx.nxv8i16(<vscale x 8 x i16> [[FALLBACK:%.*]], <vscale x 8 x i16> [[DATA:%.*]], <vscale x 8 x i16> [[INDICES:%.*]])
  36 // CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
  37 //
  38 // CPP-CHECK-LABEL: @_Z14test_svtbx_s16u11__SVInt16_tS_u12__SVUint16_t(
  39 // CPP-CHECK-NEXT:  entry:
  40 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = tail call <vscale x 8 x i16> @llvm.aarch64.sve.tbx.nxv8i16(<vscale x 8 x i16> [[FALLBACK:%.*]], <vscale x 8 x i16> [[DATA:%.*]], <vscale x 8 x i16> [[INDICES:%.*]])
  41 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
  42 //
  43 svint16_t test_svtbx_s16(svint16_t fallback, svint16_t data, svuint16_t indices)
  44 {
  45   return SVE_ACLE_FUNC(svtbx,_s16,,)(fallback, data, indices);
  46 }
  47
  48 // CHECK-LABEL: @test_svtbx_s32(
  49 // CHECK-NEXT:  entry:
  50 // CHECK-NEXT:    [[TMP0:%.*]] = tail call <vscale x 4 x i32> @llvm.aarch64.sve.tbx.nxv4i32(<vscale x 4 x i32> [[FALLBACK:%.*]], <vscale x 4 x i32> [[DATA:%.*]], <vscale x 4 x i32> [[INDICES:%.*]])
  51 // CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
  52 //
  53 // CPP-CHECK-LABEL: @_Z14test_svtbx_s32u11__SVInt32_tS_u12__SVUint32_t(
  54 // CPP-CHECK-NEXT:  entry:
  55 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = tail call <vscale x 4 x i32> @llvm.aarch64.sve.tbx.nxv4i32(<vscale x 4 x i32> [[FALLBACK:%.*]], <vscale x 4 x i32> [[DATA:%.*]], <vscale x 4 x i32> [[INDICES:%.*]])
  56 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
  57 //
  58 svint32_t test_svtbx_s32(svint32_t fallback, svint32_t data, svuint32_t indices)
  59 {
  60   return SVE_ACLE_FUNC(svtbx,_s32,,)(fallback, data, indices);
  61 }
  62
  63 // CHECK-LABEL: @test_svtbx_s64(
  64 // CHECK-NEXT:  entry:
  65 // CHECK-NEXT:    [[TMP0:%.*]] = tail call <vscale x 2 x i64> @llvm.aarch64.sve.tbx.nxv2i64(<vscale x 2 x i64> [[FALLBACK:%.*]], <vscale x 2 x i64> [[DATA:%.*]], <vscale x 2 x i64> [[INDICES:%.*]])
  66 // CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
  67 //
  68 // CPP-CHECK-LABEL: @_Z14test_svtbx_s64u11__SVInt64_tS_u12__SVUint64_t(
  69 // CPP-CHECK-NEXT:  entry:
  70 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = tail call <vscale x 2 x i64> @llvm.aarch64.sve.tbx.nxv2i64(<vscale x 2 x i64> [[FALLBACK:%.*]], <vscale x 2 x i64> [[DATA:%.*]], <vscale x 2 x i64> [[INDICES:%.*]])
  71 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
  72 //
  73 svint64_t test_svtbx_s64(svint64_t fallback, svint64_t data, svuint64_t indices)
  74 {
  75   return SVE_ACLE_FUNC(svtbx,_s64,,)(fallback, data, indices);
  76 }
  77
  78 // CHECK-LABEL: @test_svtbx_u8(
  79 // CHECK-NEXT:  entry:
  80 // CHECK-NEXT:    [[TMP0:%.*]] = tail call <vscale x 16 x i8> @llvm.aarch64.sve.tbx.nxv16i8(<vscale x 16 x i8> [[FALLBACK:%.*]], <vscale x 16 x i8> [[DATA:%.*]], <vscale x 16 x i8> [[INDICES:%.*]])
  81 // CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
  82 //
  83 // CPP-CHECK-LABEL: @_Z13test_svtbx_u8u11__SVUint8_tS_S_(
  84 // CPP-CHECK-NEXT:  entry:
  85 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = tail call <vscale x 16 x i8> @llvm.aarch64.sve.tbx.nxv16i8(<vscale x 16 x i8> [[FALLBACK:%.*]], <vscale x 16 x i8> [[DATA:%.*]], <vscale x 16 x i8> [[INDICES:%.*]])
  86 // CPP-CHECK-NEXT:    ret <vscale x 16 x i8> [[TMP0]]
  87 //
  88 svuint8_t test_svtbx_u8(svuint8_t fallback, svuint8_t data, svuint8_t indices)
  89 {
  90   return SVE_ACLE_FUNC(svtbx,_u8,,)(fallback, data, indices);
  91 }
  92
  93 // CHECK-LABEL: @test_svtbx_u16(
  94 // CHECK-NEXT:  entry:
  95 // CHECK-NEXT:    [[TMP0:%.*]] = tail call <vscale x 8 x i16> @llvm.aarch64.sve.tbx.nxv8i16(<vscale x 8 x i16> [[FALLBACK:%.*]], <vscale x 8 x i16> [[DATA:%.*]], <vscale x 8 x i16> [[INDICES:%.*]])
  96 // CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
  97 //
  98 // CPP-CHECK-LABEL: @_Z14test_svtbx_u16u12__SVUint16_tS_S_(
  99 // CPP-CHECK-NEXT:  entry:
 100 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = tail call <vscale x 8 x i16> @llvm.aarch64.sve.tbx.nxv8i16(<vscale x 8 x i16> [[FALLBACK:%.*]], <vscale x 8 x i16> [[DATA:%.*]], <vscale x 8 x i16> [[INDICES:%.*]])
 101 // CPP-CHECK-NEXT:    ret <vscale x 8 x i16> [[TMP0]]
 102 //
 103 svuint16_t test_svtbx_u16(svuint16_t fallback, svuint16_t data, svuint16_t indices)
 104 {
 105   return SVE_ACLE_FUNC(svtbx,_u16,,)(fallback, data, indices);
 106 }
 107
 108 // CHECK-LABEL: @test_svtbx_u32(
 109 // CHECK-NEXT:  entry:
 110 // CHECK-NEXT:    [[TMP0:%.*]] = tail call <vscale x 4 x i32> @llvm.aarch64.sve.tbx.nxv4i32(<vscale x 4 x i32> [[FALLBACK:%.*]], <vscale x 4 x i32> [[DATA:%.*]], <vscale x 4 x i32> [[INDICES:%.*]])
 111 // CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 112 //
 113 // CPP-CHECK-LABEL: @_Z14test_svtbx_u32u12__SVUint32_tS_S_(
 114 // CPP-CHECK-NEXT:  entry:
 115 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = tail call <vscale x 4 x i32> @llvm.aarch64.sve.tbx.nxv4i32(<vscale x 4 x i32> [[FALLBACK:%.*]], <vscale x 4 x i32> [[DATA:%.*]], <vscale x 4 x i32> [[INDICES:%.*]])
 116 // CPP-CHECK-NEXT:    ret <vscale x 4 x i32> [[TMP0]]
 117 //
 118 svuint32_t test_svtbx_u32(svuint32_t fallback, svuint32_t data, svuint32_t indices)
 119 {
 120   return SVE_ACLE_FUNC(svtbx,_u32,,)(fallback, data, indices);
 121 }
 122
 123 // CHECK-LABEL: @test_svtbx_u64(
 124 // CHECK-NEXT:  entry:
 125 // CHECK-NEXT:    [[TMP0:%.*]] = tail call <vscale x 2 x i64> @llvm.aarch64.sve.tbx.nxv2i64(<vscale x 2 x i64> [[FALLBACK:%.*]], <vscale x 2 x i64> [[DATA:%.*]], <vscale x 2 x i64> [[INDICES:%.*]])
 126 // CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
 127 //
 128 // CPP-CHECK-LABEL: @_Z14test_svtbx_u64u12__SVUint64_tS_S_(
 129 // CPP-CHECK-NEXT:  entry:
 130 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = tail call <vscale x 2 x i64> @llvm.aarch64.sve.tbx.nxv2i64(<vscale x 2 x i64> [[FALLBACK:%.*]], <vscale x 2 x i64> [[DATA:%.*]], <vscale x 2 x i64> [[INDICES:%.*]])
 131 // CPP-CHECK-NEXT:    ret <vscale x 2 x i64> [[TMP0]]
 132 //
 133 svuint64_t test_svtbx_u64(svuint64_t fallback, svuint64_t data, svuint64_t indices)
 134 {
 135   return SVE_ACLE_FUNC(svtbx,_u64,,)(fallback, data, indices);
 136 }
 137
 138 // CHECK-LABEL: @test_svtbx_f16(
 139 // CHECK-NEXT:  entry:
 140 // CHECK-NEXT:    [[TMP0:%.*]] = tail call <vscale x 8 x half> @llvm.aarch64.sve.tbx.nxv8f16(<vscale x 8 x half> [[FALLBACK:%.*]], <vscale x 8 x half> [[DATA:%.*]], <vscale x 8 x i16> [[INDICES:%.*]])
 141 // CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
 142 //
 143 // CPP-CHECK-LABEL: @_Z14test_svtbx_f16u13__SVFloat16_tS_u12__SVUint16_t(
 144 // CPP-CHECK-NEXT:  entry:
 145 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = tail call <vscale x 8 x half> @llvm.aarch64.sve.tbx.nxv8f16(<vscale x 8 x half> [[FALLBACK:%.*]], <vscale x 8 x half> [[DATA:%.*]], <vscale x 8 x i16> [[INDICES:%.*]])
 146 // CPP-CHECK-NEXT:    ret <vscale x 8 x half> [[TMP0]]
 147 //
 148 svfloat16_t test_svtbx_f16(svfloat16_t fallback, svfloat16_t data, svuint16_t indices)
 149 {
 150   return SVE_ACLE_FUNC(svtbx,_f16,,)(fallback, data, indices);
 151 }
 152
 153 // CHECK-LABEL: @test_svtbx_f32(
 154 // CHECK-NEXT:  entry:
 155 // CHECK-NEXT:    [[TMP0:%.*]] = tail call <vscale x 4 x float> @llvm.aarch64.sve.tbx.nxv4f32(<vscale x 4 x float> [[FALLBACK:%.*]], <vscale x 4 x float> [[DATA:%.*]], <vscale x 4 x i32> [[INDICES:%.*]])
 156 // CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
 157 //
 158 // CPP-CHECK-LABEL: @_Z14test_svtbx_f32u13__SVFloat32_tS_u12__SVUint32_t(
 159 // CPP-CHECK-NEXT:  entry:
 160 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = tail call <vscale x 4 x float> @llvm.aarch64.sve.tbx.nxv4f32(<vscale x 4 x float> [[FALLBACK:%.*]], <vscale x 4 x float> [[DATA:%.*]], <vscale x 4 x i32> [[INDICES:%.*]])
 161 // CPP-CHECK-NEXT:    ret <vscale x 4 x float> [[TMP0]]
 162 //
 163 svfloat32_t test_svtbx_f32(svfloat32_t fallback, svfloat32_t data, svuint32_t indices)
 164 {
 165   return SVE_ACLE_FUNC(svtbx,_f32,,)(fallback, data, indices);
 166 }
 167
 168 // CHECK-LABEL: @test_svtbx_f64(
 169 // CHECK-NEXT:  entry:
 170 // CHECK-NEXT:    [[TMP0:%.*]] = tail call <vscale x 2 x double> @llvm.aarch64.sve.tbx.nxv2f64(<vscale x 2 x double> [[FALLBACK:%.*]], <vscale x 2 x double> [[DATA:%.*]], <vscale x 2 x i64> [[INDICES:%.*]])
 171 // CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
 172 //
 173 // CPP-CHECK-LABEL: @_Z14test_svtbx_f64u13__SVFloat64_tS_u12__SVUint64_t(
 174 // CPP-CHECK-NEXT:  entry:
 175 // CPP-CHECK-NEXT:    [[TMP0:%.*]] = tail call <vscale x 2 x double> @llvm.aarch64.sve.tbx.nxv2f64(<vscale x 2 x double> [[FALLBACK:%.*]], <vscale x 2 x double> [[DATA:%.*]], <vscale x 2 x i64> [[INDICES:%.*]])
 176 // CPP-CHECK-NEXT:    ret <vscale x 2 x double> [[TMP0]]
 177 //
 178 svfloat64_t test_svtbx_f64(svfloat64_t fallback, svfloat64_t data, svuint64_t indices)
 179 {
 180   return SVE_ACLE_FUNC(svtbx,_f64,,)(fallback, data, indices);
 181 }