| /Linux-v6.6/tools/testing/selftests/arm64/signal/testcases/ |
| D | ssve_za_regs.c | 25 int vq, vl; in sme_get_vls() local
31 vl = prctl(PR_SME_SET_VL, vq * 16); in sme_get_vls()
32 if (vl == -1) in sme_get_vls()
35 vl &= PR_SME_VL_LEN_MASK; in sme_get_vls()
38 if (vq < sve_vq_from_vl(vl)) in sme_get_vls()
42 vq = sve_vq_from_vl(vl); in sme_get_vls()
44 vls[nvls++] = vl; in sme_get_vls()
68 unsigned int vl) in do_one_sme_vl() argument
77 fprintf(stderr, "Testing VL %d\n", vl); in do_one_sme_vl()
79 ret = prctl(PR_SME_SET_VL, vl); in do_one_sme_vl()
[all …]
|
| D | za_regs.c | 25 int vq, vl; in sme_get_vls() local
31 vl = prctl(PR_SME_SET_VL, vq * 16); in sme_get_vls()
32 if (vl == -1) in sme_get_vls()
35 vl &= PR_SME_VL_LEN_MASK; in sme_get_vls()
38 if (vq < sve_vq_from_vl(vl)) in sme_get_vls()
42 vq = sve_vq_from_vl(vl); in sme_get_vls()
44 vls[nvls++] = vl; in sme_get_vls()
65 unsigned int vl) in do_one_sme_vl() argument
71 fprintf(stderr, "Testing VL %d\n", vl); in do_one_sme_vl()
73 if (prctl(PR_SME_SET_VL, vl) != vl) { in do_one_sme_vl()
[all …]
|
| D | ssve_regs.c | 25 int vq, vl; in sme_get_vls() local
31 vl = prctl(PR_SME_SET_VL, vq * 16); in sme_get_vls()
32 if (vl == -1) in sme_get_vls()
35 vl &= PR_SME_VL_LEN_MASK; in sme_get_vls()
38 if (vq < sve_vq_from_vl(vl)) in sme_get_vls()
42 vq = sve_vq_from_vl(vl); in sme_get_vls()
44 vls[nvls++] = vl; in sme_get_vls()
63 unsigned int vl) in do_one_sme_vl() argument
70 fprintf(stderr, "Testing VL %d\n", vl); in do_one_sme_vl()
72 ret = prctl(PR_SME_SET_VL, vl); in do_one_sme_vl()
[all …]
|
| D | za_no_regs.c | 25 int vq, vl; in sme_get_vls() local
31 vl = prctl(PR_SME_SET_VL, vq * 16); in sme_get_vls()
32 if (vl == -1) in sme_get_vls()
35 vl &= PR_SME_VL_LEN_MASK; in sme_get_vls()
38 vq = sve_vq_from_vl(vl); in sme_get_vls()
40 vls[nvls++] = vl; in sme_get_vls()
53 unsigned int vl) in do_one_sme_vl() argument
59 fprintf(stderr, "Testing VL %d\n", vl); in do_one_sme_vl()
61 if (prctl(PR_SME_SET_VL, vl) != vl) { in do_one_sme_vl()
80 if (za->vl != vl) { in do_one_sme_vl()
[all …]
|
| D | sve_regs.c | 25 int vq, vl; in sve_get_vls() local
31 vl = prctl(PR_SVE_SET_VL, vq * 16); in sve_get_vls()
32 if (vl == -1) in sve_get_vls()
35 vl &= PR_SVE_VL_LEN_MASK; in sve_get_vls()
38 vq = sve_vq_from_vl(vl); in sve_get_vls()
40 vls[nvls++] = vl; in sve_get_vls()
59 unsigned int vl) in do_one_sve_vl() argument
65 fprintf(stderr, "Testing VL %d\n", vl); in do_one_sve_vl()
67 if (prctl(PR_SVE_SET_VL, vl) == -1) { in do_one_sve_vl()
88 if (sve->vl != vl) { in do_one_sve_vl()
[all …]
|
| D | fake_sigreturn_sme_change_vl.c | 22 int vq, vl; in sme_get_vls() local
28 vl = prctl(PR_SVE_SET_VL, vq * 16); in sme_get_vls()
29 if (vl == -1) in sme_get_vls()
32 vl &= PR_SME_VL_LEN_MASK; in sme_get_vls()
35 vq = sve_vq_from_vl(vl); in sme_get_vls()
37 vls[nvls++] = vl; in sme_get_vls()
76 sve->vl, vls[0]); in fake_sigreturn_ssve_change_vl()
77 sve->vl = vls[0]; in fake_sigreturn_ssve_change_vl()
|
| D | fake_sigreturn_sve_change_vl.c | 23 int vq, vl; in sve_get_vls() local
29 vl = prctl(PR_SVE_SET_VL, vq * 16); in sve_get_vls()
30 if (vl == -1) in sve_get_vls()
33 vl &= PR_SVE_VL_LEN_MASK; in sve_get_vls()
36 vq = sve_vq_from_vl(vl); in sve_get_vls()
38 vls[nvls++] = vl; in sve_get_vls()
78 sve->vl, vls[0]); in fake_sigreturn_sve_change_vl()
79 sve->vl = vls[0]; in fake_sigreturn_sve_change_vl()
|
| 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()
|
| 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-v6.6/tools/testing/selftests/arm64/fp/ |
| D | za-ptrace.c | 106 static void ptrace_set_get_vl(pid_t child, unsigned int vl, bool *supported) in ptrace_set_get_vl() argument
116 prctl_vl = prctl(PR_SME_SET_VL, vl); in ptrace_set_get_vl()
122 *supported = (prctl_vl == vl); in ptrace_set_get_vl()
127 za.vl = vl; in ptrace_set_get_vl()
130 ksft_test_result_fail("Failed to set VL %u\n", vl); in ptrace_set_get_vl()
139 ksft_test_result_fail("Failed to read VL %u\n", 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()
149 static void ptrace_set_no_data(pid_t child, unsigned int vl) in ptrace_set_no_data() argument
160 write_za.vl = vl; in ptrace_set_no_data()
164 ksft_test_result_fail("Failed to set VL %u no data\n", vl); in ptrace_set_no_data()
[all …]
|
| D | sve-ptrace.c | 170 sve.vl = sve_vl_from_vq(SVE_VQ_MIN); in ptrace_set_get_inherit()
215 unsigned int vl, bool *supported) in ptrace_set_get_vl() argument
225 prctl_vl = prctl(type->prctl_set, vl); in ptrace_set_get_vl()
231 *supported = (prctl_vl == vl); in ptrace_set_get_vl()
236 sve.vl = vl; in ptrace_set_get_vl()
240 type->name, vl); in ptrace_set_get_vl()
250 type->name, vl); in ptrace_set_get_vl()
254 ksft_test_result(new_sve->vl = prctl_vl, "Set %s VL %u\n", in ptrace_set_get_vl()
255 type->name, vl); in ptrace_set_get_vl()
260 static void check_u32(unsigned int vl, const char *reg, in check_u32() argument
[all …]
|
| 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()
|
| 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()
|
| D | fp-stress.c | 322 static void start_sve(struct child_data *child, int vl, int cpu) in start_sve() argument
326 ret = prctl(PR_SVE_SET_VL, vl | PR_SVE_VL_INHERIT); in start_sve()
328 ksft_exit_fail_msg("Failed to set SVE VL %d\n", vl); in start_sve()
330 ret = asprintf(&child->name, "SVE-VL-%d-%d", vl, cpu); in start_sve()
339 static void start_ssve(struct child_data *child, int vl, int cpu) in start_ssve() argument
343 ret = asprintf(&child->name, "SSVE-VL-%d-%d", vl, cpu); in start_ssve()
347 ret = prctl(PR_SME_SET_VL, vl | PR_SME_VL_INHERIT); in start_ssve()
356 static void start_za(struct child_data *child, int vl, int cpu) in start_za() argument
360 ret = prctl(PR_SME_SET_VL, vl | PR_SVE_VL_INHERIT); in start_za()
364 ret = asprintf(&child->name, "ZA-VL-%d-%d", vl, cpu); in start_za()
[all …]
|
| /Linux-v6.6/drivers/net/dsa/sja1105/ |
| D | sja1105_vl.c | 105 if (rule->vl.type != SJA1105_VL_TIME_TRIGGERED) in sja1105_compose_gating_subschedule()
108 if (max_cycle_time < rule->vl.cycle_time) { in sja1105_compose_gating_subschedule()
109 max_cycle_time = rule->vl.cycle_time; in sja1105_compose_gating_subschedule()
110 its_base_time = rule->vl.base_time; in sja1105_compose_gating_subschedule()
130 if (rule->vl.type != SJA1105_VL_TIME_TRIGGERED) in sja1105_compose_gating_subschedule()
137 rbt = future_base_time(rule->vl.base_time, rule->vl.cycle_time, in sja1105_compose_gating_subschedule()
143 for (i = 0; i < rule->vl.num_entries; i++) { in sja1105_compose_gating_subschedule()
144 u8 gate_state = rule->vl.entries[i].gate_state; in sja1105_compose_gating_subschedule()
155 entry_time += rule->vl.cycle_time; in sja1105_compose_gating_subschedule()
157 time += rule->vl.entries[i].interval; in sja1105_compose_gating_subschedule()
[all …]
|
| /Linux-v6.6/arch/arm64/kernel/ |
| D | fpsimd.c | 278 return task->thread.vl[type]; in task_get_vl()
282 unsigned long vl) in task_set_vl() argument
284 task->thread.vl[type] = vl; in task_set_vl()
294 unsigned long vl) in task_set_vl_onexec() argument
296 task->thread.vl_onexec[type] = vl; in task_set_vl_onexec()
467 unsigned int vl; in fpsimd_save() local
485 vl = last->sve_vl; in fpsimd_save()
501 vl = last->sme_vl; in fpsimd_save()
507 if (WARN_ON(sve_get_vl() != vl)) { in fpsimd_save()
518 sve_ffr_offset(vl), in fpsimd_save()
[all …]
|
| /Linux-v6.6/drivers/ata/pata_parport/ |
| 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-v6.6/tools/testing/selftests/riscv/vector/ |
| 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-v6.6/drivers/infiniband/hw/hfi1/ |
| D | chip.c | 1178 u64 (*rw_cntr)(const struct cntr_entry *, void *context, int vl,
1371 void *context, int vl, int mode, u64 data) in dev_access_u32_csr() argument
1377 if (vl == CNTR_INVALID_VL) in dev_access_u32_csr()
1379 csr += 0x100 * vl; in dev_access_u32_csr()
1381 if (vl != CNTR_INVALID_VL) in dev_access_u32_csr()
1429 int vl, int mode, u64 data) in dev_access_u64_csr() argument
1437 if (vl == CNTR_INVALID_VL) in dev_access_u64_csr()
1439 csr += 8 * vl; in dev_access_u64_csr()
1441 if (vl != CNTR_INVALID_VL) in dev_access_u64_csr()
1450 int vl, int mode, u64 data) in dc_access_lcb_cntr() argument
[all …]
|
| /Linux-v6.6/arch/arm64/include/uapi/asm/ |
| D | sve_context.h | 25 #define __sve_vl_valid(vl) \ argument
26 ((vl) % __SVE_VQ_BYTES == 0 && \
27 (vl) >= __SVE_VL_MIN && \
28 (vl) <= __SVE_VL_MAX)
30 #define __sve_vq_from_vl(vl) ((vl) / __SVE_VQ_BYTES) argument
|
| D | sigcontext.h | 140 __u16 vl; member
159 __u16 vl; member
194 #define sve_vl_valid(vl) __sve_vl_valid(vl) argument
195 #define sve_vq_from_vl(vl) __sve_vq_from_vl(vl) argument
|
| /Linux-v6.6/arch/riscv/include/asm/ |
| D | vector.h | 74 : "=r" (dest->vstart), "=r" (dest->vtype), "=r" (dest->vl), in __vstate_csr_save()
87 : : "r" (src->vstart), "r" (src->vtype), "r" (src->vl), in __vstate_csr_restore()
94 unsigned long vl; in __riscv_v_vstate_save() local
110 : "=&r" (vl) : "r" (datap) : "memory"); in __riscv_v_vstate_save()
117 unsigned long vl; in __riscv_v_vstate_restore() local
132 : "=&r" (vl) : "r" (datap) : "memory"); in __riscv_v_vstate_restore()
139 unsigned long vl, vtype_inval = 1UL << (BITS_PER_LONG - 1); in __riscv_v_vstate_discard() local
152 : "=&r" (vl) : "r" (vtype_inval) : "memory"); in __riscv_v_vstate_discard()
|
| /Linux-v6.6/tools/testing/selftests/arm64/abi/ |
| D | syscall-abi.c | 475 int vl; in sve_count_vls() local
484 vl = prctl(PR_SVE_SET_VL, vq * 16); in sve_count_vls()
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
510 vl = prctl(PR_SME_SET_VL, vq * 16); in sme_count_vls()
511 if (vl == -1) in sme_count_vls()
[all …]
|
| /Linux-v6.6/arch/arm64/include/asm/ |
| D | fpsimd.h | 91 static inline size_t sve_ffr_offset(int vl) in sve_ffr_offset() argument
93 return SVE_SIG_FFR_OFFSET(sve_vq_from_vl(vl)) - SVE_SIG_REGS_OFFSET; in sve_ffr_offset()
98 unsigned int vl; in sve_pffr() local
101 vl = thread_get_sme_vl(thread); in sve_pffr()
103 vl = thread_get_sve_vl(thread); in sve_pffr()
105 return (char *)thread->sve_state + sve_ffr_offset(vl); in sve_pffr()
181 unsigned long vl, unsigned long flags);
371 unsigned int vl = task_get_sme_vl(task); in sme_state_size() local
374 size = ZA_SIG_REGS_SIZE(sve_vq_from_vl(vl)); in sme_state_size()
|
| /Linux-v6.6/drivers/net/dsa/ |
| 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 …]
|
