Home
last modified time | relevance | path

Searched full:dq (Results 1 – 25 of 100) sorted by relevance

1234

/linux/include/soc/fsl/
H A Ddpaa2-global.h20 struct dq { struct
33 } dq; member
66 * @dq: the dequeue result.
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()
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) in dpaa2_dq_is_pull() argument
82 return (int)(dpaa2_dq_flags(dq) & DPAA2_DQ_STAT_VOLATILE); in dpaa2_dq_is_pull()
87 * @dq: the dequeue result
[all …]
/linux/lib/raid6/
H A Drecov_rvv.c11 u8 *dq, const u8 *pbmul, in __raid6_2data_recov_rvv() argument
27 * qx = qmul[*q ^ *dq]; in __raid6_2data_recov_rvv()
28 * *dq++ = db = pbmul[px] ^ qx; in __raid6_2data_recov_rvv()
36 * v2:qx, v3:dq, in __raid6_2data_recov_rvv()
48 "vle8.v v3, (%[dq])\n" in __raid6_2data_recov_rvv()
56 "vxor.vv v2, v14, v15\n" /* v2 = qmul[*q ^ *dq] */ in __raid6_2data_recov_rvv()
67 "vse8.v v3, (%[dq])\n" in __raid6_2data_recov_rvv()
74 [dq]"r"(dq), in __raid6_2data_recov_rvv()
85 dq += 16; in __raid6_2data_recov_rvv()
90 u8 *dq, const u8 *qmul) in __raid6_datap_recov_rvv() argument
[all …]
H A 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()
67 * 1 = dq[0] ^ q[0] in raid6_2data_recov_avx2()
68 * 9 = dq[32] ^ q[32] in raid6_2data_recov_avx2()
117 * 1 = db = DQ in raid6_2data_recov_avx2()
118 * 13 = db[32] = DQ[32] in raid6_2data_recov_avx2()
[all …]
H A Drecov_avx512.c25 u8 *p, *q, *dp, *dq; in raid6_2data_recov_avx512() local
42 dq = (u8 *)ptrs[failb]; in raid6_2data_recov_avx512()
44 ptrs[disks-1] = dq; in raid6_2data_recov_avx512()
50 ptrs[failb] = dq; in raid6_2data_recov_avx512()
76 "m" (p[64]), "m" (dq[0]), "m" (dq[64]), in raid6_2data_recov_avx512()
80 * 1 = dq[0] ^ q[0] in raid6_2data_recov_avx512()
81 * 9 = dq[64] ^ q[64] in raid6_2data_recov_avx512()
138 * 1 = db = DQ in raid6_2data_recov_avx512()
139 * 13 = db[64] = DQ[64] in raid6_2data_recov_avx512()
146 : "m" (dq[0]), "m" (dq[64])); in raid6_2data_recov_avx512()
[all …]
H A Drecov_s390xc.c25 u8 *p, *q, *dp, *dq; in raid6_2data_recov_s390xc() local
39 dq = (u8 *)ptrs[failb]; in raid6_2data_recov_s390xc()
41 ptrs[disks-1] = dq; in raid6_2data_recov_s390xc()
47 ptrs[failb] = dq; in raid6_2data_recov_s390xc()
58 xor_block(dq, q); in raid6_2data_recov_s390xc()
60 dq[i] = pbmul[dp[i]] ^ qmul[dq[i]]; in raid6_2data_recov_s390xc()
61 xor_block(dp, dq); in raid6_2data_recov_s390xc()
65 dq += 256; in raid6_2data_recov_s390xc()
74 u8 *p, *q, *dq; in raid6_datap_recov_s390xc() local
83 dq = (u8 *)ptrs[faila]; in raid6_datap_recov_s390xc()
[all …]
H A 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()
123 /* xmm1/9 = db = DQ */ 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()
[all …]
H A Drecov_neon_inner.c29 uint8_t *dq, const uint8_t *pbmul, in __raid6_2data_recov_neon() argument
43 * qx = qmul[*q ^ *dq]; in __raid6_2data_recov_neon()
44 * *dq++ = db = pbmul[px] ^ qx; in __raid6_2data_recov_neon()
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
87 * *p++ ^= *dq = qmul[*q ^ *dq]; in __raid6_datap_recov_neon()
88 * q++; dq++; in __raid6_datap_recov_neon()
95 vx = veorq_u8(vld1q_u8(q), vld1q_u8(dq)); in __raid6_datap_recov_neon()
[all …]
H A 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 …]
H A 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 …]
H A Drecov_neon.c25 u8 *p, *q, *dp, *dq; in raid6_2data_recov_neon() local
40 dq = (u8 *)ptrs[failb]; in raid6_2data_recov_neon()
42 ptrs[disks - 1] = dq; in raid6_2data_recov_neon()
48 ptrs[failb] = dq; in raid6_2data_recov_neon()
58 __raid6_2data_recov_neon(bytes, p, q, dp, dq, pbmul, qmul); in raid6_2data_recov_neon()
64 u8 *p, *q, *dq; in raid6_datap_recov_neon() local
74 dq = (u8 *)ptrs[faila]; in raid6_datap_recov_neon()
76 ptrs[disks - 1] = dq; in raid6_datap_recov_neon()
81 ptrs[faila] = dq; in raid6_datap_recov_neon()
88 __raid6_datap_recov_neon(bytes, p, q, dq, qmul); in raid6_datap_recov_neon()
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/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) in qbman_result_is_DQ() argument
310 return ((dq->dq.verb & QBMAN_RESULT_MASK) == QBMAN_RESULT_DQ); in qbman_result_is_DQ()
315 * @dq: the dequeue result to be checked
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()
[all …]
/linux/crypto/async_tx/
H A 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/tools/memory-model/scripts/
H A Drunlitmushist.sh68 awk -v dq='"' -v hwfnseg="$hwfnseg" -v ncpu="$LKMM_JOBS" -v t="$T" '
70 print "if test -z " dq hwfnseg dq " || scripts/simpletest.sh " dq $2 dq
72 print "\techo runtest " dq $2 dq " " hwfnseg " >> " t "/" NR % ncpu ".sh";
/linux/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/fs/xfs/scrub/
H A Ddqiterate.c150 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()
/linux/drivers/net/ethernet/cavium/liquidio/
H A 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))
H A 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/drivers/net/ethernet/mellanox/mlxsw/
H A Dcmd.h980 /* SW2HW_DQ - Software to Hardware DQ
982 * OpMod == 0 (send DQ) / OpMod == 1 (receive DQ)
983 * INMmod == DQ number
1051 /* HW2SW_DQ - Hardware to Software DQ
1053 * OpMod == 0 (send DQ) / OpMod == 1 (receive DQ)
1054 * INMmod == DQ number
1057 * software ownership. Incoming packets on the DQ are silently discarded,
1082 /* 2ERR_DQ - To Error DQ
1084 * OpMod == 0 (send DQ) / OpMod == 1 (receive DQ)
1085 * INMmod == DQ number
[all …]
/linux/Documentation/devicetree/bindings/memory-controllers/
H A Drockchip,rk3399-dmc.yaml162 When the DRAM type is DDR3, this parameter defines the PHY side DQ line
163 (including DQS/DQ/DM line) drive strength.
210 When the DRAM type is LPDDR3, this parameter defines the PHY side DQ line
211 (including DQS/DQ/DM line) drive strength.
242 DQS/DQ line strength in ohms.
273 When the DRAM type is LPDDR4, this parameter defines the PHY side DQ line
274 (including DQS/DQ/DM line) drive strength.
/linux/Documentation/devicetree/bindings/power/supply/
H A Dmaxim,ds2760.yaml25 Allow the DS2760 to enter sleep mode when the DQ line goes low for more than 2 seconds
26 and leave sleep Mode when the DQ line goes high.
/linux/Documentation/devicetree/bindings/memory-controllers/ddr/
H A Djedec,lpddr-channel.yaml10 An LPDDR channel is a completely independent set of LPDDR pins (DQ, CA, CS,
28 The number of DQ pins in the channel. If this number is different
31 channel (with the channel's DQ pins split up between the different
/linux/drivers/crypto/intel/qat/qat_common/
H A Dqat_asym_algs.c40 dma_addr_t dq; member
66 char *dq; member
877 qat_req->in.rsa.dec_crt.dq = ctx->dma_dq; in qat_rsa_dec()
1118 /* dq */ in qat_rsa_setkey_crt()
1119 ptr = rsa_key->dq; in qat_rsa_setkey_crt()
1124 ctx->dq = dma_alloc_coherent(dev, half_key_sz, &ctx->dma_dq, in qat_rsa_setkey_crt()
1126 if (!ctx->dq) in qat_rsa_setkey_crt()
1128 memcpy(ctx->dq + (half_key_sz - len), ptr, len); in qat_rsa_setkey_crt()
1146 memset(ctx->dq, '\0', half_key_sz); in qat_rsa_setkey_crt()
1147 dma_free_coherent(dev, half_key_sz, ctx->dq, ctx->dma_dq); in qat_rsa_setkey_crt()
[all …]
/linux/drivers/crypto/caam/
H A Dcaampkc.h31 * 3. The third representation consists of the quintuple (p, q, dP, dQ, qInv),
36 * dQ the second factors's CRT exponent
76 u8 *dq; member
/linux/drivers/media/common/saa7146/
H A 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()

1234