Lines Matching full:above
35 const uint8_t *above, const uint8_t *left) { in vpx_dc_predictor_4x4_neon() argument
36 const uint8x8_t a = load_unaligned_u8_4x1(above); in vpx_dc_predictor_4x4_neon()
45 const uint8_t *above, const uint8_t *left) { in vpx_dc_left_predictor_4x4_neon() argument
48 (void)above; in vpx_dc_left_predictor_4x4_neon()
53 const uint8_t *above, const uint8_t *left) { in vpx_dc_top_predictor_4x4_neon() argument
54 const uint16_t sum = dc_sum_4(above); in vpx_dc_top_predictor_4x4_neon()
61 const uint8_t *above, const uint8_t *left) { in vpx_dc_128_predictor_4x4_neon() argument
63 (void)above; in vpx_dc_128_predictor_4x4_neon()
84 const uint8_t *above, const uint8_t *left) { in vpx_dc_predictor_8x8_neon() argument
85 const uint8x8_t above_u8 = vld1_u8(above); in vpx_dc_predictor_8x8_neon()
94 const uint8_t *above, const uint8_t *left) { in vpx_dc_left_predictor_8x8_neon() argument
97 (void)above; in vpx_dc_left_predictor_8x8_neon()
102 const uint8_t *above, const uint8_t *left) { in vpx_dc_top_predictor_8x8_neon() argument
103 const uint16_t sum = dc_sum_8(above); in vpx_dc_top_predictor_8x8_neon()
110 const uint8_t *above, const uint8_t *left) { in vpx_dc_128_predictor_8x8_neon() argument
112 (void)above; in vpx_dc_128_predictor_8x8_neon()
133 const uint8_t *above, const uint8_t *left) { in vpx_dc_predictor_16x16_neon() argument
134 const uint8x16_t ref0 = vld1q_u8(above); in vpx_dc_predictor_16x16_neon()
145 const uint8_t *above, in vpx_dc_left_predictor_16x16_neon() argument
149 (void)above; in vpx_dc_left_predictor_16x16_neon()
154 const uint8_t *above, in vpx_dc_top_predictor_16x16_neon() argument
156 const uint16_t sum = dc_sum_16(above); in vpx_dc_top_predictor_16x16_neon()
163 const uint8_t *above, in vpx_dc_128_predictor_16x16_neon() argument
166 (void)above; in vpx_dc_128_predictor_16x16_neon()
191 const uint8_t *above, const uint8_t *left) { in vpx_dc_predictor_32x32_neon() argument
192 const uint8x16_t a0 = vld1q_u8(above + 0); in vpx_dc_predictor_32x32_neon()
193 const uint8x16_t a1 = vld1q_u8(above + 16); in vpx_dc_predictor_32x32_neon()
205 const uint8_t *above, in vpx_dc_left_predictor_32x32_neon() argument
209 (void)above; in vpx_dc_left_predictor_32x32_neon()
214 const uint8_t *above, in vpx_dc_top_predictor_32x32_neon() argument
216 const uint16_t sum = dc_sum_32(above); in vpx_dc_top_predictor_32x32_neon()
223 const uint8_t *above, in vpx_dc_128_predictor_32x32_neon() argument
226 (void)above; in vpx_dc_128_predictor_32x32_neon()
234 const uint8_t *above, const uint8_t *left) { in vpx_d45_predictor_4x4_neon() argument
239 a0 = vld1_u8(above); in vpx_d45_predictor_4x4_neon()
240 a7 = above[7]; in vpx_d45_predictor_4x4_neon()
242 // [ above[1], ..., above[6], x, x ] in vpx_d45_predictor_4x4_neon()
244 // [ above[2], ..., above[7], x, x ] in vpx_d45_predictor_4x4_neon()
247 // d0[0] = AVG3(above[0], above[1], above[2]); in vpx_d45_predictor_4x4_neon()
249 // d0[5] = AVG3(above[5], above[6], above[7]); in vpx_d45_predictor_4x4_neon()
258 // stride=2 [ d0[3], d0[4], d0[5], above[7] ] in vpx_d45_predictor_4x4_neon()
264 // We stored d0[6] above, so fixup into above[7]. in vpx_d45_predictor_4x4_neon()
269 const uint8_t *above, const uint8_t *left) { in vpx_d45_predictor_8x8_neon() argument
273 a0 = vld1_u8(above + 0); in vpx_d45_predictor_8x8_neon()
274 a1 = vld1_u8(above + 1); in vpx_d45_predictor_8x8_neon()
275 a7 = vld1_dup_u8(above + 7); in vpx_d45_predictor_8x8_neon()
278 // shift in above[7] later, so shift a0 across by one to get the right in vpx_d45_predictor_8x8_neon()
280 // [ x, above[0], ... , above[6] ] in vpx_d45_predictor_8x8_neon()
284 // d0[1] = AVG3(above[0], above[1], above[2]); in vpx_d45_predictor_8x8_neon()
286 // d0[7] = AVG3(above[6], above[7], above[8]); in vpx_d45_predictor_8x8_neon()
289 // Undo the earlier ext, incrementally shift in duplicates of above[7]. in vpx_d45_predictor_8x8_neon()
301 const uint8_t *above, const uint8_t *left) { in vpx_d45_predictor_16x16_neon() argument
305 a0 = vld1q_u8(above + 0); in vpx_d45_predictor_16x16_neon()
306 a1 = vld1q_u8(above + 1); in vpx_d45_predictor_16x16_neon()
307 a15 = vld1q_dup_u8(above + 15); in vpx_d45_predictor_16x16_neon()
310 // shift in above[15] later, so shift a0 across by one to get the right in vpx_d45_predictor_16x16_neon()
312 // [ x, above[0], ... , above[14] ] in vpx_d45_predictor_16x16_neon()
316 // d0[1] = AVG3(above[0], above[1], above[2]); in vpx_d45_predictor_16x16_neon()
318 // d0[15] = AVG3(above[14], above[15], above[16]); in vpx_d45_predictor_16x16_neon()
321 // Undo the earlier ext, incrementally shift in duplicates of above[15]. in vpx_d45_predictor_16x16_neon()
341 const uint8_t *above, const uint8_t *left) { in vpx_d45_predictor_32x32_neon() argument
345 a0 = vld1q_u8(above + 0); in vpx_d45_predictor_32x32_neon()
346 a1 = vld1q_u8(above + 1); in vpx_d45_predictor_32x32_neon()
347 a15 = vld1q_u8(above + 15); in vpx_d45_predictor_32x32_neon()
348 a16 = vld1q_u8(above + 16); in vpx_d45_predictor_32x32_neon()
349 a17 = vld1q_u8(above + 17); in vpx_d45_predictor_32x32_neon()
350 a31 = vld1q_dup_u8(above + 31); in vpx_d45_predictor_32x32_neon()
353 // shift in above[15] later, so shift a0 across by one to get the right in vpx_d45_predictor_32x32_neon()
355 // [ x, above[0], ... , above[14] ] in vpx_d45_predictor_32x32_neon()
359 // d0[1] = AVG3(above[0], above[1], above[2]); in vpx_d45_predictor_32x32_neon()
361 // d0[15] = AVG3(above[14], above[15], above[16]); in vpx_d45_predictor_32x32_neon()
365 // Undo the earlier ext, incrementally shift in duplicates of above[15]. in vpx_d45_predictor_32x32_neon()
436 const uint8_t *above, const uint8_t *left) { in vpx_d63_predictor_4x4_neon() argument
440 a0 = load_unaligned_u8_4x1(above + 0); in vpx_d63_predictor_4x4_neon()
441 a1 = load_unaligned_u8_4x1(above + 1); in vpx_d63_predictor_4x4_neon()
442 a2 = load_unaligned_u8_4x1(above + 2); in vpx_d63_predictor_4x4_neon()
443 a3 = load_unaligned_u8_4x1(above + 3); in vpx_d63_predictor_4x4_neon()
457 const uint8_t *above, const uint8_t *left) { in vpx_d63_predictor_8x8_neon() argument
461 a0 = vld1_u8(above + 0); in vpx_d63_predictor_8x8_neon()
462 a1 = vld1_u8(above + 1); in vpx_d63_predictor_8x8_neon()
463 a2 = vld1_u8(above + 2); in vpx_d63_predictor_8x8_neon()
464 a7 = vld1_dup_u8(above + 7); in vpx_d63_predictor_8x8_neon()
484 const uint8_t *above, const uint8_t *left) { in vpx_d63_predictor_16x16_neon() argument
488 a0 = vld1q_u8(above + 0); in vpx_d63_predictor_16x16_neon()
489 a1 = vld1q_u8(above + 1); in vpx_d63_predictor_16x16_neon()
490 a2 = vld1q_u8(above + 2); in vpx_d63_predictor_16x16_neon()
491 a15 = vld1q_dup_u8(above + 15); in vpx_d63_predictor_16x16_neon()
519 const uint8_t *above, const uint8_t *left) { in vpx_d63_predictor_32x32_neon() argument
523 a0 = vld1q_u8(above + 0); in vpx_d63_predictor_32x32_neon()
524 a1 = vld1q_u8(above + 1); in vpx_d63_predictor_32x32_neon()
525 a2 = vld1q_u8(above + 2); in vpx_d63_predictor_32x32_neon()
526 a16 = vld1q_u8(above + 16); in vpx_d63_predictor_32x32_neon()
527 a17 = vld1q_u8(above + 17); in vpx_d63_predictor_32x32_neon()
528 a18 = vld1q_u8(above + 18); in vpx_d63_predictor_32x32_neon()
529 a31 = vld1q_dup_u8(above + 31); in vpx_d63_predictor_32x32_neon()
611 const uint8_t *above, const uint8_t *left) { in vpx_d117_predictor_4x4_neon() argument
615 az = load_unaligned_u8_4x1(above - 1); in vpx_d117_predictor_4x4_neon()
616 a0 = load_unaligned_u8_4x1(above + 0); in vpx_d117_predictor_4x4_neon()
617 // [ left[0], above[-1], above[0], above[1], x, x, x, x ] in vpx_d117_predictor_4x4_neon()
620 col0 = vdup_n_u8((above[-1] + 2 * left[0] + left[1] + 2) >> 2); in vpx_d117_predictor_4x4_neon()
635 const uint8_t *above, const uint8_t *left) { in vpx_d117_predictor_8x8_neon() argument
638 az = vld1_u8(above - 1); in vpx_d117_predictor_8x8_neon()
639 a0 = vld1_u8(above + 0); in vpx_d117_predictor_8x8_neon()
640 // [ left[0], above[-1], ... , above[5] ] in vpx_d117_predictor_8x8_neon()
649 // [ above[-1], left[0], ... , left[6] ] in vpx_d117_predictor_8x8_neon()
650 azl0 = vext_u8(vld1_dup_u8(above - 1), l0, 7); in vpx_d117_predictor_8x8_neon()
652 // d0[0] = AVG2(above[-1], above[0]) in vpx_d117_predictor_8x8_neon()
653 // d0[1] = AVG2(above[0], above[1]) in vpx_d117_predictor_8x8_neon()
655 // d0[7] = AVG2(above[6], above[7]) in vpx_d117_predictor_8x8_neon()
658 // d1[0] = AVG3(left[0], above[-1], above[0]) in vpx_d117_predictor_8x8_neon()
659 // d1[1] = AVG3(above[-1], above[0], above[1]) in vpx_d117_predictor_8x8_neon()
661 // d1[7] = AVG3(above[5], above[6], above[7]) in vpx_d117_predictor_8x8_neon()
667 // col0[7] = AVG3(above[-1], left[0], left[1]) in vpx_d117_predictor_8x8_neon()
703 const uint8_t *above, const uint8_t *left) { in vpx_d117_predictor_16x16_neon() argument
707 az = vld1q_u8(above - 1); in vpx_d117_predictor_16x16_neon()
708 a0 = vld1q_u8(above + 0); in vpx_d117_predictor_16x16_neon()
709 // [ left[0], above[-1], ... , above[13] ] in vpx_d117_predictor_16x16_neon()
718 // [ above[-1], left[0], ... , left[14] ] in vpx_d117_predictor_16x16_neon()
719 azl0 = vextq_u8(vld1q_dup_u8(above - 1), l0, 15); in vpx_d117_predictor_16x16_neon()
752 const uint8_t *above, const uint8_t *left) { in vpx_d117_predictor_32x32_neon() argument
757 az = vld1q_u8(above - 1); in vpx_d117_predictor_32x32_neon()
758 a0 = vld1q_u8(above + 0); in vpx_d117_predictor_32x32_neon()
759 a14 = vld1q_u8(above + 14); in vpx_d117_predictor_32x32_neon()
760 a15 = vld1q_u8(above + 15); in vpx_d117_predictor_32x32_neon()
761 a16 = vld1q_u8(above + 16); in vpx_d117_predictor_32x32_neon()
762 // [ left[0], above[-1], ... , above[13] ] in vpx_d117_predictor_32x32_neon()
774 // [ above[-1], left[0], ... , left[14] ] in vpx_d117_predictor_32x32_neon()
775 azl0 = vextq_u8(vld1q_dup_u8(above - 1), l0, 15); in vpx_d117_predictor_32x32_neon()
863 const uint8_t *above, const uint8_t *left) { in vpx_d135_predictor_4x4_neon() argument
864 const uint8x8_t XA0123 = vld1_u8(above - 1); in vpx_d135_predictor_4x4_neon()
880 const uint8_t *above, const uint8_t *left) { in vpx_d135_predictor_8x8_neon() argument
881 const uint8x8_t XA0123456 = vld1_u8(above - 1); in vpx_d135_predictor_8x8_neon()
882 const uint8x8_t A01234567 = vld1_u8(above); in vpx_d135_predictor_8x8_neon()
883 const uint8x8_t A1234567_ = vld1_u8(above + 1); in vpx_d135_predictor_8x8_neon()
928 const uint8_t *above, const uint8_t *left) { in vpx_d135_predictor_16x16_neon() argument
929 const uint8x16_t XA0123456789abcde = vld1q_u8(above - 1); in vpx_d135_predictor_16x16_neon()
930 const uint8x16_t A0123456789abcdef = vld1q_u8(above); in vpx_d135_predictor_16x16_neon()
931 const uint8x16_t A123456789abcdef_ = vld1q_u8(above + 1); in vpx_d135_predictor_16x16_neon()
981 const uint8_t *above, const uint8_t *left) { in vpx_d135_predictor_32x32_neon() argument
997 const uint8x16_t XAL0123456789abcde = vld1q_u8(above - 1); in vpx_d135_predictor_32x32_neon()
1005 const uint8x16_t AL0123456789abcdef = vld1q_u8(above); in vpx_d135_predictor_32x32_neon()
1006 const uint8x16_t AL123456789abcdefg = vld1q_u8(above + 1); in vpx_d135_predictor_32x32_neon()
1007 const uint8x16_t ALfR0123456789abcde = vld1q_u8(above + 15); in vpx_d135_predictor_32x32_neon()
1008 const uint8x16_t AR0123456789abcdef = vld1q_u8(above + 16); in vpx_d135_predictor_32x32_neon()
1009 const uint8x16_t AR123456789abcdef_ = vld1q_u8(above + 17); in vpx_d135_predictor_32x32_neon()
1126 const uint8_t *above, const uint8_t *left) { in vpx_d153_predictor_4x4_neon() argument
1130 az = load_unaligned_u8_4x1(above - 1); in vpx_d153_predictor_4x4_neon()
1131 a0 = load_unaligned_u8_4x1(above + 0); in vpx_d153_predictor_4x4_neon()
1132 // [ left[0], above[-1], above[0], above[1], x, x, x, x ] in vpx_d153_predictor_4x4_neon()
1137 // [ above[-1], left[0], left[1], left[2], x, x, x, x ] in vpx_d153_predictor_4x4_neon()
1138 azl0 = vext_u8(vld1_dup_u8(above - 1), l0, 7); in vpx_d153_predictor_4x4_neon()
1153 const uint8_t *above, const uint8_t *left) { in vpx_d153_predictor_8x8_neon() argument
1156 az = vld1_u8(above - 1); in vpx_d153_predictor_8x8_neon()
1157 a0 = vld1_u8(above + 0); in vpx_d153_predictor_8x8_neon()
1158 // [ left[0], above[-1], ... , above[5] ] in vpx_d153_predictor_8x8_neon()
1167 // [ above[-1], left[0], ... , left[6] ] in vpx_d153_predictor_8x8_neon()
1168 azl0 = vext_u8(vld1_dup_u8(above - 1), l0, 7); in vpx_d153_predictor_8x8_neon()
1170 // d0[0] = AVG2(above[-1], left[0]) in vpx_d153_predictor_8x8_neon()
1176 // d1[0] = AVG3(left[0], above[-1], above[0]) in vpx_d153_predictor_8x8_neon()
1177 // d1[1] = AVG3(above[-1], above[0], above[1]) in vpx_d153_predictor_8x8_neon()
1179 // d1[7] = AVG3(above[5], above[6], above[7]) in vpx_d153_predictor_8x8_neon()
1182 // d2[0] = AVG3(above[-1], left[0], left[1]) in vpx_d153_predictor_8x8_neon()
1215 const uint8_t *above, const uint8_t *left) { in vpx_d153_predictor_16x16_neon() argument
1219 az = vld1q_u8(above - 1); in vpx_d153_predictor_16x16_neon()
1220 a0 = vld1q_u8(above + 0); in vpx_d153_predictor_16x16_neon()
1221 // [ left[0], above[-1], ... , above[13] ] in vpx_d153_predictor_16x16_neon()
1230 // [ above[-1], left[0], ... , left[14] ] in vpx_d153_predictor_16x16_neon()
1231 azl0 = vextq_u8(vld1q_dup_u8(above - 1), l0, 15); in vpx_d153_predictor_16x16_neon()
1263 const uint8_t *above, const uint8_t *left) { in vpx_d153_predictor_32x32_neon() argument
1269 az = vld1q_u8(above - 1); in vpx_d153_predictor_32x32_neon()
1270 a0 = vld1q_u8(above + 0); in vpx_d153_predictor_32x32_neon()
1271 a14 = vld1q_u8(above + 14); in vpx_d153_predictor_32x32_neon()
1272 a15 = vld1q_u8(above + 15); in vpx_d153_predictor_32x32_neon()
1273 a16 = vld1q_u8(above + 16); in vpx_d153_predictor_32x32_neon()
1274 // [ left[0], above[-1], ... , above[13] ] in vpx_d153_predictor_32x32_neon()
1286 // [ above[-1], left[0], ... , left[14] ] in vpx_d153_predictor_32x32_neon()
1287 azl0 = vextq_u8(vld1q_dup_u8(above - 1), l0, 15); in vpx_d153_predictor_32x32_neon()
1378 const uint8_t *above, const uint8_t *left) { in vpx_d207_predictor_4x4_neon() argument
1380 (void)above; in vpx_d207_predictor_4x4_neon()
1415 const uint8_t *above, const uint8_t *left) { in vpx_d207_predictor_8x8_neon() argument
1417 (void)above; in vpx_d207_predictor_8x8_neon()
1444 const uint8_t *above, const uint8_t *left) { in vpx_d207_predictor_16x16_neon() argument
1446 (void)above; in vpx_d207_predictor_16x16_neon()
1479 const uint8_t *above, const uint8_t *left) { in vpx_d207_predictor_32x32_neon() argument
1482 (void)above; in vpx_d207_predictor_32x32_neon()
1574 const uint8_t *above, const uint8_t *left) { in vpx_v_predictor_4x4_neon() argument
1575 const uint32_t d = *(const uint32_t *)above; in vpx_v_predictor_4x4_neon()
1585 const uint8_t *above, const uint8_t *left) { in vpx_v_predictor_8x8_neon() argument
1586 const uint8x8_t d = vld1_u8(above); in vpx_v_predictor_8x8_neon()
1596 const uint8_t *above, const uint8_t *left) { in vpx_v_predictor_16x16_neon() argument
1597 const uint8x16_t d = vld1q_u8(above); in vpx_v_predictor_16x16_neon()
1607 const uint8_t *above, const uint8_t *left) { in vpx_v_predictor_32x32_neon() argument
1608 const uint8x16_t d0 = vld1q_u8(above); in vpx_v_predictor_32x32_neon()
1609 const uint8x16_t d1 = vld1q_u8(above + 16); in vpx_v_predictor_32x32_neon()
1627 const uint8_t *above, const uint8_t *left) { in vpx_h_predictor_4x4_neon() argument
1632 (void)above; in vpx_h_predictor_4x4_neon()
1648 const uint8_t *above, const uint8_t *left) { in vpx_h_predictor_8x8_neon() argument
1651 (void)above; in vpx_h_predictor_8x8_neon()
1708 const uint8_t *above, const uint8_t *left) { in vpx_h_predictor_16x16_neon() argument
1710 (void)above; in vpx_h_predictor_16x16_neon()
1762 const uint8_t *above, const uint8_t *left) { in vpx_h_predictor_32x32_neon() argument
1764 (void)above; in vpx_h_predictor_32x32_neon()
1780 const uint8_t *above, const uint8_t *left) { in vpx_tm_predictor_4x4_neon() argument
1781 const uint8x8_t top_left = vld1_dup_u8(above - 1); in vpx_tm_predictor_4x4_neon()
1783 const uint8x8_t above_u8 = vld1_u8(above); in vpx_tm_predictor_4x4_neon()
1818 const uint8_t *above, const uint8_t *left) { in vpx_tm_predictor_8x8_neon() argument
1819 const uint8x8_t top_left = vld1_dup_u8(above - 1); in vpx_tm_predictor_8x8_neon()
1820 const uint8x8_t above_u8 = vld1_u8(above); in vpx_tm_predictor_8x8_neon()
1855 const uint8_t *above, const uint8_t *left) { in vpx_tm_predictor_16x16_neon() argument
1856 const uint8x16_t top_left = vld1q_dup_u8(above - 1); in vpx_tm_predictor_16x16_neon()
1857 const uint8x16_t above_u8 = vld1q_u8(above); in vpx_tm_predictor_16x16_neon()
1911 const uint8_t *above, const uint8_t *left) { in vpx_tm_predictor_32x32_neon() argument
1912 const uint8x16_t top_left = vld1q_dup_u8(above - 1); in vpx_tm_predictor_32x32_neon()
1913 const uint8x16_t above_low = vld1q_u8(above); in vpx_tm_predictor_32x32_neon()
1914 const uint8x16_t above_high = vld1q_u8(above + 16); in vpx_tm_predictor_32x32_neon()