Home
last modified time | relevance | path

Searched refs:local_id (Results 1 – 19 of 19) sorted by relevance

/linux/drivers/infiniband/core/
H A Dcm_trace.h146 __field(unsigned int, local_id)
154 __entry->local_id = be32_to_cpu(cm_id->local_id);
161 __entry->local_id, __entry->remote_id,
196 __field(u32, local_id)
204 __entry->local_id = be32_to_cpu(cm_id->local_id);
211 __entry->local_id, __entry->remote_id,
248 unsigned int local_id,
252 TP_ARGS(local_id, remote_id),
255 __field(unsigned int, local_id)
260 __entry->local_id = local_id;
[all …]
/linux/drivers/irqchip/
H A Dirq-riscv-imsic-early.c97 unsigned long local_id; in imsic_handle_irq() local
107 while ((local_id = csr_swap(CSR_TOPEI, 0))) { in imsic_handle_irq()
108 local_id >>= TOPEI_ID_SHIFT; in imsic_handle_irq()
110 if (!imsic_noipi && local_id == IMSIC_IPI_ID) { in imsic_handle_irq()
116 if (unlikely(local_id > imsic->global.nr_ids)) { in imsic_handle_irq()
117 pr_warn_ratelimited("vector not found for local ID 0x%lx\n", local_id); in imsic_handle_irq()
121 generic_handle_irq(lpriv->vectors[local_id].irq); in imsic_handle_irq()
H A Dirq-riscv-imsic-platform.c63 writel_relaxed(vec->local_id, local->msi_va); in imsic_irq_retrigger()
84 msg->data = vec->local_id; in imsic_irq_compose_vector_msg()
155 new_vec->local_id != old_vec->local_id) { in imsic_irq_set_affinity()
158 tmp_vec.local_id = new_vec->local_id; in imsic_irq_set_affinity()
206 d->irq, mvec->cpu, mvec->local_id); in imsic_irq_force_complete_move()
H A Dirq-riscv-imsic-state.h21 unsigned int local_id; member
/linux/tools/testing/selftests/bpf/prog_tests/
H A Dlwt_seg6local.c53 int local_id = ns * 2 - 1; in setup() local
58 NETNS_BASE, ns, local_id, peer_id, NETNS_BASE, next_ns); in setup()
60 SYS(fail, "ip -n %s%d link set dev veth%d up", NETNS_BASE, ns, local_id); in setup()
65 NETNS_BASE, ns, local_id, peer_id, local_id); in setup()
67 NETNS_BASE, next_ns, peer_id, local_id, peer_id); in setup()
/linux/tools/lib/bpf/
H A Drelo_core.h71 int __bpf_core_types_are_compat(const struct btf *local_btf, __u32 local_id,
73 int bpf_core_types_are_compat(const struct btf *local_btf, __u32 local_id,
75 int __bpf_core_types_match(const struct btf *local_btf, __u32 local_id, const struct btf *targ_btf,
77 int bpf_core_types_match(const struct btf *local_btf, __u32 local_id, const struct btf *targ_btf,
H A Drelo_core.c145 int __bpf_core_types_are_compat(const struct btf *local_btf, __u32 local_id, in __bpf_core_types_are_compat() argument
152 local_type = btf_type_by_id(local_btf, local_id); in __bpf_core_types_are_compat()
162 local_type = skip_mods_and_typedefs(local_btf, local_id, &local_id); in __bpf_core_types_are_compat()
184 local_id = local_type->type; in __bpf_core_types_are_compat()
188 local_id = btf_array(local_type)->type; in __bpf_core_types_are_compat()
205 skip_mods_and_typedefs(local_btf, local_p->type, &local_id); in __bpf_core_types_are_compat()
207 err = __bpf_core_types_are_compat(local_btf, local_id, targ_btf, targ_id, in __bpf_core_types_are_compat()
214 skip_mods_and_typedefs(local_btf, local_type->type, &local_id); in __bpf_core_types_are_compat()
220 btf_kind_str(local_type), local_id, targ_id); in __bpf_core_types_are_compat()
414 __u32 local_id, in bpf_core_fields_are_compat() argument
[all …]
H A Dlibbpf.c6031 int bpf_core_types_are_compat(const struct btf *local_btf, __u32 local_id, in bpf_core_types_are_compat() argument
6034 return __bpf_core_types_are_compat(local_btf, local_id, targ_btf, targ_id, 32); in bpf_core_types_are_compat()
6037 int bpf_core_types_match(const struct btf *local_btf, __u32 local_id, in bpf_core_types_match() argument
6040 return __bpf_core_types_match(local_btf, local_id, targ_btf, targ_id, false, 32); in bpf_core_types_match()
6099 __u32 local_id = relo->type_id; in bpf_core_resolve_relo() local
6102 local_type = btf__type_by_id(local_btf, local_id); in bpf_core_resolve_relo()
6111 !hashmap__find(cand_cache, local_id, &cands)) { in bpf_core_resolve_relo()
6112 cands = bpf_core_find_cands(prog->obj, local_btf, local_id); in bpf_core_resolve_relo()
6115 prog_name, relo_idx, local_id, btf_kind_str(local_type), in bpf_core_resolve_relo()
6119 err = hashmap__set(cand_cache, local_id, cands, NULL, NULL); in bpf_core_resolve_relo()
/linux/drivers/hwspinlock/
H A Dhwspinlock_internal.h67 int local_id = hwlock - &hwlock->bank->lock[0]; in hwlock_to_id() local
69 return hwlock->bank->base_id + local_id; in hwlock_to_id()
/linux/net/mptcp/
H A Dsyncookies.c28 u8 local_id; member
67 entry->local_id = subflow_req->local_id; in mptcp_join_store_state()
121 subflow_req->local_id = e->local_id; in mptcp_token_join_cookie_init_state()
H A Dsubflow.c89 int local_id; in subflow_token_join_request() local
97 local_id = mptcp_pm_get_local_id(msk, (struct sock_common *)req); in subflow_token_join_request()
98 if (local_id < 0) { in subflow_token_join_request()
103 subflow_req->local_id = local_id; in subflow_token_join_request()
622 static void subflow_set_local_id(struct mptcp_subflow_context *subflow, int local_id) in subflow_set_local_id() argument
624 WARN_ON_ONCE(local_id < 0 || local_id > 255); in subflow_set_local_id()
625 WRITE_ONCE(subflow->local_id, local_id); in subflow_set_local_id()
634 if (likely(subflow->local_id >= 0)) in subflow_chk_local_id()
1623 int local_id = local->addr.id; in __mptcp_subflow_connect() local
1640 msk, local_id, remote_id, err); in __mptcp_subflow_connect()
[all …]
H A Dprotocol.h510 u8 local_id; member
601 s16 local_id; /* if negative not initialized yet */
656 WRITE_ONCE(subflow->local_id, -1); in mptcp_subflow_ctx_reset()
1233 int local_id = READ_ONCE(subflow->local_id); in subflow_get_local_id() local
1235 if (local_id < 0) in subflow_get_local_id()
1237 return local_id; in subflow_get_local_id()
H A Dpm_userspace.c263 if (READ_ONCE(subflow->local_id) == 0) { in mptcp_userspace_pm_remove_id_zero_address()
H A Doptions.c493 opts->join_id = subflow->local_id; in mptcp_syn_options()
963 opts->join_id = subflow_req->local_id; in mptcp_synack_options()
H A Dprotocol.c123 WRITE_ONCE(subflow->local_id, 0); in __mptcp_socket_create()
2748 if (subflow->close_event_done || READ_ONCE(subflow->local_id) < 0) in mptcp_close_ssk()
/linux/include/rdma/
H A Dib_cm.h299 __be32 local_id; member
/linux/tools/bpf/bpftool/
H A Dgen.c2395 btfgen_find_cands(const struct btf *local_btf, const struct btf *targ_btf, __u32 local_id) in btfgen_find_cands() argument
2405 local_cand.id = local_id; in btfgen_find_cands()
2407 local_type = btf__type_by_id(local_btf, local_id); in btfgen_find_cands()
/linux/kernel/bpf/
H A Dbtf.c9392 int bpf_core_types_are_compat(const struct btf *local_btf, __u32 local_id, in bpf_core_types_are_compat() argument
9395 return __bpf_core_types_are_compat(local_btf, local_id, targ_btf, targ_id, in bpf_core_types_are_compat()
9401 int bpf_core_types_match(const struct btf *local_btf, u32 local_id, in bpf_core_types_match() argument
9404 return __bpf_core_types_match(local_btf, local_id, targ_btf, targ_id, false, in bpf_core_types_match()
/linux/net/bluetooth/
H A Dl2cap_core.c655 chan->local_id = L2CAP_BESTEFFORT_ID; in __l2cap_chan_add()
3164 efs.id = chan->local_id; in l2cap_add_opt_efs()