| /freebsd-14.2/contrib/ofed/libmlx5/ |
| H A D | mlx5.c | 775 int bfi; in mlx5_init_context() local
882 bfi = (i * context->num_uars_per_page + j) * NUM_BFREGS_PER_UAR + k; in mlx5_init_context()
883 context->bfs[bfi].reg = context->uar[i] + MLX5_ADAPTER_PAGE_SIZE * j + in mlx5_init_context()
885 context->bfs[bfi].need_lock = need_uuar_lock(context, bfi); in mlx5_init_context()
886 mlx5_spinlock_init(&context->bfs[bfi].lock); in mlx5_init_context()
887 context->bfs[bfi].offset = 0; in mlx5_init_context()
888 if (bfi) in mlx5_init_context()
889 context->bfs[bfi].buf_size = context->bf_reg_size / 2; in mlx5_init_context()
890 context->bfs[bfi].uuarn = bfi; in mlx5_init_context()
|
| /freebsd-14.2/sys/dev/ath/ |
| H A D | if_ath_tx_edma.c | 175 struct ath_buf *bfi, *bfp; in ath_tx_edma_push_staging_list() local
244 TAILQ_FOREACH(bfi, &sq, bf_list) { in ath_tx_edma_push_staging_list()
247 bfi->bf_daddr); in ath_tx_edma_push_staging_list()
249 bfp = bfi; in ath_tx_edma_push_staging_list()
253 TAILQ_FOREACH(bfi, &sq, bf_list) { in ath_tx_edma_push_staging_list()
256 ath_printtxbuf(sc, bfi, txq->axq_qnum, i, 0); in ath_tx_edma_push_staging_list()
260 ath_tx_alq_post(sc, bfi); in ath_tx_edma_push_staging_list()
|
| H A D | if_ath_beacon.c | 573 struct ath_buf *bfi; in ath_beacon_cabq_start_edma()
630 TAILQ_FOREACH(bfi, &cabq->axq_q, bf_list) { in ath_beacon_cabq_start_edma()
|
| /freebsd-14.2/contrib/llvm-project/llvm/include/llvm/CodeGen/GlobalISel/ |
| H A D | GIMatchTableExecutor.h | 567 BlockFrequencyInfo *bfi = nullptr) {
572 BFI = bfi;
|
| /freebsd-14.2/contrib/llvm-project/llvm/include/llvm/CodeGen/ |
| H A D | MachinePassRegistry.def | 105 // MACHINE_FUNCTION_ANALYSIS("lazy-machine-bfi",
107 // MACHINE_FUNCTION_ANALYSIS("machine-bfi", MachineBlockFrequencyInfoAnalysis())
|
| /freebsd-14.2/sys/arm64/arm64/ |
| H A D | locore.S | 810 bfi x2, x3, #(TCR_IPS_SHIFT), #(TCR_IPS_WIDTH)
818 bfi x2, x3, #(TCR_ASID_SHIFT), #(TCR_ASID_WIDTH)
|
| /freebsd-14.2/contrib/llvm-project/llvm/lib/Target/NVPTX/ |
| H A D | NVPTXInstrInfo.td | 1802 def bfi : SDNode<"NVPTXISD::BFI", SDTBFI>;
1832 … [(set (T RC:$f), (bfi (T RC:$a), (T RC:$b), (i32 Int32Regs:$c), (i32 Int32Regs:$d)))]>;
1837 [(set (T RC:$f), (bfi (T RC:$a), (T RC:$b), (i32 Int32Regs:$c), (i32 imm:$d)))]>;
1842 [(set (T RC:$f), (bfi (T RC:$a), (T RC:$b), (i32 imm:$c), (i32 imm:$d)))]>;
1847 … [(set (T RC:$f), (bfi (T imm:$a), (T RC:$b), (i32 Int32Regs:$c), (i32 Int32Regs:$d)))]>;
1852 [(set (T RC:$f), (bfi (T imm:$a), (T RC:$b), (i32 Int32Regs:$c), (i32 imm:$d)))]>;
1857 [(set (T RC:$f), (bfi (T imm:$a), (T RC:$b), (i32 imm:$c), (i32 imm:$d)))]>;
1884 defm BFI_B32 : BFI<"bfi.b32", i32, Int32Regs, i32imm>;
1885 defm BFI_B64 : BFI<"bfi.b64", i64, Int64Regs, i64imm>;
|
| /freebsd-14.2/contrib/llvm-project/clang/include/clang/Basic/ |
| H A D | BuiltinsAMDGPU.def | 111 BUILTIN(__builtin_amdgcn_classf, "bfi", "nc")
|
| /freebsd-14.2/sbin/camcontrol/ |
| H A D | camcontrol.c | 4379 uint32_t bfi; in readdefects() local
4381 bfi = scsi_4btoul(dlist[i].bytes_from_index); in readdefects()
4383 mads = (bfi & SDD_EXT_BFI_MADS) ? 1 : 0; in readdefects()
4384 bfi &= ~SDD_EXT_BFI_FLAG_MASK; in readdefects()
|
| /freebsd-14.2/contrib/llvm-project/llvm/lib/Target/ARM/ |
| H A D | ARMInstrThumb2.td | 2934 IIC_iBITi, "bfi", "\t$Rd, $Rn, $imm",
|
| H A D | ARMInstrInfo.td | 4213 "bfi", "\t$Rd, $Rn, $imm", "$src = $Rd",
|