/linux-master/drivers/gpu/drm/amd/display/include/ |
H A D | vector.h | 29 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 D | vector.c | 27 #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 D | local.h | 17 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 D | ipi.c | 51 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 D | x2apic_phys.c | 44 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 D | apic_noop.c | 23 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 D | apic_numachip.c | 68 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 D | event.c | 37 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 D | smp.h | 10 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 D | irq_vectors.h | 15 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 D | hyperv.h | 61 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 D | x86_irq_vectors.c | 14 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 D | idtentry.h | 21 * @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 D | irq_stack.h | 130 * 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 D | hv_apic.c | 107 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 D | ex.S | 5 * 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 D | monitor_mwait_test.c | 23 #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 D | xcr0_cpuid_test.c | 53 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 D | entry_fred.c | 17 /* 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 D | ex.S | 5 * 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 D | uv_irq.h | 16 __u64 vector : 8, member in struct:uv_IO_APIC_route_entry
|
/linux-master/include/trace/events/ |
H A D | osnoise.h | 39 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 D | event.c | 119 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 D | kvm_vcpu_vector.h | 16 #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 D | vcpu_vector.c | 16 #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...] |