2020-06-26 05:49:00 +08:00
// RUN: %clang_cc1 -triple aarch64-none-linux-gnu -target-feature +sve -target-feature +bf16 -fallow-half-arguments-and-returns -S -O1 -Werror -Wall -emit-llvm -o - %s | FileCheck %s
// RUN: %clang_cc1 -DSVE_OVERLOADED_FORMS -triple aarch64-none-linux-gnu -target-feature +sve -target-feature +bf16 -fallow-half-arguments-and-returns -S -O1 -Werror -Wall -emit-llvm -o - %s | FileCheck %s
[sve][acle] Add SVE BFloat16 extensions.
Summary:
List of intrinsics:
svfloat32_t svbfdot[_f32](svfloat32_t op1, svbfloat16_t op2, svbfloat16_t op3)
svfloat32_t svbfdot[_n_f32](svfloat32_t op1, svbfloat16_t op2, bfloat16_t op3)
svfloat32_t svbfdot_lane[_f32](svfloat32_t op1, svbfloat16_t op2, svbfloat16_t op3, uint64_t imm_index)
svfloat32_t svbfmmla[_f32](svfloat32_t op1, svbfloat16_t op2, svbfloat16_t op3)
svfloat32_t svbfmlalb[_f32](svfloat32_t op1, svbfloat16_t op2, svbfloat16_t op3)
svfloat32_t svbfmlalb[_n_f32](svfloat32_t op1, svbfloat16_t op2, bfloat16_t op3)
svfloat32_t svbfmlalb_lane[_f32](svfloat32_t op1, svbfloat16_t op2, svbfloat16_t op3, uint64_t imm_index)
svfloat32_t svbfmlalt[_f32](svfloat32_t op1, svbfloat16_t op2, svbfloat16_t op3)
svfloat32_t svbfmlalt[_n_f32](svfloat32_t op1, svbfloat16_t op2, bfloat16_t op3)
svfloat32_t svbfmlalt_lane[_f32](svfloat32_t op1, svbfloat16_t op2, svbfloat16_t op3, uint64_t imm_index)
svbfloat16_t svcvt_bf16[_f32]_m(svbfloat16_t inactive, svbool_t pg, svfloat32_t op)
svbfloat16_t svcvt_bf16[_f32]_x(svbool_t pg, svfloat32_t op)
svbfloat16_t svcvt_bf16[_f32]_z(svbool_t pg, svfloat32_t op)
svbfloat16_t svcvtnt_bf16[_f32]_m(svbfloat16_t even, svbool_t pg, svfloat32_t op)
svbfloat16_t svcvtnt_bf16[_f32]_x(svbfloat16_t even, svbool_t pg, svfloat32_t op)
For reference, see section 7.2 of "Arm C Language Extensions for SVE - Version 00bet4"
Reviewers: sdesmalen, ctetreau, efriedma, david-arm, rengolin
Subscribers: tschuett, kristof.beyls, hiraditya, rkruppe, psnobl, cfe-commits, llvm-commits
Tags: #clang, #llvm
Differential Revision: https://reviews.llvm.org/D82141
2020-06-17 06:56:00 +08:00
# include <arm_sve.h>
# ifdef SVE_OVERLOADED_FORMS
// A simple used,unused... macro, long enough to represent any SVE builtin.
# define SVE_ACLE_FUNC(A1, A2_UNUSED, A3, A4_UNUSED) A1##A3
# else
# define SVE_ACLE_FUNC(A1, A2, A3, A4) A1##A2##A3##A4
# endif
svfloat32_t test_svbfmlalt_f32 ( svfloat32_t x , svbfloat16_t y , svbfloat16_t z ) {
// CHECK-LABEL: @test_svbfmlalt_f32(
// CHECK: %[[RET:.*]] = call <vscale x 4 x float> @llvm.aarch64.sve.bfmlalt(<vscale x 4 x float> %x, <vscale x 8 x bfloat> %y, <vscale x 8 x bfloat> %z)
// CHECK: ret <vscale x 4 x float> %[[RET]]
return SVE_ACLE_FUNC ( svbfmlalt , _f32 , , ) ( x , y , z ) ;
}
svfloat32_t test_bfmlalt_lane_0_f32 ( svfloat32_t x , svbfloat16_t y , svbfloat16_t z ) {
// CHECK-LABEL: @test_bfmlalt_lane_0_f32(
// CHECK: %[[RET:.*]] = call <vscale x 4 x float> @llvm.aarch64.sve.bfmlalt.lane(<vscale x 4 x float> %x, <vscale x 8 x bfloat> %y, <vscale x 8 x bfloat> %z, i64 0)
// CHECK: ret <vscale x 4 x float> %[[RET]]
return SVE_ACLE_FUNC ( svbfmlalt_lane , _f32 , , ) ( x , y , z , 0 ) ;
}
svfloat32_t test_bfmlalt_lane_7_f32 ( svfloat32_t x , svbfloat16_t y , svbfloat16_t z ) {
// CHECK-LABEL: @test_bfmlalt_lane_7_f32(
// CHECK: %[[RET:.*]] = call <vscale x 4 x float> @llvm.aarch64.sve.bfmlalt.lane(<vscale x 4 x float> %x, <vscale x 8 x bfloat> %y, <vscale x 8 x bfloat> %z, i64 7)
// CHECK: ret <vscale x 4 x float> %[[RET]]
return SVE_ACLE_FUNC ( svbfmlalt_lane , _f32 , , ) ( x , y , z , 7 ) ;
}
svfloat32_t test_bfmlalt_n_f32 ( svfloat32_t x , svbfloat16_t y , bfloat16_t z ) {
// CHECK-LABEL: @test_bfmlalt_n_f32(
// CHECK: %[[SPLAT:.*]] = call <vscale x 8 x bfloat> @llvm.aarch64.sve.dup.x.nxv8bf16(bfloat %z)
// CHECK: %[[RET:.*]] = call <vscale x 4 x float> @llvm.aarch64.sve.bfmlalt(<vscale x 4 x float> %x, <vscale x 8 x bfloat> %y, <vscale x 8 x bfloat> %[[SPLAT]])
// CHECK: ret <vscale x 4 x float> %[[RET]]
return SVE_ACLE_FUNC ( svbfmlalt , _n_f32 , , ) ( x , y , z ) ;
}