Home
last modified time | relevance | path

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

12

/linux-6.15/drivers/infiniband/core/
H A Dcm_trace.h154 __entry->local_id = be32_to_cpu(cm_id->local_id);
196 __field(u32, local_id)
204 __entry->local_id = be32_to_cpu(cm_id->local_id);
248 unsigned int local_id,
252 TP_ARGS(local_id, remote_id),
260 __entry->local_id = local_id;
316 __be32 local_id,
320 TP_ARGS(local_id, state),
328 __entry->local_id = be32_to_cpu(local_id);
339 unsigned int local_id,
[all …]
H A Dcm.c568 static u32 cm_local_id(__be32 local_id) in cm_local_id() argument
969 timewait_info->work.local_id = local_id; in cm_create_timewait_info()
1296 low_tid = (u64)cm_id_priv->id.local_id; in cm_form_tid()
1342 be32_to_cpu(cm_id_priv->id.local_id)); in cm_format_req()
1521 id.local_id); in ib_send_cm_req()
1881 be32_to_cpu(cm_id_priv->id.local_id)); in cm_format_mra()
2122 id.local_id); in cm_req_handler()
2242 be32_to_cpu(cm_id_priv->id.local_id)); in cm_format_rep()
2338 be32_to_cpu(cm_id_priv->id.local_id)); in cm_format_rtu()
2644 be32_to_cpu(cm_id_priv->id.local_id)); in cm_format_dreq()
[all …]
/linux-6.15/drivers/irqchip/
H A Dirq-riscv-imsic-state.c179 tvec = vec->local_id == mvec->local_id ? in __imsic_local_sync()
180 NULL : &lpriv->vectors[mvec->local_id]; in __imsic_local_sync()
191 writel_relaxed(mvec->local_id, mlocal->msi_va); in __imsic_local_sync()
196 writel_relaxed(mvec->local_id, mlocal->msi_va); in __imsic_local_sync()
422 (vec->local_id <= IMSIC_IPI_ID) ? 1 : 0); in imsic_vector_debug_show()
441 if (!lpriv || imsic->global.nr_ids < local_id) in imsic_vector_from_local_id()
444 return &lpriv->vectors[local_id]; in imsic_vector_from_local_id()
453 int local_id; in imsic_vector_alloc() local
458 if (local_id < 0) in imsic_vector_alloc()
462 vec = &lpriv->vectors[local_id]; in imsic_vector_alloc()
[all …]
H A Dirq-riscv-imsic-early.c78 unsigned long local_id; in imsic_handle_irq() local
88 while ((local_id = csr_swap(CSR_TOPEI, 0))) { in imsic_handle_irq()
89 local_id >>= TOPEI_ID_SHIFT; in imsic_handle_irq()
91 if (local_id == IMSIC_IPI_ID) { in imsic_handle_irq()
100 vec = imsic_vector_from_local_id(cpu, local_id); in imsic_handle_irq()
102 pr_warn_ratelimited("vector not found for local ID 0x%lx\n", local_id); 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
97 struct imsic_vector *imsic_vector_from_local_id(unsigned int cpu, unsigned int local_id);
/linux-6.15/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-6.15/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.c163 local_type = skip_mods_and_typedefs(local_btf, local_id, &local_id); in __bpf_core_types_are_compat()
185 local_id = local_type->type; in __bpf_core_types_are_compat()
413 __u32 local_id, in bpf_core_fields_are_compat() argument
420 local_type = skip_mods_and_typedefs(local_btf, local_id, &local_id); in bpf_core_fields_are_compat()
491 __u32 local_id; in bpf_core_match_member() local
500 local_id = local_acc->type_id; in bpf_core_match_member()
1310 __u32 local_id; in bpf_core_calc_relo_insn() local
1314 local_id = relo->type_id; in bpf_core_calc_relo_insn()
1575 local_t = skip_mods_and_typedefs(local_btf, local_id, &local_id); in __bpf_core_types_match()
1656 local_id = local_t->type; in __bpf_core_types_match()
[all …]
H A Dlibbpf.c5816 int bpf_core_types_are_compat(const struct btf *local_btf, __u32 local_id, in bpf_core_types_are_compat() argument
5819 return __bpf_core_types_are_compat(local_btf, local_id, targ_btf, targ_id, 32); in bpf_core_types_are_compat()
5822 int bpf_core_types_match(const struct btf *local_btf, __u32 local_id, in bpf_core_types_match() argument
5825 return __bpf_core_types_match(local_btf, local_id, targ_btf, targ_id, false, 32); in bpf_core_types_match()
5884 __u32 local_id = relo->type_id; in bpf_core_resolve_relo() local
5887 local_type = btf__type_by_id(local_btf, local_id); in bpf_core_resolve_relo()
5896 !hashmap__find(cand_cache, local_id, &cands)) { in bpf_core_resolve_relo()
5897 cands = bpf_core_find_cands(prog->obj, local_btf, local_id); in bpf_core_resolve_relo()
5900 prog_name, relo_idx, local_id, btf_kind_str(local_type), in bpf_core_resolve_relo()
5904 err = hashmap__set(cand_cache, local_id, cands, NULL, NULL); in bpf_core_resolve_relo()
/linux-6.15/drivers/firewire/
H A Dcore-card.c327 local_id = card->local_node->node_id; in bm_work()
348 new_root_id = local_id; in bm_work()
355 new_root_id = local_id; in bm_work()
362 transaction_data[1] = cpu_to_be32(local_id); in bm_work()
380 bm_id == 0x3f ? local_id : 0xffc0 | bm_id; in bm_work()
385 if (local_id == irm_id) in bm_work()
410 new_root_id = local_id; in bm_work()
442 new_root_id = local_id; in bm_work()
453 new_root_id = local_id; in bm_work()
473 new_root_id = local_id; in bm_work()
[all …]
/linux-6.15/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-6.15/net/mptcp/
H A Dsyncookies.c28 u8 local_id; member
67 entry->local_id = subflow_req->local_id; in mptcp_join_store_state()
H A Dsubflow.c89 int local_id; in subflow_token_join_request() local
98 if (local_id < 0) { in subflow_token_join_request()
102 subflow_req->local_id = local_id; in subflow_token_join_request()
621 WARN_ON_ONCE(local_id < 0 || local_id > 255); in subflow_set_local_id()
622 WRITE_ONCE(subflow->local_id, local_id); in subflow_set_local_id()
631 if (likely(subflow->local_id >= 0)) in subflow_chk_local_id()
1598 int local_id = local->addr.id; in __mptcp_subflow_connect() local
1628 local_id = -1; in __mptcp_subflow_connect()
1632 local_id = -1; in __mptcp_subflow_connect()
1636 if (local_id >= 0) in __mptcp_subflow_connect()
[all …]
H A Dprotocol.h461 u8 local_id; member
548 s16 local_id; /* if negative not initialized yet */
599 WRITE_ONCE(subflow->local_id, -1); in mptcp_subflow_ctx_reset()
1158 int local_id = READ_ONCE(subflow->local_id); in subflow_get_local_id() local
1160 if (local_id < 0) in subflow_get_local_id()
1162 return local_id; in subflow_get_local_id()
H A Dpm_userspace.c256 if (READ_ONCE(subflow->local_id) == 0) { in mptcp_userspace_pm_remove_id_zero_address()
H A Doptions.c420 opts->join_id = subflow->local_id; in mptcp_syn_options()
917 opts->join_id = subflow_req->local_id; in mptcp_synack_options()
H A Dpm_kernel.c200 if (READ_ONCE(subflow->local_id) == local->id) in fill_remote_addresses_vec()
/linux-6.15/include/media/
H A Dv4l2-fwnode.h96 unsigned int local_id; member
H A Dmedia-entity.h462 static inline u32 media_gobj_gen_id(enum media_gobj_type type, u64 local_id) in media_gobj_gen_id() argument
467 id |= local_id & MEDIA_ID_MASK; in media_gobj_gen_id()
/linux-6.15/drivers/mailbox/
H A Dzynqmp-ipi-mailbox.c134 u32 local_id; member
154 a1 = pdata->local_id; in zynqmp_ipi_fw_call()
927 ret = of_property_read_u32(np, "xlnx,ipi-id", &pdata->local_id); in zynqmp_ipi_probe()
/linux-6.15/include/rdma/
H A Dib_cm.h299 __be32 local_id; member
/linux-6.15/tools/bpf/bpftool/
H A Dgen.c2302 btfgen_find_cands(const struct btf *local_btf, const struct btf *targ_btf, __u32 local_id) in btfgen_find_cands() argument
2312 local_cand.id = local_id; in btfgen_find_cands()
2314 local_type = btf__type_by_id(local_btf, local_id); in btfgen_find_cands()
/linux-6.15/include/net/bluetooth/
H A Dl2cap.h584 __u8 local_id; member
/linux-6.15/drivers/media/v4l2-core/
H A Dv4l2-fwnode.c609 link->local_id = fwep.id; in v4l2_fwnode_parse_link()

12