Home
last modified time | relevance | path

Searched refs:dq (Results 1 – 25 of 57) sorted by relevance

123

/linux-6.6.21/include/soc/fsl/
Ddpaa2-global.h20 struct dq { struct
33 } dq; member
68 static inline u32 dpaa2_dq_flags(const struct dpaa2_dq *dq) in dpaa2_dq_flags() argument
70 return dq->dq.stat; in dpaa2_dq_flags()
80 static inline int dpaa2_dq_is_pull(const struct dpaa2_dq *dq) in dpaa2_dq_is_pull() argument
82 return (int)(dpaa2_dq_flags(dq) & DPAA2_DQ_STAT_VOLATILE); in dpaa2_dq_is_pull()
91 static inline bool dpaa2_dq_is_pull_complete(const struct dpaa2_dq *dq) in dpaa2_dq_is_pull_complete() argument
93 return !!(dpaa2_dq_flags(dq) & DPAA2_DQ_STAT_EXPIRED); in dpaa2_dq_is_pull_complete()
104 static inline u16 dpaa2_dq_seqnum(const struct dpaa2_dq *dq) in dpaa2_dq_seqnum() argument
106 return le16_to_cpu(dq->dq.seqnum); in dpaa2_dq_seqnum()
[all …]
/linux-6.6.21/lib/raid6/
Drecov_loongarch_simd.c32 u8 *p, *q, *dp, *dq; in raid6_2data_recov_lsx() local
47 dq = (u8 *)ptrs[failb]; in raid6_2data_recov_lsx()
49 ptrs[disks - 1] = dq; in raid6_2data_recov_lsx()
55 ptrs[failb] = dq; in raid6_2data_recov_lsx()
81 asm volatile("vld $vr8, %0" : : "m" (dq[0])); in raid6_2data_recov_lsx()
82 asm volatile("vld $vr9, %0" : : "m" (dq[16])); in raid6_2data_recov_lsx()
83 asm volatile("vld $vr10, %0" : : "m" (dq[32])); in raid6_2data_recov_lsx()
84 asm volatile("vld $vr11, %0" : : "m" (dq[48])); in raid6_2data_recov_lsx()
161 asm volatile("vst $vr4, %0" : "=m" (dq[0])); in raid6_2data_recov_lsx()
162 asm volatile("vst $vr5, %0" : "=m" (dq[16])); in raid6_2data_recov_lsx()
[all …]
Drecov_avx2.c19 u8 *p, *q, *dp, *dq; in raid6_2data_recov_avx2() local
33 dq = (u8 *)ptrs[failb]; in raid6_2data_recov_avx2()
35 ptrs[disks-1] = dq; in raid6_2data_recov_avx2()
41 ptrs[failb] = dq; in raid6_2data_recov_avx2()
61 asm volatile("vpxor %0, %%ymm1, %%ymm1" : : "m" (dq[0])); in raid6_2data_recov_avx2()
62 asm volatile("vpxor %0, %%ymm9, %%ymm9" : : "m" (dq[32])); in raid6_2data_recov_avx2()
120 asm volatile("vmovdqa %%ymm1, %0" : "=m" (dq[0])); in raid6_2data_recov_avx2()
121 asm volatile("vmovdqa %%ymm13,%0" : "=m" (dq[32])); in raid6_2data_recov_avx2()
132 dq += 64; in raid6_2data_recov_avx2()
136 asm volatile("vpxor %0, %%ymm1, %%ymm1" : : "m" (*dq)); in raid6_2data_recov_avx2()
[all …]
Drecov_avx512.c27 u8 *p, *q, *dp, *dq; in raid6_2data_recov_avx512() local
44 dq = (u8 *)ptrs[failb]; in raid6_2data_recov_avx512()
46 ptrs[disks-1] = dq; in raid6_2data_recov_avx512()
52 ptrs[failb] = dq; in raid6_2data_recov_avx512()
78 "m" (p[64]), "m" (dq[0]), "m" (dq[64]), in raid6_2data_recov_avx512()
148 : "m" (dq[0]), "m" (dq[64])); in raid6_2data_recov_avx512()
159 dq += 128; in raid6_2data_recov_avx512()
166 : "m" (*q), "m" (*p), "m"(*dq), "m" (*dp)); in raid6_2data_recov_avx512()
209 : "m" (dq[0])); in raid6_2data_recov_avx512()
220 dq += 64; in raid6_2data_recov_avx512()
[all …]
Drecov_ssse3.c19 u8 *p, *q, *dp, *dq; in raid6_2data_recov_ssse3() local
35 dq = (u8 *)ptrs[failb]; in raid6_2data_recov_ssse3()
37 ptrs[disks-1] = dq; in raid6_2data_recov_ssse3()
43 ptrs[failb] = dq; in raid6_2data_recov_ssse3()
71 asm volatile("pxor %0,%%xmm1" : : "m" (dq[0])); in raid6_2data_recov_ssse3()
72 asm volatile("pxor %0,%%xmm9" : : "m" (dq[16])); in raid6_2data_recov_ssse3()
124 asm volatile("movdqa %%xmm1,%0" : "=m" (dq[0])); in raid6_2data_recov_ssse3()
125 asm volatile("movdqa %%xmm9,%0" : "=m" (dq[16])); in raid6_2data_recov_ssse3()
136 dq += 32; in raid6_2data_recov_ssse3()
140 asm volatile("pxor %0,%%xmm1" : : "m" (*dq)); in raid6_2data_recov_ssse3()
[all …]
Drecov_s390xc.c26 u8 *p, *q, *dp, *dq; in raid6_2data_recov_s390xc() local
40 dq = (u8 *)ptrs[failb]; in raid6_2data_recov_s390xc()
42 ptrs[disks-1] = dq; in raid6_2data_recov_s390xc()
48 ptrs[failb] = dq; in raid6_2data_recov_s390xc()
59 xor_block(dq, q); in raid6_2data_recov_s390xc()
61 dq[i] = pbmul[dp[i]] ^ qmul[dq[i]]; in raid6_2data_recov_s390xc()
62 xor_block(dp, dq); in raid6_2data_recov_s390xc()
66 dq += 256; in raid6_2data_recov_s390xc()
75 u8 *p, *q, *dq; in raid6_datap_recov_s390xc() local
84 dq = (u8 *)ptrs[faila]; in raid6_datap_recov_s390xc()
[all …]
Drecov.c22 u8 *p, *q, *dp, *dq; in raid6_2data_recov_intx1() local
36 dq = (u8 *)ptrs[failb]; in raid6_2data_recov_intx1()
38 ptrs[disks-1] = dq; in raid6_2data_recov_intx1()
44 ptrs[failb] = dq; in raid6_2data_recov_intx1()
55 qx = qmul[*q ^ *dq]; in raid6_2data_recov_intx1()
56 *dq++ = db = pbmul[px] ^ qx; /* Reconstructed B */ in raid6_2data_recov_intx1()
66 u8 *p, *q, *dq; in raid6_datap_recov_intx1() local
74 dq = (u8 *)ptrs[faila]; in raid6_datap_recov_intx1()
76 ptrs[disks-1] = dq; in raid6_datap_recov_intx1()
81 ptrs[faila] = dq; in raid6_datap_recov_intx1()
[all …]
Drecov_neon.c26 u8 *p, *q, *dp, *dq; in raid6_2data_recov_neon() local
41 dq = (u8 *)ptrs[failb]; in raid6_2data_recov_neon()
43 ptrs[disks - 1] = dq; in raid6_2data_recov_neon()
49 ptrs[failb] = dq; in raid6_2data_recov_neon()
59 __raid6_2data_recov_neon(bytes, p, q, dp, dq, pbmul, qmul); in raid6_2data_recov_neon()
66 u8 *p, *q, *dq; in raid6_datap_recov_neon() local
76 dq = (u8 *)ptrs[faila]; in raid6_datap_recov_neon()
78 ptrs[disks - 1] = dq; in raid6_datap_recov_neon()
83 ptrs[faila] = dq; in raid6_datap_recov_neon()
90 __raid6_datap_recov_neon(bytes, p, q, dq, qmul); in raid6_datap_recov_neon()
Drecov_neon_inner.c29 uint8_t *dq, const uint8_t *pbmul, in __raid6_2data_recov_neon() argument
54 vx = veorq_u8(vld1q_u8(q), vld1q_u8(dq)); in __raid6_2data_recov_neon()
67 vst1q_u8(dq, db); in __raid6_2data_recov_neon()
74 dq += 16; in __raid6_2data_recov_neon()
78 void __raid6_datap_recov_neon(int bytes, uint8_t *p, uint8_t *q, uint8_t *dq, in __raid6_datap_recov_neon() argument
95 vx = veorq_u8(vld1q_u8(q), vld1q_u8(dq)); in __raid6_datap_recov_neon()
103 vst1q_u8(dq, vx); in __raid6_datap_recov_neon()
109 dq += 16; in __raid6_datap_recov_neon()
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-6.6.21/fs/xfs/scrub/
Dquota.c81 struct xfs_dquot *dq, in xchk_quota_item() argument
100 offset = dq->q_id / qi->qi_dqperchunk; in xchk_quota_item()
101 if (dq->q_id && dq->q_id <= sqi->last_id) in xchk_quota_item()
104 sqi->last_id = dq->q_id; in xchk_quota_item()
114 if (dq->q_blk.hardlimit > mp->m_sb.sb_dblocks) in xchk_quota_item()
116 if (dq->q_blk.softlimit > dq->q_blk.hardlimit) in xchk_quota_item()
119 if (dq->q_ino.hardlimit > M_IGEO(mp)->maxicount) in xchk_quota_item()
121 if (dq->q_ino.softlimit > dq->q_ino.hardlimit) in xchk_quota_item()
124 if (dq->q_rtb.hardlimit > mp->m_sb.sb_rblocks) in xchk_quota_item()
126 if (dq->q_rtb.softlimit > dq->q_rtb.hardlimit) in xchk_quota_item()
[all …]
/linux-6.6.21/drivers/soc/fsl/dpio/
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);
308 static inline int qbman_result_is_DQ(const struct dpaa2_dq *dq) in qbman_result_is_DQ() argument
310 return ((dq->dq.verb & QBMAN_RESULT_MASK) == QBMAN_RESULT_DQ); in qbman_result_is_DQ()
318 static inline int qbman_result_is_SCN(const struct dpaa2_dq *dq) in qbman_result_is_SCN() argument
320 return !qbman_result_is_DQ(dq); in qbman_result_is_SCN()
324 static inline int qbman_result_is_FQDAN(const struct dpaa2_dq *dq) in qbman_result_is_FQDAN() argument
326 return ((dq->dq.verb & QBMAN_RESULT_MASK) == QBMAN_RESULT_FQDAN); in qbman_result_is_FQDAN()
330 static inline int qbman_result_is_CDAN(const struct dpaa2_dq *dq) in qbman_result_is_CDAN() argument
332 return ((dq->dq.verb & QBMAN_RESULT_MASK) == QBMAN_RESULT_CDAN); in qbman_result_is_CDAN()
[all …]
Ddpio-service.c228 const struct dpaa2_dq *dq; in dpaa2_io_irq() local
240 dq = qbman_swp_dqrr_next(swp); in dpaa2_io_irq()
241 while (dq) { in dpaa2_io_irq()
242 if (qbman_result_is_SCN(dq)) { in dpaa2_io_irq()
246 q64 = qbman_result_SCN_ctx(dq); in dpaa2_io_irq()
252 qbman_swp_dqrr_consume(swp, dq); in dpaa2_io_irq()
256 dq = qbman_swp_dqrr_next(swp); in dpaa2_io_irq()
/linux-6.6.21/crypto/async_tx/
Dasync_raid6_recov.c208 struct page *p, *q, *g, *dp, *dq; in __2data_recov_5() local
244 dq = blocks[failb]; in __2data_recov_5()
250 tx = async_mult(dq, dq_off, g, g_off, in __2data_recov_5()
263 srcs[0] = dq; in __2data_recov_5()
269 tx = async_xor_offs(dq, dq_off, srcs, src_offs, 2, bytes, submit); in __2data_recov_5()
274 srcs[1] = dq; in __2data_recov_5()
279 tx = async_sum_product(dq, dq_off, srcs, src_offs, coef, bytes, submit); in __2data_recov_5()
284 srcs[1] = dq; in __2data_recov_5()
299 struct page *p, *q, *dp, *dq; in __2data_recov_n() local
323 dq = blocks[failb]; in __2data_recov_n()
[all …]
/linux-6.6.21/drivers/net/ethernet/cavium/liquidio/
Dcn66xx_regs.h311 #define CN6XXX_DMA_CNT(dq) \ argument
312 (CN6XXX_DMA_CNT_START + ((dq) * CN6XXX_DMA_OFFSET))
314 #define CN6XXX_DMA_INT_LEVEL(dq) \ argument
315 (CN6XXX_DMA_INT_LEVEL_START + ((dq) * CN6XXX_DMA_OFFSET))
317 #define CN6XXX_DMA_PKT_INT_LEVEL(dq) \ argument
318 (CN6XXX_DMA_INT_LEVEL_START + ((dq) * CN6XXX_DMA_OFFSET))
320 #define CN6XXX_DMA_TIME_INT_LEVEL(dq) \ argument
321 (CN6XXX_DMA_INT_LEVEL_START + 4 + ((dq) * CN6XXX_DMA_OFFSET))
323 #define CN6XXX_DMA_TIM(dq) \ argument
324 (CN6XXX_DMA_TIM_START + ((dq) * CN6XXX_DMA_OFFSET))
Dcn23xx_pf_regs.h366 #define CN23XX_DMA_CNT(dq) \ argument
367 (CN23XX_DMA_CNT_START + ((dq) * CN23XX_DMA_OFFSET))
369 #define CN23XX_DMA_INT_LEVEL(dq) \ argument
370 (CN23XX_DMA_INT_LEVEL_START + ((dq) * CN23XX_DMA_OFFSET))
372 #define CN23XX_DMA_PKT_INT_LEVEL(dq) \ argument
373 (CN23XX_DMA_INT_LEVEL_START + ((dq) * CN23XX_DMA_OFFSET))
375 #define CN23XX_DMA_TIME_INT_LEVEL(dq) \ argument
376 (CN23XX_DMA_INT_LEVEL_START + 4 + ((dq) * CN23XX_DMA_OFFSET))
378 #define CN23XX_DMA_TIM(dq) \ argument
379 (CN23XX_DMA_TIM_START + ((dq) * CN23XX_DMA_OFFSET))
/linux-6.6.21/fs/xfs/
Dxfs_dquot.c70 struct xfs_dquot *dq) in xfs_qm_adjust_dqlimits() argument
72 struct xfs_mount *mp = dq->q_mount; in xfs_qm_adjust_dqlimits()
77 ASSERT(dq->q_id); in xfs_qm_adjust_dqlimits()
78 defq = xfs_get_defquota(q, xfs_dquot_type(dq)); in xfs_qm_adjust_dqlimits()
80 if (!dq->q_blk.softlimit) { in xfs_qm_adjust_dqlimits()
81 dq->q_blk.softlimit = defq->blk.soft; in xfs_qm_adjust_dqlimits()
84 if (!dq->q_blk.hardlimit) { in xfs_qm_adjust_dqlimits()
85 dq->q_blk.hardlimit = defq->blk.hard; in xfs_qm_adjust_dqlimits()
88 if (!dq->q_ino.softlimit) in xfs_qm_adjust_dqlimits()
89 dq->q_ino.softlimit = defq->ino.soft; in xfs_qm_adjust_dqlimits()
[all …]
Dxfs_iomap.c347 struct xfs_dquot *dq = xfs_inode_dquot(ip, type); in xfs_quota_need_throttle() local
349 if (!dq || !xfs_this_quota_on(ip->i_mount, type)) in xfs_quota_need_throttle()
353 if (!dq->q_prealloc_hi_wmark) in xfs_quota_need_throttle()
357 if (dq->q_blk.reserved + alloc_blocks < dq->q_prealloc_lo_wmark) in xfs_quota_need_throttle()
371 struct xfs_dquot *dq = xfs_inode_dquot(ip, type); in xfs_quota_calc_throttle() local
376 if (!dq || dq->q_blk.reserved >= dq->q_prealloc_hi_wmark) { in xfs_quota_calc_throttle()
382 freesp = dq->q_prealloc_hi_wmark - dq->q_blk.reserved; in xfs_quota_calc_throttle()
383 if (freesp < dq->q_low_space[XFS_QLOWSP_5_PCNT]) { in xfs_quota_calc_throttle()
385 if (freesp < dq->q_low_space[XFS_QLOWSP_3_PCNT]) in xfs_quota_calc_throttle()
387 if (freesp < dq->q_low_space[XFS_QLOWSP_1_PCNT]) in xfs_quota_calc_throttle()
/linux-6.6.21/drivers/s390/crypto/
Dzcrypt_msgtype50.c105 unsigned char dq[64]; member
118 unsigned char dq[128]; member
131 unsigned char dq[256]; member
263 unsigned char *p, *q, *dp, *dq, *u, *inp; in ICACRT_msg_to_type50CRT_msg() local
285 dq = crb1->dq + sizeof(crb1->dq) - short_len; in ICACRT_msg_to_type50CRT_msg()
299 dq = crb2->dq + sizeof(crb2->dq) - short_len; in ICACRT_msg_to_type50CRT_msg()
314 dq = crb3->dq + sizeof(crb3->dq) - short_len; in ICACRT_msg_to_type50CRT_msg()
328 copy_from_user(dq, crt->bq_key, short_len) || in ICACRT_msg_to_type50CRT_msg()
/linux-6.6.21/crypto/
Drsa.c23 MPI dq; member
68 ret = mpi_powm(m2, c, key->dq, key->q); in _rsa_dec_crt()
178 mpi_free(key->dq); in rsa_free_mpi_key()
186 key->dq = NULL; in rsa_free_mpi_key()
313 mpi_key->dq = mpi_read_raw_data(raw_key.dq, raw_key.dq_sz); in rsa_set_priv_key()
314 if (!mpi_key->dq) in rsa_set_priv_key()
/linux-6.6.21/drivers/scsi/hisi_sas/
Dhisi_sas_main.c400 struct hisi_sas_dq *dq, in hisi_sas_task_deliver() argument
408 spin_lock(&dq->lock); in hisi_sas_task_deliver()
409 wr_q_index = dq->wr_point; in hisi_sas_task_deliver()
410 dq->wr_point = (dq->wr_point + 1) % HISI_SAS_QUEUE_SLOTS; in hisi_sas_task_deliver()
411 list_add_tail(&slot->delivery, &dq->list); in hisi_sas_task_deliver()
412 spin_unlock(&dq->lock); in hisi_sas_task_deliver()
417 dlvry_queue = dq->id; in hisi_sas_task_deliver()
456 spin_lock(&dq->lock); in hisi_sas_task_deliver()
457 hisi_hba->hw->start_delivery(dq); in hisi_sas_task_deliver()
458 spin_unlock(&dq->lock); in hisi_sas_task_deliver()
[all …]
/linux-6.6.21/drivers/media/common/saa7146/
Dsaa7146_vbi.c293 struct saa7146_dmaqueue *dq = &dev->vv_data->vbi_dmaq; in return_buffers() local
296 if (dq->curr) { in return_buffers()
297 buf = dq->curr; in return_buffers()
298 dq->curr = NULL; in return_buffers()
301 while (!list_empty(&dq->queue)) { in return_buffers()
302 buf = list_entry(dq->queue.next, struct saa7146_buf, list); in return_buffers()
Dsaa7146_video.c638 struct saa7146_dmaqueue *dq = &dev->vv_data->video_dmaq; in return_buffers() local
641 if (dq->curr) { in return_buffers()
642 buf = dq->curr; in return_buffers()
643 dq->curr = NULL; in return_buffers()
646 while (!list_empty(&dq->queue)) { in return_buffers()
647 buf = list_entry(dq->queue.next, struct saa7146_buf, list); in return_buffers()
669 struct saa7146_dmaqueue *dq = &dev->vv_data->video_dmaq; in stop_streaming() local
671 del_timer(&dq->timeout); in stop_streaming()
/linux-6.6.21/drivers/soc/fsl/qbman/
Dqman_test_api.c212 const struct qm_dqrr_entry *dq, in cb_dqrr() argument
215 if (WARN_ON(fd_neq(&fd_dq, &dq->fd))) { in cb_dqrr()
220 if (!(dq->stat & QM_DQRR_STAT_UNSCHEDULED) && !fd_neq(&fd_dq, &fd)) { in cb_dqrr()
/linux-6.6.21/tools/testing/selftests/rcutorture/bin/
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

123