@@ -46,20 +46,19 @@ let open_test_file dir name =
failwith ("Could not create test source file " ^ name ^ ": " ^ str)
(* Emit prologue code to a test source file. *)
-let emit_prologue chan test_name effective_target =
+let emit_prologue chan test_name effective_target compile_test_optim =
Printf.fprintf chan "/* Test the `%s' ARM Neon intrinsic. */\n" test_name;
Printf.fprintf chan "/* This file was autogenerated by neon-testgen. */\n\n";
Printf.fprintf chan "/* { dg-do assemble } */\n";
Printf.fprintf chan "/* { dg-require-effective-target %s_ok } */\n"
effective_target;
- Printf.fprintf chan "/* { dg-options \"-save-temps -O0\" } */\n";
+ Printf.fprintf chan "/* { dg-options \"-save-temps %s\" } */\n" compile_test_optim;
Printf.fprintf chan "/* { dg-add-options %s } */\n" effective_target;
- Printf.fprintf chan "\n#include \"arm_neon.h\"\n\n";
- Printf.fprintf chan "void test_%s (void)\n{\n" test_name
+ Printf.fprintf chan "\n#include \"arm_neon.h\"\n\n"
-(* Emit declarations of local variables that are going to be passed
+(* Emit declarations of variables that are going to be passed
to an intrinsic, together with one to take a returned value if needed. *)
-let emit_automatics chan c_types features =
+let emit_variables chan c_types features spaces =
let emit () =
ignore (
List.fold_left (fun arg_number -> fun (flags, ty) ->
@@ -69,8 +68,8 @@ let emit_automatics chan c_types features =
(* Const arguments to builtins are directly
written in as constants. *)
if not (List.mem Const flags) then
- Printf.fprintf chan " %s %sarg%d_%s;\n"
- ty pointer_bit arg_number ty;
+ Printf.fprintf chan "%s%s %sarg%d_%s;\n"
+ spaces ty pointer_bit arg_number ty;
arg_number + 1)
0 (List.tl c_types))
in
@@ -81,13 +80,13 @@ let emit_automatics chan c_types features =
allocation for vget_low tests or they fail because of copy
elimination. *)
((if List.mem Fixed_vector_reg features then
- Printf.fprintf chan " register %s out_%s asm (\"d18\");\n"
- return_ty return_ty
+ Printf.fprintf chan "%sregister %s out_%s asm (\"d18\");\n"
+ spaces return_ty return_ty
else if List.mem Fixed_core_reg features then
- Printf.fprintf chan " register %s out_%s asm (\"r0\");\n"
- return_ty return_ty
+ Printf.fprintf chan "%sregister %s out_%s asm (\"r0\");\n"
+ spaces return_ty return_ty
else
- Printf.fprintf chan " %s out_%s;\n" return_ty return_ty);
+ Printf.fprintf chan "%s%s out_%s;\n" spaces return_ty return_ty);
emit ())
end else
(* The intrinsic does not return a value. *)
@@ -173,6 +172,17 @@ let effective_target features =
| _ -> assert false
with Not_found -> "arm_neon"
+(* Work out what the testcase optimization level should be, default to -O0. *)
+let compile_test_optim features =
+ try
+ match List.find (fun feature ->
+ match feature with Compiler_optim _ -> true
+ | _ -> false)
+ features with
+ Compiler_optim opt -> opt
+ | _ -> assert false
+ with Not_found -> "-O0"
+
(* Given an intrinsic shape, produce a regexp that will match
the right-hand sides of instructions generated by an intrinsic of
that shape. *)
@@ -280,12 +290,22 @@ let test_intrinsic dir opcode features shape name munge elt_ty =
"!?\\(\\[ \t\\]+@\\[a-zA-Z0-9 \\]+\\)?\\n")
(analyze_all_shapes features shape analyze_shape)
in
- let effective_target = effective_target features
+ let effective_target = effective_target features in
+ let compile_test_optim = compile_test_optim features
in
(* Emit file and function prologues. *)
- emit_prologue chan test_name effective_target;
- (* Emit local variable declarations. *)
- emit_automatics chan c_types features;
+ emit_prologue chan test_name effective_target compile_test_optim;
+
+ if (compare compile_test_optim "-O0") <> 0 then
+ (* Emit variable declarations. *)
+ emit_variables chan c_types features "";
+
+ Printf.fprintf chan "void test_%s (void)\n{\n" test_name;
+
+ if compare compile_test_optim "-O0" = 0 then
+ (* Emit variable declarations. *)
+ emit_variables chan c_types features " ";
+
Printf.fprintf chan "\n";
(* Emit the call to the intrinsic. *)
emit_call chan const_valuator c_types name elt_ty;
@@ -294,6 +294,8 @@ type features =
(* Mark that the intrinsic requires a particular bit in __ARM_FP to
be set. *)
| Requires_FP_bit of int
+ (* Compiler optimization level for the test. *)
+ | Compiler_optim of string
exception MixedMode of elts * elts
@@ -1941,18 +1943,18 @@ let ops =
Veor, [], All (3, Qreg), "veorQ", notype_2, su_8_64;
(* Bic (And-not). *)
- Vbic, [], All (3, Dreg), "vbic", notype_2, su_8_32;
- Vbic, [No_op], All (3, Dreg), "vbic", notype_2, [S64; U64];
- Vbic, [], All (3, Qreg), "vbicQ", notype_2, su_8_64;
+ Vbic, [Compiler_optim "-O2"], All (3, Dreg), "vbic", notype_2, su_8_32;
+ Vbic, [No_op; Compiler_optim "-O2"], All (3, Dreg), "vbic", notype_2, [S64; U64];
+ Vbic, [Compiler_optim "-O2"], All (3, Qreg), "vbicQ", notype_2, su_8_64;
(* Or-not. *)
- Vorn, [], All (3, Dreg), "vorn", notype_2, su_8_32;
- Vorn, [No_op], All (3, Dreg), "vorn", notype_2, [S64; U64];
- Vorn, [], All (3, Qreg), "vornQ", notype_2, su_8_64;
+ Vorn, [Compiler_optim "-O2"], All (3, Dreg), "vorn", notype_2, su_8_32;
+ Vorn, [No_op; Compiler_optim "-O2"], All (3, Dreg), "vorn", notype_2, [S64; U64];
+ Vorn, [Compiler_optim "-O2"], All (3, Qreg), "vornQ", notype_2, su_8_64;
]
let type_in_crypto_only t
- = (t == P64) or (t == P128)
+ = (t == P64) || (t == P128)
let cross_product s1 s2
= List.filter (fun (e, e') -> e <> e')
@@ -1963,7 +1965,7 @@ let reinterp =
let casts = cross_product elems elems in
List.map
(fun (convto, convfrom) ->
- Vreinterp, (if (type_in_crypto_only convto) or (type_in_crypto_only convfrom)
+ Vreinterp, (if (type_in_crypto_only convto) || (type_in_crypto_only convfrom)
then [Requires_feature "CRYPTO"] else []) @ [No_op], Use_operands [| Dreg; Dreg |],
"vreinterpret", conv_1, [Cast (convto, convfrom)])
casts
@@ -1973,7 +1975,7 @@ let reinterpq =
let casts = cross_product elems elems in
List.map
(fun (convto, convfrom) ->
- Vreinterp, (if (type_in_crypto_only convto) or (type_in_crypto_only convfrom)
+ Vreinterp, (if (type_in_crypto_only convto) || (type_in_crypto_only convfrom)
then [Requires_feature "CRYPTO"] else []) @ [No_op], Use_operands [| Qreg; Qreg |],
"vreinterpretQ", conv_1, [Cast (convto, convfrom)])
casts
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+int16x8_t out_int16x8_t;
+int16x8_t arg0_int16x8_t;
+int16x8_t arg1_int16x8_t;
void test_vbicQs16 (void)
{
- int16x8_t out_int16x8_t;
- int16x8_t arg0_int16x8_t;
- int16x8_t arg1_int16x8_t;
out_int16x8_t = vbicq_s16 (arg0_int16x8_t, arg1_int16x8_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+int32x4_t out_int32x4_t;
+int32x4_t arg0_int32x4_t;
+int32x4_t arg1_int32x4_t;
void test_vbicQs32 (void)
{
- int32x4_t out_int32x4_t;
- int32x4_t arg0_int32x4_t;
- int32x4_t arg1_int32x4_t;
out_int32x4_t = vbicq_s32 (arg0_int32x4_t, arg1_int32x4_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+int64x2_t out_int64x2_t;
+int64x2_t arg0_int64x2_t;
+int64x2_t arg1_int64x2_t;
void test_vbicQs64 (void)
{
- int64x2_t out_int64x2_t;
- int64x2_t arg0_int64x2_t;
- int64x2_t arg1_int64x2_t;
out_int64x2_t = vbicq_s64 (arg0_int64x2_t, arg1_int64x2_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+int8x16_t out_int8x16_t;
+int8x16_t arg0_int8x16_t;
+int8x16_t arg1_int8x16_t;
void test_vbicQs8 (void)
{
- int8x16_t out_int8x16_t;
- int8x16_t arg0_int8x16_t;
- int8x16_t arg1_int8x16_t;
out_int8x16_t = vbicq_s8 (arg0_int8x16_t, arg1_int8x16_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+uint16x8_t out_uint16x8_t;
+uint16x8_t arg0_uint16x8_t;
+uint16x8_t arg1_uint16x8_t;
void test_vbicQu16 (void)
{
- uint16x8_t out_uint16x8_t;
- uint16x8_t arg0_uint16x8_t;
- uint16x8_t arg1_uint16x8_t;
out_uint16x8_t = vbicq_u16 (arg0_uint16x8_t, arg1_uint16x8_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+uint32x4_t out_uint32x4_t;
+uint32x4_t arg0_uint32x4_t;
+uint32x4_t arg1_uint32x4_t;
void test_vbicQu32 (void)
{
- uint32x4_t out_uint32x4_t;
- uint32x4_t arg0_uint32x4_t;
- uint32x4_t arg1_uint32x4_t;
out_uint32x4_t = vbicq_u32 (arg0_uint32x4_t, arg1_uint32x4_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+uint64x2_t out_uint64x2_t;
+uint64x2_t arg0_uint64x2_t;
+uint64x2_t arg1_uint64x2_t;
void test_vbicQu64 (void)
{
- uint64x2_t out_uint64x2_t;
- uint64x2_t arg0_uint64x2_t;
- uint64x2_t arg1_uint64x2_t;
out_uint64x2_t = vbicq_u64 (arg0_uint64x2_t, arg1_uint64x2_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+uint8x16_t out_uint8x16_t;
+uint8x16_t arg0_uint8x16_t;
+uint8x16_t arg1_uint8x16_t;
void test_vbicQu8 (void)
{
- uint8x16_t out_uint8x16_t;
- uint8x16_t arg0_uint8x16_t;
- uint8x16_t arg1_uint8x16_t;
out_uint8x16_t = vbicq_u8 (arg0_uint8x16_t, arg1_uint8x16_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+int16x4_t out_int16x4_t;
+int16x4_t arg0_int16x4_t;
+int16x4_t arg1_int16x4_t;
void test_vbics16 (void)
{
- int16x4_t out_int16x4_t;
- int16x4_t arg0_int16x4_t;
- int16x4_t arg1_int16x4_t;
out_int16x4_t = vbic_s16 (arg0_int16x4_t, arg1_int16x4_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+int32x2_t out_int32x2_t;
+int32x2_t arg0_int32x2_t;
+int32x2_t arg1_int32x2_t;
void test_vbics32 (void)
{
- int32x2_t out_int32x2_t;
- int32x2_t arg0_int32x2_t;
- int32x2_t arg1_int32x2_t;
out_int32x2_t = vbic_s32 (arg0_int32x2_t, arg1_int32x2_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+int64x1_t out_int64x1_t;
+int64x1_t arg0_int64x1_t;
+int64x1_t arg1_int64x1_t;
void test_vbics64 (void)
{
- int64x1_t out_int64x1_t;
- int64x1_t arg0_int64x1_t;
- int64x1_t arg1_int64x1_t;
out_int64x1_t = vbic_s64 (arg0_int64x1_t, arg1_int64x1_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+int8x8_t out_int8x8_t;
+int8x8_t arg0_int8x8_t;
+int8x8_t arg1_int8x8_t;
void test_vbics8 (void)
{
- int8x8_t out_int8x8_t;
- int8x8_t arg0_int8x8_t;
- int8x8_t arg1_int8x8_t;
out_int8x8_t = vbic_s8 (arg0_int8x8_t, arg1_int8x8_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+uint16x4_t out_uint16x4_t;
+uint16x4_t arg0_uint16x4_t;
+uint16x4_t arg1_uint16x4_t;
void test_vbicu16 (void)
{
- uint16x4_t out_uint16x4_t;
- uint16x4_t arg0_uint16x4_t;
- uint16x4_t arg1_uint16x4_t;
out_uint16x4_t = vbic_u16 (arg0_uint16x4_t, arg1_uint16x4_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+uint32x2_t out_uint32x2_t;
+uint32x2_t arg0_uint32x2_t;
+uint32x2_t arg1_uint32x2_t;
void test_vbicu32 (void)
{
- uint32x2_t out_uint32x2_t;
- uint32x2_t arg0_uint32x2_t;
- uint32x2_t arg1_uint32x2_t;
out_uint32x2_t = vbic_u32 (arg0_uint32x2_t, arg1_uint32x2_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+uint64x1_t out_uint64x1_t;
+uint64x1_t arg0_uint64x1_t;
+uint64x1_t arg1_uint64x1_t;
void test_vbicu64 (void)
{
- uint64x1_t out_uint64x1_t;
- uint64x1_t arg0_uint64x1_t;
- uint64x1_t arg1_uint64x1_t;
out_uint64x1_t = vbic_u64 (arg0_uint64x1_t, arg1_uint64x1_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+uint8x8_t out_uint8x8_t;
+uint8x8_t arg0_uint8x8_t;
+uint8x8_t arg1_uint8x8_t;
void test_vbicu8 (void)
{
- uint8x8_t out_uint8x8_t;
- uint8x8_t arg0_uint8x8_t;
- uint8x8_t arg1_uint8x8_t;
out_uint8x8_t = vbic_u8 (arg0_uint8x8_t, arg1_uint8x8_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+int16x8_t out_int16x8_t;
+int16x8_t arg0_int16x8_t;
+int16x8_t arg1_int16x8_t;
void test_vornQs16 (void)
{
- int16x8_t out_int16x8_t;
- int16x8_t arg0_int16x8_t;
- int16x8_t arg1_int16x8_t;
out_int16x8_t = vornq_s16 (arg0_int16x8_t, arg1_int16x8_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+int32x4_t out_int32x4_t;
+int32x4_t arg0_int32x4_t;
+int32x4_t arg1_int32x4_t;
void test_vornQs32 (void)
{
- int32x4_t out_int32x4_t;
- int32x4_t arg0_int32x4_t;
- int32x4_t arg1_int32x4_t;
out_int32x4_t = vornq_s32 (arg0_int32x4_t, arg1_int32x4_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+int64x2_t out_int64x2_t;
+int64x2_t arg0_int64x2_t;
+int64x2_t arg1_int64x2_t;
void test_vornQs64 (void)
{
- int64x2_t out_int64x2_t;
- int64x2_t arg0_int64x2_t;
- int64x2_t arg1_int64x2_t;
out_int64x2_t = vornq_s64 (arg0_int64x2_t, arg1_int64x2_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+int8x16_t out_int8x16_t;
+int8x16_t arg0_int8x16_t;
+int8x16_t arg1_int8x16_t;
void test_vornQs8 (void)
{
- int8x16_t out_int8x16_t;
- int8x16_t arg0_int8x16_t;
- int8x16_t arg1_int8x16_t;
out_int8x16_t = vornq_s8 (arg0_int8x16_t, arg1_int8x16_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+uint16x8_t out_uint16x8_t;
+uint16x8_t arg0_uint16x8_t;
+uint16x8_t arg1_uint16x8_t;
void test_vornQu16 (void)
{
- uint16x8_t out_uint16x8_t;
- uint16x8_t arg0_uint16x8_t;
- uint16x8_t arg1_uint16x8_t;
out_uint16x8_t = vornq_u16 (arg0_uint16x8_t, arg1_uint16x8_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+uint32x4_t out_uint32x4_t;
+uint32x4_t arg0_uint32x4_t;
+uint32x4_t arg1_uint32x4_t;
void test_vornQu32 (void)
{
- uint32x4_t out_uint32x4_t;
- uint32x4_t arg0_uint32x4_t;
- uint32x4_t arg1_uint32x4_t;
out_uint32x4_t = vornq_u32 (arg0_uint32x4_t, arg1_uint32x4_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+uint64x2_t out_uint64x2_t;
+uint64x2_t arg0_uint64x2_t;
+uint64x2_t arg1_uint64x2_t;
void test_vornQu64 (void)
{
- uint64x2_t out_uint64x2_t;
- uint64x2_t arg0_uint64x2_t;
- uint64x2_t arg1_uint64x2_t;
out_uint64x2_t = vornq_u64 (arg0_uint64x2_t, arg1_uint64x2_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+uint8x16_t out_uint8x16_t;
+uint8x16_t arg0_uint8x16_t;
+uint8x16_t arg1_uint8x16_t;
void test_vornQu8 (void)
{
- uint8x16_t out_uint8x16_t;
- uint8x16_t arg0_uint8x16_t;
- uint8x16_t arg1_uint8x16_t;
out_uint8x16_t = vornq_u8 (arg0_uint8x16_t, arg1_uint8x16_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+int16x4_t out_int16x4_t;
+int16x4_t arg0_int16x4_t;
+int16x4_t arg1_int16x4_t;
void test_vorns16 (void)
{
- int16x4_t out_int16x4_t;
- int16x4_t arg0_int16x4_t;
- int16x4_t arg1_int16x4_t;
out_int16x4_t = vorn_s16 (arg0_int16x4_t, arg1_int16x4_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+int32x2_t out_int32x2_t;
+int32x2_t arg0_int32x2_t;
+int32x2_t arg1_int32x2_t;
void test_vorns32 (void)
{
- int32x2_t out_int32x2_t;
- int32x2_t arg0_int32x2_t;
- int32x2_t arg1_int32x2_t;
out_int32x2_t = vorn_s32 (arg0_int32x2_t, arg1_int32x2_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+int64x1_t out_int64x1_t;
+int64x1_t arg0_int64x1_t;
+int64x1_t arg1_int64x1_t;
void test_vorns64 (void)
{
- int64x1_t out_int64x1_t;
- int64x1_t arg0_int64x1_t;
- int64x1_t arg1_int64x1_t;
out_int64x1_t = vorn_s64 (arg0_int64x1_t, arg1_int64x1_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+int8x8_t out_int8x8_t;
+int8x8_t arg0_int8x8_t;
+int8x8_t arg1_int8x8_t;
void test_vorns8 (void)
{
- int8x8_t out_int8x8_t;
- int8x8_t arg0_int8x8_t;
- int8x8_t arg1_int8x8_t;
out_int8x8_t = vorn_s8 (arg0_int8x8_t, arg1_int8x8_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+uint16x4_t out_uint16x4_t;
+uint16x4_t arg0_uint16x4_t;
+uint16x4_t arg1_uint16x4_t;
void test_vornu16 (void)
{
- uint16x4_t out_uint16x4_t;
- uint16x4_t arg0_uint16x4_t;
- uint16x4_t arg1_uint16x4_t;
out_uint16x4_t = vorn_u16 (arg0_uint16x4_t, arg1_uint16x4_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+uint32x2_t out_uint32x2_t;
+uint32x2_t arg0_uint32x2_t;
+uint32x2_t arg1_uint32x2_t;
void test_vornu32 (void)
{
- uint32x2_t out_uint32x2_t;
- uint32x2_t arg0_uint32x2_t;
- uint32x2_t arg1_uint32x2_t;
out_uint32x2_t = vorn_u32 (arg0_uint32x2_t, arg1_uint32x2_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+uint64x1_t out_uint64x1_t;
+uint64x1_t arg0_uint64x1_t;
+uint64x1_t arg1_uint64x1_t;
void test_vornu64 (void)
{
- uint64x1_t out_uint64x1_t;
- uint64x1_t arg0_uint64x1_t;
- uint64x1_t arg1_uint64x1_t;
out_uint64x1_t = vorn_u64 (arg0_uint64x1_t, arg1_uint64x1_t);
}
@@ -3,16 +3,16 @@
/* { dg-do assemble } */
/* { dg-require-effective-target arm_neon_ok } */
-/* { dg-options "-save-temps -O0" } */
+/* { dg-options "-save-temps -O2" } */
/* { dg-add-options arm_neon } */
#include "arm_neon.h"
+uint8x8_t out_uint8x8_t;
+uint8x8_t arg0_uint8x8_t;
+uint8x8_t arg1_uint8x8_t;
void test_vornu8 (void)
{
- uint8x8_t out_uint8x8_t;
- uint8x8_t arg0_uint8x8_t;
- uint8x8_t arg1_uint8x8_t;
out_uint8x8_t = vorn_u8 (arg0_uint8x8_t, arg1_uint8x8_t);
}