2 /* { dg-options "-O2 -mavx512f -std=c99" } */
3 /* { dg-require-effective-target avx512f } */
4 /* { dg-require-effective-target c99_runtime } */
8 #include "avx512f-helper.h"
11 #define SIZE (AVX512F_LEN / 64)
12 #include "avx512f-mask-type.h"
14 #if AVX512F_LEN == 512
15 #define CMP(imm, rel) \
17 for (i = 0; i < 8; i++) \
19 dst_ref = (((int) rel) << i) | dst_ref; \
21 source1.x = _mm512_loadu_pd(s1); \
22 source2.x = _mm512_loadu_pd(s2); \
23 dst1 = _mm512_cmp_pd_mask(source1.x, source2.x, imm);\
24 dst2 = _mm512_mask_cmp_pd_mask(mask, source1.x, source2.x, imm);\
25 if (dst_ref != dst1) abort(); \
26 if ((dst_ref & mask) != dst2) abort();
29 #if AVX512F_LEN == 256
31 #define CMP(imm, rel) \
33 for (i = 0; i < 4; i++) \
35 dst_ref = (((int) rel) << i) | dst_ref; \
37 source1.x = _mm256_loadu_pd(s1); \
38 source2.x = _mm256_loadu_pd(s2); \
39 dst1 = _mm256_cmp_pd_mask(source1.x, source2.x, imm);\
40 dst2 = _mm256_mask_cmp_pd_mask(mask, source1.x, source2.x, imm);\
41 if (dst_ref != dst1) abort(); \
42 if ((dst_ref & mask) != dst2) abort();
45 #if AVX512F_LEN == 128
47 #define CMP(imm, rel) \
49 for (i = 0; i < 2; i++) \
51 dst_ref = (((int) rel) << i) | dst_ref; \
53 source1.x = _mm_loadu_pd(s1); \
54 source2.x = _mm_loadu_pd(s2); \
55 dst1 = _mm_cmp_pd_mask(source1.x, source2.x, imm);\
56 dst2 = _mm_mask_cmp_pd_mask(mask, source1.x, source2.x, imm);\
57 if (dst_ref != dst1) abort(); \
58 if ((dst_ref & mask) != dst2) abort();
64 UNION_TYPE (AVX512F_LEN
, d
) source1
, source2
;
65 MASK_TYPE dst1
, dst2
, dst_ref
;
66 MASK_TYPE mask
= MASK_VALUE
;
68 double s1
[8]={2134.3343, 6678.346, 453.345635, 54646.464,
69 231.23311, 5674.455, 111.111111, 23241.152};
70 double s2
[8]={41124.234, 6678.346, 8653.65635, 856.43576,
71 231.23311, 4646.123, 111.111111, 124.12455};
73 CMP(_CMP_EQ_OQ
, !isunordered(s1
[i
], s2
[i
]) && s1
[i
] == s2
[i
]);
74 CMP(_CMP_LT_OS
, !isunordered(s1
[i
], s2
[i
]) && s1
[i
] < s2
[i
]);
75 CMP(_CMP_LE_OS
, !isunordered(s1
[i
], s2
[i
]) && s1
[i
] <= s2
[i
]);
76 CMP(_CMP_UNORD_Q
, isunordered(s1
[i
], s2
[i
]));
77 CMP(_CMP_NEQ_UQ
, isunordered(s1
[i
], s2
[i
]) || s1
[i
] != s2
[i
]);
78 CMP(_CMP_NLT_US
, isunordered(s1
[i
], s2
[i
]) || s1
[i
] >= s2
[i
]);
79 CMP(_CMP_NLE_US
, isunordered(s1
[i
], s2
[i
]) || s1
[i
] > s2
[i
]);
80 CMP(_CMP_ORD_Q
, !isunordered(s1
[i
], s2
[i
]));
82 CMP(_CMP_EQ_UQ
, isunordered(s1
[i
], s2
[i
]) || s1
[i
] == s2
[i
]);
83 CMP(_CMP_NGE_US
, isunordered(s1
[i
], s2
[i
]) || s1
[i
] < s2
[i
]);
84 CMP(_CMP_NGT_US
, isunordered(s1
[i
], s2
[i
]) || s1
[i
] <= s2
[i
]);
86 CMP(_CMP_FALSE_OQ
, 0);
87 CMP(_CMP_NEQ_OQ
, !isunordered(s1
[i
], s2
[i
]) && s1
[i
] != s2
[i
]);
88 CMP(_CMP_GE_OS
, !isunordered(s1
[i
], s2
[i
]) && s1
[i
] >= s2
[i
]);
89 CMP(_CMP_GT_OS
, !isunordered(s1
[i
], s2
[i
]) && s1
[i
] > s2
[i
]);
92 CMP(_CMP_EQ_OS
, !isunordered(s1
[i
], s2
[i
]) && s1
[i
] == s2
[i
]);
93 CMP(_CMP_LT_OQ
, !isunordered(s1
[i
], s2
[i
]) && s1
[i
] < s2
[i
]);
94 CMP(_CMP_LE_OQ
, !isunordered(s1
[i
], s2
[i
]) && s1
[i
] <= s2
[i
]);
95 CMP(_CMP_UNORD_S
, isunordered(s1
[i
], s2
[i
]));
96 CMP(_CMP_NEQ_US
, isunordered(s1
[i
], s2
[i
]) || s1
[i
] != s2
[i
]);
97 CMP(_CMP_NLT_UQ
, isunordered(s1
[i
], s2
[i
]) || s1
[i
] >= s2
[i
]);
98 CMP(_CMP_NLE_UQ
, isunordered(s1
[i
], s2
[i
]) || s1
[i
] > s2
[i
]);
99 CMP(_CMP_ORD_S
, !isunordered(s1
[i
], s2
[i
]));
100 CMP(_CMP_EQ_US
, isunordered(s1
[i
], s2
[i
]) || s1
[i
] == s2
[i
]);
101 CMP(_CMP_NGE_UQ
, isunordered(s1
[i
], s2
[i
]) || s1
[i
] < s2
[i
]);
102 CMP(_CMP_NGT_UQ
, isunordered(s1
[i
], s2
[i
]) || s1
[i
] <= s2
[i
]);
103 CMP(_CMP_FALSE_OS
, 0);
104 CMP(_CMP_NEQ_OS
, !isunordered(s1
[i
], s2
[i
]) && s1
[i
] != s2
[i
]);
105 CMP(_CMP_GE_OQ
, !isunordered(s1
[i
], s2
[i
]) && s1
[i
] >= s2
[i
]);
106 CMP(_CMP_GT_OQ
, !isunordered(s1
[i
], s2
[i
]) && s1
[i
] > s2
[i
]);