Home
last modified time | relevance | path

Searched refs:pu1_src (Results 1 – 25 of 62) sorted by relevance

123

/external/libhevc/common/
Dihevc_deblk_edge_filter.c102 void ihevc_deblk_luma_vert(UWORD8 *pu1_src, in ihevc_deblk_luma_vert() argument
141 dq0 = ABS(pu1_src[2] - 2 * pu1_src[1] + pu1_src[0]); in ihevc_deblk_luma_vert()
142 dq3 = ABS(pu1_src[3 * src_strd + 2] - 2 * pu1_src[3 * src_strd + 1] in ihevc_deblk_luma_vert()
143 + pu1_src[3 * src_strd + 0]); in ihevc_deblk_luma_vert()
144 dp0 = ABS(pu1_src[-3] - 2 * pu1_src[-2] + pu1_src[-1]); in ihevc_deblk_luma_vert()
145 dp3 = ABS(pu1_src[3 * src_strd - 3] - 2 * pu1_src[3 * src_strd - 2] in ihevc_deblk_luma_vert()
146 + pu1_src[3 * src_strd - 1]); in ihevc_deblk_luma_vert()
164 && (ABS(pu1_src[3] - pu1_src[0]) + ABS(pu1_src[-1] - pu1_src[-4]) in ihevc_deblk_luma_vert()
166 && ABS(pu1_src[0] - pu1_src[-1]) < ((5 * tc + 1) >> 1)) in ihevc_deblk_luma_vert()
171 pu1_src += 3 * src_strd; in ihevc_deblk_luma_vert()
[all …]
Dihevc_sao.c72 void ihevc_sao_band_offset_luma(UWORD8 *pu1_src, in ihevc_sao_band_offset_luma() argument
90 pu1_src_left[row] = pu1_src[row * src_strd + (wd - 1)]; in ihevc_sao_band_offset_luma()
95 pu1_src_top[col] = pu1_src[(ht - 1) * src_strd + col]; in ihevc_sao_band_offset_luma()
114 band_idx = band_table[pu1_src[col] >> band_shift]; in ihevc_sao_band_offset_luma()
115 … pu1_src[col] = CLIP3(pu1_src[col] + pi1_sao_offset[band_idx], 0, (1 << (band_shift + 5)) - 1); in ihevc_sao_band_offset_luma()
117 pu1_src += src_strd; in ihevc_sao_band_offset_luma()
124 void ihevc_sao_band_offset_chroma(UWORD8 *pu1_src, in ihevc_sao_band_offset_chroma() argument
145 pu1_src_left[2 * row] = pu1_src[row * src_strd + (wd - 2)]; in ihevc_sao_band_offset_chroma()
146 pu1_src_left[2 * row + 1] = pu1_src[row * src_strd + (wd - 1)]; in ihevc_sao_band_offset_chroma()
152 pu1_src_top[col] = pu1_src[(ht - 1) * src_strd + col]; in ihevc_sao_band_offset_chroma()
[all …]
Dihevc_padding.c89 void ihevc_pad_vert(UWORD8 *pu1_src, in ihevc_pad_vert() argument
99 memcpy(pu1_src - row * src_strd, pu1_src, wd); in ihevc_pad_vert()
100 memcpy(pu1_src + (ht + row - 1) * src_strd, in ihevc_pad_vert()
101 pu1_src + (ht - 1) * src_strd, wd); in ihevc_pad_vert()
143 void ihevc_pad_horz_chroma(UWORD8 *pu1_src, in ihevc_pad_horz_chroma() argument
151 UWORD16 *pu2_src = (UWORD16 *)pu1_src; in ihevc_pad_horz_chroma()
210 void ihevc_pad_horz_luma(UWORD8 *pu1_src, in ihevc_pad_horz_luma() argument
220 memset(pu1_src - pad_size, *pu1_src, pad_size); in ihevc_pad_horz_luma()
221 memset(pu1_src + wd, *(pu1_src + wd - 1), pad_size); in ihevc_pad_horz_luma()
223 pu1_src += src_strd; in ihevc_pad_horz_luma()
[all …]
Dihevc_inter_pred_filters.c108 void ihevc_inter_pred_luma_copy(UWORD8 *pu1_src, in ihevc_inter_pred_luma_copy() argument
122 pu1_dst[col] = pu1_src[col]; in ihevc_inter_pred_luma_copy()
125 pu1_src += src_strd; in ihevc_inter_pred_luma_copy()
170 void ihevc_inter_pred_luma_horz(UWORD8 *pu1_src, in ihevc_inter_pred_luma_horz() argument
187 i2_tmp += pi1_coeff[i] * pu1_src[col + (i - 3)]; in ihevc_inter_pred_luma_horz()
195 pu1_src += src_strd; in ihevc_inter_pred_luma_horz()
243 void ihevc_inter_pred_luma_vert(UWORD8 *pu1_src, in ihevc_inter_pred_luma_vert() argument
260 i2_tmp += pi1_coeff[i] * pu1_src[col + (i - 3) * src_strd]; in ihevc_inter_pred_luma_vert()
268 pu1_src += src_strd; in ihevc_inter_pred_luma_vert()
316 void ihevc_inter_pred_luma_copy_w16out(UWORD8 *pu1_src, in ihevc_inter_pred_luma_copy_w16out() argument
[all …]
Dihevc_padding.h42 UWORD8 *pu1_src,
56 UWORD8 *pu1_src,
70 UWORD8 *pu1_src,
83 typedef void ihevc_pad_top_ft(UWORD8 *pu1_src,
93 typedef void ihevc_pad_bottom_ft(UWORD8 *pu1_src,
103 typedef void ihevc_pad_left_luma_ft(UWORD8 *pu1_src,
113 typedef void ihevc_pad_left_chroma_ft(UWORD8 *pu1_src,
123 typedef void ihevc_pad_right_luma_ft(UWORD8 *pu1_src,
133 typedef void ihevc_pad_right_chroma_ft(UWORD8 *pu1_src,
Dihevc_mem_fns.c75 void ihevc_memcpy(UWORD8 *pu1_dst, UWORD8 *pu1_src, UWORD32 num_bytes) in ihevc_memcpy() argument
77 memcpy(pu1_dst, pu1_src, num_bytes); in ihevc_memcpy()
81 void ihevc_memcpy_mul_8(UWORD8 *pu1_dst, UWORD8 *pu1_src, UWORD32 num_bytes) in ihevc_memcpy_mul_8() argument
83 memcpy(pu1_dst, pu1_src, num_bytes); in ihevc_memcpy_mul_8()
/external/libhevc/common/x86/
Dihevc_inter_pred_filters_sse42_intr.c109 void ihevc_inter_pred_luma_copy_w16out_sse42(UWORD8 *pu1_src, in ihevc_inter_pred_luma_copy_w16out_sse42() argument
130 src0_16x8b = _mm_loadl_epi64((__m128i *)(pu1_src)); /* row =0 */ in ihevc_inter_pred_luma_copy_w16out_sse42()
131 src1_16x8b = _mm_loadl_epi64((__m128i *)(pu1_src + 1 * src_strd)); /* row =1 */ in ihevc_inter_pred_luma_copy_w16out_sse42()
132 src2_16x8b = _mm_loadl_epi64((__m128i *)(pu1_src + 2 * src_strd)); /* row =2 */ in ihevc_inter_pred_luma_copy_w16out_sse42()
133 src3_16x8b = _mm_loadl_epi64((__m128i *)(pu1_src + 3 * src_strd)); /* row =3 */ in ihevc_inter_pred_luma_copy_w16out_sse42()
151 pu1_src += 8; /* pointer update */ in ihevc_inter_pred_luma_copy_w16out_sse42()
155 pu1_src += 4 * src_strd - wd; /* pointer update */ in ihevc_inter_pred_luma_copy_w16out_sse42()
166 src0_16x8b = _mm_loadl_epi64((__m128i *)(pu1_src)); /* row =0 */ in ihevc_inter_pred_luma_copy_w16out_sse42()
167 src1_16x8b = _mm_loadl_epi64((__m128i *)(pu1_src + 1 * src_strd)); /* row =1 */ in ihevc_inter_pred_luma_copy_w16out_sse42()
168 src2_16x8b = _mm_loadl_epi64((__m128i *)(pu1_src + 2 * src_strd)); /* row =2 */ in ihevc_inter_pred_luma_copy_w16out_sse42()
[all …]
Dihevc_padding_ssse3_intr.c91 void ihevc_pad_left_luma_ssse3(UWORD8 *pu1_src, in ihevc_pad_left_luma_ssse3() argument
109 src_temp0_16x8b = _mm_loadu_si128((__m128i *)pu1_src); in ihevc_pad_left_luma_ssse3()
110 pu1_dst = pu1_src - pad_size; in ihevc_pad_left_luma_ssse3()
116 pu1_src += src_strd; in ihevc_pad_left_luma_ssse3()
162 void ihevc_pad_left_chroma_ssse3(UWORD8 *pu1_src, in ihevc_pad_left_chroma_ssse3() argument
180 src_temp0_16x8b = _mm_loadu_si128((__m128i *)pu1_src); in ihevc_pad_left_chroma_ssse3()
181 pu1_dst = pu1_src - pad_size; in ihevc_pad_left_chroma_ssse3()
188 pu1_src += src_strd; in ihevc_pad_left_chroma_ssse3()
234 void ihevc_pad_right_luma_ssse3(UWORD8 *pu1_src, in ihevc_pad_right_luma_ssse3() argument
250 src_temp0_16x8b = _mm_loadu_si128((__m128i *)(pu1_src - 1)); in ihevc_pad_right_luma_ssse3()
[all …]
Dihevc_inter_pred_filters_ssse3_intr.c118 void ihevc_inter_pred_luma_copy_ssse3(UWORD8 *pu1_src, in ihevc_inter_pred_luma_copy_ssse3() argument
141 src0_16x8b = _mm_loadu_si128((__m128i *)(pu1_src)); /* row =0 */ in ihevc_inter_pred_luma_copy_ssse3()
142 src1_16x8b = _mm_loadu_si128((__m128i *)(pu1_src + 1 * src_strd)); /* row =1 */ in ihevc_inter_pred_luma_copy_ssse3()
143 src2_16x8b = _mm_loadu_si128((__m128i *)(pu1_src + 2 * src_strd)); /* row =2 */ in ihevc_inter_pred_luma_copy_ssse3()
144 src3_16x8b = _mm_loadu_si128((__m128i *)(pu1_src + 3 * src_strd)); /* row =3 */ in ihevc_inter_pred_luma_copy_ssse3()
152 pu1_src += 16; /* pointer update */ in ihevc_inter_pred_luma_copy_ssse3()
156 pu1_src += 4 * src_strd - wd; /* pointer update */ in ihevc_inter_pred_luma_copy_ssse3()
168 src0_16x8b = _mm_loadl_epi64((__m128i *)(pu1_src)); /* row =0 */ in ihevc_inter_pred_luma_copy_ssse3()
169 src1_16x8b = _mm_loadl_epi64((__m128i *)(pu1_src + 1 * src_strd)); /* row =1 */ in ihevc_inter_pred_luma_copy_ssse3()
170 src2_16x8b = _mm_loadl_epi64((__m128i *)(pu1_src + 2 * src_strd)); /* row =2 */ in ihevc_inter_pred_luma_copy_ssse3()
[all …]
Dihevc_deblk_ssse3_intr.c100 void ihevc_deblk_luma_vert_ssse3(UWORD8 *pu1_src, in ihevc_deblk_luma_vert_ssse3() argument
144 src_row0_8x16b = _mm_loadl_epi64((__m128i *)(pu1_src - 4)); in ihevc_deblk_luma_vert_ssse3()
145 src_row3_8x16b = _mm_loadl_epi64((__m128i *)((pu1_src - 4) + 3 * src_strd)); in ihevc_deblk_luma_vert_ssse3()
241 src_row1_8x16b = _mm_loadl_epi64((__m128i *)((pu1_src - 4) + src_strd)); in ihevc_deblk_luma_vert_ssse3()
242 src_row2_8x16b = _mm_loadl_epi64((__m128i *)((pu1_src - 4) + 2 * src_strd)); in ihevc_deblk_luma_vert_ssse3()
529 _mm_storel_epi64((__m128i *)(pu1_src - 4), src_row0_8x16b); in ihevc_deblk_luma_vert_ssse3()
530 _mm_storel_epi64((__m128i *)((pu1_src - 4) + src_strd), src_row1_8x16b); in ihevc_deblk_luma_vert_ssse3()
531 _mm_storel_epi64((__m128i *)((pu1_src - 4) + 2 * src_strd), src_row2_8x16b); in ihevc_deblk_luma_vert_ssse3()
532 _mm_storel_epi64((__m128i *)((pu1_src - 4) + 3 * src_strd), src_row3_8x16b); in ihevc_deblk_luma_vert_ssse3()
536 void ihevc_deblk_luma_horz_ssse3(UWORD8 *pu1_src, in ihevc_deblk_luma_horz_ssse3() argument
[all …]
Dihevc_sao_ssse3_intr.c121 void ihevc_sao_band_offset_luma_ssse3(UWORD8 *pu1_src, in ihevc_sao_band_offset_luma_ssse3() argument
146 pu1_src_left[row] = pu1_src[row * src_strd + (wd - 1)]; in ihevc_sao_band_offset_luma_ssse3()
151 tmp_set_128i_1 = _mm_loadl_epi64((__m128i *)(pu1_src + (ht - 1) * src_strd + offset)); in ihevc_sao_band_offset_luma_ssse3()
256 pu1_src_cpy = pu1_src; in ihevc_sao_band_offset_luma_ssse3()
334 pu1_src += 16; in ihevc_sao_band_offset_luma_ssse3()
338 {pu1_src_cpy = pu1_src; in ihevc_sao_band_offset_luma_ssse3()
432 pu1_src += 8; in ihevc_sao_band_offset_luma_ssse3()
438 void ihevc_sao_band_offset_chroma_ssse3(UWORD8 *pu1_src, in ihevc_sao_band_offset_chroma_ssse3() argument
466 pu1_src_left[2 * row] = pu1_src[row * src_strd + (wd - 2)]; in ihevc_sao_band_offset_chroma_ssse3()
467 pu1_src_left[2 * row + 1] = pu1_src[row * src_strd + (wd - 1)]; in ihevc_sao_band_offset_chroma_ssse3()
[all …]
/external/libhevc/decoder/
Dihevcd_deblk.c109 UWORD8 *pu1_src; in ihevcd_deblk_ctb() local
228 …pu1_src = ps_deblk->pu1_cur_pic_luma + ((ps_deblk->i4_ctb_x + ps_deblk->i4_ctb_y * ps_deblk->ps_co… in ihevcd_deblk_ctb()
229 pu1_src += i4_is_last_ctb_y ? ps_deblk->ps_codec->i4_strd << log2_ctb_size : 0; in ihevcd_deblk_ctb()
233 pu1_src -= 4 * src_strd; in ihevcd_deblk_ctb()
269 pu1_src += 4 * (ctb_size / 4 - row) * src_strd; in ihevcd_deblk_ctb()
271 pu1_src += 4 * bs_tz * src_strd; in ihevcd_deblk_ctb()
327 DUMP_DEBLK_LUMA_VERT(pu1_src, src_strd, in ihevcd_deblk_ctb()
332 ps_codec->s_func_selector.ihevc_deblk_luma_vert_fptr(pu1_src, src_strd, in ihevcd_deblk_ctb()
339 pu1_src += 4 * src_strd; in ihevcd_deblk_ctb()
349 pu1_src -= (src_strd << log2_ctb_size); in ihevcd_deblk_ctb()
[all …]
Dihevcd_debug.h150 …K_LUMA_VERT(pu1_src, src_strd, u4_bs, qp_p, qp_q, beta_offset_div2, tc_offset_div2, filter_p, filt… argument
151 …K_LUMA_HORZ(pu1_src, src_strd, u4_bs, qp_p, qp_q, beta_offset_div2, tc_offset_div2, filter_p, filt… argument
152 …A_VERT(pu1_src, src_strd, u4_bs, qp_p, qp_q, qp_offset_u, qp_offset_v, tc_offset_div2, filter_p, f… argument
153 …A_HORZ(pu1_src, src_strd, u4_bs, qp_p, qp_q, qp_offset_u, qp_offset_v, tc_offset_div2, filter_p, f… argument
157 #define DUMP_DEBLK_LUMA_VERT(pu1_src, src_strd, u4_bs3, qp_p, qp_q, beta_offset_div2, tc_offset_div… argument
158 #define DUMP_DEBLK_LUMA_HORZ(pu1_src, src_strd, u4_bs3, qp_p, qp_q, beta_offset_div2, tc_offset_div… argument
159 #define DUMP_DEBLK_CHROMA_VERT(pu1_src, src_strd, u4_bs, qp_p, qp_q, qp_offset_u, qp_offset_v, tc_o… argument
160 #define DUMP_DEBLK_CHROMA_HORZ(pu1_src, src_strd, u4_bs, qp_p, qp_q, qp_offset_u, qp_offset_v, tc_o… argument
Dihevcd_fmt_conv.c390 UWORD8 *pu1_src, *pu1_dst; in ihevcd_fmt_conv_420sp_to_420sp() local
395 pu1_src = (UWORD8 *)pu1_y_src; in ihevcd_fmt_conv_420sp_to_420sp()
406 memcpy(pu1_dst, pu1_src, num_cols); in ihevcd_fmt_conv_420sp_to_420sp()
408 pu1_src += src_strd; in ihevcd_fmt_conv_420sp_to_420sp()
412 pu1_src = (UWORD8 *)pu1_uv_src; in ihevcd_fmt_conv_420sp_to_420sp()
423 memcpy(pu1_dst, pu1_src, num_cols); in ihevcd_fmt_conv_420sp_to_420sp()
425 pu1_src += src_strd; in ihevcd_fmt_conv_420sp_to_420sp()
489 UWORD8 *pu1_src, *pu1_dst; in ihevcd_fmt_conv_420sp_to_420sp_swap_uv() local
494 pu1_src = (UWORD8 *)pu1_y_src; in ihevcd_fmt_conv_420sp_to_420sp_swap_uv()
505 memcpy(pu1_dst, pu1_src, num_cols); in ihevcd_fmt_conv_420sp_to_420sp_swap_uv()
[all …]
/external/libhevc/common/arm/
Dihevc_inter_pred_chroma_horz.s83 @void ihevc_inter_pred_chroma_horz(uword8 *pu1_src,
91 @r0 => *pu1_src
121 sub r12,r0,#2 @pu1_src - 2
123 add r4,r12,r2 @pu1_src_tmp2_8 = pu1_src + src_strd
161 vld1.u32 {q0},[r12],r11 @vector load pu1_src
163 vld1.u32 {q1},[r12],r11 @vector load pu1_src
165 vld1.u32 {q2},[r12],r11 @vector load pu1_src
167 vld1.u32 {q3},[r12],r9 @vector load pu1_src
171 vld1.u32 {q4},[r4],r11 @vector load pu1_src
173 vld1.u32 {q5},[r4],r11 @vector load pu1_src
[all …]
Dihevc_inter_pred_chroma_horz_w16out.s80 @void ihevc_inter_pred_chroma_horz_w16out(uword8 *pu1_src,
88 @r0 => *pu1_src
124 sub r12,r0,#2 @pu1_src - 2
126 add r4,r12,r2 @pu1_src_tmp2_8 = pu1_src + src_strd
178 vld1.u32 {q0},[r12],r11 @vector load pu1_src
181 vld1.u32 {q1},[r12],r11 @vector load pu1_src
184 vld1.u32 {q2},[r12],r11 @vector load pu1_src
187 vld1.u32 {q3},[r12],r9 @vector load pu1_src
191 vld1.u32 {q4},[r4],r11 @vector load pu1_src
193 vld1.u32 {q5},[r4],r11 @vector load pu1_src
[all …]
Dihevc_sao_edge_offset_class2_chroma.s39 @void ihevc_sao_edge_offset_class2_chroma(UWORD8 *pu1_src,
52 @r0 => *pu1_src
96 STR r0,[sp,#0x2C] @Store pu1_src in sp
108 MLA r11,r10,r1,r0 @pu1_src[(ht - 1) * src_strd + col]
112 VLD1.8 D0,[r11]! @pu1_src[(ht - 1) * src_strd + col]
114 … VST1.8 D0,[r12]! @au1_src_top_tmp[col] = pu1_src[(ht - 1) * src_strd + col]
120 LDRB r9,[r0] @u1_pos_0_0_tmp_u = pu1_src[0]
121 LDRB r10,[r0,#1] @u1_pos_0_0_tmp_v = pu1_src[1]
125 ADD r14,r0,r1 @pu1_src + src_strd
127 SUB r12,r9,r11 @pu1_src[0] - pu1_src_top_left[0]
[all …]
Dihevc_sao_edge_offset_class3_chroma.s39 @void ihevc_sao_edge_offset_class3_chroma(UWORD8 *pu1_src,
52 @r0 => *pu1_src
106 MLA r11,r10,r1,r0 @pu1_src[(ht - 1) * src_strd + col]
110 VLD1.8 D0,[r11]! @pu1_src[(ht - 1) * src_strd + col]
112 … VST1.8 D0,[r12]! @au1_src_top_tmp[col] = pu1_src[(ht - 1) * src_strd + col]
119 LDRB r9,[r0,r14] @u1_pos_0_0_tmp_u = pu1_src[wd - 2]
121 LDRB r10,[r0,r11] @u1_pos_0_0_tmp_v = pu1_src[wd - 1]
126 SUB r12,r9,r11 @pu1_src[wd - 2] - pu1_src_top_right[0]
129 MOVGT r12,#1 @SIGN(pu1_src[wd - 2] - pu1_src_top_right[0])
130 ADD r11,r0,r1 @pu1_src + src_strd
[all …]
Dihevc_sao_edge_offset_class2.s39 @void ihevc_sao_edge_offset_class2(UWORD8 *pu1_src,
51 @r0 => *pu1_src
88 STR r0,[sp,#0x2C] @Store pu1_src in sp
100 MLA r11,r10,r1,r0 @pu1_src[(ht - 1) * src_strd + col]
104 VLD1.8 D0,[r11]! @pu1_src[(ht - 1) * src_strd + col]
106 … VST1.8 D0,[r12]! @au1_src_top_tmp[col] = pu1_src[(ht - 1) * src_strd + col]
112 LDRB r9,[r0] @u1_pos_0_0_tmp = pu1_src[0]
116 ADD r14,r0,r1 @pu1_src + src_strd
118 SUBS r12,r9,r11 @pu1_src[0] - pu1_src_top_left[0]
119 LDRB r4,[r14,#1] @pu1_src[1 + src_strd]
[all …]
Dihevc_sao_edge_offset_class3.s39 @void ihevc_sao_edge_offset_class3(UWORD8 *pu1_src,
51 @r0 => *pu1_src
98 MLA r11,r10,r1,r0 @pu1_src[(ht - 1) * src_strd + col]
102 VLD1.8 D0,[r11]! @pu1_src[(ht - 1) * src_strd + col]
104 … VST1.8 D0,[r12]! @au1_src_top_tmp[col] = pu1_src[(ht - 1) * src_strd + col]
111 LDRB r9,[r0,r10] @u1_pos_0_0_tmp = pu1_src[wd - 1]
118 SUB r12,r9,r11 @pu1_src[wd - 1] - pu1_src_top_right[0]
120 ADD r11,r0,r1 @pu1_src + src_strd
122 LDRB r14,[r11,r10] @pu1_src[wd - 1 - 1 + src_strd]
125 SUB r11,r9,r14 @pu1_src[wd - 1] - pu1_src[wd - 1 - 1 + src_strd]
[all …]
Dihevc_deblk_luma_horz.s130 @dq0 = abs( pu1_src[2] - 2 * pu1_src[1] + pu1_src[0] )@
135 @ dp0 = abs( pu1_src[-3] - 2 * pu1_src[-2] + pu1_src[-1] )@
154 …@ dq3 = abs( pu1_src[3 * src_strd + 2] - 2 * pu1_src[3 * src_strd + 1]+ pu1_src[3 * src_strd + …
160 …@ dp3 = abs( pu1_src[3 * src_strd - 3] - 2 * pu1_src[3 * src_strd - 2] + pu1_src[3 * src_strd…
237 …@ if( (2 * d3 < (beta >> 2)&& ( abs(pu1_src[3] - pu1_src[0]) + abs(pu1_src[-1] - pu1_src[-4…
238 @ && abs(pu1_src[0] - pu1_src[-1]) < ( (5 * tc + 1) >> 1 ) )
451 @ delta = ( 9 * (pu1_src[0] - pu1_src[-1]) - 3 * (pu1_src[1] - pu1_src[-2]) + 8 ) >> 4@
502 @ d14 =tmp_p1 = clip_u8(pu1_src[-2 * src_strd] + delta_p)@
Dihevc_sao_edge_offset_class1.s39 @void ihevc_sao_edge_offset_class1(UWORD8 *pu1_src,
51 @r0 => *pu1_src
83 ADD r10,r0,r9 @pu1_src[row * src_strd + wd - 1]
87 LDRB r14,[r10],r1 @Load pu1_src[row * src_strd + wd - 1]
94 ADD r12,r12,r0 @pu1_src[(ht - 1) * src_strd]
98 ADDEQ r0,r0,r1 @pu1_src += src_strd
120 SUBEQ r9,r0,r1 @pu1_src -= src_strd
123 MOV r10,r0 @*pu1_src
125 …VLD1.8 D8,[r9]! @pu1_top_row = vld1q_u8(pu1_src_top_cpy || pu1_src - src_s…
126 …VLD1.8 D9,[r9]! @pu1_top_row = vld1q_u8(pu1_src_top_cpy || pu1_src - src_s…
[all …]
Dihevc_deblk_luma_vert.s128 @dq0 = abs( pu1_src[2] - 2 * pu1_src[1] + pu1_src[0] )@
134 @ dp0 = abs( pu1_src[-3] - 2 * pu1_src[-2] + pu1_src[-1] )@
158 @ dq3 = abs( pu1_src[3 * src_strd + 2] - 2 * pu1_src[3 * src_strd + 1]+ pu1_src[3 * src_strd + 0…
164 @ dp3 = abs( pu1_src[3 * src_strd - 3] - 2 * pu1_src[3 * src_strd - 2] + pu1_src[3 * src_strd …
241 @ if( (2 * d3 < (beta >> 2)&& ( abs(pu1_src[3] - pu1_src[0]) + abs(pu1_src[-1] - pu1_src[-4]…
242 @ && abs(pu1_src[0] - pu1_src[-1]) < ( (5 * tc + 1) >> 1 ) )
448 @ delta = ( 9 * (pu1_src[0] - pu1_src[-1]) - 3 * (pu1_src[1] - pu1_src[-2]) + 8 ) >> 4@
476 @ tmp_p0 = clip_u8(pu1_src[-1] + delta)@
477 @ tmp_q0 = clip_u8(pu1_src[0] - delta)@
Dihevc_inter_pred_chroma_vert_w16out.s83 @void ihevc_inter_pred_chroma_vert_w16out(uword8 *pu1_src,
91 @r0 => *pu1_src
114 sub r0,r0,r2 @pu1_src - src_strd
141 add r6,r0,r2 @pu1_src +src_strd
142 vld1.8 {d9},[r6],r2 @loads pu1_src
166 add r0,r0,r8 @pu1_src += (2*src_strd - 2wd)
181 add r6,r0,r2 @pu1_src + src_strd
184 add r0,r0,#4 @pu1_src + 4
207 add r0,r0,r8 @pu1_src += 2*src_strd - 2*wd
227 add r6,r0,r2 @pu1_src + src_strd
[all …]
Dihevc_sao_edge_offset_class1_chroma.s39 @void ihevc_sao_edge_offset_class1_chroma(UWORD8 *pu1_src,
52 @r0 => *pu1_src
87 ADD r11,r0,r10 @pu1_src[row * src_strd + wd - 2]
91 LDRH r10,[r11],r1 @Load pu1_src[row * src_strd + wd - 2]
98 ADD r12,r12,r0 @pu1_src[(ht - 1) * src_strd]
102 ADDEQ r0,r0,r1 @pu1_src += src_strd
125 SUBEQ r11,r0,r1 @pu1_src -= src_strd
128 MOV r10,r0 @*pu1_src
130 …VLD1.8 D28,[r11]! @pu1_top_row = vld1q_u8(pu1_src_top_cpy || pu1_src - src_s…
131 …VLD1.8 D29,[r11]! @pu1_top_row = vld1q_u8(pu1_src_top_cpy || pu1_src - src_s…
[all …]

123