Viewing file:  asm_1.c (2.42 KB) -rw-r--r--
Select action/file-type:
 (+) |  (+) |  (+) | Code (+) | Session (+) |  (+) | SDB (+) |  (+) |  (+) |  (+) |  (+) |  (+) |
/* { dg-do run { target aarch64_sve_hw } } */
/* { dg-options "-O0 -ffixed-z0 -ffixed-p0" } */
#include <arm_sve.h>
#define ASM_FUNCTION(NAME, RET_TYPE, ARG_TYPE, INSN) \
extern RET_TYPE NAME (svbool_t, ARG_TYPE); \
asm( \
" .type " #NAME ", %function\n" \
#NAME ":\n" \
" " INSN "\n" \
" ret\n" \
" .size " #NAME ", .-" #NAME "\n" \
)
ASM_FUNCTION (u8_callee, uint64_t, svuint8_t,
"uaddv d0, p0, z0.b\n\tfmov x0, d0");
ASM_FUNCTION (u16_callee, uint64_t, svuint16_t,
"uaddv d0, p0, z0.h\n\tfmov x0, d0");
ASM_FUNCTION (u32_callee, uint64_t, svuint32_t,
"uaddv d0, p0, z0.s\n\tfmov x0, d0");
ASM_FUNCTION (u64_callee, uint64_t, svuint64_t,
"uaddv d0, p0, z0.d\n\tfmov x0, d0");
ASM_FUNCTION (s8_callee, int64_t, svint8_t,
"saddv d0, p0, z0.b\n\tfmov x0, d0");
ASM_FUNCTION (s16_callee, int64_t, svint16_t,
"saddv d0, p0, z0.h\n\tfmov x0, d0");
ASM_FUNCTION (s32_callee, int64_t, svint32_t,
"saddv d0, p0, z0.s\n\tfmov x0, d0");
ASM_FUNCTION (s64_callee, int64_t, svint64_t,
"uaddv d0, p0, z0.d\n\tfmov x0, d0");
ASM_FUNCTION (f16_callee, float16_t, svfloat16_t, "faddv\th0, p0, z0.h");
ASM_FUNCTION (f32_callee, float32_t, svfloat32_t, "faddv\ts0, p0, z0.s");
ASM_FUNCTION (f64_callee, float64_t, svfloat64_t, "faddv\td0, p0, z0.d");
int
main (void)
{
if (u8_callee (svptrue_pat_b8 (SV_VL7), svdup_u8 (-1)) != 7 * 0xff)
__builtin_abort ();
if (u16_callee (svptrue_pat_b16 (SV_VL6), svdup_u16 (-1)) != 6 * 0xffff)
__builtin_abort ();
if (u32_callee (svptrue_pat_b32 (SV_VL3), svdup_u32 (-1))
!= 3 * (uint64_t) (uint32_t) -1)
__builtin_abort ();
if (u64_callee (svptrue_pat_b64 (SV_VL2), svdup_u64 ((uint64_t) 1 << 33))
!= (uint64_t) 1 << 34)
__builtin_abort ();
if (s8_callee (svptrue_pat_b8 (SV_VL7), svdup_s8 (-10)) != -70)
__builtin_abort ();
if (s16_callee (svptrue_pat_b16 (SV_VL6), svdup_s16 (-14)) != -84)
__builtin_abort ();
if (s32_callee (svptrue_pat_b32 (SV_VL3), svdup_s32 (-22)) != -66)
__builtin_abort ();
if (s64_callee (svptrue_pat_b64 (SV_VL2), svdup_s64 ((int64_t) 1 << 33))
!= (int64_t) 1 << 34)
__builtin_abort ();
if (f16_callee (svptrue_pat_b16 (SV_VL5), svdup_f16 (1.0)) != 5.0)
__builtin_abort ();
if (f32_callee (svptrue_b32 (), svdup_f32 (3.0)) != 3 * svcntw ())
__builtin_abort ();
if (f64_callee (svptrue_b64 (), svdup_f64 (11.0)) != 11 * svcntd ())
__builtin_abort ();
return 0;
}
|
