Home
last modified time | relevance | path

Searched refs:bfi (Results 1 – 14 of 14) 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.c875 int bfi; in mlx5_init_context() local
984 bfi = (i * context->num_uars_per_page + j) * NUM_BFREGS_PER_UAR + k; in mlx5_init_context()
985 context->bfs[bfi].reg = context->uar[i] + MLX5_ADAPTER_PAGE_SIZE * j + in mlx5_init_context()
987 context->bfs[bfi].need_lock = need_uuar_lock(context, bfi); in mlx5_init_context()
988 if (mlx5_spinlock_init(&context->bfs[bfi].lock)) in mlx5_init_context()
990 context->bfs[bfi].offset = 0; in mlx5_init_context()
991 if (bfi) in mlx5_init_context()
992 context->bfs[bfi].buf_size = context->bf_reg_size / 2; in mlx5_init_context()
993 context->bfs[bfi].uuarn = bfi; in mlx5_init_context()
994 context->bfs[bfi].uar_mmap_offset = get_uar_mmap_offset(i, page_size); 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/compiler-rt/lib/builtins/aarch64/
H A Dsme-libc-opt-memset-memchr.S37 bfi valw, valw, #8, #8
38 bfi valw, valw, #16, #16
39 bfi val, val, #32, #32
/freebsd/contrib/llvm-project/llvm/include/llvm/CodeGen/GlobalISel/
H A DGIMatchTableExecutor.h611 BlockFrequencyInfo *bfi = nullptr) {
616 BFI = bfi;
/freebsd/sys/arm64/arm64/
H A Dlocore.S1099 bfi x2, x3, #(TCR_IPS_SHIFT), #(TCR_IPS_WIDTH)
1107 bfi x2, x3, #(TCR_ASID_SHIFT), #(TCR_ASID_WIDTH)
/freebsd/contrib/llvm-project/llvm/lib/Target/NVPTX/
H A DNVPTXInstrInfo.td1378 def bfi : SDNode<"NVPTXISD::BFI", SDTBFI>;
1399 [(set T:$f, (bfi T:$a, T:$b, i32:$c, i32:$d))]>;
1404 [(set T:$f, (bfi T:$a, T:$b, i32:$c, imm:$d))]>;
1409 [(set T:$f, (bfi T:$a, T:$b, imm:$c, imm:$d))]>;
1414 [(set T:$f, (bfi (T imm:$a), T:$b, i32:$c, i32:$d))]>;
1419 [(set T:$f, (bfi (T imm:$a), T:$b, i32:$c, imm:$d))]>;
1424 [(set T:$f, (bfi (T imm:$a), T:$b, imm:$c, imm:$d))]>;
1441 defm BFI_B32 : BFI<"bfi.b32", i32, B32, i32imm>;
1442 defm BFI_B64 : BFI<"bfi.b64", i64, B64, i64imm>;
/freebsd/contrib/llvm-project/llvm/include/llvm/Passes/
H A DMachinePassRegistry.def90 // MACHINE_FUNCTION_ANALYSIS("lazy-machine-bfi",
/freebsd/contrib/llvm-project/clang/include/clang/Basic/
H A DBuiltinsAMDGPU.def113 BUILTIN(__builtin_amdgcn_classf, "bfi", "nc")
/freebsd/sbin/camcontrol/
H A Dcamcontrol.c4412 uint32_t bfi; in readdefects() local
4414 bfi = scsi_4btoul(dlist[i].bytes_from_index); in readdefects()
4416 mads = (bfi & SDD_EXT_BFI_MADS) ? 1 : 0; in readdefects()
4417 bfi &= ~SDD_EXT_BFI_FLAG_MASK; in readdefects()
/freebsd/contrib/llvm-project/clang/include/clang/CIR/Dialect/IR/
H A DCIROps.td1690 cir.set_bitfield(#bfi, %0 : !cir.ptr<!u32i>, %1 : !s32i) {is_volatile}
1777 cir.get_bitfield(#bfi, %0 {is_volatile} : !cir.ptr<!u64i>) -> !s32i
/freebsd/contrib/llvm-project/llvm/lib/Target/ARM/
H A DARMInstrInfo.td4227 "bfi", "\t$Rd, $Rn, $imm", "$src = $Rd",
H A DARMInstrThumb2.td2935 IIC_iBITi, "bfi", "\t$Rd, $Rn, $imm",