#define VAR1(T, N, MAP, FLAG, A) \
AARCH64_SIMD_BUILTIN_##T##_##N##A,
+#undef ENTRY
+#define ENTRY(N, S, M, U, F) \
+ AARCH64_##N,
+
+#undef ENTRY_VHSDF
+#define ENTRY_VHSDF(NAME, SIGNATURE, UNSPEC, EXTENSIONS) \
+ AARCH64_##NAME##_f16, \
+ AARCH64_##NAME##q_f16, \
+ AARCH64_##NAME##_f32, \
+ AARCH64_##NAME##q_f32, \
+ AARCH64_##NAME##q_f64,
+
enum aarch64_builtins
{
AARCH64_BUILTIN_MIN,
AARCH64_RBIT,
AARCH64_RBITL,
AARCH64_RBITLL,
+ /* Pragma builtins. */
+ AARCH64_PRAGMA_BUILTIN_START,
+#include "aarch64-simd-pragma-builtins.def"
+ AARCH64_PRAGMA_BUILTIN_END,
/* System register builtins. */
AARCH64_RSR,
AARCH64_RSRP,
extern GTY(()) aarch64_simd_type_info aarch64_simd_types[];
+#undef ENTRY
#define ENTRY(E, M, Q, G) \
{E, "__" #E, #G "__" #E, NULL_TREE, NULL_TREE, E_##M##mode, qualifier_##Q},
struct aarch64_simd_type_info aarch64_simd_types [] = {
}
}
+enum class aarch64_builtin_signatures
+{
+ binary,
+};
+
+#undef ENTRY
+#define ENTRY(N, S, M, U, F) \
+ {#N, aarch64_builtin_signatures::S, E_##M##mode, U, F},
+
+#undef ENTRY_VHSDF
+#define ENTRY_VHSDF(NAME, SIGNATURE, UNSPEC, EXTENSIONS) \
+ ENTRY (NAME##_f16, SIGNATURE, V4HF, UNSPEC, EXTENSIONS) \
+ ENTRY (NAME##q_f16, SIGNATURE, V8HF, UNSPEC, EXTENSIONS) \
+ ENTRY (NAME##_f32, SIGNATURE, V2SF, UNSPEC, EXTENSIONS) \
+ ENTRY (NAME##q_f32, SIGNATURE, V4SF, UNSPEC, EXTENSIONS) \
+ ENTRY (NAME##q_f64, SIGNATURE, V2DF, UNSPEC, EXTENSIONS)
+
+/* Initialize pragma builtins. */
+
+struct aarch64_pragma_builtins_data
+{
+ const char *name;
+ aarch64_builtin_signatures signature;
+ machine_mode mode;
+ int unspec;
+ aarch64_feature_flags required_extensions;
+};
+
+static aarch64_pragma_builtins_data aarch64_pragma_builtins[] = {
+#include "aarch64-simd-pragma-builtins.def"
+};
+
+static tree
+aarch64_fntype (const aarch64_pragma_builtins_data &builtin_data)
+{
+ auto type = aarch64_simd_builtin_type (builtin_data.mode, qualifier_none);
+ switch (builtin_data.signature)
+ {
+ case aarch64_builtin_signatures::binary:
+ return build_function_type_list (type, type, type, NULL_TREE);
+ default:
+ gcc_unreachable ();
+ }
+}
+
+static void
+aarch64_init_pragma_builtins ()
+{
+ for (size_t i = 0; i < ARRAY_SIZE (aarch64_pragma_builtins); ++i)
+ {
+ auto data = aarch64_pragma_builtins[i];
+ auto fntype = aarch64_fntype (data);
+ auto code = AARCH64_PRAGMA_BUILTIN_START + i + 1;
+ aarch64_builtin_decls[code]
+ = aarch64_general_simulate_builtin (data.name, fntype, code);
+ }
+}
+
+/* If the builtin function with code CODE has an entry in
+ aarch64_pragma_builtins, return its entry, otherwise return null. */
+
+static const aarch64_pragma_builtins_data*
+aarch64_get_pragma_builtin (int code)
+{
+ if (!(code > AARCH64_PRAGMA_BUILTIN_START
+ && code < AARCH64_PRAGMA_BUILTIN_END))
+ return NULL;
+
+ auto idx = code - (AARCH64_PRAGMA_BUILTIN_START + 1);
+ return &aarch64_pragma_builtins[idx];
+}
+
/* Register the tuple type that contains NUM_VECTORS of the AdvSIMD type
indexed by TYPE_INDEX. */
static void
aarch64_init_simd_builtin_functions (true);
aarch64_init_simd_intrinsics ();
+ aarch64_init_pragma_builtins ();
}
static void
return aarch64_check_required_extensions (location, decl,
AARCH64_FL_MEMTAG);
+ if (auto builtin_data = aarch64_get_pragma_builtin (code))
+ {
+ auto flags = builtin_data->required_extensions;
+ return aarch64_check_required_extensions (location, decl, flags);
+ }
+
return true;
}
return ops[0].value;
}
+static rtx
+aarch64_expand_pragma_builtin (tree exp, rtx target,
+ const aarch64_pragma_builtins_data *builtin_data)
+{
+ expand_operand ops[3];
+ auto mode = builtin_data->mode;
+ auto op1 = expand_normal (CALL_EXPR_ARG (exp, 0));
+ auto op2 = expand_normal (CALL_EXPR_ARG (exp, 1));
+ create_output_operand (&ops[0], target, mode);
+ create_input_operand (&ops[1], op1, mode);
+ create_input_operand (&ops[2], op2, mode);
+
+ auto unspec = builtin_data->unspec;
+ auto icode = code_for_aarch64 (unspec, mode);
+ expand_insn (icode, 3, ops);
+
+ return target;
+}
+
/* Expand an expression EXP as fpsr or fpcr setter (depending on
UNSPEC) using MODE. */
static void
&& fcode <= AARCH64_RBITLL)
return aarch64_expand_builtin_data_intrinsic (fcode, exp, target);
+ if (auto builtin_data = aarch64_get_pragma_builtin (fcode))
+ return aarch64_expand_pragma_builtin (exp, target, builtin_data);
+
gcc_unreachable ();
}
#undef CF3
#undef CF4
#undef CF10
+#undef ENTRY_VHSDF
#undef VAR1
#undef VAR2
#undef VAR3
--- /dev/null
+/* { dg-do compile } */
+/* { dg-additional-options "-O3 -march=armv9-a+faminmax" } */
+/* { dg-final { check-function-bodies "**" "" } } */
+
+#include "arm_neon.h"
+
+/*
+** test_vamax_f16:
+** famax v0.4h, v0.4h, v1.4h
+** ret
+*/
+float16x4_t
+test_vamax_f16 (float16x4_t a, float16x4_t b)
+{
+ return vamax_f16 (a, b);
+}
+
+/*
+** test_vamaxq_f16:
+** famax v0.8h, v0.8h, v1.8h
+** ret
+*/
+float16x8_t
+test_vamaxq_f16 (float16x8_t a, float16x8_t b)
+{
+ return vamaxq_f16 (a, b);
+}
+
+/*
+** test_vamax_f32:
+** famax v0.2s, v0.2s, v1.2s
+** ret
+*/
+float32x2_t
+test_vamax_f32 (float32x2_t a, float32x2_t b)
+{
+ return vamax_f32 (a, b);
+}
+
+/*
+** test_vamaxq_f32:
+** famax v0.4s, v0.4s, v1.4s
+** ret
+*/
+float32x4_t
+test_vamaxq_f32 (float32x4_t a, float32x4_t b)
+{
+ return vamaxq_f32 (a, b);
+}
+
+/*
+** test_vamaxq_f64:
+** famax v0.2d, v0.2d, v1.2d
+** ret
+*/
+float64x2_t
+test_vamaxq_f64 (float64x2_t a, float64x2_t b)
+{
+ return vamaxq_f64 (a, b);
+}
+
+/*
+** test_vamin_f16:
+** famin v0.4h, v0.4h, v1.4h
+** ret
+*/
+float16x4_t
+test_vamin_f16 (float16x4_t a, float16x4_t b)
+{
+ return vamin_f16 (a, b);
+}
+
+/*
+** test_vaminq_f16:
+** famin v0.8h, v0.8h, v1.8h
+** ret
+*/
+float16x8_t
+test_vaminq_f16 (float16x8_t a, float16x8_t b)
+{
+ return vaminq_f16 (a, b);
+}
+
+/*
+** test_vamin_f32:
+** famin v0.2s, v0.2s, v1.2s
+** ret
+*/
+float32x2_t
+test_vamin_f32 (float32x2_t a, float32x2_t b)
+{
+ return vamin_f32 (a, b);
+}
+
+/*
+** test_vaminq_f32:
+** famin v0.4s, v0.4s, v1.4s
+** ret
+*/
+float32x4_t
+test_vaminq_f32 (float32x4_t a, float32x4_t b)
+{
+ return vaminq_f32 (a, b);
+}
+
+/*
+** test_vaminq_f64:
+** famin v0.2d, v0.2d, v1.2d
+** ret
+*/
+float64x2_t
+test_vaminq_f64 (float64x2_t a, float64x2_t b)
+{
+ return vaminq_f64 (a, b);
+}
projects / thirdparty / gcc.git / commitdiff
