/aosp_15_r20/external/libhevc/common/arm/ |
H A D | ihevc_sao_edge_offset_class3_chroma.s | 365 VLD1.8 D16,[r11]! @I pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) 366 VLD1.8 D17,[r11] @I pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) 379 LDRB r8,[r0,#14] @I pu1_src_cpy[14] 382 LDRB r11,[r5,#16] @I load the value pu1_src_cpy[16 - src_strd] 384 LDRB r9,[r0,#15] @I pu1_src_cpy[15] 385 SUB r8,r8,r11 @I pu1_src_cpy[14] - pu1_src_cpy[16 - src_strd] 387 LDRB r10,[r5,#17] @I load the value pu1_src_cpy[17 - src_strd] 391 SUB r9,r9,r10 @I pu1_src_cpy[15] - pu1_src_cpy[17 - src_strd] 393 MOVGT r8,#1 @I SIGN(pu1_src_cpy[14] - pu1_src_cpy[16 - src_strd]) 397 …8 @I sign_up = sign_up = vsetq_lane_s8(SIGN(pu1_src_cpy[14] -pu1_src_cpy[16 - sr… [all …]
|
H A D | ihevc_sao_edge_offset_class3.s | 289 VLD1.8 D16,[r8]! @I pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) 290 VLD1.8 D17,[r8] @I pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) 306 LDRB r8,[r0,#15] @I pu1_src_cpy[15] 307 SUB r5,r0,r1 @I pu1_src_cpy[16 - src_strd] 310 SUB r8,r8,r5 @I pu1_src_cpy[15] - pu1_src_cpy[16 - src_strd] 313 MOVGT r8,#1 @I SIGN(pu1_src_cpy[15] - pu1_src_cpy[16 - src_strd]) 314 … D15[7],r8 @I sign_up = vsetq_lane_s8(SIGN(pu1_src_cpy[15] - pu1_src_cpy[16 - s… 354 ADD r4,r0,r1 @II pu1_src_cpy[16 - src_strd] 358 LDRB r11,[r4,#15] @II pu1_src_cpy[15] 359 VLD1.8 D16,[r8]! @II pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) [all …]
|
H A D | ihevc_sao_edge_offset_class2_chroma.s | 369 VLD1.8 D16,[r8]! @I pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) 370 VLD1.8 D17,[r8] @I pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) 375 LDRH r5,[r8] @I pu1_src_cpy[src_strd + 16] 378 …VMOV.16 D18[0],r5 @I pu1_next_row_tmp = vsetq_lane_u8(pu1_src_cpy[src_strd +… 385 LDRB r11,[r0] @I pu1_src_cpy[0] 388 LDRB r10,[r0,#1] @I pu1_src_cpy[0] 394 …SUB r8,r11,r5 @I pu1_src_cpy[0] - pu1_src_left_cpy[(ht_tmp - 1 - row) * … 398 …SUB r4,r10,r5 @I pu1_src_cpy[1] - pu1_src_left_cpy[(ht_tmp - 1 - row) * … 401 …MOVGT r8,#1 @I SIGN(pu1_src_cpy[0] - pu1_src_left_cpy[(ht_tmp - 1 - ro… 404 …VMOV.8 D14[0],r8 @I sign_up = sign_up = vsetq_lane_s8(SIGN(pu1_src_cpy[0] -… [all …]
|
H A D | ihevc_sao_edge_offset_class2.s | 278 VLD1.8 D16,[r8]! @I pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) 279 VLD1.8 D17,[r8] @I pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) 283 LDRB r5,[r8,#16] @I pu1_src_cpy[src_strd + 16] 284 …VMOV.8 D18[0],r5 @I pu1_next_row_tmp = vsetq_lane_u8(pu1_src_cpy[src_strd +… 292 LDRB r11,[r0] @I pu1_src_cpy[0] 296 SUBS r4,r11,r5 @I pu1_src_cpy[0] - pu1_src_left_cpy[ht_tmp - 1 - row] 298 …MOVGT r4,#1 @I SIGN(pu1_src_cpy[0] - pu1_src_left_cpy[ht_tmp - 1 - row… 299 …VMOV.8 D14[0],r4 @I sign_up = sign_up = vsetq_lane_s8(SIGN(pu1_src_cpy[0] -… 340 VST1.8 {Q10},[r0],r1 @I vst1q_u8(pu1_src_cpy, pu1_cur_row) 343 VLD1.8 D16,[r8]! @II pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) [all …]
|
H A D | ihevc_sao_edge_offset_class0_chroma.s | 153 MOV r12,r0 @pu1_src_cpy = pu1_src 158 VLD1.8 D12,[r12]! @pu1_cur_row = vld1q_u8(pu1_src_cpy) 159 VLD1.8 D13,[r12],r1 @pu1_cur_row = vld1q_u8(pu1_src_cpy) 167 VLD1.8 D30,[r12]! @II Iteration pu1_cur_row = vld1q_u8(pu1_src_cpy) 168 VLD1.8 D31,[r12] @II Iteration pu1_cur_row = vld1q_u8(pu1_src_cpy) 184 LDRB r11,[r12,#16] @pu1_src_cpy[16] 187 …VMOV.8 D14[0],r11 @pu1_cur_row_tmp = vsetq_lane_u8(pu1_src_cpy[16], pu1_cur_… 190 LDRB r11,[r12,#17] @pu1_src_cpy[17] 195 …VMOV.8 D14[1],r11 @pu1_cur_row_tmp = vsetq_lane_u8(pu1_src_cpy[17], pu1_cur_… 196 LDRB r11,[r12,#16] @II pu1_src_cpy[16] [all …]
|
H A D | ihevc_sao_band_offset_chroma.s | 285 MOV r4,r0 @pu1_src_cpy 289 MOV r4,r0 @pu1_src_cpy 295 VLD2.8 {D5,D6},[r4] @vld1q_u8(pu1_src_cpy) 298 VLD2.8 {D13,D14},[r5] @vld1q_u8(pu1_src_cpy) 301 VLD2.8 {D17,D18},[r6] @vld1q_u8(pu1_src_cpy) 304 VLD2.8 {D21,D22},[r7] @vld1q_u8(pu1_src_cpy) 319 VST2.8 {D5,D6},[r4] @vst1q_u8(pu1_src_cpy, au1_cur_row) 325 VST2.8 {D13,D14},[r5] @vst1q_u8(pu1_src_cpy, au1_cur_row) 331 VST2.8 {D17,D18},[r6],r1 @vst1q_u8(pu1_src_cpy, au1_cur_row) 334 VST2.8 {D21,D22},[r7] @vst1q_u8(pu1_src_cpy, au1_cur_row) [all …]
|
H A D | ihevc_sao_edge_offset_class0.s | 146 MOV r12,r0 @pu1_src_cpy = pu1_src 151 VLD1.8 D12,[r12]! @pu1_cur_row = vld1q_u8(pu1_src_cpy) 152 VLD1.8 D13,[r12], r1 @pu1_cur_row = vld1q_u8(pu1_src_cpy) 160 VLD1.8 D26,[r12]! @II Iteration pu1_cur_row = vld1q_u8(pu1_src_cpy) 161 VLD1.8 D27,[r12] @II Iteration pu1_cur_row = vld1q_u8(pu1_src_cpy) 178 LDRB r11,[r12,#16] @pu1_src_cpy[16] 183 …VMOV.8 D14[0],r11 @pu1_cur_row_tmp = vsetq_lane_u8(pu1_src_cpy[16], pu1_cur_… 186 LDRB r11,[r12,#16] @II pu1_src_cpy[16] 191 …VMOV.8 D28[0],r11 @II pu1_cur_row_tmp = vsetq_lane_u8(pu1_src_cpy[16], pu1_c… 257 VST1.8 {D18,D19},[r12],r1 @vst1q_u8(pu1_src_cpy, pu1_cur_row) [all …]
|
H A D | ihevc_sao_edge_offset_class1.s | 152 VLD1.8 D18,[r10]! @pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) 153 VLD1.8 D19,[r10] @pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) 158 VLD1.8 D30,[r6]! @II pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) 159 VLD1.8 D31,[r6] @II pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) 220 VST1.8 {Q10},[r10],r1 @vst1q_u8(pu1_src_cpy, pu1_cur_row) 226 VST1.8 {Q15},[r10],r1 @II vst1q_u8(pu1_src_cpy, pu1_cur_row) 233 VLD1.8 D18,[r10]! @pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) 234 VLD1.8 D19,[r10] @pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) 261 VST1.8 {Q15},[r10],r1 @vst1q_u8(pu1_src_cpy, pu1_cur_row) 294 VLD1.8 D18,[r10]! @pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) [all …]
|
H A D | ihevc_sao_edge_offset_class1_chroma.s | 156 VLD1.8 D18,[r10]! @pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) 157 VLD1.8 D19,[r10] @pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) 162 VLD1.8 D30,[r6]! @II pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) 163 VLD1.8 D31,[r6] @II pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) 232 VST1.8 {Q10},[r10],r1 @vst1q_u8(pu1_src_cpy, pu1_cur_row) 238 VST1.8 {Q15},[r10],r1 @II vst1q_u8(pu1_src_cpy, pu1_cur_row) 245 VLD1.8 D18,[r10]! @pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) 246 VLD1.8 D19,[r10] @pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) 278 VST1.8 {Q15},[r10],r1 @vst1q_u8(pu1_src_cpy, pu1_cur_row) 311 VLD1.8 D18,[r10]! @pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) [all …]
|
H A D | ihevc_sao_band_offset_luma.s | 193 MOV r4,r0 @pu1_src_cpy 199 VLD1.8 D13,[r4] @au1_cur_row = vld1_u8(pu1_src_cpy) 202 VLD1.8 D15,[r5] @au1_cur_row = vld1_u8(pu1_src_cpy) 204 VLD1.8 D17,[r6] @au1_cur_row = vld1_u8(pu1_src_cpy) 206 VLD1.8 D19,[r10] @au1_cur_row = vld1_u8(pu1_src_cpy) 219 VST1.8 D13,[r4],r1 @vst1_u8(pu1_src_cpy, au1_cur_row) 221 VST1.8 D15,[r5] @vst1_u8(pu1_src_cpy, au1_cur_row) 224 VST1.8 D17,[r6],r1 @vst1_u8(pu1_src_cpy, au1_cur_row) 227 VST1.8 D19,[r10] @vst1_u8(pu1_src_cpy, au1_cur_row)
|
/aosp_15_r20/external/libhevc/common/x86/ |
H A D | ihevc_sao_ssse3_intr.c | 132 UWORD8 *pu1_src_cpy; in ihevc_sao_band_offset_luma_ssse3() local 256 pu1_src_cpy = pu1_src; in ihevc_sao_band_offset_luma_ssse3() 262 src_temp0_8x16b = _mm_loadu_si128((__m128i *)(pu1_src_cpy)); in ihevc_sao_band_offset_luma_ssse3() 264 src_temp2_8x16b = _mm_loadu_si128((__m128i *)(pu1_src_cpy + src_strd)); in ihevc_sao_band_offset_luma_ssse3() 328 _mm_storeu_si128((__m128i *)(pu1_src_cpy), src_temp0_8x16b); in ihevc_sao_band_offset_luma_ssse3() 330 _mm_storeu_si128((__m128i *)(pu1_src_cpy + src_strd), src_temp2_8x16b); in ihevc_sao_band_offset_luma_ssse3() 332 pu1_src_cpy += (src_strd << 1); in ihevc_sao_band_offset_luma_ssse3() 338 {pu1_src_cpy = pu1_src; in ihevc_sao_band_offset_luma_ssse3() 344 src_temp0_8x16b = _mm_loadl_epi64((__m128i *)(pu1_src_cpy)); in ihevc_sao_band_offset_luma_ssse3() 346 src_temp1_8x16b = _mm_loadl_epi64((__m128i *)(pu1_src_cpy + src_strd)); in ihevc_sao_band_offset_luma_ssse3() [all …]
|