| /linux/include/soc/fsl/ |
| A D | dpaa2-global.h | 20 struct dq { struct
33 } dq; member
70 return dq->dq.stat; in dpaa2_dq_flags()
93 return !!(dpaa2_dq_flags(dq) & DPAA2_DQ_STAT_EXPIRED); in dpaa2_dq_is_pull_complete()
106 return le16_to_cpu(dq->dq.seqnum); in dpaa2_dq_seqnum()
119 return le16_to_cpu(dq->dq.oprid); in dpaa2_dq_odpid()
130 return le32_to_cpu(dq->dq.fqid) & DQ_FQID_MASK; in dpaa2_dq_fqid()
141 return le32_to_cpu(dq->dq.fq_byte_cnt); in dpaa2_dq_byte_count()
152 return le32_to_cpu(dq->dq.fq_frm_cnt) & DQ_FRAME_COUNT_MASK; in dpaa2_dq_frame_count()
163 return le64_to_cpu(dq->dq.fqd_ctx); in dpaa2_dq_fqd_ctx()
[all …]
|
| /linux/lib/raid6/ |
| A D | recov_loongarch_simd.c | 32 u8 *p, *q, *dp, *dq; in raid6_2data_recov_lsx() local
49 ptrs[disks - 1] = dq; in raid6_2data_recov_lsx()
55 ptrs[failb] = dq; in raid6_2data_recov_lsx()
180 dq += 64; in raid6_2data_recov_lsx()
189 u8 *p, *q, *dq; in raid6_datap_recov_lsx() local
206 ptrs[faila] = dq; in raid6_datap_recov_lsx()
282 dq += 64; in raid6_datap_recov_lsx()
329 ptrs[failb] = dq; in raid6_2data_recov_lasx()
419 dq += 64; in raid6_2data_recov_lasx()
428 u8 *p, *q, *dq; in raid6_datap_recov_lasx() local
[all …]
|
| A D | recov_avx2.c | 19 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()
132 dq += 64; in raid6_2data_recov_avx2()
179 dq += 32; in raid6_2data_recov_avx2()
189 u8 *p, *q, *dq; in raid6_datap_recov_avx2() local
200 ptrs[disks-1] = dq; in raid6_datap_recov_avx2()
205 ptrs[faila] = dq; in raid6_datap_recov_avx2()
266 dq += 64; in raid6_datap_recov_avx2()
[all …]
|
| A D | recov_avx512.c | 27 u8 *p, *q, *dp, *dq; in raid6_2data_recov_avx512() local
46 ptrs[disks-1] = 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()
220 dq += 64; in raid6_2data_recov_avx512()
230 u8 *p, *q, *dq; in raid6_datap_recov_avx512() local
266 : "m" (dq[0]), "m" (dq[64]), "m" (q[0]), in raid6_datap_recov_avx512()
316 : "m" (dq[0]), "m" (dq[64]), "m" (p[0]), in raid6_datap_recov_avx512()
322 dq += 128; in raid6_datap_recov_avx512()
[all …]
|
| A D | recov_ssse3.c | 19 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()
136 dq += 32; in raid6_2data_recov_ssse3()
183 dq += 16; in raid6_2data_recov_ssse3()
194 u8 *p, *q, *dq; in raid6_datap_recov_ssse3() local
207 ptrs[disks-1] = dq; in raid6_datap_recov_ssse3()
212 ptrs[faila] = dq; in raid6_datap_recov_ssse3()
280 dq += 32; in raid6_datap_recov_ssse3()
[all …]
|
| A D | recov_s390xc.c | 26 u8 *p, *q, *dp, *dq; in raid6_2data_recov_s390xc() local
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()
66 dq += 256; in raid6_2data_recov_s390xc()
75 u8 *p, *q, *dq; in raid6_datap_recov_s390xc() local
99 xor_block(dq, q); in raid6_datap_recov_s390xc()
101 dq[i] = qmul[dq[i]]; in raid6_datap_recov_s390xc()
102 xor_block(p, dq); in raid6_datap_recov_s390xc()
[all …]
|
| A D | recov.c | 22 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()
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()
89 *p++ ^= *dq = qmul[*q ^ *dq]; in raid6_datap_recov_intx1()
[all …]
|
| A D | recov_neon.c | 26 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()
|
| A D | recov_neon_inner.c | 29 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()
|
| 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/fs/xfs/scrub/ |
| A D | quota_repair.c | 91 xfs_qm_init_dquot_blk(sc->tp, dq->q_id, dq->q_type, bp); in xrep_quota_item_fill_bmap_hole()
200 if (dq->q_blk.softlimit > dq->q_blk.hardlimit) { in xrep_quota_item()
201 dq->q_blk.softlimit = dq->q_blk.hardlimit; in xrep_quota_item()
205 if (dq->q_ino.softlimit > dq->q_ino.hardlimit) { in xrep_quota_item()
206 dq->q_ino.softlimit = dq->q_ino.hardlimit; in xrep_quota_item()
210 if (dq->q_rtb.softlimit > dq->q_rtb.hardlimit) { in xrep_quota_item()
211 dq->q_rtb.softlimit = dq->q_rtb.hardlimit; in xrep_quota_item()
222 dq->q_blk.reserved -= dq->q_blk.count; in xrep_quota_item()
230 dq->q_ino.reserved -= dq->q_ino.count; in xrep_quota_item()
237 dq->q_rtb.reserved -= dq->q_rtb.count; in xrep_quota_item()
[all …]
|
| A D | quota.c | 84 struct xfs_dquot *dq, in xchk_quota_item_bmap() argument
161 xfs_dqunlock(dq); in xchk_quota_item()
163 xfs_dqlock(dq); in xchk_quota_item()
170 if (dq->q_id && dq->q_id <= sqi->last_id) in xchk_quota_item()
190 if (dq->q_blk.softlimit > dq->q_blk.hardlimit) in xchk_quota_item()
195 if (dq->q_ino.softlimit > dq->q_ino.hardlimit) in xchk_quota_item()
200 if (dq->q_rtb.softlimit > dq->q_rtb.hardlimit) in xchk_quota_item()
228 if (dq->q_id == 0) in xchk_quota_item()
232 dq->q_blk.count > dq->q_blk.hardlimit) in xchk_quota_item()
236 dq->q_ino.count > dq->q_ino.hardlimit) in xchk_quota_item()
[all …]
|
| A D | quotacheck_repair.c | 47 struct xfs_dquot *dq) in xqcheck_commit_dquot() argument
56 xfs_dqunlock(dq); in xqcheck_commit_dquot()
58 xfs_dqlock(dq); in xqcheck_commit_dquot()
78 dq->q_ino.count += delta; in xqcheck_commit_dquot()
111 trace_xrep_quotacheck_dquot(xqc->sc->mp, dq->q_type, dq->q_id); in xqcheck_commit_dquot()
115 if (dq->q_id) in xqcheck_commit_dquot()
125 xfs_dqlock(dq); in xqcheck_commit_dquot()
134 xfs_dqlock(dq); in xqcheck_commit_dquot()
149 struct xfs_dquot *dq; in xqcheck_commit_dqtype() local
159 xfs_qm_dqput(dq); in xqcheck_commit_dqtype()
[all …]
|
| A D | dqiterate.c | 150 struct xfs_dquot *dq; in xchk_dquot_iter_advance_incore() local
156 nr_found = radix_tree_gang_lookup(tree, (void **)&dq, cursor->id, 1); in xchk_dquot_iter_advance_incore()
158 *next_incore_id = dq->q_id; in xchk_dquot_iter_advance_incore()
176 struct xfs_dquot *dq = NULL; in xchk_dquot_iter() local
204 error = xfs_qm_dqget(mp, cursor->id, cursor->dqtype, false, &dq); in xchk_dquot_iter()
208 cursor->id = dq->q_id + 1; in xchk_dquot_iter()
209 *dqpp = dq; in xchk_dquot_iter()
|
| A D | quotacheck.c | 554 struct xfs_dquot *dq) in xqcheck_compare_dquot() argument
570 if (xcdq.icount != dq->q_ino.count) in xqcheck_compare_dquot()
573 if (xcdq.bcount != dq->q_blk.count) in xqcheck_compare_dquot()
576 if (xcdq.rtbcount != dq->q_rtb.count) in xqcheck_compare_dquot()
580 error = xfarray_store(counts, dq->q_id, &xcdq); in xqcheck_compare_dquot()
615 struct xfs_dquot *dq; in xqcheck_walk_observations() local
637 error = xqcheck_compare_dquot(xqc, dqtype, dq); in xqcheck_walk_observations()
638 xfs_qm_dqput(dq); in xqcheck_walk_observations()
660 struct xfs_dquot *dq; in xqcheck_compare_dqtype() local
675 error = xqcheck_compare_dquot(xqc, dqtype, dq); in xqcheck_compare_dqtype()
[all …]
|
| /linux/drivers/soc/fsl/dpio/ |
| A D | qbman-portal.h | 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()
320 return !qbman_result_is_DQ(dq); in qbman_result_is_SCN()
326 return ((dq->dq.verb & QBMAN_RESULT_MASK) == QBMAN_RESULT_FQDAN); in qbman_result_is_FQDAN()
332 return ((dq->dq.verb & QBMAN_RESULT_MASK) == QBMAN_RESULT_CDAN); in qbman_result_is_CDAN()
338 return ((dq->dq.verb & QBMAN_RESULT_MASK) == QBMAN_RESULT_CSCN_WQ); in qbman_result_is_CSCN()
344 return ((dq->dq.verb & QBMAN_RESULT_MASK) == QBMAN_RESULT_BPSCN); in qbman_result_is_BPSCN()
350 return ((dq->dq.verb & QBMAN_RESULT_MASK) == QBMAN_RESULT_CGCU); in qbman_result_is_CGCU()
356 return ((dq->dq.verb & QBMAN_RESULT_MASK) == QBMAN_RESULT_FQRN); in qbman_result_is_FQRN()
362 return ((dq->dq.verb & QBMAN_RESULT_MASK) == QBMAN_RESULT_FQRNI); in qbman_result_is_FQRNI()
[all …]
|
| /linux/crypto/async_tx/ |
| A D | async_raid6_recov.c | 244 dq = blocks[failb]; in __2data_recov_5()
263 srcs[0] = dq; in __2data_recov_5()
274 srcs[1] = dq; in __2data_recov_5()
284 srcs[1] = dq; in __2data_recov_5()
323 dq = blocks[failb]; in __2data_recov_n()
352 srcs[0] = dq; in __2data_recov_n()
363 srcs[1] = dq; in __2data_recov_n()
373 srcs[1] = dq; in __2data_recov_n()
569 srcs[0] = dq; in async_raid6_datap_recov()
578 tx = async_mult(dq, dq_off, dq, dq_off, coef, bytes, submit); in async_raid6_datap_recov()
[all …]
|
| /linux/drivers/net/ethernet/cavium/liquidio/ |
| A D | cn66xx_regs.h | 311 #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))
|
| A D | cn23xx_pf_regs.h | 366 #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/drivers/s390/crypto/ |
| A D | zcrypt_msgtype50.c | 105 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/fs/xfs/ |
| A D | xfs_dquot.c | 94 struct xfs_dquot *dq) in xfs_qm_adjust_dqlimits() argument
101 ASSERT(dq->q_id); in xfs_qm_adjust_dqlimits()
112 if (!dq->q_ino.softlimit) in xfs_qm_adjust_dqlimits()
114 if (!dq->q_ino.hardlimit) in xfs_qm_adjust_dqlimits()
116 if (!dq->q_rtb.softlimit) in xfs_qm_adjust_dqlimits()
118 if (!dq->q_rtb.hardlimit) in xfs_qm_adjust_dqlimits()
182 struct xfs_dquot *dq) in xfs_qm_adjust_dqtimers() argument
188 ASSERT(dq->q_id); in xfs_qm_adjust_dqtimers()
191 xfs_qm_adjust_res_timer(dq->q_mount, &dq->q_blk, &defq->blk); in xfs_qm_adjust_dqtimers()
192 xfs_qm_adjust_res_timer(dq->q_mount, &dq->q_ino, &defq->ino); in xfs_qm_adjust_dqtimers()
[all …]
|
| A D | xfs_iomap.c | 344 struct xfs_dquot *dq = xfs_inode_dquot(ip, type); in xfs_quota_need_throttle() local
346 if (!dq || !xfs_this_quota_on(ip->i_mount, type)) in xfs_quota_need_throttle()
350 if (!dq->q_prealloc_hi_wmark) in xfs_quota_need_throttle()
354 if (dq->q_blk.reserved + alloc_blocks < dq->q_prealloc_lo_wmark) in xfs_quota_need_throttle()
368 struct xfs_dquot *dq = xfs_inode_dquot(ip, type); in xfs_quota_calc_throttle() local
373 if (!dq || dq->q_blk.reserved >= dq->q_prealloc_hi_wmark) { in xfs_quota_calc_throttle()
379 freesp = dq->q_prealloc_hi_wmark - dq->q_blk.reserved; in xfs_quota_calc_throttle()
380 if (freesp < dq->q_low_space[XFS_QLOWSP_5_PCNT]) { in xfs_quota_calc_throttle()
382 if (freesp < dq->q_low_space[XFS_QLOWSP_3_PCNT]) in xfs_quota_calc_throttle()
384 if (freesp < dq->q_low_space[XFS_QLOWSP_1_PCNT]) in xfs_quota_calc_throttle()
|
| /linux/crypto/ |
| A D | rsa.c | 23 MPI dq; member
96 ret = mpi_powm(m2, c, key->dq, key->q); in _rsa_dec_crt()
205 mpi_free(key->dq); in rsa_free_mpi_key()
213 key->dq = NULL; in rsa_free_mpi_key()
346 mpi_key->dq = mpi_read_raw_data(raw_key.dq, raw_key.dq_sz); in rsa_set_priv_key()
347 if (!mpi_key->dq) in rsa_set_priv_key()
|
| /linux/drivers/scsi/hisi_sas/ |
| A D | hisi_sas_main.c | 408 spin_lock(&dq->lock); in hisi_sas_task_deliver()
410 dq->wr_point = (dq->wr_point + 1) % HISI_SAS_QUEUE_SLOTS; in hisi_sas_task_deliver()
534 dq = &hisi_hba->dq[dq_index]; in hisi_sas_queue_command()
551 dq = &hisi_hba->dq[queue]; in hisi_sas_queue_command()
567 dq = &hisi_hba->dq[task->abort_task.qid]; in hisi_sas_queue_command()
669 struct hisi_sas_dq *dq = &hisi_hba->dq[queue]; in hisi_sas_alloc_dev() local
677 sas_dev->dq = dq; in hisi_sas_alloc_dev()
2143 struct hisi_sas_dq *dq = &hisi_hba->dq[i]; in hisi_sas_init_mem() local
2150 dq->wr_point = 0; in hisi_sas_init_mem()
2195 struct hisi_sas_dq *dq = &hisi_hba->dq[i]; in hisi_sas_alloc() local
[all …]
|
| /linux/drivers/media/common/saa7146/ |
| A D | saa7146_vbi.c | 293 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()
|