Searched refs:vl (Results 1 - 25 of 99) sorted by path

1234

/linux-master/drivers/gpu/drm/nouveau/include/nvif/
H A D	unpack.h	14 #define nvif_unpack(r,d,s,m,vl,vh,x) ({ \ 16 int _ret = (r), _vl = (vl), _vh = (vh); \
/linux-master/drivers/infiniband/ulp/opa_vnic/
H A D	opa_vnic_encap.c	391 u8 vl; local 397 vl = info->vport.pcp_to_vl_mc[pcp]; 399 vl = info->vport.pcp_to_vl_uc[pcp]; 402 vl = info->vport.non_vlan_vl_mc; 404 vl = info->vport.non_vlan_vl_uc; 407 return vl; 502 mdata->vl = opa_vnic_get_vl(adapter, skb);
/linux-master/net/rose/
H A D	rose_out.c	98 rose->vl = rose->vr; 118 rose->vl = rose->vr;
/linux-master/sound/usb/6fire/
H A D	comm.h	32 u8 vh, u8 vl);
/linux-master/arch/arm64/include/asm/
H A D	fpsimd.h	116 static inline size_t sve_ffr_offset(int vl) argument 118 return SVE_SIG_FFR_OFFSET(sve_vq_from_vl(vl)) - SVE_SIG_REGS_OFFSET; 123 unsigned int vl; local 126 vl = thread_get_sme_vl(thread); 128 vl = thread_get_sve_vl(thread); 130 return (char *)thread->sve_state + sve_ffr_offset(vl); 207 unsigned long vl, unsigned long flags); 398 unsigned int vl = task_get_sme_vl(task); local 401 size = ZA_SIG_REGS_SIZE(sve_vq_from_vl(vl));
H A D	processor.h	167 unsigned int vl[ARM64_VEC_MAX]; /* vector length */ member in struct:thread_struct 168 unsigned int vl_onexec[ARM64_VEC_MAX]; /* vl after next exec */ 192 return thread->vl[type]; 215 unsigned long vl); 217 unsigned long vl); 231 static inline void task_set_sve_vl(struct task_struct *task, unsigned long vl) argument 233 task_set_vl(task, ARM64_VEC_SVE, vl); 242 unsigned long vl) 244 task_set_vl_onexec(task, ARM64_VEC_SVE, vl); 241 task_set_sve_vl_onexec(struct task_struct *task, unsigned long vl) argument
/linux-master/arch/arm64/include/uapi/asm/
H A D	ptrace.h	117 __u16 vl; /* current vector length */ member in struct:user_sve_header 276 __u16 vl; /* current vector length */ member in struct:user_za_header
H A D	sigcontext.h	47 * 0x8a0 sve_context (vl <= 64) (optional) 140 __u16 vl; member in struct:sve_context 167 __u16 vl; member in struct:za_context 202 #define sve_vl_valid(vl) __sve_vl_valid(vl) 203 #define sve_vq_from_vl(vl) __sve_vq_from_vl(vl) 209 * SVE_SIG_CONTEXT_SIZE(sve_vq_from_vl(sve_context.vl)) 213 * SVE_SIG_CONTEXT_SIZE(sve_vq_from_vl(sve_context.vl)), 225 * sve_context.vl mus [all...]
H A D	sve_context.h	36 #define __sve_vl_valid(vl) \ 37 ((vl) % __SVE_VQ_BYTES == 0 && \ 38 (vl) >= __SVE_VL_MIN && \ 39 (vl) <= __SVE_VL_MAX) 41 #define __sve_vq_from_vl(vl) ((vl) / __SVE_VQ_BYTES)
/linux-master/arch/arm64/kernel/
H A D	fpsimd.c	251 return task->thread.vl[type]; 255 unsigned long vl) 257 task->thread.vl[type] = vl; 267 unsigned long vl) 269 task->thread.vl_onexec[type] = vl; 444 unsigned int vl; local 465 vl = last->sve_vl; 481 vl = last->sme_vl; 487 if (WARN_ON(sve_get_vl() != vl)) { 254 task_set_vl(struct task_struct *task, enum vec_type type, unsigned long vl) argument 266 task_set_vl_onexec(struct task_struct *task, enum vec_type type, unsigned long vl) argument 513 find_supported_vector_length(enum vec_type type, unsigned int vl) argument 544 int vl = get_default_vl(type); local 680 unsigned int vq, vl; local 727 unsigned int vl = 0; local 832 vec_set_vector_length(struct task_struct *task, enum vec_type type, unsigned long vl, unsigned long flags) argument 951 unsigned long vl, flags; local 980 unsigned long vl, flags; local 1009 unsigned int vq, vl; local 1574 int vl, supported_vl; local [all...]
H A D	ptrace.c	797 header->vl = task_get_vl(target, type); 798 vq = sve_vq_from_vl(header->vl); 822 vq = sve_vq_from_vl(header.vl); 896 ret = vec_set_vector_length(target, type, header.vl, 957 if (count && vq != sve_vq_from_vl(header.vl)) { 1065 header.vl = task_get_sme_vl(target); 1066 vq = sve_vq_from_vl(header.vl); 1123 ret = vec_set_vector_length(target, ARM64_VEC_SME, header.vl, 1159 if (vq != sve_vq_from_vl(header.vl)) {
H A D	signal.c	268 unsigned int vl = task_get_sve_vl(current); local 272 vl = task_get_sme_vl(current); 273 vq = sve_vq_from_vl(vl); 276 vq = sve_vq_from_vl(vl); 284 __put_user_error(vl, &ctx->vl, err); 306 unsigned int vl, vq; local 313 __get_user_error(user_vl, &(user->sve->vl), err); 322 vl = task_get_sme_vl(current); 332 vl 441 unsigned int vl = task_get_sme_vl(current); local 928 int vl = max(sve_max_vl(), sme_max_vl()); local 950 unsigned int vl; local [all...]
/linux-master/arch/arm64/kvm/
H A D	reset.c	95 unsigned int vl; local 99 vl = vcpu->arch.sve_max_vl; 106 if (WARN_ON(!sve_vl_valid(vl) || vl > sve_max_virtualisable_vl() || 107 vl > VL_ARCH_MAX))
/linux-master/arch/riscv/include/asm/
H A D	vector.h	86 : "=r" (dest->vstart), "=r" (dest->vtype), "=r" (dest->vl), 99 : : "r" (src->vstart), "r" (src->vtype), "r" (src->vl), 106 unsigned long vl; local 122 : "=&r" (vl) : "r" (datap) : "memory"); 129 unsigned long vl; local 144 : "=&r" (vl) : "r" (datap) : "memory"); 151 unsigned long vl, vtype_inval = 1UL << (BITS_PER_LONG - 1); local 164 : "=&r" (vl) : "r" (vtype_inval) : "memory");
/linux-master/arch/riscv/include/uapi/asm/
H A D	ptrace.h	102 unsigned long vl; member in struct:__riscv_v_ext_state 116 unsigned long vl; member in struct:__riscv_v_regset_state
/linux-master/arch/riscv/kernel/
H A D	ptrace.c	109 ptrace_vstate.vl = vstate->vl; 143 vstate->vl = ptrace_vstate.vl;
/linux-master/arch/riscv/kvm/
H A D	vcpu_vector.c	110 case KVM_REG_RISCV_VECTOR_CSR_REG(vl): 111 *reg_addr = &cntx->vector.vl;
/linux-master/drivers/ata/pata_parport/
H A D	on20.c	24 #define vl(v) \ macro 43 op(1); vl(r); op(0); 64 op(1); vl(r); 65 op(0); vl(val); 66 op(0); vl(val); 76 op(2); vl(8); op(2); vl(9); 78 op(2); vl(0); op(2); vl(8); 93 op(1); vl( [all...]
/linux-master/drivers/infiniband/hw/hfi1/
H A D	chip.c	1178 u64 (*rw_cntr)(const struct cntr_entry *, void *context, int vl, 1371 void *context, int vl, int mode, u64 data) 1377 if (vl == CNTR_INVALID_VL) 1379 csr += 0x100 * vl; 1381 if (vl != CNTR_INVALID_VL) 1429 int vl, int mode, u64 data) 1437 if (vl == CNTR_INVALID_VL) 1439 csr += 8 * vl; 1441 if (vl != CNTR_INVALID_VL) 1450 int vl, in 1370 dev_access_u32_csr(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1428 dev_access_u64_csr(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1449 dc_access_lcb_cntr(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1474 port_access_u32_csr(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1484 port_access_u64_csr(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1524 access_sw_link_dn_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1534 access_sw_link_up_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1544 access_sw_unknown_frame_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1555 access_sw_xmit_discards(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1572 access_xmit_constraint_errs(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1585 access_rcv_constraint_errs(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1607 read_write_cpu(struct hfi1_devdata *dd, u64 *z_val, u64 __percpu *cntr, int vl, int mode, u64 data) argument 1632 access_sw_cpu_intr(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1641 access_sw_cpu_rcv_limit(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1650 access_sw_pio_wait(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1658 access_sw_pio_drain(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1666 access_sw_ctx0_seq_drop(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1674 access_sw_vtx_wait(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1682 access_sw_kmem_wait(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1690 access_sw_send_schedule(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1700 access_misc_pll_lock_fail_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1709 access_misc_mbist_fail_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1718 access_misc_invalid_eep_cmd_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1727 access_misc_efuse_done_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1736 access_misc_efuse_write_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1745 access_misc_efuse_read_bad_addr_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1754 access_misc_efuse_csr_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1763 access_misc_fw_auth_failed_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1772 access_misc_key_mismatch_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1781 access_misc_sbus_write_failed_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1790 access_misc_csr_write_bad_addr_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1799 access_misc_csr_read_bad_addr_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1808 access_misc_csr_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1821 access_sw_cce_err_status_aggregated_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1834 access_cce_msix_csr_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1843 access_cce_int_map_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1852 access_cce_int_map_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1861 access_cce_msix_table_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1870 access_cce_msix_table_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1879 access_cce_rxdma_conv_fifo_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1888 access_cce_rcpl_async_fifo_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1897 access_cce_seg_write_bad_addr_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1906 access_cce_seg_read_bad_addr_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1915 access_la_triggered_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1923 access_cce_trgt_cpl_timeout_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1932 access_pcic_receive_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1941 access_pcic_transmit_back_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1950 access_pcic_transmit_front_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1959 access_pcic_cpl_dat_q_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1968 access_pcic_cpl_hd_q_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1977 access_pcic_post_dat_q_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1986 access_pcic_post_hd_q_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 1995 access_pcic_retry_sot_mem_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2004 access_pcic_retry_mem_unc_err(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2013 access_pcic_n_post_dat_q_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2022 access_pcic_n_post_h_q_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2031 access_pcic_cpl_dat_q_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2040 access_pcic_cpl_hd_q_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2049 access_pcic_post_dat_q_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2058 access_pcic_post_hd_q_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2067 access_pcic_retry_sot_mem_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2076 access_pcic_retry_mem_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2085 access_cce_cli1_async_fifo_dbg_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2094 access_cce_cli1_async_fifo_rxdma_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2103 access_cce_cli1_async_fifo_sdma_hd_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2112 access_cce_cl1_async_fifo_pio_crdt_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2121 access_cce_cli2_async_fifo_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2130 access_cce_csr_cfg_bus_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2139 access_cce_cli0_async_fifo_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2148 access_cce_rspd_data_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2157 access_cce_trgt_access_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2166 access_cce_trgt_async_fifo_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2175 access_cce_csr_write_bad_addr_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2184 access_cce_csr_read_bad_addr_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2193 access_ccs_csr_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2206 access_rx_csr_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2215 access_rx_csr_write_bad_addr_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2224 access_rx_csr_read_bad_addr_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2233 access_rx_dma_csr_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2242 access_rx_dma_dq_fsm_encoding_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2251 access_rx_dma_eq_fsm_encoding_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2260 access_rx_dma_csr_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2269 access_rx_rbuf_data_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2278 access_rx_rbuf_data_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2287 access_rx_dma_data_fifo_rd_cor_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2296 access_rx_dma_data_fifo_rd_unc_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2305 access_rx_dma_hdr_fifo_rd_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2314 access_rx_dma_hdr_fifo_rd_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2323 access_rx_rbuf_desc_part2_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2332 access_rx_rbuf_desc_part2_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2341 access_rx_rbuf_desc_part1_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2350 access_rx_rbuf_desc_part1_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2359 access_rx_hq_intr_fsm_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2368 access_rx_hq_intr_csr_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2377 access_rx_lookup_csr_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2386 access_rx_lookup_rcv_array_cor_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2395 access_rx_lookup_rcv_array_unc_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2404 access_rx_lookup_des_part2_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2413 access_rx_lookup_des_part1_unc_cor_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2422 access_rx_lookup_des_part1_unc_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2431 access_rx_rbuf_next_free_buf_cor_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2440 access_rx_rbuf_next_free_buf_unc_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2449 access_rbuf_fl_init_wr_addr_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2458 access_rx_rbuf_fl_initdone_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2467 access_rx_rbuf_fl_write_addr_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2476 access_rx_rbuf_fl_rd_addr_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2485 access_rx_rbuf_empty_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2494 access_rx_rbuf_full_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2503 access_rbuf_bad_lookup_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2512 access_rbuf_ctx_id_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2521 access_rbuf_csr_qeopdw_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2530 access_rx_rbuf_csr_q_num_of_pkt_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2539 access_rx_rbuf_csr_q_t1_ptr_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2548 access_rx_rbuf_csr_q_hd_ptr_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2557 access_rx_rbuf_csr_q_vld_bit_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2566 access_rx_rbuf_csr_q_next_buf_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2575 access_rx_rbuf_csr_q_ent_cnt_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2584 access_rx_rbuf_csr_q_head_buf_num_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2593 access_rx_rbuf_block_list_read_cor_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2602 access_rx_rbuf_block_list_read_unc_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2611 access_rx_rbuf_lookup_des_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2620 access_rx_rbuf_lookup_des_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2629 access_rx_rbuf_lookup_des_reg_unc_cor_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2638 access_rx_rbuf_lookup_des_reg_unc_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2647 access_rx_rbuf_free_list_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2656 access_rx_rbuf_free_list_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2665 access_rx_rcv_fsm_encoding_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2674 access_rx_dma_flag_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2683 access_rx_dma_flag_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2692 access_rx_dc_sop_eop_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2701 access_rx_rcv_csr_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2710 access_rx_rcv_qp_map_table_cor_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2719 access_rx_rcv_qp_map_table_unc_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2728 access_rx_rcv_data_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2737 access_rx_rcv_data_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2746 access_rx_rcv_hdr_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2755 access_rx_rcv_hdr_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2764 access_rx_dc_intf_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2773 access_rx_dma_csr_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2786 access_pio_pec_sop_head_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2795 access_pio_pcc_sop_head_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2804 access_pio_last_returned_cnt_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2813 access_pio_current_free_cnt_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2822 access_pio_reserved_31_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2831 access_pio_reserved_30_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2840 access_pio_ppmc_sop_len_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2849 access_pio_ppmc_bqc_mem_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2858 access_pio_vl_fifo_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2867 access_pio_vlf_sop_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2876 access_pio_vlf_v1_len_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2885 access_pio_block_qw_count_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2894 access_pio_write_qw_valid_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2903 access_pio_state_machine_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2912 access_pio_write_data_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2921 access_pio_host_addr_mem_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2930 access_pio_host_addr_mem_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2939 access_pio_pkt_evict_sm_or_arb_sm_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2948 access_pio_init_sm_in_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2957 access_pio_ppmc_pbl_fifo_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2966 access_pio_credit_ret_fifo_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2975 access_pio_v1_len_mem_bank1_cor_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2984 access_pio_v1_len_mem_bank0_cor_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 2993 access_pio_v1_len_mem_bank1_unc_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3002 access_pio_v1_len_mem_bank0_unc_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3011 access_pio_sm_pkt_reset_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3020 access_pio_pkt_evict_fifo_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3029 access_pio_sbrdctrl_crrel_fifo_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3038 access_pio_sbrdctl_crrel_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3047 access_pio_pec_fifo_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3056 access_pio_pcc_fifo_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3065 access_pio_sb_mem_fifo1_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3074 access_pio_sb_mem_fifo0_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3083 access_pio_csr_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3092 access_pio_write_addr_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3101 access_pio_write_bad_ctxt_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3114 access_sdma_pcie_req_tracking_cor_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3123 access_sdma_pcie_req_tracking_unc_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3132 access_sdma_csr_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3141 access_sdma_rpy_tag_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3154 access_tx_read_pio_memory_csr_unc_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3163 access_tx_read_sdma_memory_csr_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3172 access_tx_egress_fifo_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3181 access_tx_read_pio_memory_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3190 access_tx_read_sdma_memory_cor_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3199 access_tx_sb_hdr_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3208 access_tx_credit_overrun_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3217 access_tx_launch_fifo8_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3226 access_tx_launch_fifo7_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3235 access_tx_launch_fifo6_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3244 access_tx_launch_fifo5_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3253 access_tx_launch_fifo4_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3262 access_tx_launch_fifo3_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3271 access_tx_launch_fifo2_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3280 access_tx_launch_fifo1_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3289 access_tx_launch_fifo0_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3298 access_tx_credit_return_vl_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3307 access_tx_hcrc_insertion_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3316 access_tx_egress_fifo_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3325 access_tx_read_pio_memory_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3334 access_tx_read_sdma_memory_unc_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3343 access_tx_sb_hdr_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3352 access_tx_credit_return_partiy_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3361 access_tx_launch_fifo8_unc_or_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3370 access_tx_launch_fifo7_unc_or_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3379 access_tx_launch_fifo6_unc_or_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3388 access_tx_launch_fifo5_unc_or_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3397 access_tx_launch_fifo4_unc_or_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3406 access_tx_launch_fifo3_unc_or_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3415 access_tx_launch_fifo2_unc_or_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3424 access_tx_launch_fifo1_unc_or_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3433 access_tx_launch_fifo0_unc_or_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3442 access_tx_sdma15_disallowed_packet_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3451 access_tx_sdma14_disallowed_packet_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3460 access_tx_sdma13_disallowed_packet_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3469 access_tx_sdma12_disallowed_packet_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3478 access_tx_sdma11_disallowed_packet_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3487 access_tx_sdma10_disallowed_packet_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3496 access_tx_sdma9_disallowed_packet_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3505 access_tx_sdma8_disallowed_packet_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3514 access_tx_sdma7_disallowed_packet_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3523 access_tx_sdma6_disallowed_packet_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3532 access_tx_sdma5_disallowed_packet_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3541 access_tx_sdma4_disallowed_packet_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3550 access_tx_sdma3_disallowed_packet_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3559 access_tx_sdma2_disallowed_packet_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3568 access_tx_sdma1_disallowed_packet_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3577 access_tx_sdma0_disallowed_packet_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3586 access_tx_config_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3595 access_tx_sbrd_ctl_csr_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3604 access_tx_launch_csr_parity_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3613 access_tx_illegal_vl_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3622 access_tx_sbrd_ctl_state_machine_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3631 access_egress_reserved_10_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3640 access_egress_reserved_9_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3649 access_tx_sdma_launch_intf_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3658 access_tx_pio_launch_intf_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3667 access_egress_reserved_6_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3676 access_tx_incorrect_link_state_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3685 access_tx_linkdown_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3694 access_tx_egress_fifi_underrun_or_parity_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3703 access_egress_reserved_2_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3712 access_tx_pkt_integrity_mem_unc_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3721 access_tx_pkt_integrity_mem_cor_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3734 access_send_csr_write_bad_addr_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3743 access_send_csr_read_bad_addr_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3752 access_send_csr_parity_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3765 access_pio_write_out_of_bounds_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3774 access_pio_write_overflow_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3783 access_pio_write_crosses_boundary_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3792 access_pio_disallowed_packet_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3801 access_pio_inconsistent_sop_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3814 access_sdma_header_request_fifo_cor_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3823 access_sdma_header_storage_cor_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3832 access_sdma_packet_tracking_cor_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3841 access_sdma_assembly_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3850 access_sdma_desc_table_cor_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3859 access_sdma_header_request_fifo_unc_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3868 access_sdma_header_storage_unc_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3877 access_sdma_packet_tracking_unc_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3886 access_sdma_assembly_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3895 access_sdma_desc_table_unc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3904 access_sdma_timeout_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3913 access_sdma_header_length_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3922 access_sdma_header_address_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3931 access_sdma_header_select_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3940 access_sdma_reserved_9_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3949 access_sdma_packet_desc_overflow_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3958 access_sdma_length_mismatch_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3967 access_sdma_halt_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3975 access_sdma_mem_read_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3984 access_sdma_first_desc_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 3993 access_sdma_tail_out_of_bounds_err_cnt( const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 4002 access_sdma_too_long_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 4011 access_sdma_gen_mismatch_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 4020 access_sdma_wrong_dw_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 4029 access_dc_rcv_err_cnt(const struct cntr_entry *entry, void *context, int vl, int mode, u64 data) argument 5675 handle_send_egress_err_info(struct hfi1_devdata *dd, int vl) argument 5765 int vl; local 5830 int vl = engine_to_vl(dd, disallowed_pkt_engine(shift)); local 11096 vl_arb_get_cache(struct vl_arb_cache *cache, struct ib_vl_weight_elem *vl) argument 11102 vl_arb_set_cache(struct vl_arb_cache *cache, struct ib_vl_weight_elem *vl) argument 11108 vl_arb_match_cache(struct vl_arb_cache *cache, struct ib_vl_weight_elem *vl) argument 11116 set_vl_weights(struct hfi1_pportdata *ppd, u32 target, u32 size, struct ib_vl_weight_elem *vl) argument 11241 get_vlarb_preempt(struct hfi1_devdata *dd, u32 nelems, struct ib_vl_weight_elem *vl) argument 11323 set_vl_shared(struct hfi1_devdata *dd, int vl, u16 limit) argument 11340 set_vl_dedicated(struct hfi1_devdata *dd, int vl, u16 limit) argument 12340 read_dev_port_cntr(struct hfi1_devdata *dd, struct cntr_entry *entry, u64 *psval, void *context, int vl) argument 12391 write_dev_port_cntr(struct hfi1_devdata *dd, struct cntr_entry *entry, u64 *psval, void *context, int vl, u64 data) argument 12425 read_dev_cntr(struct hfi1_devdata *dd, int index, int vl) argument 12439 write_dev_cntr(struct hfi1_devdata *dd, int index, int vl, u64 data) argument 12453 read_port_cntr(struct hfi1_pportdata *ppd, int index, int vl) argument 12473 write_port_cntr(struct hfi1_pportdata *ppd, int index, int vl, u64 data) argument 12499 int i, j, vl; local 15017 int vl; local 15363 create_pbc(struct hfi1_pportdata *ppd, u64 flags, int srate_mbs, u32 vl, u32 dw_len) argument [all...]
H A D	chip.h	666 u64 create_pbc(struct hfi1_pportdata *ppd, u64 flags, int srate_mbs, u32 vl, 786 u64 read_dev_cntr(struct hfi1_devdata *dd, int index, int vl); 787 u64 write_dev_cntr(struct hfi1_devdata *dd, int index, int vl, u64 data); 788 u64 read_port_cntr(struct hfi1_pportdata *ppd, int index, int vl); 789 u64 write_port_cntr(struct hfi1_pportdata *ppd, int index, int vl, u64 data); 812 static inline int idx_from_vl(int vl) argument 814 return (vl == 15 ? C_VL_15 : vl);
H A D	mad.c	870 pi->vl.cap = ppd->vls_supported; 871 pi->vl.high_limit = cpu_to_be16(ibp->rvp.vl_high_limit); 872 pi->vl.arb_high_cap = (u8)hfi1_get_ib_cfg(ppd, HFI1_IB_CFG_VL_HIGH_CAP); 873 pi->vl.arb_low_cap = (u8)hfi1_get_ib_cfg(ppd, HFI1_IB_CFG_VL_LOW_CAP); 1480 ibp->rvp.vl_high_limit = be16_to_cpu(pi->vl.high_limit) & 0xFF; 1505 "MTU change on vl %d from %d to %d\n", 1519 "MTU change on vl 15 from %d to %d\n", 2588 unsigned long vl; local 2592 for_each_set_bit(vl, &vl_all_mask, BITS_PER_LONG) { 2595 idx_from_vl(vl)); 2650 get_xmit_wait_counters(struct hfi1_pportdata *ppd, u16 link_width, u16 link_speed, int vl) argument 2690 unsigned long vl; local 2891 unsigned long vl; local 2949 unsigned long vl; local 3168 unsigned long vl; local 3440 unsigned long vl; local [all...]
H A D	mad.h	378 struct vl_limit vl[OPA_MAX_VLS]; member in struct:buffer_control 402 u16 link_speed, int vl);
H A D	pio.c	1755 * @vl: this vl 1757 * This function returns a send context based on the selector and a vl. 1761 u32 selector, u8 vl) 1772 if (unlikely(vl >= num_vls)) { 1783 e = m->map[vl & m->mask]; 1803 u8 vl = sc_to_vlt(dd, sc5); local 1805 return pio_select_send_context_vl(dd, selector, vl); 1850 * @vl_scontexts: per vl send context mapping (optional) 1854 * vl_scontexts is used to specify a non-uniform vl/sen 1760 pio_select_send_context_vl(struct hfi1_devdata *dd, u32 selector, u8 vl) argument [all...]
H A D	pio.h	132 * Since the mapping now allows for non-uniform send contexts per vl, the 133 * number of send contexts for a vl is either the vl_scontexts[vl] or 137 * nactual = vl_scontexts ? vl_scontexts[vl] : num_kernel_send_contexts/num_vls 142 * evenly, the extras are added from the last vl downward. 146 * for a particular vl. 194 * struct pio_map_elem - mapping for a vl 196 * @ksc - array of kernel send contexts for this vl 208 * struct pio_vl_map - mapping for a vl 210 * @mask - vl mas [all...]
H A D	qp.c	285 * fields (vl and pmtu) in ah may not be set correctly, 809 u8 sc, vl; local 813 vl = sc_to_vlt(dd, sc); 816 if (vl < PER_VL_SEND_CONTEXTS) 817 mtu = min_t(u32, mtu, dd->vld[vl].mtu);

Completed in 604 milliseconds

1234

Indexes created Sat May 11 20:17:00 MDT 2024