Home
last modified time | relevance | path

Searched refs:vl (Results 1 – 25 of 64) sorted by relevance

123

/linux/tools/testing/selftests/arm64/fp/
H A Dza-ptrace.c108 static void ptrace_set_get_vl(pid_t child, unsigned int vl, bool *supported) in ptrace_set_get_vl() argument
118 prctl_vl = prctl(PR_SME_SET_VL, vl); in ptrace_set_get_vl()
124 *supported = (prctl_vl == vl); in ptrace_set_get_vl()
129 za.vl = vl; in ptrace_set_get_vl()
132 ksft_test_result_fail("Failed to set VL %u\n", vl); in ptrace_set_get_vl()
141 ksft_test_result_fail("Failed to read VL %u\n", vl); in ptrace_set_get_vl()
145 ksft_test_result(new_za->vl = prctl_vl, "Set VL %u\n", vl); in ptrace_set_get_vl()
151 static void ptrace_set_no_data(pid_t child, unsigned int vl) in ptrace_set_no_data() argument
162 write_za.vl = vl; in ptrace_set_no_data()
166 ksft_test_result_fail("Failed to set VL %u no data\n", vl); in ptrace_set_no_data()
[all …]
H A Dsve-ptrace.c202 sve.vl = SVE_VL_MIN; in write_fails()
220 sve.vl = sve_vl_from_vq(SVE_VQ_MIN); in ptrace_set_get_inherit()
265 unsigned int vl, bool *supported) in ptrace_set_get_vl() argument
275 prctl_vl = prctl(type->prctl_set, vl); in ptrace_set_get_vl()
281 *supported = (prctl_vl == vl); in ptrace_set_get_vl()
287 sve.vl = vl; in ptrace_set_get_vl()
291 type->name, vl); in ptrace_set_get_vl()
301 type->name, vl); in ptrace_set_get_vl()
305 ksft_test_result(new_sve->vl == prctl_vl, "Set %s VL %u\n", in ptrace_set_get_vl()
306 type->name, vl); in ptrace_set_get_vl()
[all …]
H A Dsve-probe-vls.c21 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 Dvlset.c24 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 Dfp-ptrace.c220 int vl; in vl_expected()
223 vl = config->sme_vl_in; in vl_expected()
225 vl = config->sve_vl_in; in run_child()
227 return vl; in run_child()
232 int vl; in run_child()
235 vl = config->sme_vl_expected; in run_child()
237 vl = config->sve_vl_expected; in run_child()
239 return vl; in run_child()
450 if (sve->vl != config->sve_vl_in) { in check_ptrace_values_sve()
452 sve->vl, confi in check_ptrace_values_sve()
203 int vl; vl_in() local
215 int vl; vl_expected() local
889 fpsimd_to_sve(__uint128_t * v,char * z,int vl) fpsimd_to_sve() argument
1091 int vl; fpsimd_write_expected() local
1154 int vl = vl_expected(config); sve_write_expected() local
1182 int ret, vl, vq, regset; sve_write_sve() local
1229 int ret, vl, vq; sve_write_fpsimd() local
1484 int vl; probe_vls() local
[all...]
H A Dfp-stress.c337 static void start_sve(struct child_data *child, int vl, int cpu) in start_sve() argument
341 ret = prctl(PR_SVE_SET_VL, vl | PR_SVE_VL_INHERIT); in start_sve()
343 ksft_exit_fail_msg("Failed to set SVE VL %d\n", vl); in start_sve()
345 ret = asprintf(&child->name, "SVE-VL-%d-%d", vl, cpu); in start_sve()
354 static void start_ssve(struct child_data *child, int vl, int cpu) in start_ssve() argument
358 ret = asprintf(&child->name, "SSVE-VL-%d-%d", vl, cpu); in start_ssve()
362 ret = prctl(PR_SME_SET_VL, vl | PR_SME_VL_INHERIT); in start_ssve()
371 static void start_za(struct child_data *child, int vl, int cpu) in start_za() argument
375 ret = prctl(PR_SME_SET_VL, vl | PR_SVE_VL_INHERIT); in start_za()
379 ret = asprintf(&child->name, "ZA-VL-%d-%d", vl, cpu); in start_za()
[all …]
H A Dvec-syscfg.c562 int ret, vq, vl, new_vl, i; in prctl_set_all_vqs() local
579 vl = sve_vl_from_vq(vq); in prctl_set_all_vqs()
582 ret = prctl(data->prctl_set, vl); in prctl_set_all_vqs()
586 data->name, vl, in prctl_set_all_vqs()
617 if (new_vl == vl) in prctl_set_all_vqs()
621 if (vl < data->min_vl) { in prctl_set_all_vqs()
624 data->name, vl, new_vl, in prctl_set_all_vqs()
633 if (vl > data->max_vl) { in prctl_set_all_vqs()
636 data->name, vl, new_vl, in prctl_set_all_vqs()
645 if (!(new_vl < vl)) { in prctl_set_all_vqs()
[all …]
/linux/tools/testing/selftests/arm64/signal/testcases/
H A Dssve_za_regs.c48 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 Dza_regs.c45 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 Dza_no_regs.c37 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 Dssve_regs.c43 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 Dsve_regs.c43 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 Dsve_vl.c17 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()
H A Dsme_vl.c17 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()
/linux/tools/testing/selftests/riscv/vector/
H A Dvalidate_v_ptrace.c89 static volatile unsigned long vl; in TEST() local
115 : [vtype] "=r"(vtype), [vstart] "=r"(vstart), [vl] "=r"(vl) in TEST()
176 vl_csr = ptrace(PTRACE_PEEKDATA, pid, &vl, NULL); in TEST()
207 EXPECT_EQ(vl_csr, regset_data->vl); in TEST()
228 unsigned long vl; in TEST() local
239 : [new_vl] "=r" (vl) : : "t4"); in TEST()
246 : [new_vl] "=r"(vl) : : ); in TEST()
300 EXPECT_EQ(regset_data->vlenb, regset_data->vl); in TEST()
331 EXPECT_EQ(0UL, regset_data->vl); in TEST()
361 unsigned long vl; in FIXTURE_VARIANT() local
[all …]
H A Dv_exec_initval_nolibc.c18 unsigned long vl; in main() local
26 : [vl] "=r" (vl) : : "t4" in main()
34 : [vl] "=r" (vl) in main()
38 for (int i = 0; i < vl; i++) { \ in main()
/linux/arch/arm64/kernel/
H A Dfpsimd.c259 return task->thread.vl[type]; in task_get_vl()
263 unsigned long vl) in task_set_vl() argument
265 task->thread.vl[type] = vl; in task_set_vl()
275 unsigned long vl) in task_set_vl_onexec() argument
277 task->thread.vl_onexec[type] = vl; in task_set_vl_onexec()
453 unsigned int vl; in fpsimd_save_user_state() local
477 vl = last->sve_vl; in fpsimd_save_user_state()
493 vl = last->sme_vl; in fpsimd_save_user_state()
499 if (WARN_ON(sve_get_vl() != vl)) { in fpsimd_save_user_state()
525 unsigned int vl) in find_supported_vector_length() argument
[all …]
/linux/tools/testing/selftests/arm64/signal/
H A Dsve_helpers.c18 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 Don20.c24 #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/lib/raid/raid6/riscv/
H A Drvv.c23 unsigned long vl, d, nsize; in raid6_rvv1_gen_syndrome_real() local
34 : "=&r" (vl) in raid6_rvv1_gen_syndrome_real()
37 nsize = vl; in raid6_rvv1_gen_syndrome_real()
98 unsigned long vl, d, nsize; in raid6_rvv1_xor_syndrome_real() local
109 : "=&r" (vl) in raid6_rvv1_xor_syndrome_real()
112 nsize = vl; in raid6_rvv1_xor_syndrome_real()
198 unsigned long vl, d, nsize; in raid6_rvv2_gen_syndrome_real() local
209 : "=&r" (vl) in raid6_rvv2_gen_syndrome_real()
212 nsize = vl; in raid6_rvv2_gen_syndrome_real()
292 unsigned long vl, d, nsize; in raid6_rvv2_xor_syndrome_real() local
[all …]
/linux/arch/arm64/include/uapi/asm/
H A Dsve_context.h36 #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
/linux/lib/crc/x86/
H A Dcrc-pclmul-template.S90 .macro _load_data vl, src, bswap_mask, dst
91 .if \vl < 64
101 .macro _prepare_v0 vl, v0, v1, bswap_mask
103 .if \vl < 64
109 _load_data \vl, (BUF), \bswap_mask, \v1
110 .if \vl < 64
154 .macro _fold_vec_mem vl, acc, data, consts, bswap_mask, tmp1, tmp2
156 _load_data \vl, \data, \bswap_mask, \tmp1
174 .macro _fold_vec_final vl, v0, v1, consts, bswap_mask, tmp1, tmp2
176 test $\vl, LEN8
[all …]
/linux/tools/testing/selftests/arm64/abi/
H A Dsyscall-abi.c475 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/arch/riscv/include/asm/
H A Dvector.h135 : "=r" (dest->vstart), "=r" (dest->vtype), "=r" (dest->vl), in __vstate_csr_save()
175 : : "r" (src->vstart), "r" (src->vtype), "r" (src->vl)); in __vstate_csr_restore()
199 unsigned long vl; in __riscv_v_vstate_save() local
228 : "=&r" (vl) : "r" (datap) : "memory"); in __riscv_v_vstate_save()
236 unsigned long vl; in __riscv_v_vstate_restore() local
264 : "=&r" (vl) : "r" (datap) : "memory"); in __riscv_v_vstate_restore()
272 unsigned long vl, vtype_inval = 1UL << (BITS_PER_LONG - 1); in __riscv_v_vstate_discard() local
282 ".option pop\n\t": "=&r" (vl)); in __riscv_v_vstate_discard()
293 : "=&r" (vl) : "r" (vtype_inval)); in __riscv_v_vstate_discard()
/linux/sound/usb/6fire/
H A Dcomm.c59 u8 reg, u8 vl, u8 vh) in usb6fire_comm_init_buffer()
68 buffer[5] = vl; in usb6fire_comm_init_buffer()
82 buffer[12] = vl; in usb6fire_comm_init_buffer()
90 buffer[5] = vl; in usb6fire_comm_init_buffer()
128 u8 reg, u8 vl, u8 vh) in usb6fire_comm_write16()
138 usb6fire_comm_init_buffer(buffer, 0x00, request, reg, vl, vh); in usb6fire_comm_write16()
56 usb6fire_comm_init_buffer(u8 * buffer,u8 id,u8 request,u8 reg,u8 vl,u8 vh) usb6fire_comm_init_buffer() argument
125 usb6fire_comm_write16(struct comm_runtime * rt,u8 request,u8 reg,u8 vl,u8 vh) usb6fire_comm_write16() argument

123