| /hardware/intel/common/omx-components/videocodec/libvpx_internal/libvpx/vp8/common/mips/dspr2/ |
| D | loopfilter_filters_dspr2.c | 355 uint32_t pm1, p0, p1, p2, p3, p4, p5, p6; in vp8_loop_filter_horizontal_edge_mips() local
363 p4 = 0; in vp8_loop_filter_horizontal_edge_mips()
387 p4 = *((uint32_t *)(s4)); in vp8_loop_filter_horizontal_edge_mips()
392 if (!(((p1 - p4) == 0) && ((p2 - p3) == 0))) in vp8_loop_filter_horizontal_edge_mips()
400 vp8_filter_mask_vec_mips(limit, flimit, p1, p2, pm1, p0, p3, p4, p5, p6, in vp8_loop_filter_horizontal_edge_mips()
407 vp8_filter_mips(mask, hev, &p1, &p2, &p3, &p4); in vp8_loop_filter_horizontal_edge_mips()
413 *((uint32_t *)s4) = p4; in vp8_loop_filter_horizontal_edge_mips()
432 p4 = *((uint32_t *)(s4)); in vp8_loop_filter_horizontal_edge_mips()
437 if (!(((p1 - p4) == 0) && ((p2 - p3) == 0))) in vp8_loop_filter_horizontal_edge_mips()
445 vp8_filter_mask_vec_mips(limit, flimit, p1, p2, pm1, p0, p3, p4, p5, p6, in vp8_loop_filter_horizontal_edge_mips()
[all …]
|
| D | filter_dspr2.c | 328 unsigned int p1, p2, p3, p4; in vp8_filter_block2d_first_pass_8_all() local
469 [p4] "=&r" (p4), [n4] "=&r" (n4), in vp8_filter_block2d_first_pass_8_all()
546 [p3] "=&r" (p3), [p4] "=&r" (p4), [n1] "=&r" (n1), in vp8_filter_block2d_first_pass_8_all()
591 : [tp1] "r" (tp1), [p3] "r" (p3), [p4] "r" (p4), in vp8_filter_block2d_first_pass_8_all()
628 unsigned int p1, p2, p3, p4; in vp8_filter_block2d_first_pass16_6tap() local
742 [p4] "=&r" (p4), [n4] "=&r" (n4), in vp8_filter_block2d_first_pass16_6tap()
800 [p4] "r" (p4), [n4] "r" (n4), [p1] "r" (p1), [src_ptr] "r" (src_ptr), in vp8_filter_block2d_first_pass16_6tap()
857 [tp1] "r" (tp1), [p4] "r" (p4), [n1] "r" (n1), [p1] "r" (p1), in vp8_filter_block2d_first_pass16_6tap()
|
| /hardware/intel/common/omx-components/videocodec/libvpx_internal/libvpx/vp9/common/mips/dspr2/ |
| D | vp9_loopfilter_filters_dspr2.c | 32 uint32_t pm1, p0, p1, p2, p3, p4, p5, p6; in vp9_lpf_horizontal_4_dspr2() local
73 : [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4) in vp9_lpf_horizontal_4_dspr2()
79 if (!(((p1 - p4) == 0) && ((p2 - p3) == 0))) { in vp9_lpf_horizontal_4_dspr2()
92 pm1, p0, p3, p4, p5, p6, in vp9_lpf_horizontal_4_dspr2()
98 vp9_filter_dspr2(mask, hev, &p1, &p2, &p3, &p4); in vp9_lpf_horizontal_4_dspr2()
107 : [p1] "r" (p1), [p2] "r" (p2), [p3] "r" (p3), [p4] "r" (p4), in vp9_lpf_horizontal_4_dspr2()
125 uint32_t pm1, p0, p1, p2, p3, p4, p5, p6; in vp9_lpf_vertical_4_dspr2() local
164 p4 = *((uint32_t *)(s3)); in vp9_lpf_vertical_4_dspr2()
211 [p6] "+r" (p6), [p5] "+r" (p5), [p4] "+r" (p4), [p3] "+r" (p3), in vp9_lpf_vertical_4_dspr2()
219 if (!(((p1 - p4) == 0) && ((p2 - p3) == 0))) { in vp9_lpf_vertical_4_dspr2()
[all …]
|
| D | vp9_convolve8_horiz_dspr2.c | 35 uint32_t p1, p2, p3, p4; in convolve_horiz_4_dspr2() local
118 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4), in convolve_horiz_4_dspr2()
146 uint32_t p1, p2, p3, p4, n1; in convolve_horiz_8_dspr2() local
283 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4), in convolve_horiz_8_dspr2()
313 uint32_t p1, p2, p3, p4, p5; in convolve_horiz_16_dspr2() local
549 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4), in convolve_horiz_16_dspr2()
583 uint32_t p1, p2, p3, p4, p5; in convolve_horiz_64_dspr2() local
821 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4), in convolve_horiz_64_dspr2()
|
| D | vp9_convolve8_avg_horiz_dspr2.c | 35 uint32_t p1, p2, p3, p4; in convolve_avg_horiz_4_dspr2() local
129 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4), in convolve_avg_horiz_4_dspr2()
157 uint32_t p1, p2, p3, p4, n1; in convolve_avg_horiz_8_dspr2() local
317 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4), in convolve_avg_horiz_8_dspr2()
347 uint32_t p1, p2, p3, p4, p5; in convolve_avg_horiz_16_dspr2() local
625 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4), in convolve_avg_horiz_16_dspr2()
658 uint32_t p1, p2, p3, p4, p5; in convolve_avg_horiz_64_dspr2() local
938 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4), in convolve_avg_horiz_64_dspr2()
|
| D | vp9_convolve2_horiz_dspr2.c | 116 uint32_t p1, p2, p3, p4; in convolve_bi_horiz_8_dspr2() local
217 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4), in convolve_bi_horiz_8_dspr2()
243 uint32_t p1, p2, p3, p4, p5; in convolve_bi_horiz_16_dspr2() local
420 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4), in convolve_bi_horiz_16_dspr2()
450 uint32_t p1, p2, p3, p4, p5; in convolve_bi_horiz_64_dspr2() local
629 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4), in convolve_bi_horiz_64_dspr2()
|
| D | vp9_convolve2_avg_horiz_dspr2.c | 129 uint32_t p1, p2, p3, p4, n1; in convolve_bi_avg_horiz_8_dspr2() local
254 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4), in convolve_bi_avg_horiz_8_dspr2()
281 uint32_t p1, p2, p3, p4, p5; in convolve_bi_avg_horiz_16_dspr2() local
500 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4), in convolve_bi_avg_horiz_16_dspr2()
530 uint32_t p1, p2, p3, p4, p5; in convolve_bi_avg_horiz_64_dspr2() local
751 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4), in convolve_bi_avg_horiz_64_dspr2()
|
| D | vp9_convolve2_dspr2.c | 125 uint32_t p1, p2, p3, p4; in convolve_bi_horiz_8_transposed_dspr2() local
237 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4), in convolve_bi_horiz_8_transposed_dspr2()
264 uint32_t p1, p2, p3, p4, p5; in convolve_bi_horiz_16_transposed_dspr2() local
464 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4), in convolve_bi_horiz_16_transposed_dspr2()
496 uint32_t p1, p2, p3, p4, p5; in convolve_bi_horiz_64_transposed_dspr2() local
697 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4), in convolve_bi_horiz_64_transposed_dspr2()
|
| D | vp9_convolve8_dspr2.c | 52 uint32_t p1, p2, p3, p4; in convolve_horiz_4_transposed_dspr2() local
140 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4), in convolve_horiz_4_transposed_dspr2()
168 uint32_t p1, p2, p3, p4, n1; in convolve_horiz_8_transposed_dspr2() local
315 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4), in convolve_horiz_8_transposed_dspr2()
346 uint32_t p1, p2, p3, p4, p5; in convolve_horiz_16_transposed_dspr2() local
601 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4), in convolve_horiz_16_transposed_dspr2()
636 uint32_t p1, p2, p3, p4, p5; in convolve_horiz_64_transposed_dspr2() local
892 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4), in convolve_horiz_64_transposed_dspr2()
|
| D | vp9_loopfilter_macros_dspr2.h | 382 : [p7] "r" (p7), [p6] "r" (p6), [p5] "r" (p5), [p4] "r" (p4), \
422 : [p7] "r" (p7), [p6] "r" (p6), [p5] "r" (p5), [p4] "r" (p4), \
459 [p4] "=&r" (p4),[p3] "=&r" (p3), \
|
| D | vp9_loopfilter_masks_dspr2.h | 282 static INLINE void vp9_flatmask5(uint32_t p4, uint32_t p3, in vp9_flatmask5() argument
360 : [p4] "r" (p4), [p3] "r" (p3), [p2] "r" (p2), in vp9_flatmask5()
|
| D | vp9_loopfilter_filters_dspr2.h | 534 const uint32_t p7 = *op7, p6 = *op6, p5 = *op5, p4 = *op4; in vp9_wide_mbfilter_dspr2() local
563 : [p6] "r" (p6), [p5] "r" (p5), [p4] "r" (p4), in vp9_wide_mbfilter_dspr2()
649 : [p7] "r" (p7), [p6] "r" (p6), [p5] "r" (p5), [p4] "r" (p4), in vp9_wide_mbfilter_dspr2()
746 [p3] "r" (p3), [p4] "r" (p4), [p5] "r" (p5), [p6] "r" (p6), in vp9_wide_mbfilter_dspr2()
|
| D | vp9_mblpf_vert_loopfilter_dspr2.c | 34 uint32_t p7, p6, p5, p4, p3, p2, p1, p0, q0, q1, q2, q3, q4, q5, q6, q7; in vp9_lpf_vertical_16_dspr2() local
79 [p5] "=&r" (p5), [p4] "=&r" (p4) in vp9_lpf_vertical_16_dspr2()
208 [p4] "+r" (p4), [p5] "+r" (p5), [p6] "+r" (p6), [p7] "+r" (p7), in vp9_lpf_vertical_16_dspr2()
255 vp9_flatmask5(p7, p6, p5, p4, p0, q0, q4, q5, q6, q7, &flat2); in vp9_lpf_vertical_16_dspr2()
|
| D | vp9_mblpf_horiz_loopfilter_dspr2.c | 36 uint32_t p7, p6, p5, p4, p3, p2, p1, p0, q0, q1, q2, q3, q4, q5, q6, q7; in vp9_lpf_horizontal_16_dspr2() local
92 [p7] "=&r" (p7), [p6] "=&r" (p6), [p5] "=&r" (p5), [p4] "=&r" (p4) in vp9_lpf_horizontal_16_dspr2()
117 vp9_flatmask5(p7, p6, p5, p4, p0, q0, q4, q5, q6, q7, &flat2); in vp9_lpf_horizontal_16_dspr2()
167 : [p6] "r" (p6), [p5] "r" (p5), [p4] "r" (p4), [p3] "r" (p3), in vp9_lpf_horizontal_16_dspr2()
|
| /hardware/intel/common/libmix/mix_vbp/viddec_fw/fw/parser/include/ |
| D | viddec_fw_debug.h | 21 …RITE_SVEN(event, p1, p2, p3, p4, p5, p6) DEB("Sven evnt=0x%.8X p1=%d p2=%d p3=%d p4=%d p5=%d p6=%d… argument
36 #define WRITE_SVEN(event, p1, p2, p3, p4, p5, p6) devh_SVEN_WriteModuleEvent( NULL, event, p1, p2, … argument
44 #define WRITE_SVEN(event, p1, p2, p3, p4, p5, p6) argument
54 static inline void DEBUG_WRITE(uint32_t p1, uint32_t p2, uint32_t p3, uint32_t p4, uint32_t p5, uin… in DEBUG_WRITE() argument
61 DUMP_TO_MEM(p4); in DEBUG_WRITE()
|
| /hardware/intel/common/omx-components/videocodec/libvpx_internal/libvpx/vp8/common/arm/armv6/ |
| D | intra4x4_predict_v6.asm | 301 add r4, r4, r6 ; [p2+2*p3+p4 | p0+2*p1+p2]
302 uxtab16 r4, r4, r12 ; [p2+2*p3+p4+2 | p0+2*p1+p2+2]
304 add r5, r5, r6, lsl #1 ; [p3+2*p4 | p1+2*p2]
305 add r5, r5, r7 ; [p3+2*p4+p5 | p1+2*p2+p3]
306 uxtab16 r5, r5, r12 ; [p3+2*p4+p5+2 | p1+2*p2+p3+2]
308 add r6, r7, r8, lsl #1 ; [p5+2*p6 | p3+2*p4]
309 add r6, r6, r9 ; [p5+2*p6+p7 | p3+2*p4+p5]
310 uxtab16 r6, r6, r12 ; [p5+2*p6+p7+2 | p3+2*p4+p5+2]
312 add r7, r8, r9, lsl #1 ; [p6+2*p7 | p4+2*p5]
313 add r7, r7, r10 ; [p6+2*p7+p8 | p4+2*p5+p6]
[all …]
|
| /hardware/intel/common/omx-components/videocodec/libvpx_internal/libvpx/vp9/common/ |
| D | vp9_loopfilter_filters.c | 53 uint8_t p4, uint8_t p3, in flat_mask5() argument
59 mask |= (abs(p4 - p0) > thresh) * -1; in flat_mask5()
242 const uint8_t p7 = *op7, p6 = *op6, p5 = *op5, p4 = *op4, in filter16() local
249 *op6 = ROUND_POWER_OF_TWO(p7 * 7 + p6 * 2 + p5 + p4 + p3 + p2 + p1 + p0 + in filter16()
251 *op5 = ROUND_POWER_OF_TWO(p7 * 6 + p6 + p5 * 2 + p4 + p3 + p2 + p1 + p0 + in filter16()
253 *op4 = ROUND_POWER_OF_TWO(p7 * 5 + p6 + p5 + p4 * 2 + p3 + p2 + p1 + p0 + in filter16()
255 *op3 = ROUND_POWER_OF_TWO(p7 * 4 + p6 + p5 + p4 + p3 * 2 + p2 + p1 + p0 + in filter16()
257 *op2 = ROUND_POWER_OF_TWO(p7 * 3 + p6 + p5 + p4 + p3 + p2 * 2 + p1 + p0 + in filter16()
259 *op1 = ROUND_POWER_OF_TWO(p7 * 2 + p6 + p5 + p4 + p3 + p2 + p1 * 2 + p0 + in filter16()
261 *op0 = ROUND_POWER_OF_TWO(p7 + p6 + p5 + p4 + p3 + p2 + p1 + p0 * 2 + in filter16()
[all …]
|
| /hardware/intel/common/libmix/mix_vbp/viddec_fw/fw/codecs/h264/include/ |
| D | h264parse.h | 40 int p1,p2,p3,p4,p5,p6; in MFD_PARSER_DEBUG() local
45 p4=p5=p6 = 0; in MFD_PARSER_DEBUG()
47 DEBUG_WRITE(p1,p2,p3,p4,p5,p6); in MFD_PARSER_DEBUG()
|
| /hardware/intel/common/omx-components/videocodec/libvpx_internal/libvpx/vp9/common/x86/ |
| D | vp9_loopfilter_intrin_avx2.c | 402 __m128i p4, p3, p2, p1, p0, q0, q1, q2, q3, q4; in mb_lpf_horizontal_edge_w_avx2_16() local
412 p4 = _mm_loadu_si128((__m128i *) (s - 5 * p)); in mb_lpf_horizontal_edge_w_avx2_16()
531 _mm_or_si128(_mm_subs_epu8(p4, p0), _mm_subs_epu8(p0, p4)), in mb_lpf_horizontal_edge_w_avx2_16()
579 p256_4 = _mm256_cvtepu8_epi16(p4); in mb_lpf_horizontal_edge_w_avx2_16()
874 p4 = _mm_andnot_si128(flat2, p4); in mb_lpf_horizontal_edge_w_avx2_16()
876 p4 = _mm_or_si128(flat2_p4, p4); in mb_lpf_horizontal_edge_w_avx2_16()
877 _mm_storeu_si128((__m128i *) (s - 5 * p), p4); in mb_lpf_horizontal_edge_w_avx2_16()
|
| D | vp9_loopfilter_intrin_sse2.c | 388 __m128i p4, p3, p2, p1, p0, q0, q1, q2, q3, q4; in mb_lpf_horizontal_edge_w_sse2_16() local
392 p4 = _mm_loadu_si128((__m128i *)(s - 5 * p)); in mb_lpf_horizontal_edge_w_sse2_16()
403 _mm_store_si128((__m128i *)&ap[4 * 16], p4); in mb_lpf_horizontal_edge_w_sse2_16()
522 work = _mm_max_epu8(_mm_or_si128(_mm_subs_epu8(p4, p0), in mb_lpf_horizontal_edge_w_sse2_16()
523 _mm_subs_epu8(p0, p4)), in mb_lpf_horizontal_edge_w_sse2_16()
582 p4 = _mm_unpacklo_epi8(_mm_loadl_epi64((__m128i *)(&ap[4 * 16] + off)), in mb_lpf_horizontal_edge_w_sse2_16()
610 c = _mm_add_epi16(_mm_slli_epi16(p6, 1), _mm_add_epi16(p4, c)); in mb_lpf_horizontal_edge_w_sse2_16()
642 c = _mm_add_epi16(_mm_sub_epi16(c, _mm_add_epi16(p7, p5)), p4); in mb_lpf_horizontal_edge_w_sse2_16()
653 c = _mm_add_epi16(_mm_sub_epi16(c, _mm_add_epi16(p7, p4)), p3); in mb_lpf_horizontal_edge_w_sse2_16()
706 c = _mm_add_epi16(_mm_sub_epi16(c, _mm_add_epi16(p4, q2)), q3); in mb_lpf_horizontal_edge_w_sse2_16()
|
| /hardware/intel/common/omx-components/videocodec/libvpx_internal/libvpx/vp9/common/arm/neon/ |
| D | vp9_mb_lpf_neon.asm | 43 vld1.u8 {d3}, [r8@64], r1 ; p4
295 ; d3 p4
365 ; flatmask5(1, p7, p6, p5, p4, p0, q0, q4, q5, q6, q7)
366 vabd.u8 d22, d3, d7 ; abs(p4 - p0)
376 vmax.u8 d22, d22, d23 ; max(abs(p4 - p0), abs(q4 - q0))
595 vbif d25, d3, d17 ; op4 |= p4 & ~(f2 & f & m)
|
| /hardware/intel/common/omx-components/videocodec/libvpx_internal/libvpx/vp8/common/x86/ |
| D | subpixel_mmx.asm | 74 punpcklbw mm4, mm0 ; mm4 = p1..p4
|