2020-06-24 23:52:41 +08:00
|
|
|
// RUN: %clang_cc1 -triple aarch64-none-linux-gnu -target-feature +sve2 -fallow-half-arguments-and-returns -fsyntax-only -verify %s
|
|
|
|
// RUN: %clang_cc1 -DSVE_OVERLOADED_FORMS -triple aarch64-none-linux-gnu -target-feature +sve2 -fallow-half-arguments-and-returns -fsyntax-only -verify %s
|
[SveEmitter] Add builtins for SVE2 Widening DSP operations
This patch adds builtins for:
- svabalb
- svabalt
- svabdlb
- svabdlt
- svaddlb
- svaddlt
- svaddwb
- svaddwt
- svmlalb, svmlalb_lane
- svmlalt, svmlalt_lane
- svmlslb, svmlslb_lane
- svmlslt, svmlslt_lane
- svmullb, svmullb_lane
- svmullt, svmullt_lane
- svqdmlalb, svqdmlalb_lane
- svqdmlalt, svqdmlalt_lane
- svqdmlslb, svqdmlslb_lane
- svqdmlslt, svqdmlslt_lane
- svqdmullb, svqdmullb_lane
- svqdmullt, svqdmullt_lane
- svshllb
- svshllt
- svsublb
- svsublt
- svsubwb
- svsubwt
2020-05-05 22:10:48 +08:00
|
|
|
|
|
|
|
#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
|
|
|
|
|
|
|
|
#include <arm_sve.h>
|
|
|
|
|
|
|
|
svint32_t test_svmlalb_lane_s32(svint32_t op1, svint16_t op2, svint16_t op3)
|
|
|
|
{
|
|
|
|
// expected-error-re@+1 {{argument value {{[0-9]+}} is outside the valid range [0, 7]}}
|
|
|
|
return SVE_ACLE_FUNC(svmlalb_lane,_s32,,)(op1, op2, op3, -1);
|
|
|
|
}
|
|
|
|
|
|
|
|
svint64_t test_svmlalb_lane_s64(svint64_t op1, svint32_t op2, svint32_t op3)
|
|
|
|
{
|
|
|
|
// expected-error-re@+1 {{argument value {{[0-9]+}} is outside the valid range [0, 3]}}
|
|
|
|
return SVE_ACLE_FUNC(svmlalb_lane,_s64,,)(op1, op2, op3, -1);
|
|
|
|
}
|
|
|
|
|
|
|
|
svuint32_t test_svmlalb_lane_u32(svuint32_t op1, svuint16_t op2, svuint16_t op3)
|
|
|
|
{
|
|
|
|
// expected-error-re@+1 {{argument value {{[0-9]+}} is outside the valid range [0, 7]}}
|
|
|
|
return SVE_ACLE_FUNC(svmlalb_lane,_u32,,)(op1, op2, op3, 8);
|
|
|
|
}
|
|
|
|
|
|
|
|
svuint64_t test_svmlalb_lane_u64(svuint64_t op1, svuint32_t op2, svuint32_t op3)
|
|
|
|
{
|
|
|
|
// expected-error-re@+1 {{argument value {{[0-9]+}} is outside the valid range [0, 3]}}
|
|
|
|
return SVE_ACLE_FUNC(svmlalb_lane,_u64,,)(op1, op2, op3, 4);
|
|
|
|
}
|
2020-05-05 23:07:09 +08:00
|
|
|
|
|
|
|
svfloat32_t test_svmlalb_lane_f32(svfloat32_t op1, svfloat16_t op2, svfloat16_t op3)
|
|
|
|
{
|
|
|
|
// expected-error-re@+1 {{argument value {{[0-9]+}} is outside the valid range [0, 7]}}
|
|
|
|
return SVE_ACLE_FUNC(svmlalb_lane,_f32,,)(op1, op2, op3, -1);
|
|
|
|
}
|
|
|
|
|
|
|
|
svfloat32_t test_svmlalb_lane_f32_1(svfloat32_t op1, svfloat16_t op2, svfloat16_t op3)
|
|
|
|
{
|
|
|
|
// expected-error-re@+1 {{argument value {{[0-9]+}} is outside the valid range [0, 7]}}
|
|
|
|
return SVE_ACLE_FUNC(svmlalb_lane,_f32,,)(op1, op2, op3, 8);
|
|
|
|
}
|