Searched defs:p3 (Results 1 - 21 of 21) sorted by relevance

/hardware/intel/common/omx-components/videocodec/libvpx_internal/libvpx/vp9/common/mips/dspr2/
H A Dvp9_loopfilter_masks_dspr2.h29 uint32_t p3, uint32_t p2,
40 /* mask |= (abs(p3 - p2) > limit) */
41 "subu_s.qb %[c], %[p3], %[p2] \n\t"
42 "subu_s.qb %[r_k], %[p2], %[p3] \n\t"
93 : [limit] "r" (limit), [p3] "r" (p3), [p2] "r" (p2),
136 uint32_t p3, uint32_t p2,
150 /* mask |= (abs(p3 - p2) > limit) */
151 "subu_s.qb %[c], %[p3], %[p2] \n\t"
152 "subu_s.qb %[r_k], %[p2], %[p3] \
27 vp9_filter_hev_mask_dspr2(uint32_t limit, uint32_t flimit, uint32_t p1, uint32_t p0, uint32_t p3, uint32_t p2, uint32_t q0, uint32_t q1, uint32_t q2, uint32_t q3, uint32_t thresh, uint32_t *hev, uint32_t *mask) argument
132 vp9_filter_hev_mask_flatmask4_dspr2(uint32_t limit, uint32_t flimit, uint32_t thresh, uint32_t p1, uint32_t p0, uint32_t p3, uint32_t p2, uint32_t q0, uint32_t q1, uint32_t q2, uint32_t q3, uint32_t *hev, uint32_t *mask, uint32_t *flat) argument
282 vp9_flatmask5(uint32_t p4, uint32_t p3, uint32_t p2, uint32_t p1, uint32_t p0, uint32_t q0, uint32_t q1, uint32_t q2, uint32_t q3, uint32_t q4, uint32_t *flat2) argument
[all...]
H A Dvp9_convolve2_avg_horiz_dspr2.c34 uint32_t p1, p2, p3; local
74 "preceu.ph.qbl %[p3], %[tp2] \n\t"
86 "dpa.w.ph $ac2, %[p3], %[filter45] \n\t"
94 "lbux %[p3], %[Temp4](%[cm]) \n\t" /* odd 2 */
100 "addqh_r.w %[p2], %[p2], %[p3] \n\t" /* average odd 2 */
105 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3),
129 uint32_t p1, p2, p3, p4, n1; local
153 "preceu.ph.qbr %[p3], %[tp2] \n\t"
170 "dpa.w.ph $ac1, %[p3],
281 uint32_t p1, p2, p3, p4, p5; local
530 uint32_t p1, p2, p3, p4, p5; local
[all...]
H A Dvp9_convolve2_dspr2.c125 uint32_t p1, p2, p3, p4; local
152 "preceu.ph.qbr %[p3], %[tp2] \n\t"
168 "dpa.w.ph $ac1, %[p3], %[filter45] \n\t"
170 "extp %[p3], $ac1, 31 \n\t"
185 "lbux %[Temp1], %[p3](%[cm]) \n\t"
192 "preceu.ph.qbr %[p3], %[tp3] \n\t"
213 "dpa.w.ph $ac3, %[p3], %[filter45] \n\t"
237 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4),
264 uint32_t p1, p2, p3, p local
496 uint32_t p1, p2, p3, p4, p5; local
[all...]
H A Dvp9_convolve2_horiz_dspr2.c116 uint32_t p1, p2, p3, p4; local
140 "preceu.ph.qbr %[p3], %[tp2] \n\t"
154 "dpa.w.ph $ac1, %[p3], %[filter45] \n\t"
179 "preceu.ph.qbr %[p3], %[tp3] \n\t"
196 "dpa.w.ph $ac3, %[p3], %[filter45] \n\t"
217 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4),
243 uint32_t p1, p2, p3, p4, p5; local
271 "preceu.ph.qbr %[p3], %[qload2] \n\t"
292 "dpa.w.ph $ac3, %[p3],
450 uint32_t p1, p2, p3, p4, p5; local
[all...]
H A Dvp9_convolve8_avg_horiz_dspr2.c35 uint32_t p1, p2, p3, p4; local
59 "preceu.ph.qbr %[p3], %[tp2] \n\t"
63 "dpa.w.ph $ac3, %[p3], %[vector3b] \n\t"
76 "dpa.w.ph $ac2, %[p3], %[vector2b] \n\t"
129 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4),
157 uint32_t p1, p2, p3, p4, n1; local
183 "preceu.ph.qbr %[p3], %[tp2] \n\t"
188 "dpa.w.ph $ac3, %[p3], %[vector3b] \n\t"
199 "dpa.w.ph $ac2, %[p3],
347 uint32_t p1, p2, p3, p4, p5; local
658 uint32_t p1, p2, p3, p4, p5; local
[all...]
H A Dvp9_convolve8_horiz_dspr2.c35 uint32_t p1, p2, p3, p4; local
59 "preceu.ph.qbr %[p3], %[tp2] \n\t"
63 "dpa.w.ph $ac3, %[p3], %[vector3b] \n\t"
76 "dpa.w.ph $ac2, %[p3], %[vector2b] \n\t"
118 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4),
146 uint32_t p1, p2, p3, p4, n1; local
172 "preceu.ph.qbr %[p3], %[tp2] \n\t"
177 "dpa.w.ph $ac3, %[p3], %[vector3b] \n\t"
186 "dpa.w.ph $ac2, %[p3],
313 uint32_t p1, p2, p3, p4, p5; local
583 uint32_t p1, p2, p3, p4, p5; local
[all...]
H A Dvp9_loopfilter_filters_dspr2.c32 uint32_t pm1, p0, p1, p2, p3, p4, p5, p6; local
70 "lw %[p3], (%[s3]) \n\t"
73 : [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4)
77 /* if (p1 - p4 == 0) and (p2 - p3 == 0)
79 if (!(((p1 - p4) == 0) && ((p2 - p3) == 0))) {
92 pm1, p0, p3, p4, p5, p6,
98 vp9_filter_dspr2(mask, hev, &p1, &p2, &p3, &p4);
103 "sw %[p3], (%[s3]) \n\t"
107 : [p1] "r" (p1), [p2] "r" (p2), [p3] "
125 uint32_t pm1, p0, p1, p2, p3, p4, p5, p6; local
[all...]
H A Dvp9_mbloop_loopfilter_dspr2.c36 uint32_t p3, p2, p1, p0, q0, q1, q2, q3; local
69 "lw %[p3], (%[sp3]) \n\t"
78 : [p3] "=&r" (p3), [p2] "=&r" (p2), [p1] "=&r" (p1), [p0] "=&r" (p0),
85 p1, p0, p3, p2, q0, q1, q2, q3,
334 uint32_t p3, p2, p1, p0, q3, q2, q1, q0; local
367 "lw %[p3], -4(%[s4]) \n\t"
373 : [p3] "=&r" (p3), [p2] "=&r" (p2), [p1] "=&r" (p1), [p0] "=&r" (p0),
378 /* transpose p3, p
[all...]
H A Dvp9_convolve8_dspr2.c52 uint32_t p1, p2, p3, p4; local
75 "preceu.ph.qbr %[p3], %[tp2] \n\t"
79 "dpa.w.ph $ac3, %[p3], %[vector3b] \n\t"
92 "dpa.w.ph $ac2, %[p3], %[vector2b] \n\t"
103 "preceu.ph.qbr %[p3], %[tn2] \n\t"
107 "dpa.w.ph $ac3, %[p3], %[vector3b] \n\t"
117 "dpa.w.ph $ac2, %[p3], %[vector2b] \n\t"
140 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3), [p4] "=&r" (p4),
168 uint32_t p1, p2, p3, p local
346 uint32_t p1, p2, p3, p4, p5; local
636 uint32_t p1, p2, p3, p4, p5; local
[all...]
H A Dvp9_loopfilter_filters_dspr2.h376 const uint32_t p3 = *op3, p2 = *op2, p1 = *op1, p0 = *op0; local
384 /* *op2 = ROUND_POWER_OF_TWO(p3 + p3 + p3 + p2 + p2 + p1 + p0 + q0, 3) 1 */
385 /* *op1 = ROUND_POWER_OF_TWO(p3 + p3 + p2 + p1 + p1 + p0 + q0 + q1, 3) 2 */
386 /* *op0 = ROUND_POWER_OF_TWO(p3 + p2 + p1 + p0 + p0 + q0 + q1 + q2, 3) 3 */
399 "shll.ph %[tmp], %[p3], 1 \n\t"
400 "addu.ph %[res_op2], %[tmp], %[p3] \n\t"
401 "addu.ph %[res_op1], %[p3],
448 vp9_mbfilter1_dspr2(uint32_t p3, uint32_t p2, uint32_t p1, uint32_t p0, uint32_t q0, uint32_t q1, uint32_t q2, uint32_t q3, uint32_t *op2_f1, uint32_t *op1_f1, uint32_t *op0_f1, uint32_t *oq0_f1, uint32_t *oq1_f1, uint32_t *oq2_f1) argument
535 const uint32_t p3 = *op3, p2 = *op2, p1 = *op1, p0 = *op0; local
[all...]
H A Dvp9_mblpf_horiz_loopfilter_dspr2.c36 uint32_t p7, p6, p5, p4, p3, p2, p1, p0, q0, q1, q2, q3, q4, q5, q6, q7; local
86 "lw %[p3], (%[sp3]) \n\t"
91 : [p3] "=&r" (p3), [p2] "=&r" (p2), [p1] "=&r" (p1), [p0] "=&r" (p0),
114 p1, p0, p3, p2, q0, q1, q2, q3,
161 "sw %[p3], (%[sp3]) \n\t"
167 : [p6] "r" (p6), [p5] "r" (p5), [p4] "r" (p4), [p3] "r" (p3),
H A Dvp9_mblpf_vert_loopfilter_dspr2.c34 uint32_t p7, p6, p5, p4, p3, p2, p1, p0, q0, q1, q2, q3, q4, q5, q6, q7; local
71 "lw %[p3], -4(%[s4]) \n\t"
77 : [p3] "=&r" (p3), [p2] "=&r" (p2), [p1] "=&r" (p1),
99 /* transpose p3, p2, p1, p0
105 p3 p3_0 p3_1 p3_2 p3_3
112 p3 p3_0 p2_0 p1_0 p0_0
117 "precrq.qb.ph %[prim3], %[p2], %[p3] \n\t"
118 "precr.qb.ph %[prim4], %[p2], %[p3] \n\t"
121 "precr.qb.ph %[p3],
[all...]
/hardware/intel/common/omx-components/videocodec/libvpx_internal/libvpx/vp8/common/
H A Dloopfilter_filters.c28 uc p3, uc p2, uc p1, uc p0,
32 mask |= (abs(p3 - p2) > limit);
27 vp8_filter_mask(uc limit, uc blimit, uc p3, uc p2, uc p1, uc p0, uc q0, uc q1, uc q2, uc q3) argument
/hardware/intel/common/omx-components/videocodec/libvpx_internal/libvpx/vp8/common/mips/dspr2/
H A Dfilter_dspr2.c132 unsigned int p1, p2, p3; local
178 "preceu.ph.qbr %[p3], %[tp2] \n\t"
181 "dpa.w.ph $ac3, %[p3], %[vector3b] \n\t"
189 "dpa.w.ph $ac2, %[p3], %[vector2b] \n\t"
226 [p3] "=&r" (p3), [n1] "=&r" (n1), [n2] "=&r" (n2),
257 "preceu.ph.qbr %[p3], %[tp2] \n\t"
264 "dpa.w.ph $ac2, %[p3], %[vector2b] \n\t"
296 [p1] "=&r" (p1), [p2] "=&r" (p2), [p3] "=&r" (p3),
328 unsigned int p1, p2, p3, p4; local
628 unsigned int p1, p2, p3, p4; local
960 unsigned int p1, p2, p3; local
[all...]
H A Dloopfilter_filters_dspr2.c49 uint32_t p3,
66 /* mask |= (abs(p3 - p2) > limit) */
67 "subu_s.qb %[c], %[p3], %[p2] \n\t"
68 "subu_s.qb %[r_k], %[p2], %[p3] \n\t"
119 : [limit] "r" (limit), [p3] "r" (p3), [p2] "r" (p2),
355 uint32_t pm1, p0, p1, p2, p3, p4, p5, p6; local
362 p3 = 0;
386 p3 = *((uint32_t *)(s3));
389 /* if (p1 - p4 == 0) and (p2 - p3
43 vp8_filter_mask_vec_mips( uint32_t limit, uint32_t flimit, uint32_t p1, uint32_t p0, uint32_t p3, uint32_t p2, uint32_t q0, uint32_t q1, uint32_t q2, uint32_t q3, uint32_t thresh, uint32_t *hev, uint32_t *mask ) argument
565 uint32_t pm1, p0, p1, p2, p3, p4, p5, p6; local
682 uint32_t pm1, p0, p1, p2, p3, p4, p5, p6; local
1032 uint32_t pm1, p0, p1, p2, p3, p4, p5, p6; local
1643 uint32_t pm1, p0, p1, p2, p3, p4, p5, p6; local
1788 uint32_t pm1, p0, p1, p2, p3, p4, p5, p6; local
1915 uint32_t pm1, p0, p1, p2, p3, p4, p5, p6; local
2125 uint32_t pm1, p0, p1, p2, p3, p4, p5, p6; local
[all...]
/hardware/intel/common/omx-components/videocodec/libvpx_internal/libvpx/vp9/common/
H A Dvp9_loopfilter_filters.c22 uint8_t p3, uint8_t p2,
27 mask |= (abs(p3 - p2) > limit) * -1;
38 uint8_t p3, uint8_t p2,
47 mask |= (abs(p3 - p0) > thresh) * -1;
53 uint8_t p4, uint8_t p3,
58 int8_t mask = ~flat_mask4(thresh, p3, p2, p1, p0, q0, q1, q2, q3);
113 const uint8_t p3 = s[-4 * p], p2 = s[-3 * p], p1 = s[-2 * p], p0 = s[-p]; local
116 p3, p2, p1, p0, q0, q1, q2, q3);
138 const uint8_t p3 = s[-4], p2 = s[-3], p1 = s[-2], p0 = s[-1]; local
141 p3, p
21 filter_mask(uint8_t limit, uint8_t blimit, uint8_t p3, uint8_t p2, uint8_t p1, uint8_t p0, uint8_t q0, uint8_t q1, uint8_t q2, uint8_t q3) argument
37 flat_mask4(uint8_t thresh, uint8_t p3, uint8_t p2, uint8_t p1, uint8_t p0, uint8_t q0, uint8_t q1, uint8_t q2, uint8_t q3) argument
52 flat_mask5(uint8_t thresh, uint8_t p4, uint8_t p3, uint8_t p2, uint8_t p1, uint8_t p0, uint8_t q0, uint8_t q1, uint8_t q2, uint8_t q3, uint8_t q4) argument
162 const uint8_t p3 = *op3, p2 = *op2, p1 = *op1, p0 = *op0; local
185 const uint8_t p3 = s[-4 * p], p2 = s[-3 * p], p1 = s[-2 * p], p0 = s[-p]; local
211 const uint8_t p3 = s[-4], p2 = s[-3], p1 = s[-2], p0 = s[-1]; local
243 p3 = *op3, p2 = *op2, p1 = *op1, p0 = *op0; local
290 const uint8_t p3 = s[-4 * p], p2 = s[-3 * p], p1 = s[-2 * p], p0 = s[-p]; local
316 const uint8_t p3 = s[-4], p2 = s[-3], p1 = s[-2], p0 = s[-1]; local
[all...]
/hardware/intel/common/omx-components/videocodec/libvpx_internal/libvpx/test/
H A Dconvolve_test.cc326 const int p3 = filters[i][6] + filters[i][7]; local
330 EXPECT_LE(p3, 128);
331 EXPECT_LE(p0 + p3, 128);
332 EXPECT_LE(p0 + p3 + p1, 128);
333 EXPECT_LE(p0 + p3 + p1 + p2, 128);
334 EXPECT_EQ(p0 + p1 + p2 + p3, 128);
/hardware/intel/common/omx-components/videocodec/libvpx_internal/libvpx/vp9/common/x86/
H A Dvp9_loopfilter_intrin_avx2.c402 __m128i p4, p3, p2, p1, p0, q0, q1, q2, q3, q4; local
413 p3 = _mm_loadu_si128((__m128i *) (s - 4 * p));
449 _mm_or_si128(_mm_subs_epu8(p3, p2), _mm_subs_epu8(p2, p3)));
527 _mm_or_si128(_mm_subs_epu8(p3, p0), _mm_subs_epu8(p0, p3)),
580 p256_3 = _mm256_cvtepu8_epi16(p3);
879 p3 = _mm_andnot_si128(flat2, p3);
881 p3
[all...]
H A Dvp9_loopfilter_intrin_sse2.c388 __m128i p4, p3, p2, p1, p0, q0, q1, q2, q3, q4; local
393 p3 = _mm_loadu_si128((__m128i *)(s - 4 * p));
404 _mm_store_si128((__m128i *)&ap[3 * 16], p3);
441 _mm_or_si128(_mm_subs_epu8(p3, p2),
442 _mm_subs_epu8(p2, p3)));
517 work = _mm_max_epu8(_mm_or_si128(_mm_subs_epu8(p3, p0),
518 _mm_subs_epu8(p0, p3)),
584 p3 = _mm_unpacklo_epi8(_mm_loadl_epi64((__m128i *)(&ap[3 * 16] + off)),
612 b = _mm_add_epi16(_mm_add_epi16(p3, four), _mm_add_epi16(p3, p
874 __m128i p3, p2, p1, p0, q0, q1, q2, q3; local
1107 __m128i p3, p2, p1, p0, q0, q1, q2, q3; local
1346 __m128i p3, p2, p1, p0, q0, q1, q2, q3; local
[all...]
/hardware/ril/include/telephony/
H A Dril.h486 int p3; member in struct:__anon2409
500 int p3; member in struct:__anon2410
518 int p3; /* A negative P3 implies a 4 byte APDU. */ member in struct:__anon2411
/hardware/ril/reference-ril/
H A Dril.h486 int p3; member in struct:__anon2585
500 int p3; member in struct:__anon2586
518 int p3; /* A negative P3 implies a 4 byte APDU. */ member in struct:__anon2587

Completed in 1489 milliseconds