/linux-master/include/soc/fsl/ |
H A D | dpaa2-global.h | 20 struct dq { struct in union:dpaa2_dq::__anon12452 33 } dq; member in union:dpaa2_dq::__anon12452 66 * @dq: the dequeue result. 68 static inline u32 dpaa2_dq_flags(const struct dpaa2_dq *dq) argument 70 return dq->dq.stat; 74 * dpaa2_dq_is_pull() - Check whether the dq response is from a pull 76 * @dq: the dequeue result 80 static inline int dpaa2_dq_is_pull(const struct dpaa2_dq *dq) argument 82 return (int)(dpaa2_dq_flags(dq) 91 dpaa2_dq_is_pull_complete(const struct dpaa2_dq *dq) argument 104 dpaa2_dq_seqnum(const struct dpaa2_dq *dq) argument 117 dpaa2_dq_odpid(const struct dpaa2_dq *dq) argument 128 dpaa2_dq_fqid(const struct dpaa2_dq *dq) argument 139 dpaa2_dq_byte_count(const struct dpaa2_dq *dq) argument 150 dpaa2_dq_frame_count(const struct dpaa2_dq *dq) argument 161 dpaa2_dq_fqd_ctx(const struct dpaa2_dq *dq) argument 172 dpaa2_dq_fd(const struct dpaa2_dq *dq) argument [all...] |
/linux-master/lib/raid6/ |
H A D | recov_avx2.c | 19 u8 *p, *q, *dp, *dq; local 33 dq = (u8 *)ptrs[failb]; 35 ptrs[disks-1] = dq; 41 ptrs[failb] = dq; 61 asm volatile("vpxor %0, %%ymm1, %%ymm1" : : "m" (dq[0])); 62 asm volatile("vpxor %0, %%ymm9, %%ymm9" : : "m" (dq[32])); 67 * 1 = dq[0] ^ q[0] 68 * 9 = dq[32] ^ q[32] 120 asm volatile("vmovdqa %%ymm1, %0" : "=m" (dq[0])); 121 asm volatile("vmovdqa %%ymm13,%0" : "=m" (dq[3 189 u8 *p, *q, *dq; local [all...] |
H A D | recov_loongarch_simd.c | 32 u8 *p, *q, *dp, *dq; local 47 dq = (u8 *)ptrs[failb]; 49 ptrs[disks - 1] = dq; 55 ptrs[failb] = dq; 81 asm volatile("vld $vr8, %0" : : "m" (dq[0])); 82 asm volatile("vld $vr9, %0" : : "m" (dq[16])); 83 asm volatile("vld $vr10, %0" : : "m" (dq[32])); 84 asm volatile("vld $vr11, %0" : : "m" (dq[48])); 161 asm volatile("vst $vr4, %0" : "=m" (dq[0])); 162 asm volatile("vst $vr5, %0" : "=m" (dq[1 189 u8 *p, *q, *dq; local 306 u8 *p, *q, *dp, *dq; local 428 u8 *p, *q, *dq; local [all...] |
H A D | recov_s390xc.c | 26 u8 *p, *q, *dp, *dq; local 40 dq = (u8 *)ptrs[failb]; 42 ptrs[disks-1] = dq; 48 ptrs[failb] = dq; 59 xor_block(dq, q); 61 dq[i] = pbmul[dp[i]] ^ qmul[dq[i]]; 62 xor_block(dp, dq); 66 dq += 256; 75 u8 *p, *q, *dq; local [all...] |
H A D | recov_avx512.c | 27 u8 *p, *q, *dp, *dq; local 44 dq = (u8 *)ptrs[failb]; 46 ptrs[disks-1] = dq; 52 ptrs[failb] = dq; 78 "m" (p[64]), "m" (dq[0]), "m" (dq[64]), 82 * 1 = dq[0] ^ q[0] 83 * 9 = dq[64] ^ q[64] 148 : "m" (dq[0]), "m" (dq[6 230 u8 *p, *q, *dq; local [all...] |
H A D | recov_ssse3.c | 19 u8 *p, *q, *dp, *dq; local 35 dq = (u8 *)ptrs[failb]; 37 ptrs[disks-1] = dq; 43 ptrs[failb] = dq; 71 asm volatile("pxor %0,%%xmm1" : : "m" (dq[0])); 72 asm volatile("pxor %0,%%xmm9" : : "m" (dq[16])); 124 asm volatile("movdqa %%xmm1,%0" : "=m" (dq[0])); 125 asm volatile("movdqa %%xmm9,%0" : "=m" (dq[16])); 136 dq += 32; 140 asm volatile("pxor %0,%%xmm1" : : "m" (*dq)); 194 u8 *p, *q, *dq; local [all...] |
H A D | recov_neon.c | 26 u8 *p, *q, *dp, *dq; local 41 dq = (u8 *)ptrs[failb]; 43 ptrs[disks - 1] = dq; 49 ptrs[failb] = dq; 59 __raid6_2data_recov_neon(bytes, p, q, dp, dq, pbmul, qmul); 66 u8 *p, *q, *dq; local 76 dq = (u8 *)ptrs[faila]; 78 ptrs[disks - 1] = dq; 83 ptrs[faila] = dq; 90 __raid6_datap_recov_neon(bytes, p, q, dq, qmu [all...] |
H A D | recov.c | 22 u8 *p, *q, *dp, *dq; local 36 dq = (u8 *)ptrs[failb]; 38 ptrs[disks-1] = dq; 44 ptrs[failb] = dq; 55 qx = qmul[*q ^ *dq]; 56 *dq++ = db = pbmul[px] ^ qx; /* Reconstructed B */ 66 u8 *p, *q, *dq; local 74 dq = (u8 *)ptrs[faila]; 76 ptrs[disks-1] = dq; 81 ptrs[faila] = dq; [all...] |
H A D | recov_neon_inner.c | 29 uint8_t *dq, const uint8_t *pbmul, 43 * qx = qmul[*q ^ *dq]; 44 * *dq++ = db = pbmul[px] ^ qx; 54 vx = veorq_u8(vld1q_u8(q), vld1q_u8(dq)); 67 vst1q_u8(dq, db); 74 dq += 16; 78 void __raid6_datap_recov_neon(int bytes, uint8_t *p, uint8_t *q, uint8_t *dq, argument 87 * *p++ ^= *dq = qmul[*q ^ *dq]; 88 * q++; dq 28 __raid6_2data_recov_neon(int bytes, uint8_t *p, uint8_t *q, uint8_t *dp, uint8_t *dq, const uint8_t *pbmul, const uint8_t *qmul) argument [all...] |
H A D | neon.h | 16 uint8_t *dq, const uint8_t *pbmul, 19 void __raid6_datap_recov_neon(int bytes, uint8_t *p, uint8_t *q, uint8_t *dq,
|
/linux-master/fs/xfs/scrub/ |
H A D | quotacheck_repair.c | 47 struct xfs_dquot *dq) 56 xfs_dqunlock(dq); 58 xfs_dqlock(dq); 62 xfs_trans_dqjoin(xqc->sc->tp, dq); 70 error = xfarray_load_sparse(counts, dq->q_id, &xcdq); 75 delta = (int64_t)xcdq.icount - dq->q_ino.count; 77 dq->q_ino.reserved += delta; 78 dq->q_ino.count += delta; 82 delta = (int64_t)xcdq.bcount - dq->q_blk.count; 84 dq 44 xqcheck_commit_dquot( struct xqcheck *xqc, xfs_dqtype_t dqtype, struct xfs_dquot *dq) argument 149 struct xfs_dquot *dq; local [all...] |
H A D | quota.c | 84 struct xfs_dquot *dq, 97 if (dq->q_fileoffset != offset) { 113 if (XFS_FSB_TO_DADDR(mp, irec.br_startblock) != dq->q_blkno) 142 struct xfs_dquot *dq) 161 xfs_dqunlock(dq); 163 xfs_dqlock(dq); 169 offset = dq->q_id / qi->qi_dqperchunk; 170 if (dq->q_id && dq->q_id <= sqi->last_id) 173 sqi->last_id = dq 82 xchk_quota_item_bmap( struct xfs_scrub *sc, struct xfs_dquot *dq, xfs_fileoff_t offset) argument 140 xchk_quota_item( struct xchk_quota_info *sqi, struct xfs_dquot *dq) argument 303 struct xfs_dquot *dq; local [all...] |
H A D | quota_repair.c | 59 struct xfs_dquot *dq, 75 error = xfs_bmapi_write(sc->tp, sc->ip, dq->q_fileoffset, 83 dq->q_blkno = XFS_FSB_TO_DADDR(mp, irec->br_startblock); 85 trace_xrep_dquot_item_fill_bmap_hole(sc->mp, dq->q_type, dq->q_id); 88 error = xfs_trans_get_buf(sc->tp, mp->m_ddev_targp, dq->q_blkno, 94 xfs_qm_init_dquot_blk(sc->tp, dq->q_id, dq->q_type, bp); 111 struct xfs_dquot *dq, 117 xfs_fileoff_t offset = dq 57 xrep_quota_item_fill_bmap_hole( struct xfs_scrub *sc, struct xfs_dquot *dq, struct xfs_bmbt_irec *irec) argument 109 xrep_quota_item_bmap( struct xfs_scrub *sc, struct xfs_dquot *dq, bool *dirty) argument 173 xrep_quota_item( struct xrep_quota_info *rqi, struct xfs_dquot *dq) argument 517 struct xfs_dquot *dq; local [all...] |
H A D | dqiterate.c | 150 struct xfs_dquot *dq; local 156 nr_found = radix_tree_gang_lookup(tree, (void **)&dq, cursor->id, 1); 158 *next_incore_id = dq->q_id; 176 struct xfs_dquot *dq = NULL; local 204 error = xfs_qm_dqget(mp, cursor->id, cursor->dqtype, false, &dq); 208 cursor->id = dq->q_id + 1; 209 *dqpp = dq;
|
H A D | quotacheck.c | 554 struct xfs_dquot *dq) 566 error = xfarray_load_sparse(counts, dq->q_id, &xcdq); 570 if (xcdq.icount != dq->q_ino.count) 571 xchk_qcheck_set_corrupt(xqc->sc, dqtype, dq->q_id); 573 if (xcdq.bcount != dq->q_blk.count) 574 xchk_qcheck_set_corrupt(xqc->sc, dqtype, dq->q_id); 576 if (xcdq.rtbcount != dq->q_rtb.count) 577 xchk_qcheck_set_corrupt(xqc->sc, dqtype, dq->q_id); 580 error = xfarray_store(counts, dq->q_id, &xcdq); 615 struct xfs_dquot *dq; local 551 xqcheck_compare_dquot( struct xqcheck *xqc, xfs_dqtype_t dqtype, struct xfs_dquot *dq) argument 660 struct xfs_dquot *dq; local [all...] |
/linux-master/drivers/soc/fsl/dpio/ |
H A D | qbman-portal.h | 219 void qbman_swp_dqrr_consume(struct qbman_swp *s, const struct dpaa2_dq *dq); 221 int qbman_result_has_new_result(struct qbman_swp *p, const struct dpaa2_dq *dq); 304 * @dq: the dequeue result to be checked 308 static inline int qbman_result_is_DQ(const struct dpaa2_dq *dq) argument 310 return ((dq->dq.verb & QBMAN_RESULT_MASK) == QBMAN_RESULT_DQ); 315 * @dq: the dequeue result to be checked 318 static inline int qbman_result_is_SCN(const struct dpaa2_dq *dq) argument 320 return !qbman_result_is_DQ(dq); 324 static inline int qbman_result_is_FQDAN(const struct dpaa2_dq *dq) argument 330 qbman_result_is_CDAN(const struct dpaa2_dq *dq) argument 336 qbman_result_is_CSCN(const struct dpaa2_dq *dq) argument 342 qbman_result_is_BPSCN(const struct dpaa2_dq *dq) argument 348 qbman_result_is_CGCU(const struct dpaa2_dq *dq) argument 354 qbman_result_is_FQRN(const struct dpaa2_dq *dq) argument 360 qbman_result_is_FQRNI(const struct dpaa2_dq *dq) argument 366 qbman_result_is_FQPN(const struct dpaa2_dq *dq) argument [all...] |
/linux-master/crypto/async_tx/ |
H A D | async_raid6_recov.c | 208 struct page *p, *q, *g, *dp, *dq; local 244 dq = blocks[failb]; 250 tx = async_mult(dq, dq_off, g, g_off, 263 srcs[0] = dq; 269 tx = async_xor_offs(dq, dq_off, srcs, src_offs, 2, bytes, submit); 274 srcs[1] = dq; 279 tx = async_sum_product(dq, dq_off, srcs, src_offs, coef, bytes, submit); 284 srcs[1] = dq; 299 struct page *p, *q, *dp, *dq; local 323 dq 476 struct page *p, *q, *dq; local [all...] |
/linux-master/include/crypto/internal/ |
H A D | rsa.h | 20 * @dq : RSA exponent d mod (q - 1) raw byte stream 28 * @dq_sz : length in bytes of dq field 38 const u8 *dq; member in struct:rsa_key
|
/linux-master/drivers/net/ethernet/cavium/liquidio/ |
H A D | cn66xx_regs.h | 311 #define CN6XXX_DMA_CNT(dq) \ 312 (CN6XXX_DMA_CNT_START + ((dq) * CN6XXX_DMA_OFFSET)) 314 #define CN6XXX_DMA_INT_LEVEL(dq) \ 315 (CN6XXX_DMA_INT_LEVEL_START + ((dq) * CN6XXX_DMA_OFFSET)) 317 #define CN6XXX_DMA_PKT_INT_LEVEL(dq) \ 318 (CN6XXX_DMA_INT_LEVEL_START + ((dq) * CN6XXX_DMA_OFFSET)) 320 #define CN6XXX_DMA_TIME_INT_LEVEL(dq) \ 321 (CN6XXX_DMA_INT_LEVEL_START + 4 + ((dq) * CN6XXX_DMA_OFFSET)) 323 #define CN6XXX_DMA_TIM(dq) \ 324 (CN6XXX_DMA_TIM_START + ((dq) * CN6XXX_DMA_OFFSE [all...] |
H A D | cn23xx_pf_regs.h | 366 #define CN23XX_DMA_CNT(dq) \ 367 (CN23XX_DMA_CNT_START + ((dq) * CN23XX_DMA_OFFSET)) 369 #define CN23XX_DMA_INT_LEVEL(dq) \ 370 (CN23XX_DMA_INT_LEVEL_START + ((dq) * CN23XX_DMA_OFFSET)) 372 #define CN23XX_DMA_PKT_INT_LEVEL(dq) \ 373 (CN23XX_DMA_INT_LEVEL_START + ((dq) * CN23XX_DMA_OFFSET)) 375 #define CN23XX_DMA_TIME_INT_LEVEL(dq) \ 376 (CN23XX_DMA_INT_LEVEL_START + 4 + ((dq) * CN23XX_DMA_OFFSET)) 378 #define CN23XX_DMA_TIM(dq) \ 379 (CN23XX_DMA_TIM_START + ((dq) * CN23XX_DMA_OFFSE [all...] |
/linux-master/fs/xfs/ |
H A D | xfs_dquot.c | 94 struct xfs_dquot *dq) 96 struct xfs_mount *mp = dq->q_mount; 101 ASSERT(dq->q_id); 102 defq = xfs_get_defquota(q, xfs_dquot_type(dq)); 104 if (!dq->q_blk.softlimit) { 105 dq->q_blk.softlimit = defq->blk.soft; 108 if (!dq->q_blk.hardlimit) { 109 dq->q_blk.hardlimit = defq->blk.hard; 112 if (!dq->q_ino.softlimit) 113 dq 93 xfs_qm_adjust_dqlimits( struct xfs_dquot *dq) argument 181 xfs_qm_adjust_dqtimers( struct xfs_dquot *dq) argument [all...] |
/linux-master/tools/testing/selftests/rcutorture/bin/ |
H A D | kvm-transform.sh | 56 awk -v dq='"' '/./ { print "\tbootarg[" NR "] = " dq $1 dq ";" }' >> $T/bootarg.awk 58 awk -v dq='"' '/./ { print "\tbootpar[" NR "] = " dq $1 dq ";" }' >> $T/bootarg.awk
|
/linux-master/drivers/s390/crypto/ |
H A D | zcrypt_msgtype50.c | 105 unsigned char dq[64]; member in struct:type50_crb1_msg 118 unsigned char dq[128]; member in struct:type50_crb2_msg 131 unsigned char dq[256]; member in struct:type50_crb3_msg 263 unsigned char *p, *q, *dp, *dq, *u, *inp; local 285 dq = crb1->dq + sizeof(crb1->dq) - short_len; 299 dq = crb2->dq + sizeof(crb2->dq) [all...] |
/linux-master/crypto/ |
H A D | rsa.c | 23 MPI dq; member in struct:rsa_mpi_key 96 ret = mpi_powm(m2, c, key->dq, key->q); 206 mpi_free(key->dq); 214 key->dq = NULL; 341 mpi_key->dq = mpi_read_raw_data(raw_key.dq, raw_key.dq_sz); 342 if (!mpi_key->dq)
|
/linux-master/drivers/soc/fsl/qbman/ |
H A D | qman_test_api.c | 212 const struct qm_dqrr_entry *dq, 215 if (WARN_ON(fd_neq(&fd_dq, &dq->fd))) { 220 if (!(dq->stat & QM_DQRR_STAT_UNSCHEDULED) && !fd_neq(&fd_dq, &fd)) { 210 cb_dqrr(struct qman_portal *p, struct qman_fq *fq, const struct qm_dqrr_entry *dq, bool sched_napi) argument
|