/external/boringssl/linux-aarch64/crypto/modes/ |
D | ghashv8-armx64.S | 17 ushr v18.2d,v19.2d,#63 19 ext v16.16b,v18.16b,v19.16b,#8 //t0=0xc2....01 20 ushr v18.2d,v3.2d,#63 22 and v18.16b,v18.16b,v16.16b 24 ext v18.16b,v18.16b,v18.16b,#8 26 orr v3.16b,v3.16b,v18.16b //H<<<=1 38 eor v18.16b,v0.16b,v2.16b 40 eor v1.16b,v1.16b,v18.16b 41 pmull v18.1q,v0.1d,v19.1d //1st phase 45 eor v0.16b,v1.16b,v18.16b [all …]
|
/external/libavc/common/armv8/ |
D | ih264_inter_pred_luma_horz_qpel_vert_hpel_av8.s | 177 uaddl v18.8h, v0.8b, v10.8b 179 mla v18.8h, v20.8h , v28.8h 185 mls v18.8h, v22.8h , v30.8h 191 st1 {v18.4s }, [x9], #16 193 ext v24.16b, v18.16b , v20.16b , #4 194 ext v26.16b, v18.16b , v20.16b , #6 196 ext v22.16b, v18.16b , v20.16b , #10 198 ext v24.16b, v18.16b , v20.16b , #2 199 ext v26.16b, v18.16b , v20.16b , #8 202 saddl v26.4s, v18.4h, v22.4h [all …]
|
D | ih264_inter_pred_luma_horz_qpel_vert_qpel_av8.s | 156 ld1 {v18.2s, v19.2s}, [x6], x2 // horz row0, col 0 162 ext v23.8b, v18.8b , v19.8b , #5 163 ext v20.8b, v18.8b , v19.8b , #2 164 ext v21.8b, v18.8b , v19.8b , #3 165 ext v22.8b, v18.8b , v19.8b , #4 166 ext v19.8b, v18.8b , v19.8b , #1 168 uaddl v28.8h, v18.8b, v23.8b 173 ld1 {v18.2s, v19.2s}, [x11], x2 // horz row 0, col 1 180 ext v23.8b, v18.8b , v19.8b , #5 181 ext v20.8b, v18.8b , v19.8b , #2 [all …]
|
D | ih264_inter_pred_luma_horz_hpel_vert_hpel_av8.s | 115 uaddl v18.8h, v0.8b, v10.8b 117 mla v18.8h, v20.8h , v28.8h 123 mls v18.8h, v22.8h , v30.8h 130 ext v24.16b, v18.16b , v20.16b , #4 131 ext v26.16b, v18.16b , v20.16b , #6 133 ext v23.16b, v18.16b , v20.16b , #10 135 ext v24.16b, v18.16b , v20.16b , #2 136 ext v26.16b, v18.16b , v20.16b , #8 139 saddl v26.4s, v18.4h, v23.4h 143 saddl2 v23.4s, v18.8h, v23.8h [all …]
|
D | ih264_inter_pred_luma_horz_hpel_vert_qpel_av8.s | 242 uaddl v18.8h, v2.8b, v3.8b 244 mla v16.8h, v18.8h , v22.8h 247 uaddl v18.8h, v1.8b, v4.8b 249 mls v16.8h, v18.8h , v24.8h 258 saddl v18.4s, v6.4h, v16.4h 266 smlal v18.4s, v30.4h, v22.4h 267 smlsl v18.4s, v28.4h, v24.4h 273 sqrshrun v18.4h, v18.4s, #10 281 uqxtn v18.8b, v18.8h 283 mov v18.s[1], v19.s[0] [all …]
|
D | ih264_inter_pred_luma_vert_qpel_av8.s | 151 uaddl v18.8h, v5.8b, v7.8b // temp3 = src[2_8] + src[3_8] 152 mla v20.8h, v18.8h , v22.8h // temp4 += temp3 * 20 158 uaddl v18.8h, v4.8b, v10.8b 167 mls v16.8h, v18.8h , v24.8h 172 uaddl v18.8h, v4.8b, v2.8b 175 mla v18.8h, v12.8h , v22.8h 183 mls v18.8h, v20.8h , v24.8h 195 sqrshrun v30.8b, v18.8h, #5 196 uaddl v18.8h, v7.8b, v5.8b 198 mla v18.8h, v12.8h , v22.8h [all …]
|
D | ih264_inter_pred_filters_luma_vert_av8.s | 144 uaddl v18.8h, v5.8b, v7.8b // temp3 = src[2_8] + src[3_8] 145 mla v20.8h, v18.8h , v22.8h // temp4 += temp3 * 20 151 uaddl v18.8h, v4.8b, v10.8b 160 mls v16.8h, v18.8h , v24.8h 162 uaddl v18.8h, v4.8b, v2.8b 166 mla v18.8h, v12.8h , v22.8h 174 mls v18.8h, v20.8h , v24.8h 184 sqrshrun v30.8b, v18.8h, #5 185 uaddl v18.8h, v7.8b, v5.8b 187 mla v18.8h, v12.8h , v22.8h [all …]
|
D | ih264_deblk_luma_av8.s | 129 cmhs v18.16b, v22.16b, v20.16b 135 orr v18.16b, v18.16b , v24.16b //Q9 = ( ABS(p0 - q0) >= Alpha ) | ( ABS(q1 - q0) >= Beta ) 138 …orr v18.16b, v18.16b , v26.16b //Q9 = ( ABS(p0 - q0) >= Alpha ) | ( ABS(q1 - q0) >= Beta ) |… 143 bic v12.16b, v12.16b , v18.16b //final condition 146 sub v18.16b, v14.16b , v20.16b //Q9 = C0 + (Ap < Beta) 152 sub v18.16b, v18.16b , v22.16b //Q9 = C0 + (Ap < Beta) + (Aq < Beta) 159 umin v18.16b, v26.16b , v18.16b //Q9 = delta = (ABS(i_macro) > C) ? C : ABS(i_macro) 163 … and v18.16b, v18.16b , v12.16b //Making delta zero in places where values shouldn be filterd 180 uqadd v16.16b, v6.16b , v18.16b //Q8 = p0 + delta 181 uqsub v6.16b, v6.16b , v18.16b //Q3 = p0 - delta [all …]
|
/external/libhevc/common/arm64/ |
D | ihevc_sao_edge_offset_class3_chroma.s | 363 movi v18.16b, #0 394 movi v18.16b, #0 //I 404 mov v18.h[7], w5 //I vsetq_lane_u8 408 …EXT v18.16b, v18.16b , v16.16b,#14 //I pu1_next_row_tmp = vextq_u8(pu1_next_row_tmp, pu1… 441 cmhi v20.16b, v5.16b , v18.16b //I vcgtq_u8(pu1_cur_row, pu1_next_row_tmp) 443 cmhi v22.16b, v18.16b , v5.16b //I vcltq_u8(pu1_cur_row, pu1_next_row_tmp) 446 ADD v18.16b, v0.16b , v17.16b //I edge_idx = vaddq_s8(const_2, sign_up) 447 ADD v18.16b, v18.16b , v22.16b //I edge_idx = vaddq_s8(edge_idx, sign_down) 448 TBL v18.16b, {v28.16b},v18.16b //I vtbl1_s8(edge_idx_tbl, vget_low_s8(edge_idx)) 455 AND v18.16b, v18.16b , v1.16b //I edge_idx = vandq_s8(edge_idx, au1_mask) [all …]
|
D | ihevc_sao_edge_offset_class2.s | 290 movi v18.16b, #0 298 …mov v18.b[0], w5 //I pu1_next_row_tmp = vsetq_lane_u8(pu1_src_cpy[src_strd … 300 …EXT v18.16b, v16.16b , v18.16b,#1 //I pu1_next_row_tmp = vextq_u8(pu1_next_row, pu1_next… 319 cmhi v3.16b, v5.16b , v18.16b //I vcgtq_u8(pu1_cur_row, pu1_next_row_tmp) 322 cmhi v18.16b, v18.16b , v5.16b //I vcltq_u8(pu1_cur_row, pu1_next_row_tmp) 323 …SUB v3.16b, v18.16b , v3.16b //I sign_down = vreinterpretq_s8_u8(vsubq_u8(cmp_lt, cmp_g… 326 TBL v18.16b, {v6.16b},v24.16b //I vtbl1_s8(edge_idx_tbl, vget_low_s8(edge_idx)) 329 AND v18.16b, v18.16b , v1.16b //I edge_idx = vandq_s8(edge_idx, au1_mask) 332 TBL v3.16b, {v7.16b},v18.16b //I offset = vtbl1_s8(offset_tbl, vget_low_s8(edge_idx)) 376 …mov v18.b[0], w8 //III pu1_next_row_tmp = vsetq_lane_u8(pu1_src_cpy[src_str… [all …]
|
D | ihevc_sao_edge_offset_class2_chroma.s | 411 movi v18.16b, #0 415 …mov v18.h[0], w5 //I pu1_next_row_tmp = vsetq_lane_u8(pu1_src_cpy[src_strd … 419 …EXT v18.16b, v16.16b , v18.16b,#2 //I pu1_next_row_tmp = vextq_u8(pu1_next_row, pu1_next… 455 cmhi v20.16b, v5.16b , v18.16b //I vcgtq_u8(pu1_cur_row, pu1_next_row_tmp) 457 cmhi v22.16b, v18.16b , v5.16b //I vcltq_u8(pu1_cur_row, pu1_next_row_tmp) 460 ADD v18.16b, v0.16b , v17.16b //I edge_idx = vaddq_s8(const_2, sign_up) 461 ADD v18.16b, v18.16b , v22.16b //I edge_idx = vaddq_s8(edge_idx, sign_down) 463 TBL v18.16b, {v30.16b},v18.16b //I vtbl1_s8(edge_idx_tbl, vget_low_s8(edge_idx)) 470 AND v22.16b, v18.16b , v1.16b //I edge_idx = vandq_s8(edge_idx, au1_mask) 473 …Uxtl2 v18.8h, v5.16b //I pi2_tmp_cur_row.val[1] = vreinterpretq_s16_u16(vmovl_u… [all …]
|
D | ihevc_sao_edge_offset_class3.s | 296 movi v18.16b, #0 311 mov v18.b[15], w8 //I vsetq_lane_u8 314 …EXT v18.16b, v18.16b , v16.16b,#15 //I pu1_next_row_tmp = vextq_u8(pu1_next_row_tmp, pu1… 332 cmhi v3.16b, v5.16b , v18.16b //I vcgtq_u8(pu1_cur_row, pu1_next_row_tmp) 333 cmhi v18.16b, v18.16b , v5.16b //I vcltq_u8(pu1_cur_row, pu1_next_row_tmp) 334 …SUB v3.16b, v18.16b , v3.16b //I sign_down = vreinterpretq_s8_u8(vsubq_u8(cmp_lt, cmp_g… 336 ADD v18.16b, v0.16b , v17.16b //I edge_idx = vaddq_s8(const_2, sign_up) 337 ADD v18.16b, v18.16b , v3.16b //I edge_idx = vaddq_s8(edge_idx, sign_down) 338 TBL v18.16b, {v6.16b},v18.16b //I vtbl1_s8(edge_idx_tbl, vget_low_s8(edge_idx)) 345 AND v18.16b, v18.16b , v1.16b //I edge_idx = vandq_s8(edge_idx, au1_mask) [all …]
|
D | ihevc_sao_edge_offset_class0.s | 162 cmhi v18.16b, v21.16b , v17.16b //vcltq_u8(pu1_cur_row, pu1_cur_row_tmp) 165 …SUB v20.16b, v18.16b , v16.16b //sign_left = vreinterpretq_s8_u8(vsubq_u8(cmp_lt, cmp_gt… 188 cmhi v18.16b, v21.16b , v17.16b //vcltq_u8(pu1_cur_row, pu1_cur_row_tmp) 192 …SUB v22.16b, v18.16b , v16.16b //sign_right = vreinterpretq_s8_u8(vsubq_u8(cmp_lt, cmp_g… 199 …Uxtl v18.8h, v17.8b //pi2_tmp_cur_row.val[0] = vreinterpretq_s16_u16(vmovl_u8(… 216 SADDW v18.8h, v18.8h , v16.8b 218 …SMAX v18.8h, v18.8h , v4.8h //pi2_tmp_cur_row.val[0] = vmaxq_s16(pi2_tmp_cur_row.val[0… 221 …UMIN v18.8h, v18.8h , v6.8h //pi2_tmp_cur_row.val[0] = vreinterpretq_s16_u16(vminq_u16… 234 xtn v18.8b, v18.8h //vmovn_s16(pi2_tmp_cur_row.val[0]) 247 ST1 {v18.8b, v19.8b},[x12],x1 //vst1q_u8(pu1_src_cpy, pu1_cur_row) [all …]
|
D | ihevc_itrans_recon_32x32.s | 240 smull v18.4s, v10.4h, v0.h[0] 241 smlal v18.4s, v11.4h, v3.h[2] 274 smlal v18.4s, v12.4h, v7.h[0] 275 smlsl v18.4s, v13.4h, v5.h[2] 310 smlsl v18.4s, v10.4h, v2.h[0] 311 smlsl v18.4s, v11.4h, v1.h[2] 348 smlsl v18.4s, v12.4h, v5.h[0] 349 smlal v18.4s, v13.4h, v7.h[2] 386 smlal v18.4s, v10.4h, v0.h[0] 387 smlal v18.4s, v11.4h, v0.h[2] [all …]
|
D | ihevc_sao_edge_offset_class0_chroma.s | 185 cmhi v18.16b, v21.16b , v19.16b //vcltq_u8(pu1_cur_row, pu1_cur_row_tmp) 188 …SUB v20.16b, v18.16b , v16.16b //sign_left = vreinterpretq_s8_u8(vsubq_u8(cmp_lt, cmp_gt… 212 cmhi v18.16b, v21.16b , v19.16b //vcltq_u8(pu1_cur_row, pu1_cur_row_tmp) 215 …SUB v22.16b, v18.16b , v16.16b //sign_right = vreinterpretq_s8_u8(vsubq_u8(cmp_lt, cmp_g… 241 …Uxtl v18.8h, v19.8b //pi2_tmp_cur_row.val[0] = vreinterpretq_s16_u16(vmovl_u8(… 253 …SADDW v18.8h, v18.8h , v16.8b //pi2_tmp_cur_row.val[0] = vaddw_s8(pi2_tmp_cur_row.val[0]… 255 …SMAX v18.8h, v18.8h , v4.8h //pi2_tmp_cur_row.val[0] = vmaxq_s16(pi2_tmp_cur_row.val[0… 259 …UMIN v18.8h, v18.8h , v6.8h //pi2_tmp_cur_row.val[0] = vreinterpretq_s16_u16(vminq_u16… 271 xtn v21.8b, v18.8h //vmovn_s16(pi2_tmp_cur_row.val[0]) 368 cmhi v18.16b, v21.16b , v19.16b //vcltq_u8(pu1_cur_row, pu1_cur_row_tmp) [all …]
|
D | ihevc_itrans_recon_8x8.s | 189 smull v18.4s, v3.4h, v1.h[2] //// y2 * sin2 (q3 is freed by this time)(part of d1) 239 smlsl v18.4s, v11.4h, v0.h[2] //// d1 = y2 * sin2 - y6 * cos2(part of a0 and a1) 252 sub v22.4s, v20.4s , v18.4s //// a2 = c1 - d1(part of x2,x5) 253 add v18.4s, v20.4s , v18.4s //// a1 = c1 + d1(part of x1,x6) 261 add v28.4s, v18.4s , v26.4s //// a1 + b1(part of x1) 262 sub v18.4s, v18.4s , v26.4s //// a1 - b1(part of x6) 272 sqrshrn v11.4h, v18.4s,#shift_stage1_idct //// x6 = (a1 - b1 + rnd) >> 7(shift_stage1_idct) 314 smull v18.4s, v3.4h, v1.h[2] //// y2 * sin2 (q3 is freed by this time)(part of d1) 322 sub v22.4s, v20.4s , v18.4s //// a2 = c1 - d1(part of x2,x5) 323 add v18.4s, v20.4s , v18.4s //// a1 = c1 + d1(part of x1,x6) [all …]
|
D | ihevc_sao_edge_offset_class1.s | 145 LD1 {v18.16b},[x10] //pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) 148 cmhi v5.16b, v3.16b , v18.16b //vcgtq_u8(pu1_cur_row, pu1_top_row) 151 cmhi v17.16b, v18.16b , v3.16b //vcltq_u8(pu1_cur_row, pu1_top_row) 155 …Uxtl v26.8h, v18.8b //II pi2_tmp_cur_row.val[0] = vreinterpretq_s16_u16(vmovl_… 158 …Uxtl2 v28.8h, v18.16b //II pi2_tmp_cur_row.val[1] = vreinterpretq_s16_u16(vmovl_… 161 cmhi v22.16b, v18.16b , v30.16b //II vcgtq_u8(pu1_cur_row, pu1_top_row) 165 cmhi v24.16b, v30.16b , v18.16b //II vcltq_u8(pu1_cur_row, pu1_top_row) 222 LD1 {v18.16b},[x10] //pu1_next_row = vld1q_u8(pu1_src_cpy + src_strd) 223 cmhi v5.16b, v3.16b , v18.16b //vcgtq_u8(pu1_cur_row, pu1_top_row) 224 cmhi v17.16b, v18.16b , v3.16b //vcltq_u8(pu1_cur_row, pu1_top_row) [all …]
|
D | ihevc_weighted_pred_bi.s | 251 … smull v18.4s, v2.4h, v7.h[0] //vmull_n_s16(pi2_src1_val2, (int16_t) wgt0) iv iteration 263 add v18.4s, v18.4s , v20.4s //vaddq_s32(i4_tmp2_t1, i4_tmp2_t2) iv iteration 266 add v18.4s, v18.4s , v30.4s //vaddq_s32(i4_tmp2_t1, tmp_lvl_shift_t) iv iteration 271 sshl v18.4s,v18.4s,v28.4s 279 sqxtun v18.4h, v18.4s //vqmovun_s32(sto_res_tmp1) iv iteration 282 uqxtn v18.8b,v18.8h 285 st1 {v18.s}[0],[x10],x5 //store pu1_dst iv iteration
|
D | ihevc_intra_pred_luma_mode_3_to_9.s | 222 umull v18.8h, v23.8b, v7.8b //mul (row 3) 223 umlal v18.8h, v25.8b, v6.8b //mul (row 3) 230 rshrn v18.8b, v18.8h,#5 //round shft (row 3) 240 st1 {v18.8b},[x2], x3 //st (row 3) 259 umull v18.8h, v23.8b, v7.8b //mul (row 7) 260 umlal v18.8h, v25.8b, v6.8b //mul (row 7) 264 rshrn v18.8b, v18.8h,#5 //round shft (row 7) 270 st1 {v18.8b},[x2], x3 //st (row 7) 343 umull v18.8h, v23.8b, v7.8b //mul (row 7) 345 umlal v18.8h, v25.8b, v6.8b //mul (row 7) [all …]
|
D | ihevc_itrans_recon_16x16.s | 276 smull v18.4s, v10.4h, v0.h[0] 277 smlal v18.4s, v11.4h, v3.h[2] 303 smlsl v18.4s, v4.4h, v1.h[0] 304 smlsl v18.4s, v5.4h, v2.h[2] 378 smlal v18.4s, v10.4h, v0.h[0] 379 smlal v18.4s, v11.4h, v1.h[2] 380 smlsl v18.4s, v4.4h, v3.h[0] 381 smlsl v18.4s, v5.4h, v0.h[2] 394 add v16.4s, v18.4s , v30.4s 395 sub v28.4s, v18.4s , v30.4s [all …]
|
D | ihevc_intra_pred_chroma_horz.s | 120 ld1 { v18.8h},[x12] //load 16 values. d1[7] will have the 1st value. 149 dup v2.8h, v18.h[7] 153 dup v4.8h, v18.h[6] 157 dup v6.8h, v18.h[5] 161 dup v1.8h, v18.h[4] 165 dup v2.8h, v18.h[3] 169 dup v4.8h, v18.h[2] 173 dup v6.8h, v18.h[1] 178 dup v1.8h, v18.h[0] 206 dup v18.8h, v0.h[7] [all …]
|
/external/boringssl/linux-aarch64/crypto/aes/ |
D | aesv8-armx64.S | 305 ld1 {v18.4s,v19.4s},[x7],#32 361 aese v0.16b,v18.16b 400 aese v0.16b,v18.16b 420 ld1 {v18.16b},[x0],#16 425 orr v19.16b,v18.16b,v18.16b 428 orr v1.16b,v18.16b,v18.16b 429 ld1 {v18.16b},[x0],#16 432 orr v19.16b,v18.16b,v18.16b 439 aesd v18.16b,v16.16b 440 aesimc v18.16b,v18.16b [all …]
|
/external/llvm/test/MC/SystemZ/ |
D | insn-good-z13.s | 25 #CHECK: vab %v18, %v3, %v20 # encoding: [0xe7,0x23,0x40,0x00,0x0a,0xf3] 31 vab %v18, %v3, %v20 37 #CHECK: vaccb %v18, %v3, %v20 # encoding: [0xe7,0x23,0x40,0x00,0x0a,0xf1] 43 vaccb %v18, %v3, %v20 63 #CHECK: vaccf %v18, %v3, %v20 # encoding: [0xe7,0x23,0x40,0x00,0x2a,0xf1] 69 vaccf %v18, %v3, %v20 75 #CHECK: vaccg %v18, %v3, %v20 # encoding: [0xe7,0x23,0x40,0x00,0x3a,0xf1] 81 vaccg %v18, %v3, %v20 87 #CHECK: vacch %v18, %v3, %v20 # encoding: [0xe7,0x23,0x40,0x00,0x1a,0xf1] 93 vacch %v18, %v3, %v20 [all …]
|
/external/libmpeg2/common/armv8/ |
D | ideint_spatial_filter_av8.s | 69 movi v18.8h, #0 112 uabal v18.8h, v1.8b, v5.8b 126 addp v18.8h, v18.8h, v18.8h 130 uaddlp v18.2s, v18.4h 137 mul v18.2s, v18.2s, v31.2s 148 smov x6, v18.s[0] 176 smov x6, v18.s[1]
|
/external/llvm/test/MC/Disassembler/SystemZ/ |
D | insns-z13.txt | 17 #CHECK: vab %v18, %v3, %v20 26 #CHECK: vaccb %v18, %v3, %v20 44 #CHECK: vaccf %v18, %v3, %v20 53 #CHECK: vaccg %v18, %v3, %v20 62 #CHECK: vacch %v18, %v3, %v20 71 #CHECK: vaccq %v18, %v3, %v20 89 #CHECK: vaf %v18, %v3, %v20 98 #CHECK: vag %v18, %v3, %v20 107 #CHECK: vah %v18, %v3, %v20 116 #CHECK: vaq %v18, %v3, %v20 [all …]
|