Home
last modified time | relevance | path

Searched refs:vector (Results 1 – 25 of 201) sorted by relevance

123456789

/arch/x86/kernel/apic/
A Dlocal.h20 void x2apic_send_IPI_all(int vector);
21 void x2apic_send_IPI_allbutself(int vector);
22 void x2apic_send_IPI_self(int vector);
29 static inline unsigned int __prepare_ICR(unsigned int shortcut, int vector, in __prepare_ICR() argument
34 switch (vector) { in __prepare_ICR()
36 icr |= APIC_DM_FIXED | vector; in __prepare_ICR()
56 void default_send_IPI_single(int cpu, int vector);
57 void default_send_IPI_single_phys(int cpu, int vector);
60 void default_send_IPI_allbutself(int vector);
61 void default_send_IPI_all(int vector);
[all …]
A Dipi.c58 __apic_send_IPI_allbutself(vector); in apic_send_IPI_allbutself()
161 if (unlikely(vector == NMI_VECTOR)) in __default_send_IPI_shortcut()
178 if (unlikely(vector == NMI_VECTOR)) in __default_send_IPI_dest_field()
195 vector, APIC_DEST_PHYSICAL); in default_send_IPI_single_phys()
207 cpu), vector, APIC_DEST_PHYSICAL); in default_send_IPI_mask_sequence_phys()
213 int vector) in default_send_IPI_mask_allbutself_phys() argument
223 cpu), vector, APIC_DEST_PHYSICAL); in default_send_IPI_mask_allbutself_phys()
236 void default_send_IPI_allbutself(int vector) in default_send_IPI_allbutself() argument
241 void default_send_IPI_all(int vector) in default_send_IPI_all() argument
246 void default_send_IPI_self(int vector) in default_send_IPI_self() argument
[all …]
A Dx2apic_phys.c44 static void x2apic_send_IPI(int cpu, int vector) in x2apic_send_IPI() argument
70 vector, APIC_DEST_PHYSICAL); in __x2apic_send_IPI_mask()
77 __x2apic_send_IPI_mask(mask, vector, APIC_DEST_ALLINC); in x2apic_send_IPI_mask()
88 unsigned long cfg = __prepare_ICR(which, vector, 0); in __x2apic_send_IPI_shorthand()
95 void x2apic_send_IPI_allbutself(int vector) in x2apic_send_IPI_allbutself() argument
97 __x2apic_send_IPI_shorthand(vector, APIC_DEST_ALLBUT); in x2apic_send_IPI_allbutself()
100 void x2apic_send_IPI_all(int vector) in x2apic_send_IPI_all() argument
102 __x2apic_send_IPI_shorthand(vector, APIC_DEST_ALLINC); in x2apic_send_IPI_all()
105 void x2apic_send_IPI_self(int vector) in x2apic_send_IPI_self() argument
107 apic_write(APIC_SELF_IPI, vector); in x2apic_send_IPI_self()
[all …]
A Dvector.c135 apicd->hw_irq_cfg.vector = vector; in apic_update_irq_cfg()
239 int vector = apicd->vector; in assign_vector_locked() local
261 trace_vector_alloc(irqd->irq, vector, resvd, vector); in assign_vector_locked()
262 if (vector < 0) in assign_vector_locked()
263 return vector; in assign_vector_locked()
337 trace_vector_alloc_managed(irqd->irq, vector, vector); in assign_managed_vector()
338 if (vector < 0) in assign_managed_vector()
349 unsigned int vector = apicd->vector; in clear_irq_vector() local
353 if (!vector) in clear_irq_vector()
365 if (!vector) in clear_irq_vector()
[all …]
A Dapic_numachip.c82 __default_send_IPI_dest_field(apicid, vector, in numachip_send_IPI_one()
91 numachip_apic_icr_write(apicid, dmode | vector); in numachip_send_IPI_one()
99 numachip_send_IPI_one(cpu, vector); in numachip_send_IPI_mask()
103 int vector) in numachip_send_IPI_mask_allbutself() argument
110 numachip_send_IPI_one(cpu, vector); in numachip_send_IPI_mask_allbutself()
114 static void numachip_send_IPI_allbutself(int vector) in numachip_send_IPI_allbutself() argument
121 numachip_send_IPI_one(cpu, vector); in numachip_send_IPI_allbutself()
125 static void numachip_send_IPI_all(int vector) in numachip_send_IPI_all() argument
127 numachip_send_IPI_mask(cpu_online_mask, vector); in numachip_send_IPI_all()
130 static void numachip_send_IPI_self(int vector) in numachip_send_IPI_self() argument
[all …]
A Dapic_noop.c23 static void noop_send_IPI(int cpu, int vector) { } in noop_send_IPI() argument
24 static void noop_send_IPI_mask(const struct cpumask *cpumask, int vector) { } in noop_send_IPI_mask() argument
25 static void noop_send_IPI_mask_allbutself(const struct cpumask *cpumask, int vector) { } in noop_send_IPI_mask_allbutself() argument
26 static void noop_send_IPI_allbutself(int vector) { } in noop_send_IPI_allbutself() argument
27 static void noop_send_IPI_all(int vector) { } in noop_send_IPI_all() argument
28 static void noop_send_IPI_self(int vector) { } in noop_send_IPI_self() argument
A Dx2apic_cluster.c29 static void x2apic_send_IPI(int cpu, int vector) in x2apic_send_IPI() argument
35 __x2apic_send_IPI_dest(dest, vector, APIC_DEST_LOGICAL); in x2apic_send_IPI()
39 __x2apic_send_IPI_mask(const struct cpumask *mask, int vector, int apic_dest) in __x2apic_send_IPI_mask() argument
67 __x2apic_send_IPI_dest(dest, vector, APIC_DEST_LOGICAL); in __x2apic_send_IPI_mask()
75 static void x2apic_send_IPI_mask(const struct cpumask *mask, int vector) in x2apic_send_IPI_mask() argument
77 __x2apic_send_IPI_mask(mask, vector, APIC_DEST_ALLINC); in x2apic_send_IPI_mask()
81 x2apic_send_IPI_mask_allbutself(const struct cpumask *mask, int vector) in x2apic_send_IPI_mask_allbutself() argument
83 __x2apic_send_IPI_mask(mask, vector, APIC_DEST_ALLBUT); in x2apic_send_IPI_mask_allbutself()
/arch/x86/hyperv/
A Dhv_apic.c124 ipi_arg->vector = vector; in __send_ipi_mask_ex()
189 if (vector < HV_IPI_LOW_VECTOR || vector > HV_IPI_HIGH_VECTOR) in __send_ipi_mask()
205 ipi_arg.vector = vector; in __send_ipi_mask()
238 trace_hyperv_send_ipi_one(cpu, vector); in __send_ipi_one()
249 if (vector < HV_IPI_LOW_VECTOR || vector > HV_IPI_HIGH_VECTOR) in __send_ipi_one()
261 if (!__send_ipi_one(cpu, vector)) in hv_send_ipi()
262 orig_apic.send_IPI(cpu, vector); in hv_send_ipi()
268 orig_apic.send_IPI_mask(mask, vector); in hv_send_ipi_mask()
282 static void hv_send_ipi_all(int vector) in hv_send_ipi_all() argument
285 orig_apic.send_IPI_all(vector); in hv_send_ipi_all()
[all …]
/arch/x86/include/asm/
A Didtentry.h125 DECLARE_IDTENTRY(vector, func)
237 DECLARE_IDTENTRY(vector, func)
327 DECLARE_IDTENTRY(vector, func)
492 DECLARE_IDTENTRY(vector, func)
499 idtentry_irq vector func
503 DECLARE_IDTENTRY(vector, func)
557 .byte 0x6a, vector
561 vector = vector+1
568 vector=FIRST_SYSTEM_VECTOR
573 .byte 0x6a, vector
[all …]
A Dapic.h285 void (*send_IPI)(int cpu, int vector);
288 void (*send_IPI_allbutself)(int vector);
289 void (*send_IPI_all)(int vector);
290 void (*send_IPI_self)(int vector);
328 void (*send_IPI)(int cpu, int vector);
331 void (*send_IPI_allbutself)(int vector);
332 void (*send_IPI_all)(int vector);
333 void (*send_IPI_self)(int vector);
430 static_call(apic_call_send_IPI)(cpu, vector); in __apic_send_IPI()
450 static_call(apic_call_send_IPI_all)(vector); in __apic_send_IPI_all()
[all …]
A Dposted_intr.h108 static inline bool pi_test_and_set_pir(int vector, struct pi_desc *pi_desc) in pi_test_and_set_pir() argument
110 return test_and_set_bit(vector, pi_desc->pir); in pi_test_and_set_pir()
148 static inline bool pi_test_pir(int vector, struct pi_desc *pi_desc) in pi_test_pir() argument
150 return test_bit(vector, (unsigned long *)pi_desc->pir); in pi_test_pir()
170 static inline bool pi_pending_this_cpu(unsigned int vector) in pi_pending_this_cpu() argument
174 if (WARN_ON_ONCE(vector > NR_VECTORS || vector < FIRST_EXTERNAL_VECTOR)) in pi_pending_this_cpu()
177 return test_bit(vector, pid->pir); in pi_pending_this_cpu()
182 static inline bool pi_pending_this_cpu(unsigned int vector) { return false; } in pi_pending_this_cpu() argument
A Dirq_stack.h194 #define IRQ_CONSTRAINTS , [arg1] "r" (regs), [arg2] "r" ((unsigned long)vector)
196 #define run_irq_on_irqstack_cond(func, regs, vector) \ argument
200 assert_arg_type(vector, u32); \
203 IRQ_CONSTRAINTS, regs, vector); \
232 #define run_irq_on_irqstack_cond(func, regs, vector) \ argument
235 func(regs, vector); \
/arch/x86/include/asm/trace/
A Dirq_vectors.h14 TP_PROTO(int vector),
16 TP_ARGS(vector),
19 __field( int, vector )
23 __entry->vector = vector;
30 TP_PROTO(int vector), \
33 TP_PROTO(int vector), \
141 __entry->vector = vector;
169 __entry->vector = vector;
234 __entry->vector = ret < 0 ? 0 : vector;
259 __entry->vector = ret < 0 ? 0 : vector;
[all …]
A Dhyperv.h61 int vector),
62 TP_ARGS(cpus, vector),
65 __field(int, vector)
68 __entry->vector = vector;
71 __entry->ncpus, __entry->vector)
76 int vector),
77 TP_ARGS(cpu, vector),
80 __field(int, vector)
83 __entry->vector = vector;
86 __entry->cpu, __entry->vector)
/arch/x86/entry/
A Dentry_fred.c56 switch (regs->fred_ss.vector) { in fred_intx()
145 unsigned int vector; in fred_complete_exception_setup() local
147 for (vector = 0; vector < FIRST_EXTERNAL_VECTOR; vector++) in fred_complete_exception_setup()
148 set_bit(vector, system_vectors); in fred_complete_exception_setup()
150 for (vector = 0; vector < NR_SYSTEM_VECTORS; vector++) { in fred_complete_exception_setup()
151 if (sysvec_table[vector]) in fred_complete_exception_setup()
161 unsigned int vector = regs->fred_ss.vector; in fred_extint() local
168 if (likely(vector >= FIRST_SYSTEM_VECTOR)) { in fred_extint()
176 common_interrupt(regs, vector); in fred_extint()
186 switch (regs->fred_ss.vector) { in fred_hwexc()
[all …]
/arch/riscv/kvm/
A Dvcpu_vector.c26 cntx->vector.vlenb = riscv_v_vsize / 32; in kvm_riscv_vcpu_vector_reset()
30 WARN_ON(!cntx->vector.datap); in kvm_riscv_vcpu_vector_reset()
79 if (!vcpu->arch.guest_context.vector.datap) in kvm_riscv_vcpu_alloc_vector_context()
83 if (!vcpu->arch.host_context.vector.datap) in kvm_riscv_vcpu_alloc_vector_context()
109 *reg_addr = &cntx->vector.vstart; in kvm_riscv_vcpu_vreg_addr()
112 *reg_addr = &cntx->vector.vl; in kvm_riscv_vcpu_vreg_addr()
115 *reg_addr = &cntx->vector.vtype; in kvm_riscv_vcpu_vreg_addr()
118 *reg_addr = &cntx->vector.vcsr; in kvm_riscv_vcpu_vreg_addr()
121 *reg_addr = &cntx->vector.vlenb; in kvm_riscv_vcpu_vreg_addr()
130 *reg_addr = cntx->vector.datap + in kvm_riscv_vcpu_vreg_addr()
[all …]
/arch/sh/kernel/cpu/sh2a/
A Dex.S61 vector = 0 define
63 .long exception_entry0 + vector * 6
64 vector = vector + 1 define
66 vector = 0 define
68 .long exception_entry1 + vector * 6
69 vector = vector + 1 define
/arch/x86/xen/
A Dsmp.c145 int vector) in __xen_send_IPI_mask() argument
150 xen_send_IPI_one(cpu, vector); in __xen_send_IPI_mask()
178 switch (vector) { in xen_map_vector()
200 vector); in xen_map_vector()
207 int vector) in xen_send_IPI_mask() argument
209 int xen_vector = xen_map_vector(vector); in xen_send_IPI_mask()
215 void xen_send_IPI_all(int vector) in xen_send_IPI_all() argument
217 int xen_vector = xen_map_vector(vector); in xen_send_IPI_all()
223 void xen_send_IPI_self(int vector) in xen_send_IPI_self() argument
232 int vector) in xen_send_IPI_mask_allbutself() argument
[all …]
/arch/riscv/crypto/
A DKconfig16 - Zvkned vector crypto extension
17 - Zvbb vector extension (XTS)
18 - Zvkb vector crypto extension (CTR)
19 - Zvkg vector crypto extension (XTS)
29 - Zvkg vector crypto extension
40 - Zvksh vector crypto extension
41 - Zvkb vector crypto extension
57 - Zvksed vector crypto extension
58 - Zvkb vector crypto extension
/arch/x86/kernel/
A Dirq.c259 static struct irq_desc *reevaluate_vector(int vector) in reevaluate_vector() argument
261 struct irq_desc *desc = __this_cpu_read(vector_irq[vector]); in reevaluate_vector()
269 __this_cpu_write(vector_irq[vector], VECTOR_UNUSED); in reevaluate_vector()
304 desc = reevaluate_vector(vector); in call_irq_handler()
325 if (unlikely(!call_irq_handler(vector, regs))) in DEFINE_IDTENTRY_IRQ()
484 unsigned int vector; in fixup_irqs() local
507 for (vector = FIRST_EXTERNAL_VECTOR; vector < NR_VECTORS; vector++) { in fixup_irqs()
508 if (IS_ERR_OR_NULL(__this_cpu_read(vector_irq[vector]))) in fixup_irqs()
511 if (is_vector_pending(vector)) { in fixup_irqs()
512 desc = __this_cpu_read(vector_irq[vector]); in fixup_irqs()
[all …]
/arch/alpha/kernel/
A Dirq_alpha.c31 dummy_perf(unsigned long vector, struct pt_regs *regs) in dummy_perf() argument
45 do_entInt(unsigned long type, unsigned long vector, in do_entInt() argument
75 alpha_mv.machine_check(vector, la_ptr); in do_entInt()
80 alpha_mv.device_interrupt(vector); in do_entInt()
88 type, vector); in do_entInt()
128 process_mcheck_info(unsigned long vector, unsigned long la_ptr, in process_mcheck_info() argument
156 machine, vector, get_irq_regs()->pc, mchk_header->code); in process_mcheck_info()
A Dsys_nautilus.c120 naut_sys_machine_check(unsigned long vector, unsigned long la_ptr, in naut_sys_machine_check() argument
131 nautilus_machine_check(unsigned long vector, unsigned long la_ptr) in nautilus_machine_check() argument
139 if (vector == SCB_Q_SYSMCHK in nautilus_machine_check()
166 if (vector == SCB_Q_SYSERR) in nautilus_machine_check()
168 else if (vector == SCB_Q_SYSMCHK) in nautilus_machine_check()
171 ev6_machine_check(vector, la_ptr); in nautilus_machine_check()
177 vector, mchk_class); in nautilus_machine_check()
179 naut_sys_machine_check(vector, la_ptr, get_irq_regs()); in nautilus_machine_check()
/arch/sh/kernel/cpu/sh2/
A Dex.S40 vector = 0 define
42 .long exception_entry + vector * 6
43 vector = vector + 1 define
/arch/riscv/include/asm/
A Dkvm_vcpu_vector.h21 __riscv_v_vstate_save(&context->vector, context->vector.datap); in __kvm_riscv_vector_save()
26 __riscv_v_vstate_restore(&context->vector, context->vector.datap); in __kvm_riscv_vector_restore()
/arch/x86/kvm/
A Dirq.c49 int vector = vcpu->arch.pending_external_vector; in get_userspace_extint() local
52 return vector; in get_userspace_extint()
158 int vector = kvm_cpu_get_extint(v); in kvm_cpu_get_interrupt() local
159 if (vector != -1) in kvm_cpu_get_interrupt()
160 return vector; /* PIC */ in kvm_cpu_get_interrupt()
163 if (vector != -1) in kvm_cpu_get_interrupt()
164 kvm_apic_ack_interrupt(v, vector); in kvm_cpu_get_interrupt()
166 return vector; in kvm_cpu_get_interrupt()
267 irq->vector = msg.arch_data.vector; in kvm_msi_to_lapic_irq()
453 __set_bit(vector, ioapic_handled_vectors); in kvm_scan_ioapic_irq()
[all …]

Completed in 53 milliseconds

123456789