1 #include <arm_neon.h> 2 #include "arm-neon-ref.h" 3 #include "compute-ref-data.h" 4 5 /* Expected results splitted in several chunks. */ 6 /* Chunk 0. */ 7 VECT_VAR_DECL(expected0,int,8,8) [] = { 0xf0, 0xf1, 0xf2, 0xf3, 8 0xf4, 0xf5, 0xf6, 0xf7 }; 9 VECT_VAR_DECL(expected0,int,16,4) [] = { 0xfff0, 0xfff1, 10 0xfff2, 0xfff3 }; 11 VECT_VAR_DECL(expected0,int,32,2) [] = { 0xfffffff0, 0xfffffff1 }; 12 VECT_VAR_DECL(expected0,uint,8,8) [] = { 0xf0, 0xf1, 0xf2, 0xf3, 13 0xf4, 0xf5, 0xf6, 0xf7 }; 14 VECT_VAR_DECL(expected0,uint,16,4) [] = { 0xfff0, 0xfff1, 15 0xfff2, 0xfff3 }; 16 VECT_VAR_DECL(expected0,uint,32,2) [] = { 0xfffffff0, 17 0xfffffff1 }; 18 VECT_VAR_DECL(expected0,poly,8,8) [] = { 0xf0, 0xf1, 0xf2, 0xf3, 19 0xf4, 0xf5, 0xf6, 0xf7 }; 20 VECT_VAR_DECL(expected0,poly,16,4) [] = { 0xfff0, 0xfff1, 21 0xfff2, 0xfff3 }; 22 #if defined (FP16_SUPPORTED) 23 VECT_VAR_DECL (expected0, hfloat, 16, 4) [] = { 0xcc00, 0xcb80, 24 0xcb00, 0xca80 }; 25 #endif 26 VECT_VAR_DECL(expected0,hfloat,32,2) [] = { 0xc1800000, 0xc1700000 }; 27 VECT_VAR_DECL(expected0,int,8,16) [] = { 0xf0, 0xf1, 0xf2, 0xf3, 28 0xf4, 0xf5, 0xf6, 0xf7, 29 0xf8, 0xf9, 0xfa, 0xfb, 30 0xfc, 0xfd, 0xfe, 0xff }; 31 VECT_VAR_DECL(expected0,int,16,8) [] = { 0xfff0, 0xfff1, 32 0xfff2, 0xfff3, 33 0xfff4, 0xfff5, 34 0xfff6, 0xfff7 }; 35 VECT_VAR_DECL(expected0,int,32,4) [] = { 0xfffffff0, 0xfffffff1, 36 0xfffffff2, 0xfffffff3 }; 37 VECT_VAR_DECL(expected0,uint,8,16) [] = { 0xf0, 0xf1, 0xf2, 0xf3, 38 0xf4, 0xf5, 0xf6, 0xf7, 39 0xf8, 0xf9, 0xfa, 0xfb, 40 0xfc, 0xfd, 0xfe, 0xff }; 41 VECT_VAR_DECL(expected0,uint,16,8) [] = { 0xfff0, 0xfff1, 42 0xfff2, 0xfff3, 43 0xfff4, 0xfff5, 44 0xfff6, 0xfff7 }; 45 VECT_VAR_DECL(expected0,uint,32,4) [] = { 0xfffffff0, 0xfffffff1, 46 0xfffffff2, 0xfffffff3 }; 47 VECT_VAR_DECL(expected0,poly,8,16) [] = { 0xf0, 0xf1, 0xf2, 0xf3, 48 0xf4, 0xf5, 0xf6, 0xf7, 49 0xf8, 0xf9, 0xfa, 0xfb, 50 0xfc, 0xfd, 0xfe, 0xff }; 51 VECT_VAR_DECL(expected0,poly,16,8) [] = { 0xfff0, 0xfff1, 52 0xfff2, 0xfff3, 53 0xfff4, 0xfff5, 54 0xfff6, 0xfff7 }; 55 #if defined (FP16_SUPPORTED) 56 VECT_VAR_DECL (expected0, hfloat, 16, 8) [] = { 0xcc00, 0xcb80, 57 0xcb00, 0xca80, 58 0xca00, 0xc980, 59 0xc900, 0xc880 }; 60 #endif 61 VECT_VAR_DECL(expected0,hfloat,32,4) [] = { 0xc1800000, 0xc1700000, 62 0xc1600000, 0xc1500000 }; 63 64 /* Chunk 1. */ 65 VECT_VAR_DECL(expected1,int,8,8) [] = { 0x11, 0x11, 0x11, 0x11, 66 0x11, 0x11, 0x11, 0x11 }; 67 VECT_VAR_DECL(expected1,int,16,4) [] = { 0x22, 0x22, 0x22, 0x22 }; 68 VECT_VAR_DECL(expected1,int,32,2) [] = { 0x33, 0x33 }; 69 VECT_VAR_DECL(expected1,uint,8,8) [] = { 0x55, 0x55, 0x55, 0x55, 70 0x55, 0x55, 0x55, 0x55 }; 71 VECT_VAR_DECL(expected1,uint,16,4) [] = { 0x66, 0x66, 0x66, 0x66 }; 72 VECT_VAR_DECL(expected1,uint,32,2) [] = { 0x77, 0x77 }; 73 VECT_VAR_DECL(expected1,poly,8,8) [] = { 0x55, 0x55, 0x55, 0x55, 74 0x55, 0x55, 0x55, 0x55 }; 75 VECT_VAR_DECL(expected1,poly,16,4) [] = { 0x66, 0x66, 0x66, 0x66 }; 76 #if defined (FP16_SUPPORTED) 77 VECT_VAR_DECL (expected1, hfloat, 16, 4) [] = { 0x4b4d, 0x4b4d, 78 0x4b4d, 0x4b4d }; 79 #endif 80 VECT_VAR_DECL(expected1,hfloat,32,2) [] = { 0x42066666, 0x42066666 }; 81 VECT_VAR_DECL(expected1,int,8,16) [] = { 0x11, 0x11, 0x11, 0x11, 82 0x11, 0x11, 0x11, 0x11, 83 0x11, 0x11, 0x11, 0x11, 84 0x11, 0x11, 0x11, 0x11 }; 85 VECT_VAR_DECL(expected1,int,16,8) [] = { 0x22, 0x22, 0x22, 0x22, 86 0x22, 0x22, 0x22, 0x22 }; 87 VECT_VAR_DECL(expected1,int,32,4) [] = { 0x33, 0x33, 0x33, 0x33 }; 88 VECT_VAR_DECL(expected1,uint,8,16) [] = { 0x55, 0x55, 0x55, 0x55, 89 0x55, 0x55, 0x55, 0x55, 90 0x55, 0x55, 0x55, 0x55, 91 0x55, 0x55, 0x55, 0x55 }; 92 VECT_VAR_DECL(expected1,uint,16,8) [] = { 0x66, 0x66, 0x66, 0x66, 93 0x66, 0x66, 0x66, 0x66 }; 94 VECT_VAR_DECL(expected1,uint,32,4) [] = { 0x77, 0x77, 0x77, 0x77 }; 95 VECT_VAR_DECL(expected1,poly,8,16) [] = { 0x55, 0x55, 0x55, 0x55, 96 0x55, 0x55, 0x55, 0x55, 97 0x55, 0x55, 0x55, 0x55, 98 0x55, 0x55, 0x55, 0x55 }; 99 VECT_VAR_DECL(expected1,poly,16,8) [] = { 0x66, 0x66, 0x66, 0x66, 100 0x66, 0x66, 0x66, 0x66 }; 101 #if defined (FP16_SUPPORTED) 102 VECT_VAR_DECL (expected1, hfloat, 16, 8) [] = { 0x4b4d, 0x4b4d, 103 0x4b4d, 0x4b4d, 104 0x4b4d, 0x4b4d, 105 0x4b4d, 0x4b4d }; 106 #endif 107 VECT_VAR_DECL(expected1,hfloat,32,4) [] = { 0x42073333, 0x42073333, 108 0x42073333, 0x42073333 }; 109 110 #define INSN_NAME vuzp 111 #define TEST_MSG "VUZP/VUZPQ" 112 113 #include "vshuffle.inc" 114