| /openbmc/linux/include/soc/fsl/ |
| H A D | dpaa2-global.h | 20 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 …]
|
| /openbmc/u-boot/drivers/ddr/marvell/axp/ |
| H A D | ddr3_pbs.c | 44 /* PBS locked dq (per pup) */
96 u32 pup, dq, pups, cur_max_pup, valid_pup, reg; in ddr3_pbs_tx() local
125 for (dq = 0; dq < DQ_NUM; dq++) in ddr3_pbs_tx()
126 skew_sum_array[pup][dq] = 0; in ddr3_pbs_tx()
173 for (dq = 0; dq < DQ_NUM; dq++) { in ddr3_pbs_tx()
176 (max_pup - 1)][dq] = in ddr3_pbs_tx()
200 for (dq = 0; dq < DQ_NUM; dq++) { in ddr3_pbs_tx()
206 [dq], CS0, (1 - ecc) * in ddr3_pbs_tx()
212 * Shift DQ ADLL right, One step before in ddr3_pbs_tx()
253 for (dq = 0; dq < DQ_NUM; dq++) { in ddr3_pbs_tx()
[all …]
|
| H A D | ddr3_dqs.c | 312 u32 dq; in ddr3_find_adll_limits() local
346 for (dq = 0; dq < DQ_NUM; dq++) { in ddr3_find_adll_limits()
347 analog_pbs_sum[pup][dq][0] = adll_start_val; in ddr3_find_adll_limits()
348 analog_pbs_sum[pup][dq][1] = adll_end_val; in ddr3_find_adll_limits()
354 DEBUG_DQS_FULL_C("DDR3 - DQS Find Limits - Victim DQ - ", in ddr3_find_adll_limits()
378 for (dq = 0; dq < DQ_NUM; dq++) { in ddr3_find_adll_limits()
379 analog_pbs[victim_dq][pup][dq][0] = in ddr3_find_adll_limits()
381 analog_pbs[victim_dq][pup][dq][1] = in ddr3_find_adll_limits()
383 per_bit_data[pup][dq] = 0; in ddr3_find_adll_limits()
453 DEBUG_DQS_S(", DQ - "); in ddr3_find_adll_limits()
[all …]
|
| H A D | ddr3_sdram.c | 27 /* PBS locked dq (per pup) */
98 __maybe_unused u32 dq; in compare_pattern_v1() local
114 for (dq = 0; dq < DQ_NUM; dq++) { in compare_pattern_v1()
117 if (((var1 >> dq) & 0x1) != in compare_pattern_v1()
118 ((var2 >> dq) & 0x1)) in compare_pattern_v1()
119 per_bit_data[val][dq] = 1; in compare_pattern_v1()
121 per_bit_data[val][dq] = 0; in compare_pattern_v1()
171 __maybe_unused u32 dq; in ddr3_sdram_compare() local
269 * Desc: Execute SRAM compare per PUP and DQ.
276 * ai_unlock_pup_dq_array bit array of the locked / unlocked pups per dq.
[all …]
|
| /openbmc/linux/fs/xfs/scrub/ |
| H A D | quota.c | 21 /* Convert a scrub type code to a DQ flag, or return 0 if error. */
81 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()
[all …]
|
| /openbmc/linux/lib/raid6/ |
| H A D | recov_avx512.c | 27 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()
82 * 1 = dq[0] ^ q[0] in raid6_2data_recov_avx512()
83 * 9 = dq[64] ^ q[64] in raid6_2data_recov_avx512()
140 * 1 = db = DQ in raid6_2data_recov_avx512()
141 * 13 = db[64] = DQ[64] in raid6_2data_recov_avx512()
148 : "m" (dq[0]), "m" (dq[64])); in raid6_2data_recov_avx512()
[all …]
|
| H 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()
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 D | recov_s390xc.c | 26 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 …]
|
| H 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()
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 D | recov_neon_inner.c | 29 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 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()
|
| H 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()
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 D | recov_loongarch_simd.c | 32 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 …]
|
| /openbmc/linux/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) 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 …]
|
| /openbmc/u-boot/board/gateworks/gw_ventana/ |
| H A D | gw_ventana_spl.c | 214 /* Read Calibration: DQS delay relative to DQ read access */
216 /* Write Calibration: DQ/DM delay relative to DQS write access */
232 /* Read Calibration: DQS delay relative to DQ read access */
235 /* Write Calibration: DQ/DM delay relative to DQS write access */
252 /* Read Calibration: DQS delay relative to DQ read access */
255 /* Write Calibration: DQ/DM delay relative to DQS write access */
267 /* Read Calibration: DQS delay relative to DQ read access */
269 /* Write Calibration: DQ/DM delay relative to DQS write access */
280 /* Read Calibration: DQS delay relative to DQ read access */
282 /* Write Calibration: DQ/DM delay relative to DQS write access */
[all …]
|
| /openbmc/linux/crypto/async_tx/ |
| H A D | async_raid6_recov.c | 208 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 …]
|
| /openbmc/linux/tools/memory-model/scripts/ |
| H A D | runlitmushist.sh | 68 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";
|
| /openbmc/u-boot/drivers/net/fsl-mc/dpio/ |
| H A D | qbman_portal.c | 374 const struct ldpaa_dq *dq; in qbman_swp_dqrr_next() local
377 dq = qbman_cena_read(&s->sys, QBMAN_CENA_SWP_DQRR(s->dqrr.next_idx)); in qbman_swp_dqrr_next()
378 p = qb_cl(dq); in qbman_swp_dqrr_next()
404 flags = ldpaa_dq_flags(dq); in qbman_swp_dqrr_next()
413 return dq; in qbman_swp_dqrr_next()
417 void qbman_swp_dqrr_consume(struct qbman_swp *s, const struct ldpaa_dq *dq) in qbman_swp_dqrr_consume() argument
419 qbman_cinh_write(&s->sys, QBMAN_CINH_SWP_DCAP, QBMAN_IDX_FROM_DQRR(dq)); in qbman_swp_dqrr_consume()
426 void qbman_dq_entry_set_oldtoken(struct ldpaa_dq *dq, in qbman_dq_entry_set_oldtoken() argument
430 memset(dq, oldtoken, num_entries * sizeof(*dq)); in qbman_dq_entry_set_oldtoken()
434 const struct ldpaa_dq *dq, in qbman_dq_entry_has_newtoken() argument
[all …]
|
| /openbmc/linux/fs/xfs/ |
| H A D | xfs_dquot.c | 70 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 …]
|
| /openbmc/linux/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
|
| /openbmc/phosphor-fan-presence/control/ |
| H A D | fanctl.cpp | 585 void queryDumpFile(const DumpQuery& dq) in queryDumpFile() argument
598 if (!dumpData.contains(dq.section)) in queryDumpFile()
600 std::cerr << "Error: Dump file does not contain " << dq.section in queryDumpFile()
606 const auto& section = dumpData.at(dq.section); in queryDumpFile()
612 if (!entry.is_string() || dq.name.empty() || in queryDumpFile()
613 (entry.get<std::string>().find(dq.name) != std::string::npos)) in queryDumpFile()
615 output[dq.section].push_back(entry); in queryDumpFile()
624 if (dq.name.empty() || (key1.find(dq.name) != std::string::npos)) in queryDumpFile()
627 if (dq.properties.empty()) in queryDumpFile()
637 for (const auto& prop : dq.properties) in queryDumpFile()
[all …]
|
| /openbmc/linux/crypto/ |
| H A D | rsa.c | 23 MPI dq; member
44 * m_2 = c^dQ mod q;
67 /* (2i) m_2 = c^dQ mod q */ in _rsa_dec_crt()
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()
|
| /openbmc/linux/drivers/s390/crypto/ |
| H 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()
|
| /openbmc/u-boot/drivers/ddr/altera/ |
| H A D | sequencer.c | 353 /* load up dq config settings */
469 * bits: 1:1 = 1'b1 - DQ bypass in scc_mgr_set_hhp_extras()
534 /* Multicast to all DQ enables. */ in scc_set_bypass_mode()
574 * Zero DQ, DM, DQS and OCT configs for a group.
582 /* Zero all DQ config settings. */ in scc_mgr_zero_group()
589 /* Multicast to all DQ enables. */ in scc_mgr_zero_group()
620 * apply and load a particular input delay for the DQ pins in a group
621 * group_bgn is the index of the first dq pin (in the write group)
634 * scc_mgr_apply_group_dq_out1_delay() - Apply and load an output delay for the DQ pins in a group
637 * Apply and load a particular output delay for the DQ pins in a group.
[all …]
|
| /openbmc/u-boot/include/fsl-mc/ |
| H A D | fsl_dpaa_fd.h | 100 static inline int ldpaa_dq_is_pull(const struct ldpaa_dq *dq) in ldpaa_dq_is_pull() argument
102 return (int)(ldpaa_dq_flags(dq) & LDPAA_DQ_STAT_VOLATILE); in ldpaa_dq_is_pull()
105 const struct ldpaa_dq *dq) in ldpaa_dq_is_pull_complete() argument
107 return (int)(ldpaa_dq_flags(dq) & LDPAA_DQ_STAT_EXPIRED); in ldpaa_dq_is_pull_complete()
|