Home
last modified time | relevance | path

Searched refs:bfi (Results 1 – 13 of 13) sorted by relevance

/freebsd/lib/libc/aarch64/string/
H A Dtimingsafe_memcmp.S32 bfi w5, w3, #8, #8 // join bytes in big endian
33 bfi w6, w4, #8, #8
43 bfi w3, w5, #16, #16 // join halfwords in little endian
44 bfi w4, w6, #16, #16
57 bfi x3, x5, #32, #32 // join words in little endian
58 bfi x4, x6, #32, #32
/freebsd/contrib/ofed/libmlx5/
H A Dmlx5.c775 int bfi; in mlx5_init_context() local
886 bfi = (i * context->num_uars_per_page + j) * NUM_BFREGS_PER_UAR + k; in mlx5_init_context()
887 context->bfs[bfi].reg = context->uar[i] + MLX5_ADAPTER_PAGE_SIZE * j + in mlx5_init_context()
889 context->bfs[bfi].need_lock = need_uuar_lock(context, bfi); in mlx5_init_context()
890 if (mlx5_spinlock_init(&context->bfs[bfi].lock)) in mlx5_init_context()
892 context->bfs[bfi].offset = 0; in mlx5_init_context()
893 if (bfi) in mlx5_init_context()
894 context->bfs[bfi].buf_size = context->bf_reg_size / 2; in mlx5_init_context()
895 context->bfs[bfi].uuarn = bfi; in mlx5_init_context()
961 bfi = (i * context->num_uars_per_page + j) * NUM_BFREGS_PER_UAR + k; in mlx5_init_context()
[all …]
/freebsd/sys/dev/ath/
H A Dif_ath_tx_edma.c175 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 Dif_ath_beacon.c573 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/contrib/llvm-project/llvm/include/llvm/CodeGen/GlobalISel/
H A DGIMatchTableExecutor.h585 BlockFrequencyInfo *bfi = nullptr) {
590 BFI = bfi;
/freebsd/contrib/llvm-project/compiler-rt/lib/builtins/aarch64/
H A Dsme-libc-mem-routines.S258 bfi valw, valw, #8, #8
259 bfi valw, valw, #16, #16
260 bfi val, val, #32, #32
/freebsd/sys/arm64/arm64/
H A Dlocore.S938 bfi x2, x3, #(TCR_IPS_SHIFT), #(TCR_IPS_WIDTH)
946 bfi x2, x3, #(TCR_ASID_SHIFT), #(TCR_ASID_WIDTH)
/freebsd/contrib/llvm-project/llvm/include/llvm/Passes/
H A DMachinePassRegistry.def112 // MACHINE_FUNCTION_ANALYSIS("lazy-machine-bfi",
/freebsd/contrib/llvm-project/llvm/lib/Target/NVPTX/
H A DNVPTXInstrInfo.td1835 def bfi : SDNode<"NVPTXISD::BFI", SDTBFI>;
1865 … [(set (T RC:$f), (bfi (T RC:$a), (T RC:$b), (i32 Int32Regs:$c), (i32 Int32Regs:$d)))]>;
1870 [(set (T RC:$f), (bfi (T RC:$a), (T RC:$b), (i32 Int32Regs:$c), (i32 imm:$d)))]>;
1875 [(set (T RC:$f), (bfi (T RC:$a), (T RC:$b), (i32 imm:$c), (i32 imm:$d)))]>;
1880 … [(set (T RC:$f), (bfi (T imm:$a), (T RC:$b), (i32 Int32Regs:$c), (i32 Int32Regs:$d)))]>;
1885 [(set (T RC:$f), (bfi (T imm:$a), (T RC:$b), (i32 Int32Regs:$c), (i32 imm:$d)))]>;
1890 [(set (T RC:$f), (bfi (T imm:$a), (T RC:$b), (i32 imm:$c), (i32 imm:$d)))]>;
1921 defm BFI_B32 : BFI<"bfi.b32", i32, Int32Regs, i32imm>;
1922 defm BFI_B64 : BFI<"bfi.b64", i64, Int64Regs, i64imm>;
/freebsd/contrib/llvm-project/clang/include/clang/Basic/
H A DBuiltinsAMDGPU.def113 BUILTIN(__builtin_amdgcn_classf, "bfi", "nc")
/freebsd/sbin/camcontrol/
H A Dcamcontrol.c3920 { "bfi", SRDD10_BYTES_FROM_INDEX_FORMAT }, in scanlun_or_reset_dev()
4381 uint32_t bfi; in readdefects()
4383 bfi = scsi_4btoul(dlist[i].bytes_from_index); in readdefects()
4385 mads = (bfi & SDD_EXT_BFI_MADS) ? 1 : 0; in readdefects()
4386 bfi &= ~SDD_EXT_BFI_FLAG_MASK; in readdefects()
10138 "-f format specify defect list format (block, bfi or phys)\n" in usage()
4391 uint32_t bfi; readdefects() local
/freebsd/contrib/llvm-project/llvm/lib/Target/ARM/
H A DARMInstrInfo.td4209 "bfi", "\t$Rd, $Rn, $imm", "$src = $Rd",
H A DARMInstrThumb2.td2928 IIC_iBITi, "bfi", "\t$Rd, $Rn, $imm",