| /kernel/linux/linux-5.10/arch/arm64/lib/ |
| H A D | xor-neon.c | 16 uint64_t *dp1 = (uint64_t *)p1; in xor_arm64_neon_2() local
24 v0 = veorq_u64(vld1q_u64(dp1 + 0), vld1q_u64(dp2 + 0)); in xor_arm64_neon_2()
25 v1 = veorq_u64(vld1q_u64(dp1 + 2), vld1q_u64(dp2 + 2)); in xor_arm64_neon_2()
26 v2 = veorq_u64(vld1q_u64(dp1 + 4), vld1q_u64(dp2 + 4)); in xor_arm64_neon_2()
27 v3 = veorq_u64(vld1q_u64(dp1 + 6), vld1q_u64(dp2 + 6)); in xor_arm64_neon_2()
30 vst1q_u64(dp1 + 0, v0); in xor_arm64_neon_2()
31 vst1q_u64(dp1 + 2, v1); in xor_arm64_neon_2()
32 vst1q_u64(dp1 + 4, v2); in xor_arm64_neon_2()
33 vst1q_u64(dp1 + 6, v3); in xor_arm64_neon_2()
35 dp1 in xor_arm64_neon_2()
43 uint64_t *dp1 = (uint64_t *)p1; xor_arm64_neon_3() local
78 uint64_t *dp1 = (uint64_t *)p1; xor_arm64_neon_4() local
122 uint64_t *dp1 = (uint64_t *)p1; xor_arm64_neon_5() local
[all...] |
| /kernel/linux/linux-6.6/arch/arm64/lib/ |
| H A D | xor-neon.c | 16 uint64_t *dp1 = (uint64_t *)p1; in xor_arm64_neon_2() local
24 v0 = veorq_u64(vld1q_u64(dp1 + 0), vld1q_u64(dp2 + 0)); in xor_arm64_neon_2()
25 v1 = veorq_u64(vld1q_u64(dp1 + 2), vld1q_u64(dp2 + 2)); in xor_arm64_neon_2()
26 v2 = veorq_u64(vld1q_u64(dp1 + 4), vld1q_u64(dp2 + 4)); in xor_arm64_neon_2()
27 v3 = veorq_u64(vld1q_u64(dp1 + 6), vld1q_u64(dp2 + 6)); in xor_arm64_neon_2()
30 vst1q_u64(dp1 + 0, v0); in xor_arm64_neon_2()
31 vst1q_u64(dp1 + 2, v1); in xor_arm64_neon_2()
32 vst1q_u64(dp1 + 4, v2); in xor_arm64_neon_2()
33 vst1q_u64(dp1 + 6, v3); in xor_arm64_neon_2()
35 dp1 in xor_arm64_neon_2()
44 uint64_t *dp1 = (uint64_t *)p1; xor_arm64_neon_3() local
81 uint64_t *dp1 = (uint64_t *)p1; xor_arm64_neon_4() local
127 uint64_t *dp1 = (uint64_t *)p1; xor_arm64_neon_5() local
199 uint64_t *dp1 = (uint64_t *)p1; xor_arm64_eor3_3() local
235 uint64_t *dp1 = (uint64_t *)p1; xor_arm64_eor3_4() local
280 uint64_t *dp1 = (uint64_t *)p1; xor_arm64_eor3_5() local
[all...] |
| /kernel/linux/linux-5.10/drivers/parisc/ |
| H A D | iosapic.c | 526 static void iosapic_rd_irt_entry(struct vector_info *vi , u32 *dp0, u32 *dp1) in iosapic_rd_irt_entry() argument
532 *dp1 = iosapic_read(isp->addr, IOSAPIC_IRDT_ENTRY_HI(idx)); in iosapic_rd_irt_entry()
536 static void iosapic_wr_irt_entry(struct vector_info *vi, u32 dp0, u32 dp1) in iosapic_wr_irt_entry() argument
541 vi->irqline, isp->isi_hpa, dp0, dp1); in iosapic_wr_irt_entry()
548 iosapic_write(isp->addr, IOSAPIC_IRDT_ENTRY_HI(vi->irqline), dp1); in iosapic_wr_irt_entry()
551 dp1 = readl(isp->addr+IOSAPIC_REG_WINDOW); in iosapic_wr_irt_entry()
555 ** set_irt prepares the data (dp0, dp1) according to the vector_info
556 ** and target cpu (id_eid). dp0/dp1 are then used to program I/O SAPIC
560 iosapic_set_irt_data( struct vector_info *vi, u32 *dp0, u32 *dp1) in iosapic_set_irt_data() argument
587 *dp1 in iosapic_set_irt_data()
[all...] |
| /kernel/linux/linux-6.6/drivers/parisc/ |
| H A D | iosapic.c | 517 static void iosapic_rd_irt_entry(struct vector_info *vi , u32 *dp0, u32 *dp1) in iosapic_rd_irt_entry() argument
523 *dp1 = iosapic_read(isp->addr, IOSAPIC_IRDT_ENTRY_HI(idx)); in iosapic_rd_irt_entry()
527 static void iosapic_wr_irt_entry(struct vector_info *vi, u32 dp0, u32 dp1) in iosapic_wr_irt_entry() argument
532 vi->irqline, isp->isi_hpa, dp0, dp1); in iosapic_wr_irt_entry()
539 iosapic_write(isp->addr, IOSAPIC_IRDT_ENTRY_HI(vi->irqline), dp1); in iosapic_wr_irt_entry()
542 dp1 = readl(isp->addr+IOSAPIC_REG_WINDOW); in iosapic_wr_irt_entry()
546 ** set_irt prepares the data (dp0, dp1) according to the vector_info
547 ** and target cpu (id_eid). dp0/dp1 are then used to program I/O SAPIC
551 iosapic_set_irt_data( struct vector_info *vi, u32 *dp0, u32 *dp1) in iosapic_set_irt_data() argument
578 *dp1 in iosapic_set_irt_data()
[all...] |
| /kernel/linux/linux-5.10/fs/xfs/ |
| H A D | xfs_inode.c | 2939 struct xfs_inode *dp1, /* in: old (source) directory inode */ in xfs_sort_for_rename()
2957 * Note that the table may contain duplicates. e.g., dp1 == dp2. in xfs_sort_for_rename()
2960 i_tab[i++] = dp1; in xfs_sort_for_rename()
3006 struct xfs_inode *dp1, in xfs_cross_rename()
3020 error = xfs_dir_replace(tp, dp1, name1, ip2->i_ino, spaceres); in xfs_cross_rename()
3034 if (dp1 != dp2) { in xfs_cross_rename()
3039 dp1->i_ino, spaceres); in xfs_cross_rename()
3043 /* transfer ip2 ".." reference to dp1 */ in xfs_cross_rename()
3048 xfs_bumplink(tp, dp1); in xfs_cross_rename()
3069 error = xfs_droplink(tp, dp1); in xfs_cross_rename()
2938 xfs_sort_for_rename( struct xfs_inode *dp1, struct xfs_inode *dp2, struct xfs_inode *ip1, struct xfs_inode *ip2, struct xfs_inode *wip, struct xfs_inode **i_tab, int *num_inodes) xfs_sort_for_rename() argument
3004 xfs_cross_rename( struct xfs_trans *tp, struct xfs_inode *dp1, struct xfs_name *name1, struct xfs_inode *ip1, struct xfs_inode *dp2, struct xfs_name *name2, struct xfs_inode *ip2, int spaceres) xfs_cross_rename() argument
[all...] |
| /kernel/linux/linux-6.6/fs/xfs/ |
| H A D | xfs_inode.c | 2623 struct xfs_inode *dp1, /* in: old (source) directory inode */ in xfs_sort_for_rename()
2641 * Note that the table may contain duplicates. e.g., dp1 == dp2. in xfs_sort_for_rename()
2644 i_tab[i++] = dp1; in xfs_sort_for_rename()
2690 struct xfs_inode *dp1, in xfs_cross_rename()
2704 error = xfs_dir_replace(tp, dp1, name1, ip2->i_ino, spaceres); in xfs_cross_rename()
2718 if (dp1 != dp2) { in xfs_cross_rename()
2723 dp1->i_ino, spaceres); in xfs_cross_rename()
2727 /* transfer ip2 ".." reference to dp1 */ in xfs_cross_rename()
2732 xfs_bumplink(tp, dp1); in xfs_cross_rename()
2753 error = xfs_droplink(tp, dp1); in xfs_cross_rename()
2622 xfs_sort_for_rename( struct xfs_inode *dp1, struct xfs_inode *dp2, struct xfs_inode *ip1, struct xfs_inode *ip2, struct xfs_inode *wip, struct xfs_inode **i_tab, int *num_inodes) xfs_sort_for_rename() argument
2688 xfs_cross_rename( struct xfs_trans *tp, struct xfs_inode *dp1, struct xfs_name *name1, struct xfs_inode *ip1, struct xfs_inode *dp2, struct xfs_name *name2, struct xfs_inode *ip2, int spaceres) xfs_cross_rename() argument
[all...] |
| /kernel/linux/linux-5.10/drivers/net/ethernet/marvell/octeontx2/af/ |
| H A D | npc.h | 157 u16 dp1; member
|
| H A D | rvu_npc.c | 882 cam1.dp1_data = kpucam->dp1 & kpucam->dp1_mask; in npc_config_kpucam()
887 cam0.dp1_data = ~kpucam->dp1 & kpucam->dp1_mask; in npc_config_kpucam()
|
| /kernel/linux/linux-6.6/drivers/net/ethernet/marvell/octeontx2/af/ |
| H A D | npc.h | 246 u16 dp1; member
|
| H A D | rvu_npc.c | 1487 cam1.dp1_data = kpucam->dp1 & kpucam->dp1_mask; in npc_config_kpucam()
1492 cam0.dp1_data = ~kpucam->dp1 & kpucam->dp1_mask; in npc_config_kpucam()
|