| /linux-master/arch/powerpc/include/asm/ |
| H A D | spu.h | 129 struct spu_context *ctx; member in struct:spu
|
| /linux-master/arch/powerpc/kernel/ |
| H A D | uprobes.c | 210 bool arch_uretprobe_is_alive(struct return_instance *ret, enum rp_check ctx, argument
|
| /linux-master/arch/powerpc/kvm/ |
| H A D | book3s_64_mmu_hv.c | 1728 struct kvm_htab_ctx *ctx = file->private_data; local
1827 struct kvm_htab_ctx *ctx = file->private_data; local
1949 struct kvm_htab_ctx *ctx local
1969 struct kvm_htab_ctx *ctx; local
[all...] |
| /linux-master/arch/powerpc/mm/book3s32/ |
| H A D | mmu_context.c | 53 unsigned long ctx = next_mmu_context; local
85 void __destroy_context(unsigned long ctx) argument
[all...] |
| H A D | tlb.c | 55 unsigned int ctx = mm->context.id; local
|
| /linux-master/arch/powerpc/mm/book3s64/ |
| H A D | mmu_context.c | 57 static int realloc_context_ids(mm_context_t *ctx) argument
226 static void destroy_contexts(mm_context_t *ctx) argument
[all...] |
| /linux-master/arch/powerpc/net/ |
| H A D | bpf_jit.h | 147 bpf_is_seen_register(struct codegen_context *ctx, int i) argument
152 bpf_set_seen_register(struct codegen_context *ctx, int i) argument
157 bpf_clear_seen_register(struct codegen_context *ctx, int i) argument
[all...] |
| H A D | bpf_jit_comp.c | 30 int bpf_jit_emit_exit_insn(u32 *image, struct codegen_context *ctx, int tmp_reg, long exit_addr) argument
54 struct codegen_context ctx; member in struct:powerpc_jit_data
257 bpf_add_extable_entry(struct bpf_prog *fp, u32 *image, u32 *fimage, int pass, struct codegen_context *ctx, int insn_idx, int jmp_off, int dst_reg) argument
[all...] |
| H A D | bpf_jit_comp32.c | 46 void bpf_jit_init_reg_mapping(struct codegen_context *ctx) argument
68 bpf_jit_stack_offsetof(struct codegen_context *ctx, int reg) argument
82 bpf_has_stack_frame(struct codegen_context *ctx) argument
96 bpf_jit_realloc_regs(struct codegen_context *ctx) argument
126 bpf_jit_build_prologue(u32 *image, struct codegen_context *ctx) argument
173 bpf_jit_emit_common_epilogue(u32 *image, struct codegen_context *ctx) argument
194 bpf_jit_build_epilogue(u32 *image, struct codegen_context *ctx) argument
204 bpf_jit_emit_func_call_rel(u32 *image, u32 *fimage, struct codegen_context *ctx, u64 func) argument
221 bpf_jit_emit_tail_call(u32 *image, struct codegen_context *ctx, u32 out) argument
282 bpf_jit_build_body(struct bpf_prog *fp, u32 *image, u32 *fimage, struct codegen_context *ctx, u32 *addrs, int pass, bool extra_pass) argument
[all...] |
| H A D | bpf_jit_comp64.c | 49 void bpf_jit_init_reg_mapping(struct codegen_context *ctx) argument
75 bpf_has_stack_frame(struct codegen_context *ctx) argument
97 bpf_jit_stack_local(struct codegen_context *ctx) argument
105 bpf_jit_stack_tailcallcnt(struct codegen_context *ctx) argument
110 bpf_jit_stack_offsetof(struct codegen_context *ctx, int reg) argument
121 bpf_jit_realloc_regs(struct codegen_context *ctx) argument
125 bpf_jit_build_prologue(u32 *image, struct codegen_context *ctx) argument
176 bpf_jit_emit_common_epilogue(u32 *image, struct codegen_context *ctx) argument
195 bpf_jit_build_epilogue(u32 *image, struct codegen_context *ctx) argument
205 bpf_jit_emit_func_call_hlp(u32 *image, struct codegen_context *ctx, u64 func) argument
243 bpf_jit_emit_func_call_rel(u32 *image, u32 *fimage, struct codegen_context *ctx, u64 func) argument
276 bpf_jit_emit_tail_call(u32 *image, struct codegen_context *ctx, u32 out) argument
364 bpf_jit_build_body(struct bpf_prog *fp, u32 *image, u32 *fimage, struct codegen_context *ctx, u32 *addrs, int pass, bool extra_pass) argument
[all...] |
| /linux-master/arch/powerpc/platforms/cell/ |
| H A D | spu_manage.c | 351 static void enable_spu_by_master_run(struct spu_context *ctx) argument
356 static void disable_spu_by_master_run(struct spu_context *ctx) argument
|
| /linux-master/arch/powerpc/platforms/cell/spufs/ |
| H A D | coredump.c | 24 static int spufs_ctx_note_size(struct spu_context *ctx, int dfd) argument
46 struct spu_context *ctx; local
69 struct spu_context *ctx = NULL; local
90 struct spu_context *ctx; local
118 spufs_arch_write_note(struct spu_context *ctx, int i, struct coredump_params *cprm, int dfd) argument
161 struct spu_context *ctx; local
[all...] |
| H A D | file.c | 160 struct spu_context *ctx = i->i_ctx; local
174 struct spu_context *ctx = i->i_ctx; local
184 spufs_mem_dump(struct spu_context *ctx, struc argument
193 struct spu_context *ctx = file->private_data; local
210 struct spu_context *ctx = file->private_data; local
233 struct spu_context *ctx = vma->vm_file->private_data; local
265 struct spu_context *ctx = vma->vm_file->private_data; local
314 struct spu_context *ctx = vmf->vma->vm_file->private_data; local
396 struct spu_context *ctx = data; local
410 struct spu_context *ctx = data; local
425 struct spu_context *ctx = i->i_ctx; local
440 struct spu_context *ctx = i->i_ctx; local
469 spufs_regs_dump(struct spu_context *ctx, struct coredump_params *cprm) argument
480 struct spu_context *ctx = file->private_data; local
500 struct spu_context *ctx = file->private_data; local
526 spufs_fpcr_dump(struct spu_context *ctx, struct coredump_params *cprm) argument
537 struct spu_context *ctx = file->private_data; local
552 struct spu_context *ctx = file->private_data; local
597 struct spu_context *ctx = file->private_data; local
643 struct spu_context *ctx = file->private_data; local
671 spu_ibox_read(struct spu_context *ctx, u32 *data) argument
679 struct spu_context *ctx = spu->ctx; local
700 struct spu_context *ctx = file->private_data; local
752 struct spu_context *ctx = file->private_data; local
778 struct spu_context *ctx = file->private_data; local
804 spu_wbox_write(struct spu_context *ctx, u32 data) argument
812 struct spu_context *ctx = spu->ctx; local
833 struct spu_context *ctx = file->private_data; local
884 struct spu_context *ctx = file->private_data; local
910 struct spu_context *ctx = file->private_data; local
938 struct spu_context *ctx = i->i_ctx; local
952 struct spu_context *ctx = i->i_ctx; local
961 spufs_signal1_dump(struct spu_context *ctx, struct coredump_params *cprm) argument
970 __spufs_signal1_read(struct spu_context *ctx, char __user *buf, size_t len) argument
987 struct spu_context *ctx = file->private_data; local
1001 struct spu_context *ctx; local
1073 struct spu_context *ctx = i->i_ctx; local
1087 struct spu_context *ctx = i->i_ctx; local
1096 spufs_signal2_dump(struct spu_context *ctx, struct coredump_params *cprm) argument
1105 __spufs_signal2_read(struct spu_context *ctx, char __user *buf, size_t len) argument
1121 struct spu_context *ctx = file->private_data; local
1136 struct spu_context *ctx; local
1245 struct spu_context *ctx = data; local
1257 spufs_signal1_type_get(struct spu_context *ctx) argument
1267 struct spu_context *ctx = data; local
1279 spufs_signal2_type_get(struct spu_context *ctx) argument
1318 struct spu_context *ctx = i->i_ctx; local
1333 struct spu_context *ctx = i->i_ctx; local
1377 struct spu_context *ctx = i->i_ctx; local
1391 struct spu_context *ctx = i->i_ctx; local
1440 struct spu_context *ctx = i->i_ctx; local
1461 struct spu_context *ctx = i->i_ctx; local
1473 struct spu_context *ctx = spu->ctx; local
1479 spufs_read_mfc_tagstatus(struct spu_context *ctx, u32 *status) argument
1497 struct spu_context *ctx = file->private_data; local
1602 spu_send_mfc_command(struct spu_context *ctx, struct mfc_dma_command cmd, int *error) argument
1623 struct spu_context *ctx = file->private_data; local
1672 struct spu_context *ctx = file->private_data; local
1702 struct spu_context *ctx = file->private_data; local
1752 struct spu_context *ctx = data; local
1764 spufs_npc_get(struct spu_context *ctx) argument
1773 struct spu_context *ctx = data; local
1786 spufs_decr_get(struct spu_context *ctx) argument
1796 struct spu_context *ctx = data; local
1811 spufs_decr_status_get(struct spu_context *ctx) argument
1824 struct spu_context *ctx = data; local
1837 spufs_event_mask_get(struct spu_context *ctx) argument
1847 spufs_event_status_get(struct spu_context *ctx) argument
1861 struct spu_context *ctx = data; local
1874 spufs_srr0_get(struct spu_context *ctx) argument
1882 spufs_id_get(struct spu_context *ctx) argument
1896 spufs_object_id_get(struct spu_context *ctx) argument
1904 struct spu_context *ctx = data; local
1913 spufs_lslr_get(struct spu_context *ctx) argument
1923 struct spu_context *ctx = i->i_ctx; local
1930 struct spu_context *ctx = s->private; local
1951 spufs_mbox_info_dump(struct spu_context *ctx, struct coredump_params *cprm) argument
1963 struct spu_context *ctx = file->private_data; local
1989 spufs_ibox_info_dump(struct spu_context *ctx, struct coredump_params *cprm) argument
2001 struct spu_context *ctx = file->private_data; local
2027 spufs_wbox_info_cnt(struct spu_context *ctx) argument
2032 spufs_wbox_info_dump(struct spu_context *ctx, struct coredump_params *cprm) argument
2042 struct spu_context *ctx = file->private_data; local
2065 spufs_get_dma_info(struct spu_context *ctx, struct spu_dma_info *info) argument
2086 spufs_dma_info_dump(struct spu_context *ctx, struct coredump_params *cprm) argument
2098 struct spu_context *ctx = file->private_data; local
2120 spufs_get_proxydma_info(struct spu_context *ctx, struct spu_proxydma_info *info) argument
2140 spufs_proxydma_info_dump(struct spu_context *ctx, struct coredump_params *cprm) argument
2152 struct spu_context *ctx = file->private_data; local
2179 struct spu_context *ctx = s->private; local
2201 spufs_acct_time(struct spu_context *ctx, enum spu_utilization_state state) argument
2222 spufs_slb_flts(struct spu_context *ctx) argument
2234 spufs_class2_intrs(struct spu_context *ctx) argument
2249 struct spu_context *ctx = s->private; local
2287 spufs_switch_log_used(struct spu_context *ctx) argument
2293 spufs_switch_log_avail(struct spu_context *ctx) argument
2300 struct spu_context *ctx = SPUFS_I(inode)->i_ctx; local
2331 struct spu_context *ctx = SPUFS_I(inode)->i_ctx; local
2345 switch_log_sprint(struct spu_context *ctx, char *tbuf, int n) argument
2364 struct spu_context *ctx = SPUFS_I(inode)->i_ctx; local
2434 struct spu_context *ctx = SPUFS_I(inode)->i_ctx; local
2465 spu_switch_log_notify(struct spu *spu, struct spu_context *ctx, u32 type, u32 val) argument
2490 struct spu_context *ctx = s->private; local
[all...] |
| H A D | inode.c | 235 struct spu_context *ctx; local
110 spufs_new_file(struct super_block *sb, struct dentry *dentry, const struct file_operations *fops, umode_t mode, size_t size, struct spu_context *ctx) argument
184 spufs_fill_dir(struct dentry *dir, const struct spufs_tree_descr *files, umode_t mode, struct spu_context *ctx) argument
371 spufs_set_affinity(unsigned int flags, struct spu_context *ctx, struct spu_context *neighbor) argument
611 struct spufs_fs_context *ctx = fc->fs_private; local
680 struct spufs_fs_context *ctx = fc->fs_private; local
740 struct spufs_fs_context *ctx; local
[all...] |
| H A D | run.c | 17 struct spu_context *ctx = spu->ctx; local
49 int spu_stopped(struct spu_context *ctx, u32 *stat) argument
82 spu_setup_isolated(struct spu_context *ctx) argument
176 spu_run_init(struct spu_context *ctx, u32 *npc) argument
244 spu_run_fini(struct spu_context *ctx, u32 *npc, u32 *status) argument
273 spu_handle_restartsys(struct spu_context *ctx, long *spu_ret, unsigned int *npc) argument
309 spu_process_callback(struct spu_context *ctx) argument
353 spufs_run_spu(struct spu_context *ctx, u32 *npc, u32 *event) argument
[all...] |
| H A D | sched.c | 85 void spu_set_timeslice(struct spu_context *ctx) argument
96 void __spu_update_sched_info(struct spu_context *ctx) argument
137 spu_update_sched_info(struct spu_context *ctx) argument
155 __node_allowed(struct spu_context *ctx, int node) argument
167 node_allowed(struct spu_context *ctx, int node) argument
191 struct spu_context *ctx = spu->ctx; local
207 spu_bind_context(struct spu *spu, struct spu_context *ctx) argument
256 struct spu_context *ctx; local
267 struct spu_context *ctx; local
288 aff_ref_location(struct spu_context *ctx, int mem_aff, int group_size, int lowest_offset) argument
343 struct spu_context *tmp, *ctx; local
393 has_affinity(struct spu_context *ctx) argument
419 spu_unbind_context(struct spu *spu, struct spu_context *ctx) argument
475 __spu_add_to_rq(struct spu_context *ctx) argument
498 spu_add_to_rq(struct spu_context *ctx) argument
505 __spu_del_from_rq(struct spu_context *ctx) argument
519 spu_del_from_rq(struct spu_context *ctx) argument
526 spu_prio_wait(struct spu_context *ctx) argument
553 spu_get_idle(struct spu_context *ctx) argument
611 find_victim(struct spu_context *ctx) argument
699 __spu_schedule(struct spu *spu, struct spu_context *ctx) argument
721 spu_schedule(struct spu *spu, struct spu_context *ctx) argument
744 spu_unschedule(struct spu *spu, struct spu_context *ctx, int free_spu) argument
768 spu_activate(struct spu_context *ctx, unsigned long flags) argument
821 struct spu_context *ctx; local
844 __spu_deactivate(struct spu_context *ctx, int force, int max_prio) argument
877 spu_deactivate(struct spu_context *ctx) argument
891 spu_yield(struct spu_context *ctx) argument
901 spusched_tick(struct spu_context *ctx) argument
1002 struct spu_context *ctx = spu->ctx; local
1019 spuctx_switch_state(struct spu_context *ctx, enum spu_utilization_state new_state) argument
[all...] |
| H A D | spufs.h | 259 spu_acquire(struct spu_context *ctx) argument
264 spu_release(struct spu_context *ctx) argument
[all...] |
| H A D | switch.c | 1698 struct spu_context *ctx = spu->ctx; local
|
| /linux-master/arch/powerpc/platforms/ps3/ |
| H A D | spu.c | 442 static void ps3_enable_spu(struct spu_context *ctx) argument
446 static void ps3_disable_spu(struct spu_context *ctx) argument
|
| /linux-master/arch/riscv/crypto/ |
| H A D | aes-riscv64-glue.c | 63 static int riscv64_aes_setkey(struct crypto_aes_ctx *ctx, argument
92 struct crypto_aes_ctx *ctx = crypto_tfm_ctx(tfm); local
100 struct crypto_aes_ctx *ctx = crypto_skcipher_ctx(tfm); local
109 const struct crypto_aes_ctx *ctx = crypto_tfm_ctx(tfm); local
122 const struct crypto_aes_ctx *ctx local
138 const struct crypto_aes_ctx *ctx = crypto_skcipher_ctx(tfm); local
176 const struct crypto_aes_ctx *ctx = crypto_skcipher_ctx(tfm); local
216 const struct crypto_aes_ctx *ctx = crypto_skcipher_ctx(tfm); local
280 const struct crypto_aes_ctx *ctx = crypto_skcipher_ctx(tfm); local
347 struct riscv64_aes_xts_ctx *ctx = crypto_skcipher_ctx(tfm); local
357 const struct riscv64_aes_xts_ctx *ctx = crypto_skcipher_ctx(tfm); local
[all...] |
| H A D | chacha-riscv64-glue.c | 24 const struct chacha_ctx *ctx = crypto_skcipher_ctx(tfm); local
|
| H A D | sm3-riscv64-glue.c | 49 struct sm3_state *ctx; local
|
| H A D | sm4-riscv64-glue.c | 30 struct sm4_ctx *ctx = crypto_tfm_ctx(tfm); local
45 const struct sm4_ctx *ctx = crypto_tfm_ctx(tfm); local
58 const struct sm4_ctx *ctx = crypto_tfm_ctx(tfm); local
[all...] |
| /linux-master/arch/riscv/kernel/probes/ |
| H A D | uprobes.c | 120 bool arch_uretprobe_is_alive(struct return_instance *ret, enum rp_check ctx, argument
|
| /linux-master/arch/riscv/kernel/ |
| H A D | vector.c | 102 riscv_v_thread_zalloc(struct kmem_cache *cache, struct __riscv_v_ext_state *ctx) argument
|