Searched refs:vector (Results 1 - 25 of 498) sorted by relevance

1234567891011>>

/linux-master/drivers/gpu/drm/amd/display/include/
H A Dvector.h29 struct vector { struct
38 struct vector *vector,
43 struct vector *dal_vector_create(
49 * each "structure" in the vector will contain zeros by default. */
50 struct vector *dal_vector_presized_create(
57 struct vector *vector);
60 struct vector **vector);
[all...]
/linux-master/drivers/gpu/drm/amd/display/dc/basics/
H A Dvector.c27 #include "include/vector.h"
30 struct vector *vector,
35 vector->container = NULL;
43 vector->container = kcalloc(capacity, struct_size, GFP_KERNEL);
44 if (vector->container == NULL)
46 vector->capacity = capacity;
47 vector->struct_size = struct_size;
48 vector->count = 0;
49 vector
29 dal_vector_construct( struct vector *vector, struct dc_context *ctx, uint32_t capacity, uint32_t struct_size) argument
53 dal_vector_presized_costruct(struct vector *vector, struct dc_context *ctx, uint32_t count, void *initial_value, uint32_t struct_size) argument
97 struct vector *vector = kzalloc(sizeof(struct vector), GFP_KERNEL); local
116 struct vector *vector = kzalloc(sizeof(struct vector), GFP_KERNEL); local
129 dal_vector_destruct( struct vector *vector) argument
137 dal_vector_destroy( struct vector **vector) argument
147 dal_vector_get_count( const struct vector *vector) argument
153 dal_vector_at_index( const struct vector *vector, uint32_t index) argument
162 dal_vector_remove_at_index( struct vector *vector, uint32_t index) argument
179 dal_vector_set_at_index( const struct vector *vector, const void *what, uint32_t index) argument
202 dal_vector_insert_at( struct vector *vector, const void *what, uint32_t position) argument
234 dal_vector_append( struct vector *vector, const void *item) argument
241 dal_vector_clone( const struct vector *vector) argument
279 dal_vector_capacity(const struct vector *vector) argument
284 dal_vector_reserve(struct vector *vector, uint32_t capacity) argument
303 dal_vector_clear(struct vector *vector) argument
[all...]
/linux-master/arch/x86/kernel/apic/
H A Dlocal.h17 void __x2apic_send_IPI_dest(unsigned int apicid, int vector, unsigned int dest);
20 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, argument
34 switch (vector) {
36 icr |= APIC_DM_FIXED | vector;
54 void __default_send_IPI_dest_field(unsigned int mask, int vector, unsigned int dest);
56 void default_send_IPI_single(int cpu, int vector);
57 void default_send_IPI_single_phys(int cpu, int vector);
[all...]
H A Dipi.c51 void apic_send_IPI_allbutself(unsigned int vector) argument
57 __apic_send_IPI_allbutself(vector);
59 __apic_send_IPI_mask_allbutself(cpu_online_mask, vector);
152 static void __default_send_IPI_shortcut(unsigned int shortcut, int vector) argument
156 * safe_apic_wait_icr_idle() for the NMI vector as there have been
160 if (unlikely(vector == NMI_VECTOR))
166 native_apic_mem_write(APIC_ICR, __prepare_ICR(shortcut, vector, 0));
173 void __default_send_IPI_dest_field(unsigned int dest_mask, int vector, argument
177 if (unlikely(vector == NMI_VECTOR))
185 native_apic_mem_write(APIC_ICR, __prepare_ICR(0, vector, dest_mod
188 default_send_IPI_single_phys(int cpu, int vector) argument
194 vector, APIC_DEST_PHYSICAL); local
198 default_send_IPI_mask_sequence_phys(const struct cpumask *mask, int vector) argument
206 cpu), vector, APIC_DEST_PHYSICAL); local
211 default_send_IPI_mask_allbutself_phys(const struct cpumask *mask, int vector) argument
222 cpu), vector, APIC_DEST_PHYSICAL); local
230 default_send_IPI_single(int cpu, int vector) argument
232 __apic_send_IPI_mask(cpumask_of(cpu), vector); local
235 default_send_IPI_allbutself(int vector) argument
240 default_send_IPI_all(int vector) argument
245 default_send_IPI_self(int vector) argument
251 default_send_IPI_mask_sequence_logical(const struct cpumask *mask, int vector) argument
262 default_send_IPI_mask_allbutself_logical(const struct cpumask *mask, int vector) argument
277 default_send_IPI_mask_logical(const struct cpumask *cpumask, int vector) argument
[all...]
H A Dx2apic_phys.c44 static void x2apic_send_IPI(int cpu, int vector) argument
50 __x2apic_send_IPI_dest(dest, vector, APIC_DEST_PHYSICAL);
54 __x2apic_send_IPI_mask(const struct cpumask *mask, int vector, int apic_dest) argument
70 vector, APIC_DEST_PHYSICAL); local
75 static void x2apic_send_IPI_mask(const struct cpumask *mask, int vector) argument
77 __x2apic_send_IPI_mask(mask, vector, APIC_DEST_ALLINC);
81 x2apic_send_IPI_mask_allbutself(const struct cpumask *mask, int vector) argument
83 __x2apic_send_IPI_mask(mask, vector, APIC_DEST_ALLBUT);
86 static void __x2apic_send_IPI_shorthand(int vector, u32 which) argument
88 unsigned long cfg = __prepare_ICR(which, vector,
95 x2apic_send_IPI_allbutself(int vector) argument
100 x2apic_send_IPI_all(int vector) argument
105 x2apic_send_IPI_self(int vector) argument
110 __x2apic_send_IPI_dest(unsigned int apicid, int vector, unsigned int dest) argument
[all...]
H A Dapic_noop.c23 static void noop_send_IPI(int cpu, int vector) { } argument
24 static void noop_send_IPI_mask(const struct cpumask *cpumask, int vector) { } argument
25 static void noop_send_IPI_mask_allbutself(const struct cpumask *cpumask, int vector) { } argument
26 static void noop_send_IPI_allbutself(int vector) { } argument
27 static void noop_send_IPI_all(int vector) { } argument
28 static void noop_send_IPI_self(int vector) { } argument
H A Dapic_numachip.c68 static void numachip_send_IPI_one(int cpu, int vector) argument
81 __default_send_IPI_dest_field(apicid, vector,
89 dmode = (vector == NMI_VECTOR) ? APIC_DM_NMI : APIC_DM_FIXED;
90 numachip_apic_icr_write(apicid, dmode | vector);
93 static void numachip_send_IPI_mask(const struct cpumask *mask, int vector) argument
98 numachip_send_IPI_one(cpu, vector);
102 int vector)
109 numachip_send_IPI_one(cpu, vector);
113 static void numachip_send_IPI_allbutself(int vector) argument
120 numachip_send_IPI_one(cpu, vector);
101 numachip_send_IPI_mask_allbutself(const struct cpumask *mask, int vector) argument
124 numachip_send_IPI_all(int vector) argument
129 numachip_send_IPI_self(int vector) argument
[all...]
/linux-master/drivers/net/wireless/ti/wl12xx/
H A Devent.c37 u32 vector; local
40 vector = le32_to_cpu(mbox->events_vector);
41 vector &= ~(le32_to_cpu(mbox->events_mask));
43 wl1271_debug(DEBUG_EVENT, "MBOX vector: 0x%x", vector);
45 if (vector & SCAN_COMPLETE_EVENT_ID) {
53 if (vector & PERIODIC_SCAN_REPORT_EVENT_ID) {
61 if (vector & PERIODIC_SCAN_COMPLETE_EVENT_ID)
64 if (vector & SOFT_GEMINI_SENSE_EVENT_ID)
68 if (vector
[all...]
/linux-master/arch/x86/xen/
H A Dsmp.h10 int vector);
12 int vector);
13 extern void xen_send_IPI_allbutself(int vector);
14 extern void xen_send_IPI_all(int vector);
15 extern void xen_send_IPI_self(int vector);
/linux-master/arch/x86/include/asm/trace/
H A Dirq_vectors.h15 TP_PROTO(int vector),
17 TP_ARGS(vector),
20 __field( int, vector )
24 __entry->vector = vector;
27 TP_printk("vector=%d", __entry->vector) );
31 TP_PROTO(int vector), \
32 TP_ARGS(vector), NULL, NULL); \
34 TP_PROTO(int vector), \
[all...]
H A Dhyperv.h61 int vector),
62 TP_ARGS(cpus, vector),
65 __field(int, vector)
68 __entry->vector = vector;
70 TP_printk("ncpus %d vector %x",
71 __entry->ncpus, __entry->vector)
76 int vector),
77 TP_ARGS(cpu, vector),
80 __field(int, vector)
[all...]
/linux-master/tools/perf/trace/beauty/tracepoints/
H A Dx86_irq_vectors.c14 static size_t x86_irq_vectors__scnprintf(unsigned long vector, char *bf, size_t size, bool show_prefix) argument
16 return strarray__scnprintf_suffix(&strarray__x86_irq_vectors, bf, size, "%#x", show_prefix, vector);
21 unsigned long vector = arg->val; local
23 return x86_irq_vectors__scnprintf(vector, bf, size, arg->show_string_prefix);
/linux-master/arch/x86/include/asm/
H A Didtentry.h21 * @vector: Vector number (ignored for C)
34 #define DECLARE_IDTENTRY(vector, func) \
75 * @vector: Vector number (ignored for C)
86 #define DECLARE_IDTENTRY_ERRORCODE(vector, func) \
119 * @vector: Vector number (ignored for C)
124 #define DECLARE_IDTENTRY_RAW(vector, func) \
125 DECLARE_IDTENTRY(vector, func)
158 * @vector: Vector number (ignored for C)
163 #define DECLARE_IDTENTRY_RAW_ERRORCODE(vector, func) \
164 DECLARE_IDTENTRY_ERRORCODE(vector, fun
467 fred_install_sysvec(unsigned int vector, const idtentry_t function) argument
561 vector = vector+1 variable
577 vector = vector+1 variable
[all...]
H A Dirq_stack.h130 * Macro to invoke system vector and device interrupt C handlers.
187 * @regs and @vector in callee saved registers.
194 #define IRQ_CONSTRAINTS , [arg1] "r" (regs), [arg2] "r" ((unsigned long)vector)
196 #define run_irq_on_irqstack_cond(func, regs, vector) \
200 assert_arg_type(vector, u32); \
203 IRQ_CONSTRAINTS, regs, vector); \
223 /* System vector handlers always run on the stack they interrupted. */
232 #define run_irq_on_irqstack_cond(func, regs, vector) \
235 func(regs, vector); \
/linux-master/arch/x86/hyperv/
H A Dhv_apic.c107 static bool __send_ipi_mask_ex(const struct cpumask *mask, int vector, argument
124 ipi_arg->vector = vector;
157 static bool __send_ipi_mask(const struct cpumask *mask, int vector, argument
165 trace_hyperv_send_ipi_mask(mask, vector);
184 if (vector < HV_IPI_LOW_VECTOR || vector > HV_IPI_HIGH_VECTOR)
200 ipi_arg.vector = vector;
220 status = hv_do_fast_hypercall16(HVCALL_SEND_IPI, ipi_arg.vector,
228 __send_ipi_one(int cpu, int vector) argument
254 hv_send_ipi(int cpu, int vector) argument
260 hv_send_ipi_mask(const struct cpumask *mask, int vector) argument
266 hv_send_ipi_mask_allbutself(const struct cpumask *mask, int vector) argument
272 hv_send_ipi_allbutself(int vector) argument
277 hv_send_ipi_all(int vector) argument
283 hv_send_ipi_self(int vector) argument
[all...]
/linux-master/arch/sh/kernel/cpu/sh2a/
H A Dex.S5 * The SH-2A exception vector table
61 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
/linux-master/tools/testing/selftests/kvm/x86_64/
H A Dmonitor_mwait_test.c23 #define GUEST_ASSERT_MONITOR_MWAIT(insn, testcase, vector) \
29 __GUEST_ASSERT((vector) == UD_VECTOR, \
31 testcase, vector); \
33 __GUEST_ASSERT(!(vector), \
35 testcase, vector); \
40 u8 vector; local
48 vector = kvm_asm_safe("monitor", "a"(guest_monitor_wait), "c"(0), "d"(0));
49 GUEST_ASSERT_MONITOR_MWAIT("MONITOR", testcase, vector);
51 vector = kvm_asm_safe("mwait", "a"(guest_monitor_wait), "c"(0), "d"(0));
52 GUEST_ASSERT_MONITOR_MWAIT("MWAIT", testcase, vector);
[all...]
H A Dxcr0_cpuid_test.c53 int i, vector; local
82 vector = xsetbv_safe(0, supported_xcr0);
83 __GUEST_ASSERT(!vector,
84 "Expected success on XSETBV(0x%lx), got vector '0x%x'",
85 supported_xcr0, vector);
91 vector = xsetbv_safe(0, supported_xcr0 | BIT_ULL(i));
92 __GUEST_ASSERT(vector == GP_VECTOR,
93 "Expected #GP on XSETBV(0x%llx), supported XCR0 = %lx, got vector '0x%x'",
94 BIT_ULL(i), supported_xcr0, vector);
/linux-master/arch/x86/entry/
H A Dentry_fred.c17 /* FRED EVENT_TYPE_OTHER vector numbers */
30 "vector %u error 0x%lx aux 0x%lx at %04x:%016lx\n",
31 regs->fred_ss.type, regs->fred_ss.vector, error_code,
40 "vector %u error 0x%lx aux 0x%lx at %04x:%016lx\n",
41 regs->fred_ss.type, regs->fred_ss.vector, error_code,
56 switch (regs->fred_ss.vector) {
81 if (likely(regs->fred_ss.vector == FRED_SYSCALL && regs->fred_ss.lm)) {
87 likely(regs->fred_ss.vector == FRED_SYSENTER && !regs->fred_ss.lm)) {
138 spurious_interrupt(regs, regs->fred_ss.vector);
143 unsigned int vector; local
159 unsigned int vector = regs->fred_ss.vector; local
[all...]
/linux-master/arch/sh/kernel/cpu/sh2/
H A Dex.S5 * The SH-2 exception vector table
40 vector = 0 define
42 .long exception_entry + vector * 6
43 vector = vector + 1 define
/linux-master/arch/x86/include/asm/uv/
H A Duv_irq.h16 __u64 vector : 8, member in struct:uv_IO_APIC_route_entry
/linux-master/include/trace/events/
H A Dosnoise.h39 TP_PROTO(int vector, u64 start, u64 duration),
41 TP_ARGS(vector, start, duration),
46 __field( int, vector )
50 __entry->vector = vector;
56 show_softirq_name(__entry->vector),
57 __entry->vector,
65 TP_PROTO(int vector, const char *desc, u64 start, u64 duration),
67 TP_ARGS(vector, desc, start, duration),
73 __field( int, vector )
[all...]
/linux-master/drivers/net/wireless/ti/wl18xx/
H A Devent.c119 u32 vector; local
121 vector = le32_to_cpu(mbox->events_vector);
122 wl1271_debug(DEBUG_EVENT, "MBOX vector: 0x%x", vector);
124 if (vector & SCAN_COMPLETE_EVENT_ID) {
132 if (vector & TIME_SYNC_EVENT_ID)
139 if (vector & RADAR_DETECTED_EVENT_ID) {
148 if (vector & PERIODIC_SCAN_REPORT_EVENT_ID) {
156 if (vector & PERIODIC_SCAN_COMPLETE_EVENT_ID)
159 if (vector
[all...]
/linux-master/arch/riscv/include/asm/
H A Dkvm_vcpu_vector.h16 #include <asm/vector.h>
21 __riscv_v_vstate_save(&context->vector, context->vector.datap);
26 __riscv_v_vstate_restore(&context->vector, context->vector.datap);
/linux-master/arch/riscv/kvm/
H A Dvcpu_vector.c16 #include <asm/vector.h>
27 WARN_ON(!cntx->vector.datap);
28 memset(cntx->vector.datap, 0, riscv_v_vsize);
76 cntx->vector.datap = kmalloc(riscv_v_vsize, GFP_KERNEL);
77 if (!cntx->vector.datap)
79 cntx->vector.vlenb = riscv_v_vsize / 32;
81 vcpu->arch.host_context.vector.datap = kzalloc(riscv_v_vsize, GFP_KERNEL);
82 if (!vcpu->arch.host_context.vector.datap)
90 kfree(vcpu->arch.guest_reset_context.vector.datap);
91 kfree(vcpu->arch.host_context.vector
[all...]

Completed in 248 milliseconds

1234567891011>>