/hardware/intel/common/omx-components/videocodec/libvpx_internal/libvpx/vp9/common/mips/dspr2/ |
H A D | vp9_loopfilter_masks_dspr2.h | 29 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 D | vp9_convolve2_avg_horiz_dspr2.c | 34 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 D | vp9_convolve2_dspr2.c | 125 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 D | vp9_convolve2_horiz_dspr2.c | 116 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 D | vp9_convolve8_avg_horiz_dspr2.c | 35 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 D | vp9_convolve8_horiz_dspr2.c | 35 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 D | vp9_loopfilter_filters_dspr2.c | 32 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 D | vp9_mbloop_loopfilter_dspr2.c | 36 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 D | vp9_convolve8_dspr2.c | 52 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 D | vp9_loopfilter_filters_dspr2.h | 376 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 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; 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 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; 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 D | loopfilter_filters.c | 28 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 D | filter_dspr2.c | 132 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 D | loopfilter_filters_dspr2.c | 49 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 D | vp9_loopfilter_filters.c | 22 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 D | convolve_test.cc | 326 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 D | vp9_loopfilter_intrin_avx2.c | 402 __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 D | vp9_loopfilter_intrin_sse2.c | 388 __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 D | ril.h | 486 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 D | ril.h | 486 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
|