1178479Sjb/* { dg-do run } */ 2178479Sjb/* { dg-require-effective-target avx } */ 3178479Sjb/* { dg-require-effective-target c99_runtime } */ 4178479Sjb/* { dg-options "-O2 -mavx -std=c99" } */ 5178479Sjb 6178479Sjb#include "avx-check.h" 7178479Sjb#include <math.h> 8178479Sjb 9178479Sjbdouble s1[4]={2134.3343,6678.346,453.345635,54646.464356}; 10178479Sjbdouble s2[4]={41124.234,6678.346,8653.65635,856.43576}; 11178479Sjblong long e[4]; 12178479Sjb 13178479Sjbunion 14178479Sjb{ 15178479Sjb double d[4]; 16178479Sjb long long ll[4]; 17178479Sjb}d; 18178479Sjb 19178479Sjbvoid check(unsigned imm, char *id) 20178479Sjb{ 21178479Sjb if(checkVl(d.ll, e, 4)){ 22210767Srpaulo printf("mm256_cmp_pd(%s: 0x%x) FAILED\n", id, imm); 23178479Sjb } 24178479Sjb} 25178479Sjb 26237624Spfg#define CMP(imm, rel) \ 27237624Spfg for (i = 0; i < 4; i++) e[i] = rel ? -1 : 0; \ 28250574Smarkj source1 = _mm256_loadu_pd(s1); \ 29237624Spfg source2 = _mm256_loadu_pd(s2); \ 30237624Spfg dest = _mm256_cmp_pd(source1, source2, imm); \ 31178479Sjb _mm256_storeu_pd(d.d, dest); \ 32178479Sjb check(imm, "" #imm ""); 33178479Sjb 34178479Sjbstatic void 35178479Sjbavx_test () 36178479Sjb{ 37178479Sjb __m256d source1, source2, dest; 38178576Sjb int i; 39178479Sjb 40178576Sjb CMP(_CMP_EQ_OQ, !isunordered(s1[i], s2[i]) && s1[i] == s2[i]); 41178479Sjb CMP(_CMP_LT_OS, !isunordered(s1[i], s2[i]) && s1[i] < s2[i]); 42250574Smarkj CMP(_CMP_LE_OS, !isunordered(s1[i], s2[i]) && s1[i] <= s2[i]); 43211554Srpaulo CMP(_CMP_UNORD_Q, isunordered(s1[i], s2[i])); 44211554Srpaulo CMP(_CMP_NEQ_UQ, isunordered(s1[i], s2[i]) || s1[i] != s2[i]); 45211554Srpaulo CMP(_CMP_NLT_US, isunordered(s1[i], s2[i]) || s1[i] >= s2[i]); 46178479Sjb CMP(_CMP_NLE_US, isunordered(s1[i], s2[i]) || s1[i] > s2[i]); 47178479Sjb CMP(_CMP_ORD_Q, !isunordered(s1[i], s2[i])); 48178479Sjb 49178479Sjb CMP(_CMP_EQ_UQ, isunordered(s1[i], s2[i]) || s1[i] == s2[i]); 50178479Sjb CMP(_CMP_NGE_US, isunordered(s1[i], s2[i]) || s1[i] < s2[i]); 51178479Sjb CMP(_CMP_NGT_US, isunordered(s1[i], s2[i]) || s1[i] <= s2[i]); 52178479Sjb 53178479Sjb CMP(_CMP_FALSE_OQ, 0); 54178479Sjb CMP(_CMP_NEQ_OQ, !isunordered(s1[i], s2[i]) && s1[i] != s2[i]); 55178479Sjb CMP(_CMP_GE_OS, !isunordered(s1[i], s2[i]) && s1[i] >= s2[i]); 56178479Sjb CMP(_CMP_GT_OS, !isunordered(s1[i], s2[i]) && s1[i] > s2[i]); 57178479Sjb CMP(_CMP_TRUE_UQ, 1); 58178479Sjb 59178479Sjb CMP(_CMP_EQ_OS, !isunordered(s1[i], s2[i]) && s1[i] == s2[i]); 60178479Sjb CMP(_CMP_LT_OQ, !isunordered(s1[i], s2[i]) && s1[i] < s2[i]); 61178479Sjb CMP(_CMP_LE_OQ, !isunordered(s1[i], s2[i]) && s1[i] <= s2[i]); 62178479Sjb CMP(_CMP_UNORD_S, isunordered(s1[i], s2[i])); 63178479Sjb CMP(_CMP_NEQ_US, isunordered(s1[i], s2[i]) || s1[i] != s2[i]); 64178479Sjb CMP(_CMP_NLT_UQ, isunordered(s1[i], s2[i]) || s1[i] >= s2[i]); 65178479Sjb CMP(_CMP_NLE_UQ, isunordered(s1[i], s2[i]) || s1[i] > s2[i]); 66178479Sjb CMP(_CMP_ORD_S, !isunordered(s1[i], s2[i])); 67178479Sjb CMP(_CMP_EQ_US, isunordered(s1[i], s2[i]) || s1[i] == s2[i]); 68178479Sjb CMP(_CMP_NGE_UQ, isunordered(s1[i], s2[i]) || s1[i] < s2[i]); 69178479Sjb CMP(_CMP_NGT_UQ, isunordered(s1[i], s2[i]) || s1[i] <= s2[i]); 70178479Sjb CMP(_CMP_FALSE_OS, 0); 71178479Sjb CMP(_CMP_NEQ_OS, !isunordered(s1[i], s2[i]) && s1[i] != s2[i]); 72178479Sjb CMP(_CMP_GE_OQ, !isunordered(s1[i], s2[i]) && s1[i] >= s2[i]); 73178479Sjb CMP(_CMP_GT_OQ, !isunordered(s1[i], s2[i]) && s1[i] > s2[i]); 74178479Sjb CMP(_CMP_TRUE_US, 1); 75178479Sjb 76178479Sjb} 77178479Sjb