Searched refs:dq (Results 1 - 25 of 58) sorted by relevance

123

/linux-master/include/soc/fsl/
H A Ddpaa2-global.h20 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 Drecov_avx2.c19 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 Drecov_loongarch_simd.c32 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 Drecov_s390xc.c26 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 Drecov_avx512.c27 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 Drecov_ssse3.c19 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 Drecov_neon.c26 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 Drecov.c22 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 Drecov_neon_inner.c29 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 Dneon.h16 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 Dquotacheck_repair.c47 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 Dquota.c84 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 Dquota_repair.c59 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 Ddqiterate.c150 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 Dquotacheck.c554 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 Dqbman-portal.h219 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 Dasync_raid6_recov.c208 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 Drsa.h20 * @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 Dcn66xx_regs.h311 #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 Dcn23xx_pf_regs.h366 #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 Dxfs_dquot.c94 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 Dkvm-transform.sh56 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 Dzcrypt_msgtype50.c105 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 Drsa.c23 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 Dqman_test_api.c212 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

Completed in 342 milliseconds

123