/linux/tools/testing/selftests/arm64/fp/ |
H A D | za-ptrace.c | 122 *supported = (prctl_vl == vl); in ptrace_set_get_vl() 127 za.vl = vl; in ptrace_set_get_vl() 143 ksft_test_result(new_za->vl = prctl_vl, "Set VL %u\n", vl); in ptrace_set_get_vl() 160 write_za.vl = vl; in ptrace_set_no_data() 205 data_size, vl); in ptrace_set_get_data() 213 write_za->vl = vl; in ptrace_set_get_data() 240 "Data match for VL %u\n", vl); in ptrace_set_get_data() 254 unsigned int vq, vl; in do_parent() local 315 vl = sve_vl_from_vq(vq); in do_parent() 322 ptrace_set_no_data(child, vl); in do_parent() [all …]
|
H A D | sve-ptrace.c | 236 sve.vl = vl; in ptrace_set_get_vl() 255 type->name, vl); in ptrace_set_get_vl() 328 unsigned int vl) in ptrace_set_sve_get_sve_data() argument 352 write_sve->vl = vl; in ptrace_set_sve_get_sve_data() 415 type->name, vl); in ptrace_set_sve_get_sve_data() 453 write_sve->vl = vl; in ptrace_set_sve_get_fpsimd_data() 500 type->name, vl); in ptrace_set_sve_get_fpsimd_data() 547 if (read_sve->vl != vl) { in ptrace_set_fpsimd_get_sve_data() 549 read_sve->vl, vl); in ptrace_set_fpsimd_get_sve_data() 609 type->name, vl); in ptrace_set_fpsimd_get_sve_data() [all …]
|
H A D | sve-probe-vls.c | 21 int vl; in main() local 35 vl = prctl(PR_SVE_SET_VL, vq * 16); in main() 36 if (vl == -1) in main() 40 vl &= PR_SVE_VL_LEN_MASK; in main() 42 if (rdvl_sve() != vl) in main() 44 vl, rdvl_sve()); in main() 46 if (!sve_vl_valid(vl)) in main() 47 ksft_exit_fail_msg("VL %d invalid\n", vl); in main() 48 vq = sve_vq_from_vl(vl); in main()
|
H A D | vlset.c | 24 static unsigned long vl; variable 53 case 'M': vl = SVE_VL_MAX; break; in parse_options() 66 if (!vl) { in parse_options() 72 vl = strtoul(argv[optind], &rest, 0); in parse_options() 74 vl = ULONG_MAX; in parse_options() 77 if (vl == ULONG_MAX && errno) { in parse_options() 112 if (vl & ~(vl & PR_SVE_VL_LEN_MASK)) { in main() 114 program_name, vl); in main() 134 t = prctl(set_ctl, vl | flags); in main()
|
H A D | fp-ptrace.c | 177 int vl; in vl_in() local 180 vl = config->sme_vl_in; in vl_in() 182 vl = config->sve_vl_in; in vl_in() 184 return vl; in vl_in() 189 int vl; in vl_expected() local 196 return vl; in vl_expected() 813 if (!vl) in fpsimd_to_sve() 973 int vl; in fpsimd_write_expected() local 1048 sve->vl = vl; in sve_write() 1297 int vl; in probe_vls() local [all …]
|
H A D | fp-stress.c | 339 ret = prctl(PR_SVE_SET_VL, vl | PR_SVE_VL_INHERIT); in start_sve() 341 ksft_exit_fail_msg("Failed to set SVE VL %d\n", vl); in start_sve() 360 ret = prctl(PR_SME_SET_VL, vl | PR_SME_VL_INHERIT); in start_ssve() 373 ret = prctl(PR_SME_SET_VL, vl | PR_SVE_VL_INHERIT); in start_za() 402 int vl; in probe_vls() local 407 vl = prctl(set_vl, vq * 16); in probe_vls() 408 if (vl == -1) in probe_vls() 412 vl &= PR_SVE_VL_LEN_MASK; in probe_vls() 414 if (*vl_count && (vl == vls[*vl_count - 1])) in probe_vls() 417 vq = sve_vq_from_vl(vl); in probe_vls() [all …]
|
/linux/tools/testing/selftests/arm64/signal/testcases/ |
H A D | ssve_za_regs.c | 48 unsigned int vl) in do_one_sme_vl() argument 57 fprintf(stderr, "Testing VL %d\n", vl); in do_one_sme_vl() 59 ret = prctl(PR_SME_SET_VL, vl); in do_one_sme_vl() 60 if (ret != vl) { in do_one_sme_vl() 81 if (ssve->vl != vl) { in do_one_sme_vl() 82 fprintf(stderr, "Got SSVE VL %d, expected %d\n", ssve->vl, vl); in do_one_sme_vl() 92 regs->size, ssve->vl); in do_one_sme_vl() 102 if (za->vl != vl) { in do_one_sme_vl() 103 fprintf(stderr, "Got ZA VL %d, expected %d\n", za->vl, vl); in do_one_sme_vl() 108 regs->size, za->vl); in do_one_sme_vl() [all …]
|
H A D | za_regs.c | 45 unsigned int vl) in do_one_sme_vl() argument 51 fprintf(stderr, "Testing VL %d\n", vl); in do_one_sme_vl() 53 if (prctl(PR_SME_SET_VL, vl) != vl) { in do_one_sme_vl() 73 if (za->vl != vl) { in do_one_sme_vl() 74 fprintf(stderr, "Got VL %d, expected %d\n", za->vl, vl); in do_one_sme_vl() 78 if (head->size != ZA_SIG_CONTEXT_SIZE(sve_vq_from_vl(vl))) { in do_one_sme_vl() 80 head->size, ZA_SIG_CONTEXT_SIZE(sve_vq_from_vl(vl))); in do_one_sme_vl() 85 head->size, za->vl); in do_one_sme_vl() 89 ZA_SIG_REGS_SIZE(sve_vq_from_vl(za->vl))) != 0) { in do_one_sme_vl()
|
H A D | ssve_regs.c | 43 unsigned int vl) in do_one_sme_vl() argument 50 fprintf(stderr, "Testing VL %d\n", vl); in do_one_sme_vl() 52 ret = prctl(PR_SME_SET_VL, vl); in do_one_sme_vl() 53 if (ret != vl) { in do_one_sme_vl() 74 if (ssve->vl != vl) { in do_one_sme_vl() 75 fprintf(stderr, "Got VL %d, expected %d\n", ssve->vl, vl); in do_one_sme_vl() 86 head->size, ssve->vl); in do_one_sme_vl()
|
H A D | za_no_regs.c | 37 unsigned int vl) in do_one_sme_vl() argument 43 fprintf(stderr, "Testing VL %d\n", vl); in do_one_sme_vl() 45 if (prctl(PR_SME_SET_VL, vl) != vl) { in do_one_sme_vl() 64 if (za->vl != vl) { in do_one_sme_vl() 65 fprintf(stderr, "Got VL %d, expected %d\n", za->vl, vl); in do_one_sme_vl() 77 head->size, za->vl); in do_one_sme_vl()
|
H A D | sve_regs.c | 43 unsigned int vl) in do_one_sve_vl() argument 49 fprintf(stderr, "Testing VL %d\n", vl); in do_one_sve_vl() 51 if (prctl(PR_SVE_SET_VL, vl) == -1) { in do_one_sve_vl() 72 if (sve->vl != vl) { in do_one_sve_vl() 73 fprintf(stderr, "Got VL %d, expected %d\n", sve->vl, vl); in do_one_sve_vl() 79 head->size, sve->vl); in do_one_sve_vl()
|
H A D | sme_vl.c | 17 unsigned int vl; variable 25 vl = ret; in get_sme_vl() 48 if (za->vl != vl) { in sme_vl() 50 za->vl, vl); in sme_vl() 53 fprintf(stderr, "got expected VL %u\n", vl); in sme_vl()
|
H A D | sve_vl.c | 17 unsigned int vl; variable 25 vl = ret; in get_sve_vl() 48 if (sve->vl != vl) { in sve_vl() 50 sve->vl, vl); in sve_vl() 53 fprintf(stderr, "got expected VL %u\n", vl); in sve_vl()
|
/linux/drivers/net/dsa/sja1105/ |
H A D | sja1105_vl.c | 110 its_base_time = rule->vl.base_time; in sja1105_compose_gating_subschedule() 137 rbt = future_base_time(rule->vl.base_time, rule->vl.cycle_time, in sja1105_compose_gating_subschedule() 539 rule->vl.destports |= destports; in sja1105_vl_redirect() 541 rule->vl.destports = destports; in sja1105_vl_redirect() 634 rule->vl.sharindx = index; in sja1105_vl_gate() 635 rule->vl.base_time = base_time; in sja1105_vl_gate() 641 if (!rule->vl.entries) { in sja1105_vl_gate() 692 ipv = key->vl.pcp; in sja1105_vl_gate() 699 rule->vl.ipv = ipv; in sja1105_vl_gate() 723 kfree(rule->vl.entries); in sja1105_vl_gate() [all …]
|
/linux/arch/arm64/kernel/ |
H A D | fpsimd.c | 255 unsigned long vl) in task_set_vl() argument 257 task->thread.vl[type] = vl; in task_set_vl() 444 unsigned int vl; in fpsimd_save_user_state() local 526 if (vl > max_vl) in find_supported_vector_length() 527 vl = max_vl; in find_supported_vector_length() 546 .data = &vl, in vec_proc_do_default_vl() 555 if (vl == -1) in vec_proc_do_default_vl() 732 vl = max(vl, task_get_sme_vl(task)); in sve_state_size() 853 vl = find_supported_vector_length(type, vl); in vec_set_vector_length() 1024 vl = 0; in vec_probe_vqs() [all …]
|
/linux/tools/testing/selftests/arm64/signal/ |
H A D | sve_helpers.c | 18 int vq, vl; in sve_fill_vls() local 26 vl = prctl(pr_set_vl, vq * 16); in sve_fill_vls() 27 if (vl == -1) in sve_fill_vls() 30 vl &= len_mask; in sve_fill_vls() 41 if (vq < sve_vq_from_vl(vl)) in sve_fill_vls() 45 vq = sve_vq_from_vl(vl); in sve_fill_vls() 47 vls[nvls++] = vl; in sve_fill_vls()
|
/linux/drivers/ata/pata_parport/ |
H A D | on20.c | 24 #define vl(v) \ macro 43 op(1); vl(r); op(0); in on20_read_regr() 64 op(1); vl(r); in on20_write_regr() 65 op(0); vl(val); in on20_write_regr() 66 op(0); vl(val); in on20_write_regr() 76 op(2); vl(8); op(2); vl(9); in on20_connect() 78 op(2); vl(0); op(2); vl(8); in on20_connect() 93 op(1); vl(1); op(0); in on20_read_block() 111 op(1); vl(1); op(0); in on20_write_block()
|
/linux/tools/testing/selftests/riscv/vector/ |
H A D | v_initval_nolibc.c | 25 unsigned long vl; in main() local 47 : "=&r" (vl), "=r" (tmp) : "r" (datap) : "memory"); in main() 49 ksft_print_msg("vl = %lu\n", vl); in main() 53 dump(datap, vl * 4); in main() 57 for (i = 1; i < vl * 4; i++) { in main() 60 dump(datap, vl * 4); in main()
|
/linux/arch/arm64/include/uapi/asm/ |
H A D | sve_context.h | 36 #define __sve_vl_valid(vl) \ argument 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) argument
|
H A D | sigcontext.h | 147 __u16 vl; member 174 __u16 vl; member 209 #define sve_vl_valid(vl) __sve_vl_valid(vl) argument 210 #define sve_vq_from_vl(vl) __sve_vq_from_vl(vl) argument
|
/linux/drivers/infiniband/hw/hfi1/ |
H A D | chip.c | 1564 else if (vl >= 0 && vl < C_VL_COUNT) in access_sw_xmit_discards() 5676 int vl) in handle_send_egress_err_info() argument 5719 if (vl >= 0 && vl < TXE_NUM_DATA_VL) in handle_send_egress_err_info() 5765 int vl; in engine_to_vl() local 5776 return vl; in engine_to_vl() 11153 reg = (((u64)vl->vl & SEND_LOW_PRIORITY_LIST_VL_MASK) in set_vl_weights() 11247 vl->vl = 0xf; in get_vlarb_preempt() 12547 for (vl = 0; vl < C_VL_COUNT; vl++) in do_update_synth_timer() 12558 for (vl = 0; vl < C_VL_COUNT; vl++) in do_update_synth_timer() 15017 int vl; in hfi1_init_dd() local [all …]
|
/linux/arch/riscv/include/asm/ |
H A D | vector.h | 86 : "=r" (dest->vstart), "=r" (dest->vtype), "=r" (dest->vl), in __vstate_csr_save() 99 : : "r" (src->vstart), "r" (src->vtype), "r" (src->vl), in __vstate_csr_restore() 106 unsigned long vl; in __riscv_v_vstate_save() local 122 : "=&r" (vl) : "r" (datap) : "memory"); in __riscv_v_vstate_save() 129 unsigned long vl; in __riscv_v_vstate_restore() local 144 : "=&r" (vl) : "r" (datap) : "memory"); in __riscv_v_vstate_restore() 151 unsigned long vl, vtype_inval = 1UL << (BITS_PER_LONG - 1); in __riscv_v_vstate_discard() local 164 : "=&r" (vl) : "r" (vtype_inval) : "memory"); in __riscv_v_vstate_discard()
|
/linux/tools/testing/selftests/arm64/abi/ |
H A D | syscall-abi.c | 475 int vl; in sve_count_vls() local 485 if (vl == -1) in sve_count_vls() 489 vl &= PR_SVE_VL_LEN_MASK; in sve_count_vls() 491 if (vq != sve_vq_from_vl(vl)) in sve_count_vls() 492 vq = sve_vq_from_vl(vl); in sve_count_vls() 494 sve_vls[sve_vl_count++] = vl; in sve_count_vls() 501 int vl; in sme_count_vls() local 511 if (vl == -1) in sme_count_vls() 515 vl &= PR_SME_VL_LEN_MASK; in sme_count_vls() 518 if (sve_vq_from_vl(vl) > vq) in sme_count_vls() [all …]
|
/linux/arch/arm64/include/asm/ |
H A D | fpsimd.h | 116 static inline size_t sve_ffr_offset(int vl) in sve_ffr_offset() argument 118 return SVE_SIG_FFR_OFFSET(sve_vq_from_vl(vl)) - SVE_SIG_REGS_OFFSET; in sve_ffr_offset() 123 unsigned int vl; in sve_pffr() local 126 vl = thread_get_sme_vl(thread); in sve_pffr() 128 vl = thread_get_sve_vl(thread); in sve_pffr() 130 return (char *)thread->sve_state + sve_ffr_offset(vl); in sve_pffr() 205 unsigned long vl, unsigned long flags); 396 unsigned int vl = task_get_sme_vl(task); in sme_state_size() local 399 size = ZA_SIG_REGS_SIZE(sve_vq_from_vl(vl)); in sme_state_size()
|
/linux/drivers/net/dsa/ |
H A D | dsa_loop.c | 39 struct dsa_loop_vlan *vl; in dsa_loop_devlink_vtu_get() local 42 vl = &ps->vlans[i]; in dsa_loop_devlink_vtu_get() 43 if (vl->members) in dsa_loop_devlink_vtu_get() 212 struct dsa_loop_vlan *vl; in dsa_loop_port_vlan_add() local 220 vl = &ps->vlans[vlan->vid]; in dsa_loop_port_vlan_add() 222 vl->members |= BIT(port); in dsa_loop_port_vlan_add() 224 vl->untagged |= BIT(port); in dsa_loop_port_vlan_add() 226 vl->untagged &= ~BIT(port); in dsa_loop_port_vlan_add() 244 struct dsa_loop_vlan *vl; in dsa_loop_port_vlan_del() local 249 vl = &ps->vlans[vlan->vid]; in dsa_loop_port_vlan_del() [all …]
|