arch/arm/mach-davinci/common.c
45
for (i = 0, dip = soc_info->ids; i < soc_info->ids_num;
arch/arm/mach-davinci/common.h
38
struct davinci_id *ids;
arch/arm/mach-davinci/da850.c
349
.ids = da850_ids,
arch/arm/mach-rpc/ecard.c
1027
ecard_match_device(const struct ecard_id *ids, struct expansion_card *ec)
arch/arm/mach-rpc/ecard.c
1031
for (i = 0; ids[i].manufacturer != 65535; i++)
arch/arm/mach-rpc/ecard.c
1032
if (ec->cid.manufacturer == ids[i].manufacturer &&
arch/arm/mach-rpc/ecard.c
1033
ec->cid.product == ids[i].product)
arch/arm/mach-rpc/ecard.c
1034
return ids + i;
arch/mips/sgi-ip22/ip22-gio.c
46
const struct gio_device_id *ids;
arch/mips/sgi-ip22/ip22-gio.c
48
for (ids = match; ids->id != 0xff; ids++)
arch/mips/sgi-ip22/ip22-gio.c
49
if (ids->id == dev->id.id)
arch/mips/sgi-ip22/ip22-gio.c
50
return ids;
arch/parisc/kernel/drivers.c
100
const struct parisc_device_id *ids;
arch/parisc/kernel/drivers.c
102
for (ids = driver->id_table; ids->sversion; ids++) {
arch/parisc/kernel/drivers.c
103
if ((ids->sversion != SVERSION_ANY_ID) &&
arch/parisc/kernel/drivers.c
104
(ids->sversion != dev->id.sversion))
arch/parisc/kernel/drivers.c
107
if ((ids->hw_type != HWTYPE_ANY_ID) &&
arch/parisc/kernel/drivers.c
108
(ids->hw_type != dev->id.hw_type))
arch/parisc/kernel/drivers.c
111
if ((ids->hversion != HVERSION_ANY_ID) &&
arch/parisc/kernel/drivers.c
112
(ids->hversion != dev->id.hversion))
arch/powerpc/kernel/secure_boot.c
14
static const struct of_device_id ids[] = {
arch/powerpc/kernel/secure_boot.c
21
return of_find_matching_node(NULL, ids);
arch/powerpc/kvm/book3s_hv_nestedv2.c
37
u16 ids[] = {
arch/powerpc/kvm/book3s_hv_nestedv2.c
45
for (int i = 0; i < ARRAY_SIZE(ids); i++)
arch/powerpc/kvm/book3s_hv_nestedv2.c
46
size += kvmppc_gse_total_size(kvmppc_gsid_size(ids[i]));
arch/powerpc/kvm/test-guest-state-buffer.c
223
u16 ids[] = {
arch/powerpc/kvm/test-guest-state-buffer.c
231
for (int i = 0; i < ARRAY_SIZE(ids); i++)
arch/powerpc/kvm/test-guest-state-buffer.c
232
size += kvmppc_gse_total_size(kvmppc_gsid_size(ids[i]));
arch/powerpc/kvm/test-guest-state-buffer.c
336
u16 ids[] = {
arch/powerpc/kvm/test-guest-state-buffer.c
344
for (int i = 0; i < ARRAY_SIZE(ids); i++)
arch/powerpc/kvm/test-guest-state-buffer.c
345
size += kvmppc_gse_total_size(kvmppc_gsid_size(ids[i]));
arch/powerpc/perf/kvm-hv-pmu.c
218
const u16 ids[] = {
arch/powerpc/perf/kvm-hv-pmu.c
226
for (int i = 0; i < ARRAY_SIZE(ids); i++)
arch/powerpc/perf/kvm-hv-pmu.c
227
size += kvmppc_gse_total_size(kvmppc_gsid_size(ids[i]));
arch/powerpc/platforms/pseries/vio.c
1205
const struct vio_device_id *ids, const struct vio_dev *dev)
arch/powerpc/platforms/pseries/vio.c
1207
while (ids->type[0] != '\0') {
arch/powerpc/platforms/pseries/vio.c
1208
if ((strncmp(dev->type, ids->type, strlen(ids->type)) == 0) &&
arch/powerpc/platforms/pseries/vio.c
1210
ids->compat))
arch/powerpc/platforms/pseries/vio.c
1211
return ids;
arch/powerpc/platforms/pseries/vio.c
1212
ids++;
arch/powerpc/platforms/pseries/vio.c
1582
const struct vio_device_id *ids = vio_drv->id_table;
arch/powerpc/platforms/pseries/vio.c
1584
return (ids != NULL) && (vio_match_device(ids, vio_dev) != NULL);
arch/s390/include/asm/ccwdev.h
136
struct ccw_device_id *ids;
arch/um/drivers/virtio_uml.c
1316
const char *ids = strchr(device, ':');
arch/um/drivers/virtio_uml.c
1323
if (!ids || ids == device)
arch/um/drivers/virtio_uml.c
1328
processed = sscanf(ids, ":%u%n:%d%n",
arch/um/drivers/virtio_uml.c
1332
if (processed < 1 || ids[consumed])
arch/um/drivers/virtio_uml.c
1345
socket_path = kmemdup_nul(device, ids - device, GFP_KERNEL);
arch/x86/events/intel/uncore.c
1124
uncore_pci_find_dev_pmu(struct pci_dev *pdev, const struct pci_device_id *ids)
arch/x86/events/intel/uncore.c
1131
if (!ids)
arch/x86/events/intel/uncore.c
1134
while (ids && ids->vendor) {
arch/x86/events/intel/uncore.c
1135
if ((ids->vendor == pdev->vendor) &&
arch/x86/events/intel/uncore.c
1136
(ids->device == pdev->device)) {
arch/x86/events/intel/uncore.c
1137
data = ids->driver_data;
arch/x86/events/intel/uncore.c
1146
ids++;
arch/x86/events/intel/uncore.c
1288
const struct pci_device_id *ids)
arch/x86/events/intel/uncore.c
1299
pmu = uncore_pci_find_dev_pmu(pdev, ids);
arch/x86/events/intel/uncore.c
1324
const struct pci_device_id *ids = uncore_pci_sub_driver->id_table;
arch/x86/events/intel/uncore.c
1332
while (ids && ids->vendor) {
arch/x86/events/intel/uncore.c
1334
type = uncore_pci_uncores[UNCORE_PCI_DEV_TYPE(ids->driver_data)];
arch/x86/events/intel/uncore.c
1340
ids->device, pci_sub_dev))) {
arch/x86/events/intel/uncore.c
1341
devfn = PCI_DEVFN(UNCORE_PCI_DEV_DEV(ids->driver_data),
arch/x86/events/intel/uncore.c
1342
UNCORE_PCI_DEV_FUNC(ids->driver_data));
arch/x86/events/intel/uncore.c
1346
pmu = &type->pmus[UNCORE_PCI_DEV_IDX(ids->driver_data)];
arch/x86/events/intel/uncore.c
1355
ids++;
arch/x86/events/intel/uncore_snb.c
1515
const struct pci_device_id *ids = tgl_uncore_pci_ids;
arch/x86/events/intel/uncore_snb.c
1518
while (ids && ids->vendor) {
arch/x86/events/intel/uncore_snb.c
1519
mc_dev = pci_get_device(PCI_VENDOR_ID_INTEL, ids->device, NULL);
arch/x86/events/intel/uncore_snb.c
1522
ids++;
drivers/accel/habanalabs/common/habanalabs_drv.c
68
static const struct pci_device_id ids[] = {
drivers/accel/habanalabs/common/habanalabs_drv.c
724
.id_table = ids,
drivers/accel/habanalabs/common/habanalabs_drv.c
75
MODULE_DEVICE_TABLE(pci, ids);
drivers/acpi/acpi_apd.c
273
.ids = acpi_apd_device_ids,
drivers/acpi/acpi_memhotplug.c
35
.ids = memory_device_ids,
drivers/acpi/acpi_memhotplug.c
359
.ids = memory_device_ids,
drivers/acpi/acpi_pnp.c
349
.ids = acpi_pnp_device_ids,
drivers/acpi/acpi_processor.c
641
.ids = processor_device_ids,
drivers/acpi/acpi_processor.c
663
.ids = processor_container_ids,
drivers/acpi/acpi_video.c
1096
struct acpi_video_enumerated_device *ids;
drivers/acpi/acpi_video.c
1100
ids = &video->attached_array[i];
drivers/acpi/acpi_video.c
1101
if ((ids->value.int_val & 0xffff) == device_id)
drivers/acpi/acpi_video.c
1102
return &ids->value.attrib;
drivers/acpi/acpi_video.c
1112
struct acpi_video_enumerated_device *ids;
drivers/acpi/acpi_video.c
1116
ids = &video->attached_array[i];
drivers/acpi/acpi_video.c
1117
if ((ids->value.int_val & 0xffff) == device_id)
drivers/acpi/acpi_video.c
1118
return ids->value.int_val;
drivers/acpi/acpi_video.c
1245
struct acpi_video_enumerated_device *ids;
drivers/acpi/acpi_video.c
1249
ids = &video->attached_array[i];
drivers/acpi/acpi_video.c
1250
if (device->device_id == (ids->value.int_val & 0xffff)) {
drivers/acpi/acpi_video.c
1251
ids->bind_info = device;
drivers/acpi/acpica/dbdisply.c
632
info->compatible_id_list.ids[i].string);
drivers/acpi/acpica/dbnames.c
1010
info->compatible_id_list.ids[i].string);
drivers/acpi/acpica/evrgnini.c
345
if (acpi_ut_is_pci_root_bridge(cid->ids[i].string)) {
drivers/acpi/acpica/nsxfeval.c
705
if (strcmp(cid->ids[i].string, info->hid) == 0) {
drivers/acpi/acpica/nsxfname.c
379
next_id_string = ACPI_CAST_PTR(char, info->compatible_id_list.ids);
drivers/acpi/acpica/nsxfname.c
418
ids[i], &cid_list->ids[i],
drivers/acpi/acpica/nsxfname.c
421
if (acpi_ut_is_pci_root_bridge(cid_list->ids[i].string)) {
drivers/acpi/acpica/utids.c
276
next_id_string = ACPI_CAST_PTR(char, cid_list->ids) +
drivers/acpi/acpica/utids.c
296
cid_list->ids[i].string = next_id_string;
drivers/acpi/acpica/utids.c
297
cid_list->ids[i].length = length;
drivers/acpi/arm64/amba.c
109
.ids = amba_id_list,
drivers/acpi/arm64/iort.c
1092
if (fwspec->ids[i] >= id_start &&
drivers/acpi/arm64/iort.c
1093
fwspec->ids[i] <= id_start + id_count)
drivers/acpi/arm64/iort.c
1254
fwspec->ids[i],
drivers/acpi/bus.c
1019
list_for_each_entry(hwid, &device->pnp.ids, list) {
drivers/acpi/bus.c
1055
const struct acpi_device_id *acpi_match_acpi_device(const struct acpi_device_id *ids,
drivers/acpi/bus.c
1060
__acpi_match_device(adev, ids, NULL, &id, NULL);
drivers/acpi/bus.c
1076
const struct acpi_device_id *acpi_match_device(const struct acpi_device_id *ids,
drivers/acpi/bus.c
1079
return acpi_match_acpi_device(ids, acpi_companion_match(dev));
drivers/acpi/bus.c
1105
const struct acpi_device_id *ids)
drivers/acpi/bus.c
1107
return __acpi_match_device(device, ids, NULL, NULL, NULL) ? 0 : -ENOENT;
drivers/acpi/bus.c
1174
&& !acpi_match_device_ids(acpi_dev, acpi_drv->ids);
drivers/acpi/bus.c
885
if (list_empty(&adev->pnp.ids))
drivers/acpi/container.c
109
.ids = container_device_ids,
drivers/acpi/container.c
91
.ids = container_device_ids,
drivers/acpi/device_sysfs.c
153
list_for_each_entry(id, &acpi_dev->pnp.ids, list)
drivers/acpi/device_sysfs.c
166
list_for_each_entry(id, &acpi_dev->pnp.ids, list) {
drivers/acpi/device_sysfs.c
248
if (list_empty(&adev->pnp.ids))
drivers/acpi/device_sysfs.c
291
if (list_empty(&adev->pnp.ids))
drivers/acpi/device_sysfs.c
422
len += sysfs_emit_at(buf, len, "%s,", cid_list->ids[i].string);
drivers/acpi/device_sysfs.c
424
len += sysfs_emit_at(buf, len, "%s\n", cid_list->ids[i].string);
drivers/acpi/device_sysfs.c
573
return !list_empty(&dev->pnp.ids);
drivers/acpi/pci_link.c
44
.ids = link_device_ids,
drivers/acpi/pci_root.c
48
.ids = root_device_ids,
drivers/acpi/property.c
602
list_for_each_entry(hwid, &adev->pnp.ids, list) {
drivers/acpi/scan.c
1244
list_for_each_entry(hwid, &adev->pnp.ids, list)
drivers/acpi/scan.c
1323
hid = list_first_entry_or_null(&device->pnp.ids, struct acpi_hardware_id, list);
drivers/acpi/scan.c
1345
list_add_tail(&id->list, &pnp->ids);
drivers/acpi/scan.c
1417
acpi_add_id(pnp, cid_list->ids[i].string);
drivers/acpi/scan.c
1446
else if (list_empty(&pnp->ids) &&
drivers/acpi/scan.c
1481
list_for_each_entry_safe(id, tmp, &pnp->ids, list) {
drivers/acpi/scan.c
1811
INIT_LIST_HEAD(&device->pnp.ids);
drivers/acpi/scan.c
1974
for (devid = handler->ids; devid->id[0]; devid++)
drivers/acpi/scan.c
2060
list_for_each_entry(hwid, &adev->pnp.ids, list) {
drivers/acpi/scan.c
2305
.ids = generic_device_ids,
drivers/acpi/scan.c
2314
list_for_each_entry(hwid, &device->pnp.ids, list) {
drivers/acpi/scan.c
820
const char * const ids[])
drivers/acpi/scan.c
828
index = match_string(ids, -1, info->hardware_id.string);
drivers/acpi/scan.c
839
index = match_string(ids, -1, cid_list->ids[i].string);
drivers/acpi/x86/cmos_rtc.c
99
.ids = acpi_cmos_rtc_ids,
drivers/acpi/x86/lpss.c
1318
.ids = acpi_lpss_device_ids,
drivers/acpi/x86/lpss.c
1344
.ids = acpi_lpss_device_ids,
drivers/acpi/x86/s2idle.c
514
.ids = lps0_device_ids,
drivers/block/xen-blkback/xenbus.c
1160
.ids = xen_blkbk_ids,
drivers/block/xen-blkfront.c
2520
.ids = blkfront_ids,
drivers/cdx/cdx.c
211
cdx_match_id(const struct cdx_device_id *ids, struct cdx_device *dev)
drivers/cdx/cdx.c
213
if (ids) {
drivers/cdx/cdx.c
214
while (ids->vendor || ids->device) {
drivers/cdx/cdx.c
215
if (cdx_match_one_device(ids, dev))
drivers/cdx/cdx.c
216
return ids;
drivers/cdx/cdx.c
217
ids++;
drivers/cdx/cdx.c
268
const struct cdx_device_id *ids;
drivers/cdx/cdx.c
274
ids = cdx_drv->match_id_table;
drivers/cdx/cdx.c
281
found_id = cdx_match_id(ids, cdx_dev);
drivers/cdx/cdx.c
295
ids = found_id + 1;
drivers/cdx/cdx.c
296
found_id = cdx_match_id(ids, cdx_dev);
drivers/char/tpm/tpm_tis.c
109
list_for_each_entry(id, &dev->pnp.ids, list)
drivers/char/tpm/xen-tpmfront.c
415
.ids = tpmfront_ids,
drivers/clk/renesas/renesas-cpg-mssr.c
1184
unsigned int *ids = NULL;
drivers/clk/renesas/renesas-cpg-mssr.c
1223
new_ids = krealloc_array(ids, (num + 1), sizeof(*ids), GFP_KERNEL);
drivers/clk/renesas/renesas-cpg-mssr.c
1226
kfree(ids);
drivers/clk/renesas/renesas-cpg-mssr.c
1229
ids = new_ids;
drivers/clk/renesas/renesas-cpg-mssr.c
1236
ids[num] = info->num_total_core_clks + idx;
drivers/clk/renesas/renesas-cpg-mssr.c
1243
priv->reserved_ids = ids;
drivers/crypto/ccp/sev-dev-tio.c
807
int sev_tio_dev_connect(struct tsm_dsm_tio *dev_data, u8 tc_mask, u8 ids[8], u8 cert_slot)
drivers/crypto/ccp/sev-dev-tio.c
815
ids[0], ids[1], ids[2], ids[3],
drivers/crypto/ccp/sev-dev-tio.c
816
ids[4], ids[5], ids[6], ids[7]
drivers/crypto/ccp/sev-dev-tio.h
119
int sev_tio_dev_connect(struct tsm_dsm_tio *dev_data, u8 tc_mask, u8 ids[8], u8 cert_slot);
drivers/crypto/ccp/sev-dev-tsm.c
119
static u8 streams_setup(struct pci_ide **ide, u8 *ids)
drivers/crypto/ccp/sev-dev-tsm.c
127
ids[i] = 0xFF;
drivers/crypto/ccp/sev-dev-tsm.c
132
ids[i] = ide[i]->stream_id;
drivers/crypto/ccp/sev-dev-tsm.c
277
u8 ids[TIO_IDE_MAX_TC];
drivers/crypto/ccp/sev-dev-tsm.c
295
tc_mask = streams_setup(dev_data->ide, ids);
drivers/crypto/ccp/sev-dev-tsm.c
297
ret = sev_tio_dev_connect(dev_data, tc_mask, ids, dev_data->cert_slot);
drivers/dax/bus.c
115
list_add(&dax_id->list, &dax_drv->ids);
drivers/dax/bus.c
1592
INIT_LIST_HEAD(&dax_drv->ids);
drivers/dax/bus.c
1608
list_for_each_entry_safe(dax_id, _id, &dax_drv->ids, list) {
drivers/dax/bus.c
50
list_for_each_entry(dax_id, &dax_drv->ids, list)
drivers/dax/bus.h
41
struct list_head ids;
drivers/dio/dio-driver.c
117
const struct dio_device_id *ids = dio_drv->id_table;
drivers/dio/dio-driver.c
119
if (!ids)
drivers/dio/dio-driver.c
122
return dio_match_device(ids, d) ? 1 : 0;
drivers/dio/dio-driver.c
29
dio_match_device(const struct dio_device_id *ids,
drivers/dio/dio-driver.c
32
while (ids->id) {
drivers/dio/dio-driver.c
33
if (ids->id == DIO_WILDCARD)
drivers/dio/dio-driver.c
34
return ids;
drivers/dio/dio-driver.c
35
if (DIO_NEEDSSECID(ids->id & 0xff)) {
drivers/dio/dio-driver.c
36
if (ids->id == d->id)
drivers/dio/dio-driver.c
37
return ids;
drivers/dio/dio-driver.c
39
if ((ids->id & 0xff) == (d->id & 0xff))
drivers/dio/dio-driver.c
40
return ids;
drivers/dio/dio-driver.c
42
ids++;
drivers/firewire/device-attribute-test.c
103
int ids[4] = {0, 0, 0, 0};
drivers/firewire/device-attribute-test.c
160
get_modalias_ids(&unit0, ids);
drivers/firewire/device-attribute-test.c
161
KUNIT_EXPECT_MEMEQ(test, ids, unit0_expected_ids, sizeof(ids));
drivers/firewire/device-attribute-test.c
185
int ids[4] = {0, 0, 0, 0};
drivers/firewire/device-attribute-test.c
239
get_modalias_ids(&unit0, ids);
drivers/firewire/device-attribute-test.c
240
KUNIT_EXPECT_MEMEQ(test, ids, unit0_expected_ids, sizeof(ids));
drivers/fpga/dfl.c
543
const struct dfl_feature_id *ids = driver->id_table;
drivers/fpga/dfl.c
545
if (ids) {
drivers/fpga/dfl.c
546
while (ids->id) {
drivers/fpga/dfl.c
547
if (ids->id == feature->id)
drivers/fpga/dfl.c
549
ids++;
drivers/gpio/gpio-virtuser.c
1432
char **ids __free(kfree) = kcalloc(num_ids + 1, sizeof(*ids),
drivers/gpio/gpio-virtuser.c
1434
if (!ids)
drivers/gpio/gpio-virtuser.c
1438
ids[i++] = lookup->con_id;
drivers/gpio/gpio-virtuser.c
1441
ids, num_ids);
drivers/gpio/gpio-virtuser.c
870
static int gpio_virtuser_get_ids(struct device *dev, const char **ids,
drivers/gpio/gpio-virtuser.c
881
ids, num_ids);
drivers/gpio/gpio-virtuser.c
896
ids[pos++] = tmp;
drivers/gpio/gpio-virtuser.c
908
const char **ids;
drivers/gpio/gpio-virtuser.c
919
ids = devm_kcalloc(dev, num_ids, sizeof(*ids), GFP_KERNEL);
drivers/gpio/gpio-virtuser.c
920
if (!ids)
drivers/gpio/gpio-virtuser.c
923
ret = gpio_virtuser_get_ids(dev, ids, num_ids);
drivers/gpio/gpio-virtuser.c
935
descs = devm_gpiod_get_array(dev, ids[i], GPIOD_ASIS);
drivers/gpio/gpio-virtuser.c
939
ids[i]);
drivers/gpio/gpio-virtuser.c
942
ids[i],
drivers/gpio/gpio-virtuser.c
947
ids[i]);
drivers/gpio/gpio-virtuser.c
951
descs->desc[j], ids[i],
drivers/gpio/gpio-virtuser.c
956
ids[i]);
drivers/gpu/drm/amd/amdgpu/amdgpu_ids.c
432
job->vmid = id - id_mgr->ids;
drivers/gpu/drm/amd/amdgpu/amdgpu_ids.c
534
struct amdgpu_vmid *id = &id_mgr->ids[vmid];
drivers/gpu/drm/amd/amdgpu/amdgpu_ids.c
599
amdgpu_sync_create(&id_mgr->ids[j].active);
drivers/gpu/drm/amd/amdgpu/amdgpu_ids.c
600
list_add_tail(&id_mgr->ids[j].list, &id_mgr->ids_lru);
drivers/gpu/drm/amd/amdgpu/amdgpu_ids.c
622
struct amdgpu_vmid *id = &id_mgr->ids[j];
drivers/gpu/drm/amd/amdgpu/amdgpu_ids.h
69
struct amdgpu_vmid ids[AMDGPU_NUM_VMID];
drivers/gpu/drm/amd/amdgpu/amdgpu_vm.c
757
if (amdgpu_vmid_had_gpu_reset(adev, &id_mgr->ids[job->vmid]))
drivers/gpu/drm/amd/amdgpu/amdgpu_vm.c
779
struct amdgpu_vmid *id = &id_mgr->ids[job->vmid];
drivers/gpu/drm/i915/display/intel_display_device.c
1437
static const struct pci_device_id ids[] = {
drivers/gpu/drm/i915/display/intel_display_device.c
1442
return pci_match_id(ids, pdev);
drivers/gpu/drm/i915/i915_query.c
400
u64 *ids;
drivers/gpu/drm/i915/i915_query.c
403
ids = krealloc(oa_config_ids,
drivers/gpu/drm/i915/i915_query.c
406
if (!ids)
drivers/gpu/drm/i915/i915_query.c
411
ids[n_configs++] = 1ull; /* reserved for test_config */
drivers/gpu/drm/i915/i915_query.c
415
ids[n_configs] = id;
drivers/gpu/drm/i915/i915_query.c
420
oa_config_ids = ids;
drivers/gpu/drm/nouveau/nvkm/subdev/i2c/base.c
267
int ret, i, ids;
drivers/gpu/drm/nouveau/nvkm/subdev/i2c/base.c
410
ids = 0;
drivers/gpu/drm/nouveau/nvkm/subdev/i2c/base.c
412
ids = max(ids, aux->id + 1);
drivers/gpu/drm/nouveau/nvkm/subdev/i2c/base.c
413
if (!ids)
drivers/gpu/drm/nouveau/nvkm/subdev/i2c/base.c
416
return nvkm_event_init(&nvkm_i2c_intr_func, &i2c->subdev, 4, ids, &i2c->event);
drivers/gpu/drm/panel/panel-sitronix-st7789v.c
215
u8 ids[3];
drivers/gpu/drm/panel/panel-sitronix-st7789v.c
220
ret = st7789v_read_data(ctx, MIPI_DCS_GET_DISPLAY_ID, ids, ST7789V_IDS_SIZE);
drivers/gpu/drm/panel/panel-sitronix-st7789v.c
225
if (ids[i] != st7789v_ids[i]) {
drivers/gpu/drm/radeon/cik.c
3722
unsigned vm_id = ib->vm ? ib->vm->ids[ib->ring].id : 0;
drivers/gpu/drm/radeon/cik_sdma.c
136
u32 extra_bits = (ib->vm ? ib->vm->ids[ib->ring].id : 0) & 0xf;
drivers/gpu/drm/radeon/ni.c
1402
unsigned vm_id = ib->vm ? ib->vm->ids[ib->ring].id : 0;
drivers/gpu/drm/radeon/ni_dma.c
125
unsigned vm_id = ib->vm ? ib->vm->ids[ib->ring].id : 0;
drivers/gpu/drm/radeon/radeon.h
902
struct radeon_vm_id ids[RADEON_NUM_RINGS];
drivers/gpu/drm/radeon/radeon_vm.c
1005
radeon_sync_fence(&ib.sync, vm->ids[i].last_id_use);
drivers/gpu/drm/radeon/radeon_vm.c
1179
vm->ids[i].id = 0;
drivers/gpu/drm/radeon/radeon_vm.c
1180
vm->ids[i].flushed_updates = NULL;
drivers/gpu/drm/radeon/radeon_vm.c
1181
vm->ids[i].last_id_use = NULL;
drivers/gpu/drm/radeon/radeon_vm.c
1262
radeon_fence_unref(&vm->ids[i].flushed_updates);
drivers/gpu/drm/radeon/radeon_vm.c
1263
radeon_fence_unref(&vm->ids[i].last_id_use);
drivers/gpu/drm/radeon/radeon_vm.c
179
struct radeon_vm_id *vm_id = &vm->ids[ring];
drivers/gpu/drm/radeon/radeon_vm.c
239
struct radeon_vm_id *vm_id = &vm->ids[ring];
drivers/gpu/drm/radeon/radeon_vm.c
244
trace_radeon_vm_flush(pd_addr, ring, vm->ids[ring].id);
drivers/gpu/drm/radeon/radeon_vm.c
270
unsigned vm_id = vm->ids[fence->ring].id;
drivers/gpu/drm/radeon/radeon_vm.c
275
radeon_fence_unref(&vm->ids[fence->ring].last_id_use);
drivers/gpu/drm/radeon/radeon_vm.c
276
vm->ids[fence->ring].last_id_use = radeon_fence_ref(fence);
drivers/gpu/drm/radeon/si.c
3383
unsigned vm_id = ib->vm ? ib->vm->ids[ib->ring].id : 0;
drivers/gpu/drm/v3d/v3d_submit.c
703
u64 ids;
drivers/gpu/drm/v3d/v3d_submit.c
710
if (get_user(ids, kperfmon_ids++)) {
drivers/gpu/drm/v3d/v3d_submit.c
724
ids_pointer = u64_to_user_ptr(ids);
drivers/gpu/drm/xe/tests/xe_pci.c
87
const struct pci_device_id *ids;
drivers/gpu/drm/xe/tests/xe_pci.c
89
for (ids = pciidlist; ids->driver_data; ids++) {
drivers/gpu/drm/xe/tests/xe_pci.c
90
desc = (const void *)ids->driver_data;
drivers/gpu/drm/xe/xe_configfs.c
967
const struct pci_device_id *ids = drv ? drv->id_table : NULL;
drivers/gpu/drm/xe/xe_configfs.c
968
const struct pci_device_id *found = pci_match_id(ids, pdev);
drivers/gpu/drm/xen/xen_drm_front.c
753
.ids = xen_driver_ids,
drivers/hwtracing/stm/core.c
1003
char *ids[] = { NULL, "default", NULL };
drivers/hwtracing/stm/core.c
1018
ids[0] = kstrdup(src->data->name, GFP_KERNEL);
drivers/hwtracing/stm/core.c
1019
if (!ids[0])
drivers/hwtracing/stm/core.c
1022
err = stm_assign_first_policy(stm, &src->output, ids,
drivers/hwtracing/stm/core.c
1024
kfree(ids[0]);
drivers/hwtracing/stm/core.c
543
char **ids, unsigned int width)
drivers/hwtracing/stm/core.c
554
for (n = 0, pn = NULL; ids[n] && !pn; n++)
drivers/hwtracing/stm/core.c
555
pn = stp_policy_node_lookup(stm, ids[n]);
drivers/hwtracing/stm/core.c
635
char *ids[] = { comm, "default", NULL };
drivers/hwtracing/stm/core.c
639
err = stm_assign_first_policy(stmf->stm, &stmf->output, ids, 1);
drivers/hwtracing/stm/core.c
740
char *ids[] = { NULL, NULL };
drivers/hwtracing/stm/core.c
775
ids[0] = id->id;
drivers/hwtracing/stm/core.c
776
ret = stm_assign_first_policy(stmf->stm, &stmf->output, ids,
drivers/iio/adc/ad4030.c
1270
static const char * const ids[] = { "vdd-5v", "vdd-1v8" };
drivers/iio/adc/ad4030.c
1273
ret = devm_regulator_bulk_get_enable(dev, ARRAY_SIZE(ids), ids);
drivers/iio/adc/mcp3564.c
1111
enum mcp3564_ids ids;
drivers/iio/adc/mcp3564.c
1161
ids = mcp3461r;
drivers/iio/adc/mcp3564.c
1163
ids = mcp3461;
drivers/iio/adc/mcp3564.c
1167
ids = mcp3462r;
drivers/iio/adc/mcp3564.c
1169
ids = mcp3462;
drivers/iio/adc/mcp3564.c
1173
ids = mcp3464r;
drivers/iio/adc/mcp3564.c
1175
ids = mcp3464;
drivers/iio/adc/mcp3564.c
1179
ids = mcp3561r;
drivers/iio/adc/mcp3564.c
1181
ids = mcp3561;
drivers/iio/adc/mcp3564.c
1185
ids = mcp3562r;
drivers/iio/adc/mcp3564.c
1187
ids = mcp3562;
drivers/iio/adc/mcp3564.c
1191
ids = mcp3564r;
drivers/iio/adc/mcp3564.c
1193
ids = mcp3564;
drivers/iio/adc/mcp3564.c
1209
adc->chip_info = &mcp3564_chip_infos_tbl[ids];
drivers/infiniband/core/uverbs_ioctl.c
168
val_spec = &spec->u2.enum_def.ids[uattr->attr_data.enum_data.elem_id];
drivers/infiniband/core/uverbs_uapi.c
746
elm->spec.u2.enum_def.ids = NULL;
drivers/infiniband/hw/hfi1/affinity.c
121
const struct pci_device_id *ids = hfi1_pci_tbl;
drivers/infiniband/hw/hfi1/affinity.c
147
while (ids->vendor) {
drivers/infiniband/hw/hfi1/affinity.c
149
while ((dev = pci_get_device(ids->vendor, ids->device, dev))) {
drivers/infiniband/hw/hfi1/affinity.c
156
ids++;
drivers/infiniband/ulp/srp/ib_srp.c
3130
struct srp_rport_identifiers ids;
drivers/infiniband/ulp/srp/ib_srp.c
3140
memcpy(ids.port_id, &target->id_ext, 8);
drivers/infiniband/ulp/srp/ib_srp.c
3141
memcpy(ids.port_id + 8, &target->ioc_guid, 8);
drivers/infiniband/ulp/srp/ib_srp.c
3142
ids.roles = SRP_RPORT_ROLE_TARGET;
drivers/infiniband/ulp/srp/ib_srp.c
3143
rport = srp_rport_add(target->scsi_host, &ids);
drivers/input/misc/xen-kbdfront.c
539
.ids = xenkbd_ids,
drivers/input/mouse/psmouse-base.c
487
static bool psmouse_check_pnp_id(const char *id, const char * const ids[])
drivers/input/mouse/psmouse-base.c
491
for (i = 0; ids[i]; i++)
drivers/input/mouse/psmouse-base.c
492
if (!strcasecmp(id, ids[i]))
drivers/input/mouse/psmouse-base.c
501
bool psmouse_matches_pnp_id(struct psmouse *psmouse, const char * const ids[])
drivers/input/mouse/psmouse-base.c
518
if (psmouse_check_pnp_id(p, ids)) {
drivers/input/mouse/psmouse.h
141
bool psmouse_matches_pnp_id(struct psmouse *psmouse, const char * const ids[]);
drivers/input/serio/serio.c
65
static int serio_match_port(const struct serio_device_id *ids, struct serio *serio)
drivers/input/serio/serio.c
67
while (ids->type || ids->proto) {
drivers/input/serio/serio.c
68
if ((ids->type == SERIO_ANY || ids->type == serio->id.type) &&
drivers/input/serio/serio.c
69
(ids->proto == SERIO_ANY || ids->proto == serio->id.proto) &&
drivers/input/serio/serio.c
70
(ids->extra == SERIO_ANY || ids->extra == serio->id.extra) &&
drivers/input/serio/serio.c
71
(ids->id == SERIO_ANY || ids->id == serio->id.id))
drivers/input/serio/serio.c
73
ids++;
drivers/input/touchscreen/cyttsp5.c
295
DECLARE_BITMAP(ids, MAX_CY_TCH_T_IDS);
drivers/input/touchscreen/cyttsp5.c
299
bitmap_zero(ids, MAX_CY_TCH_T_IDS);
drivers/input/touchscreen/cyttsp5.c
324
__set_bit(t, ids);
drivers/input/touchscreen/cyttsp_core.c
290
static void cyttsp_extract_track_ids(struct cyttsp_xydata *xy_data, int *ids)
drivers/input/touchscreen/cyttsp_core.c
292
ids[0] = xy_data->touch12_id >> 4;
drivers/input/touchscreen/cyttsp_core.c
293
ids[1] = xy_data->touch12_id & 0xF;
drivers/input/touchscreen/cyttsp_core.c
294
ids[2] = xy_data->touch34_id >> 4;
drivers/input/touchscreen/cyttsp_core.c
295
ids[3] = xy_data->touch34_id & 0xF;
drivers/input/touchscreen/cyttsp_core.c
321
int ids[CY_MAX_ID];
drivers/input/touchscreen/cyttsp_core.c
339
cyttsp_extract_track_ids(xy_data, ids);
drivers/input/touchscreen/cyttsp_core.c
346
input_mt_slot(input, ids[i]);
drivers/input/touchscreen/cyttsp_core.c
352
__set_bit(ids[i], used);
drivers/input/touchscreen/pixcir_i2c_ts.c
139
report->ids[i] = bufptr[4];
drivers/input/touchscreen/pixcir_i2c_ts.c
165
report->ids[i]);
drivers/input/touchscreen/pixcir_i2c_ts.c
168
report->ids[i]);
drivers/input/touchscreen/pixcir_i2c_ts.c
90
int ids[PIXCIR_MAX_SLOTS];
drivers/iommu/arm/arm-smmu-v3/arm-smmu-v3-test.c
643
const int *ids, const int *users,
drivers/iommu/arm/arm-smmu-v3/arm-smmu-v3-test.c
649
KUNIT_EXPECT_EQ(test, invs->inv[num_invs].id, ids[num_invs]);
drivers/iommu/arm/arm-smmu-v3/arm-smmu-v3.c
4045
new_stream->id = fwspec->ids[i];
drivers/iommu/arm/arm-smmu/arm-smmu-qcom.c
233
u16 sid = FIELD_GET(ARM_SMMU_SMR_ID, fwspec->ids[i]);
drivers/iommu/arm/arm-smmu/arm-smmu.c
1096
u16 sid = FIELD_GET(ARM_SMMU_SMR_ID, fwspec->ids[i]);
drivers/iommu/arm/arm-smmu/arm-smmu.c
1097
u16 mask = FIELD_GET(ARM_SMMU_SMR_MASK, fwspec->ids[i]);
drivers/iommu/arm/arm-smmu/arm-smmu.c
1458
u16 sid = FIELD_GET(ARM_SMMU_SMR_ID, fwspec->ids[i]);
drivers/iommu/arm/arm-smmu/arm-smmu.c
1459
u16 mask = FIELD_GET(ARM_SMMU_SMR_MASK, fwspec->ids[i]);
drivers/iommu/arm/arm-smmu/qcom_iommu.c
121
struct qcom_iommu_ctx *ctx = to_ctx(qcom_domain, fwspec->ids[i]);
drivers/iommu/arm/arm-smmu/qcom_iommu.c
140
struct qcom_iommu_ctx *ctx = to_ctx(qcom_domain, fwspec->ids[i]);
drivers/iommu/arm/arm-smmu/qcom_iommu.c
157
struct qcom_iommu_ctx *ctx = to_ctx(qcom_domain, fwspec->ids[i]);
drivers/iommu/arm/arm-smmu/qcom_iommu.c
253
struct qcom_iommu_ctx *ctx = to_ctx(qcom_domain, fwspec->ids[i]);
drivers/iommu/arm/arm-smmu/qcom_iommu.c
409
struct qcom_iommu_ctx *ctx = to_ctx(qcom_domain, fwspec->ids[i]);
drivers/iommu/iommu.c
3090
fwspec = kzalloc_flex(*fwspec, ids, 1);
drivers/iommu/iommu.c
3112
int iommu_fwspec_add_ids(struct device *dev, const u32 *ids, int num_ids)
drivers/iommu/iommu.c
3122
fwspec = krealloc(fwspec, struct_size(fwspec, ids, new_num),
drivers/iommu/iommu.c
3131
fwspec->ids[fwspec->num_ids + i] = ids[i];
drivers/iommu/ipmmu-vmsa.c
634
ipmmu_utlb_enable(domain, fwspec->ids[i]);
drivers/iommu/ipmmu-vmsa.c
652
ipmmu_utlb_disable(domain, fwspec->ids[i]);
drivers/iommu/ipmmu-vmsa.c
867
unsigned int utlb = fwspec->ids[i];
drivers/iommu/mtk_iommu.c
551
portmsk |= BIT(MTK_M4U_TO_PORT(fwspec->ids[i]));
drivers/iommu/mtk_iommu.c
576
larbid = MTK_M4U_TO_LARB(fwspec->ids[0]);
drivers/iommu/mtk_iommu.c
578
portidmsk |= BIT(MTK_M4U_TO_PORT(fwspec->ids[i]));
drivers/iommu/mtk_iommu.c
606
portid = MTK_M4U_TO_PORT(fwspec->ids[i]);
drivers/iommu/mtk_iommu.c
612
larbid = MTK_M4U_TO_LARB(fwspec->ids[0]);
drivers/iommu/mtk_iommu.c
895
larbid = MTK_M4U_TO_LARB(fwspec->ids[0]);
drivers/iommu/mtk_iommu.c
902
larbidx = MTK_M4U_TO_LARB(fwspec->ids[i]);
drivers/iommu/mtk_iommu.c
949
larbid = MTK_M4U_TO_LARB(fwspec->ids[i]);
drivers/iommu/mtk_iommu_v1.c
251
larbid = mt2701_m4u_to_larb(fwspec->ids[i]);
drivers/iommu/mtk_iommu_v1.c
252
portid = mt2701_m4u_to_port(fwspec->ids[i]);
drivers/iommu/mtk_iommu_v1.c
492
larbid = mt2701_m4u_to_larb(fwspec->ids[0]);
drivers/iommu/mtk_iommu_v1.c
497
larbidx = mt2701_m4u_to_larb(fwspec->ids[idx]);
drivers/iommu/mtk_iommu_v1.c
535
larbid = mt2701_m4u_to_larb(fwspec->ids[0]);
drivers/iommu/riscv/iommu.c
1178
dc = riscv_iommu_get_dc(iommu, fwspec->ids[i]);
drivers/iommu/riscv/iommu.c
1187
riscv_iommu_cmd_iodir_set_did(&cmd, fwspec->ids[i]);
drivers/iommu/riscv/iommu.c
1205
dc = riscv_iommu_get_dc(iommu, fwspec->ids[i]);
drivers/iommu/riscv/iommu.c
1217
riscv_iommu_cmd_iodir_set_did(&cmd, fwspec->ids[i]);
drivers/iommu/riscv/iommu.c
1462
dc = riscv_iommu_get_dc(iommu, fwspec->ids[i]);
drivers/iommu/tegra-smmu.c
509
tegra_smmu_enable(smmu, fwspec->ids[index], as->id);
drivers/iommu/tegra-smmu.c
519
tegra_smmu_disable(smmu, fwspec->ids[index], as->id);
drivers/iommu/tegra-smmu.c
544
tegra_smmu_disable(smmu, fwspec->ids[index], as->id);
drivers/iommu/tegra-smmu.c
920
unsigned int swgroup = fwspec->ids[0];
drivers/iommu/virtio-iommu.c
317
req->endpoint = cpu_to_le32(fwspec->ids[i]);
drivers/iommu/virtio-iommu.c
556
probe->endpoint = cpu_to_le32(fwspec->ids[0]);
drivers/iommu/virtio-iommu.c
835
req.endpoint = cpu_to_le32(fwspec->ids[i]);
drivers/ipack/ipack.c
40
ipack_match_id(const struct ipack_device_id *ids, struct ipack_device *idev)
drivers/ipack/ipack.c
42
if (ids) {
drivers/ipack/ipack.c
43
while (ids->vendor || ids->device) {
drivers/ipack/ipack.c
44
if (ipack_match_one_device(ids, idev))
drivers/ipack/ipack.c
45
return ids;
drivers/ipack/ipack.c
46
ids++;
drivers/irqchip/irq-gic-v3-its.c
2492
u32 *order, u32 ids)
drivers/irqchip/irq-gic-v3-its.c
2503
if ((esz << ids) > (psz * 2)) {
drivers/irqchip/irq-gic-v3-its.c
2519
ids -= ilog2(psz / (int)esz);
drivers/irqchip/irq-gic-v3-its.c
2531
new_order = max_t(u32, get_order(esz << ids), new_order);
drivers/irqchip/irq-gic-v3-its.c
2534
ids = ilog2(PAGE_ORDER_TO_SIZE(new_order) / (int)esz);
drivers/irqchip/irq-gic-v3-its.c
2537
device_ids(its), ids);
drivers/irqchip/irq-gic-v3-its.c
4828
u32 ids;
drivers/irqchip/irq-gic-v3-its.c
4838
ids = ilog2(pre_its_window[1]) - 2;
drivers/irqchip/irq-gic-v3-its.c
4839
if (device_ids(its) > ids)
drivers/irqchip/irq-gic-v3-its.c
4840
FIELD_MODIFY(GITS_TYPER_DEVBITS, &its->typer, ids - 1);
drivers/macintosh/adb.c
472
adb_register(int default_id, int handler_id, struct adb_ids *ids,
drivers/macintosh/adb.c
478
ids->nids = 0;
drivers/macintosh/adb.c
491
ids->id[ids->nids++] = i;
drivers/macintosh/adb.c
495
return ids->nids;
drivers/mcb/mcb-core.c
17
static const struct mcb_device_id *mcb_match_id(const struct mcb_device_id *ids,
drivers/mcb/mcb-core.c
20
if (ids) {
drivers/mcb/mcb-core.c
21
while (ids->device) {
drivers/mcb/mcb-core.c
22
if (ids->device == dev->id)
drivers/mcb/mcb-core.c
23
return ids;
drivers/mcb/mcb-core.c
24
ids++;
drivers/media/pci/ddbridge/ddbridge-core.c
1443
struct ddb_ids *devids = &input->port->dev->link[input->port->lnr].ids;
drivers/media/pci/ddbridge/ddbridge-core.c
1850
link->ids.device == 0x0005) {
drivers/media/pci/ddbridge/ddbridge-core.c
3005
dev->link[0].ids.hwid, dev->link[0].ids.regmapid);
drivers/media/pci/ddbridge/ddbridge-core.c
3013
return sprintf(buf, "0x%08X\n", dev->link[0].ids.hwid);
drivers/media/pci/ddbridge/ddbridge-core.c
3021
return sprintf(buf, "0x%08X\n", dev->link[0].ids.regmapid);
drivers/media/pci/ddbridge/ddbridge-core.c
3039
return sprintf(buf, "%08x\n", dev->link[num].ids.devid);
drivers/media/pci/ddbridge/ddbridge-core.c
3317
if (link->ids.regmapid < 0x00010002)
drivers/media/pci/ddbridge/ddbridge-core.c
395
if (dev->link[0].ids.regmapid >= 0x10003 && !(flags & 1)) {
drivers/media/pci/ddbridge/ddbridge-main.c
188
dev->link[0].ids.vendor = id->vendor;
drivers/media/pci/ddbridge/ddbridge-main.c
189
dev->link[0].ids.device = id->device;
drivers/media/pci/ddbridge/ddbridge-main.c
190
dev->link[0].ids.subvendor = id->subvendor;
drivers/media/pci/ddbridge/ddbridge-main.c
191
dev->link[0].ids.subdevice = pdev->subsystem_device;
drivers/media/pci/ddbridge/ddbridge-main.c
192
dev->link[0].ids.devid = (id->device << 16) | id->vendor;
drivers/media/pci/ddbridge/ddbridge-main.c
215
dev->link[0].ids.hwid = ddbreadl(dev, 0);
drivers/media/pci/ddbridge/ddbridge-main.c
216
dev->link[0].ids.regmapid = ddbreadl(dev, 4);
drivers/media/pci/ddbridge/ddbridge-main.c
219
dev->link[0].ids.hwid, dev->link[0].ids.regmapid);
drivers/media/pci/ddbridge/ddbridge-mci.c
37
if (link->ids.device == 0x0009)
drivers/media/pci/ddbridge/ddbridge-mci.c
46
if (link->ids.device != 0x0009)
drivers/media/pci/ddbridge/ddbridge.h
302
struct ddb_ids ids;
drivers/memstick/core/memstick.c
47
const struct memstick_device_id *ids = ms_drv->id_table;
drivers/memstick/core/memstick.c
49
if (ids) {
drivers/memstick/core/memstick.c
50
while (ids->match_flags) {
drivers/memstick/core/memstick.c
51
if (memstick_dev_match(card, ids))
drivers/memstick/core/memstick.c
53
++ids;
drivers/mfd/mfd-core.c
39
struct acpi_device_id *ids;
drivers/mfd/mfd-core.c
47
if (!acpi_match_device_ids(adev, wd->ids)) {
drivers/mfd/mfd-core.c
77
struct acpi_device_id ids[2] = {};
drivers/mfd/mfd-core.c
80
.ids = ids,
drivers/mfd/mfd-core.c
83
strscpy(ids[0].id, match->pnpid, sizeof(ids[0].id));
drivers/misc/tifm_core.c
46
const struct tifm_device_id *ids = fm_drv->id_table;
drivers/misc/tifm_core.c
48
if (ids) {
drivers/misc/tifm_core.c
49
while (ids->type) {
drivers/misc/tifm_core.c
50
if (tifm_dev_match(sock, ids))
drivers/misc/tifm_core.c
52
++ids;
drivers/mmc/core/sdio_bus.c
100
if (ids) {
drivers/mmc/core/sdio_bus.c
101
while (ids->class || ids->vendor || ids->device) {
drivers/mmc/core/sdio_bus.c
102
if (sdio_match_one(func, ids))
drivers/mmc/core/sdio_bus.c
103
return ids;
drivers/mmc/core/sdio_bus.c
104
ids++;
drivers/mmc/core/sdio_bus.c
96
const struct sdio_device_id *ids;
drivers/mmc/core/sdio_bus.c
98
ids = sdrv->id_table;
drivers/mtd/nand/raw/loongson-nand-controller.c
519
char ids[6];
drivers/mtd/nand/raw/loongson-nand-controller.c
539
op.buf[i] = nand_id.ids[host->data->max_id_cycle - 1 - i];
drivers/mtd/nand/raw/nand_base.c
6532
struct nand_flash_dev *ids)
drivers/mtd/nand/raw/nand_base.c
6539
ret = nand_scan_ident(chip, maxchips, ids);
drivers/mtd/nand/raw/nandsim.c
1906
outb = ns->ids[ns->regs.count];
drivers/mtd/nand/raw/nandsim.c
2313
memcpy(ns->ids, id_bytes, sizeof(ns->ids));
drivers/mtd/nand/raw/nandsim.c
296
u_char ids[8]; /* chip's ID bytes */
drivers/net/dsa/sja1105/sja1105_spi.c
234
u64 ids;
drivers/net/dsa/sja1105/sja1105_spi.c
255
sja1105_unpack(p + 0x1, &status->ids, 29, 29, 4);
drivers/net/dsa/sja1105/sja1105_spi.c
373
if (status.ids == 1) {
drivers/net/ethernet/broadcom/bnxt/bnxt_ethtool.c
1071
int tbl_size, u32 *ids, u32 start,
drivers/net/ethernet/broadcom/bnxt/bnxt_ethtool.c
1087
ids[j++] = fltr->sw_id;
drivers/net/ethernet/chelsio/cxgb4/cxgb4_uld.c
113
unsigned short *ids = rxq_info->rspq_id;
drivers/net/ethernet/chelsio/cxgb4/cxgb4_uld.c
157
if (ids)
drivers/net/ethernet/chelsio/cxgb4/cxgb4_uld.c
158
ids[i] = q->rspq.abs_id;
drivers/net/ethernet/ec_bhf.c
583
.id_table = ids,
drivers/net/ethernet/ec_bhf.c
67
static const struct pci_device_id ids[] = {
drivers/net/ethernet/ec_bhf.c
71
MODULE_DEVICE_TABLE(pci, ids);
drivers/net/ethernet/intel/ice/ice_flow.c
1458
struct ice_prof_id *ids;
drivers/net/ethernet/intel/ice/ice_flow.c
1466
ids = &hw->blk[blk].prof_id;
drivers/net/ethernet/intel/ice/ice_flow.c
1467
prof_id = find_first_zero_bit(ids->id, ids->count);
drivers/net/ethernet/intel/ice/ice_flow.c
1468
if (prof_id >= ids->count)
drivers/net/ethernet/intel/ice/ice_flow.c
1517
set_bit(prof_id, ids->id);
drivers/net/ethernet/mellanox/mlx5/core/diag/en_tc_tracepoint.c
14
ids[i] = entries[i].id;
drivers/net/ethernet/mellanox/mlx5/core/diag/en_tc_tracepoint.c
43
int *ids,
drivers/net/ethernet/mellanox/mlx5/core/diag/en_tc_tracepoint.c
50
if (ids[i] < NUM_FLOW_ACTIONS)
drivers/net/ethernet/mellanox/mlx5/core/diag/en_tc_tracepoint.c
51
trace_seq_printf(p, "%s ", FLOWACT2STR[ids[i]]);
drivers/net/ethernet/mellanox/mlx5/core/diag/en_tc_tracepoint.c
7
void put_ids_to_array(int *ids,
drivers/net/ethernet/mellanox/mlx5/core/diag/en_tc_tracepoint.h
15
#define __parse_action(ids, num) parse_action(p, ids, num)
drivers/net/ethernet/mellanox/mlx5/core/diag/en_tc_tracepoint.h
17
void put_ids_to_array(int *ids,
drivers/net/ethernet/mellanox/mlx5/core/diag/en_tc_tracepoint.h
22
int *ids,
drivers/net/ethernet/mellanox/mlx5/core/diag/en_tc_tracepoint.h
30
__dynamic_array(int, ids, f->rule ?
drivers/net/ethernet/mellanox/mlx5/core/diag/en_tc_tracepoint.h
37
put_ids_to_array(__get_dynamic_array(ids),
drivers/net/ethernet/mellanox/mlx5/core/diag/en_tc_tracepoint.h
43
__parse_action(__get_dynamic_array(ids),
drivers/net/ethernet/mellanox/mlx5/core/en/tc/post_act.c
137
err = xa_alloc(&post_act->ids, &handle->id, post_attr,
drivers/net/ethernet/mellanox/mlx5/core/en/tc/post_act.c
15
struct xarray ids;
drivers/net/ethernet/mellanox/mlx5/core/en/tc/post_act.c
164
xa_erase(&post_act->ids, handle->id);
drivers/net/ethernet/mellanox/mlx5/core/en/tc/post_act.c
59
xa_init_flags(&post_act->ids, XA_FLAGS_ALLOC1);
drivers/net/ethernet/mellanox/mlx5/core/en/tc/post_act.c
74
xa_destroy(&post_act->ids);
drivers/net/ethernet/sfc/mcdi_filters.c
754
u16 *ids;
drivers/net/ethernet/sfc/mcdi_filters.c
760
ids = vlan->mc;
drivers/net/ethernet/sfc/mcdi_filters.c
764
ids = vlan->uc;
drivers/net/ethernet/sfc/mcdi_filters.c
771
EFX_WARN_ON_PARANOID(ids[i] != EFX_EF10_FILTER_ID_INVALID);
drivers/net/ethernet/sfc/mcdi_filters.c
784
ids[j]);
drivers/net/ethernet/sfc/mcdi_filters.c
785
ids[j] = EFX_EF10_FILTER_ID_INVALID;
drivers/net/ethernet/sfc/mcdi_filters.c
792
ids[i] = efx_mcdi_filter_get_unsafe_id(rc);
drivers/net/ethernet/sfc/mcdi_filters.c
811
ids[j]);
drivers/net/ethernet/sfc/mcdi_filters.c
812
ids[j] = EFX_EF10_FILTER_ID_INVALID;
drivers/net/ethernet/sis/sis190.c
1631
static const u16 ids[] = { 0x0965, 0x0966, 0x0968 };
drivers/net/ethernet/sis/sis190.c
1641
for (i = 0; i < ARRAY_SIZE(ids); i++) {
drivers/net/ethernet/sis/sis190.c
1642
isa_bridge = pci_get_device(PCI_VENDOR_ID_SI, ids[i], NULL);
drivers/net/pcs/pcs-xpcs.c
1533
static const char *ids[DW_XPCS_NUM_CLKS] = {
drivers/net/pcs/pcs-xpcs.c
1541
xpcs->clks[i].id = ids[i];
drivers/net/wireless/intel/iwlwifi/mvm/binding.c
127
data.ids[data.idx] = mvmvif->id;
drivers/net/wireless/intel/iwlwifi/mvm/binding.c
17
u16 ids[MAX_MACS_IN_BINDING];
drivers/net/wireless/intel/iwlwifi/mvm/binding.c
50
cmd.macs[i] = cpu_to_le32(FW_CMD_ID_AND_COLOR(data->ids[i],
drivers/net/wireless/intel/iwlwifi/mvm/binding.c
88
data->ids[data->idx] = mvmvif->id;
drivers/net/wireless/realtek/rtw89/fw.c
2145
log->fmt_ids = suit_hdr->ids;
drivers/net/wireless/realtek/rtw89/fw.c
2146
fmts_ptr = &suit_hdr->ids[fmt_count];
drivers/net/wireless/realtek/rtw89/fw.h
4323
__le32 ids[];
drivers/net/xen-netback/xenbus.c
1164
.ids = netback_ids,
drivers/net/xen-netfront.c
2681
.ids = netfront_ids,
drivers/nvme/host/core.c
1501
static int nvme_process_ns_desc(struct nvme_ctrl *ctrl, struct nvme_ns_ids *ids,
drivers/nvme/host/core.c
1516
memcpy(ids->eui64, data + sizeof(*cur), NVME_NIDT_EUI64_LEN);
drivers/nvme/host/core.c
1526
memcpy(ids->nguid, data + sizeof(*cur), NVME_NIDT_NGUID_LEN);
drivers/nvme/host/core.c
1536
uuid_copy(&ids->uuid, data + sizeof(*cur));
drivers/nvme/host/core.c
1544
memcpy(&ids->csi, data + sizeof(*cur), NVME_NIDT_CSI_LEN);
drivers/nvme/host/core.c
1589
len = nvme_process_ns_desc(ctrl, &info->ids, cur, &csi_seen);
drivers/nvme/host/core.c
1634
struct nvme_ns_ids *ids = &info->ids;
drivers/nvme/host/core.c
1659
!memchr_inv(ids->eui64, 0, sizeof(ids->eui64)))
drivers/nvme/host/core.c
1660
memcpy(ids->eui64, id->eui64, sizeof(ids->eui64));
drivers/nvme/host/core.c
1662
!memchr_inv(ids->nguid, 0, sizeof(ids->nguid)))
drivers/nvme/host/core.c
1663
memcpy(ids->nguid, id->nguid, sizeof(ids->nguid));
drivers/nvme/host/core.c
2418
ns->head->ids.csi == NVME_CSI_ZNS) {
drivers/nvme/host/core.c
2451
ns->head->ids.csi == NVME_CSI_ZNS)
drivers/nvme/host/core.c
2525
switch (info->ids.csi) {
drivers/nvme/host/core.c
2542
info->nsid, info->ids.csi);
drivers/nvme/host/core.c
2609
struct nvme_ns_ids *ids = &ns->head->ids;
drivers/nvme/host/core.c
2614
if (memchr_inv(ids->nguid, 0, sizeof(ids->nguid))) {
drivers/nvme/host/core.c
2615
memcpy(id, &ids->nguid, sizeof(ids->nguid));
drivers/nvme/host/core.c
2616
return sizeof(ids->nguid);
drivers/nvme/host/core.c
2618
if (memchr_inv(ids->eui64, 0, sizeof(ids->eui64))) {
drivers/nvme/host/core.c
2619
memcpy(id, &ids->eui64, sizeof(ids->eui64));
drivers/nvme/host/core.c
2620
return sizeof(ids->eui64);
drivers/nvme/host/core.c
37
struct nvme_ns_ids ids;
drivers/nvme/host/core.c
3867
struct nvme_ns_ids *ids)
drivers/nvme/host/core.c
3869
bool has_uuid = !uuid_is_null(&ids->uuid);
drivers/nvme/host/core.c
3870
bool has_nguid = memchr_inv(ids->nguid, 0, sizeof(ids->nguid));
drivers/nvme/host/core.c
3871
bool has_eui64 = memchr_inv(ids->eui64, 0, sizeof(ids->eui64));
drivers/nvme/host/core.c
3877
if (has_uuid && uuid_equal(&ids->uuid, &h->ids.uuid))
drivers/nvme/host/core.c
3880
memcmp(&ids->nguid, &h->ids.nguid, sizeof(ids->nguid)) == 0)
drivers/nvme/host/core.c
3883
memcmp(&ids->eui64, &h->ids.eui64, sizeof(ids->eui64)) == 0)
drivers/nvme/host/core.c
3991
head->ids = info->ids;
drivers/nvme/host/core.c
3998
if (head->ids.csi) {
drivers/nvme/host/core.c
3999
ret = nvme_get_effects_log(ctrl, head->ids.csi, &head->effects);
drivers/nvme/host/core.c
4027
struct nvme_ns_ids *ids)
drivers/nvme/host/core.c
4042
ret = nvme_subsys_check_duplicate_ids(s, ids);
drivers/nvme/host/core.c
4058
ret = nvme_global_check_duplicate_ids(ctrl->subsys, &info->ids);
drivers/nvme/host/core.c
4090
memset(&info->ids.nguid, 0, sizeof(info->ids.nguid));
drivers/nvme/host/core.c
4091
memset(&info->ids.uuid, 0, sizeof(info->ids.uuid));
drivers/nvme/host/core.c
4092
memset(&info->ids.eui64, 0, sizeof(info->ids.eui64));
drivers/nvme/host/core.c
4099
ret = nvme_subsys_check_duplicate_ids(ctrl->subsys, &info->ids);
drivers/nvme/host/core.c
4120
if (!nvme_ns_ids_equal(&head->ids, &info->ids)) {
drivers/nvme/host/core.c
4373
if (!nvme_ns_ids_equal(&ns->head->ids, &info->ids)) {
drivers/nvme/host/core.c
4400
if (info.ids.csi != NVME_CSI_NVM && !nvme_multi_css(ctrl)) {
drivers/nvme/host/core.c
4412
(info.ids.csi != NVME_CSI_NVM && info.ids.csi != NVME_CSI_ZNS) ||
drivers/nvme/host/multipath.c
760
if (head->ids.csi == NVME_CSI_ZNS)
drivers/nvme/host/nvme.h
534
struct nvme_ns_ids ids;
drivers/nvme/host/sysfs.c
108
struct nvme_ns_ids *ids = &head->ids;
drivers/nvme/host/sysfs.c
113
if (!uuid_is_null(&ids->uuid))
drivers/nvme/host/sysfs.c
114
return sysfs_emit(buf, "uuid.%pU\n", &ids->uuid);
drivers/nvme/host/sysfs.c
116
if (memchr_inv(ids->nguid, 0, sizeof(ids->nguid)))
drivers/nvme/host/sysfs.c
117
return sysfs_emit(buf, "eui.%16phN\n", ids->nguid);
drivers/nvme/host/sysfs.c
119
if (memchr_inv(ids->eui64, 0, sizeof(ids->eui64)))
drivers/nvme/host/sysfs.c
120
return sysfs_emit(buf, "eui.%8phN\n", ids->eui64);
drivers/nvme/host/sysfs.c
138
return sysfs_emit(buf, "%pU\n", dev_to_ns_head(dev)->ids.nguid);
drivers/nvme/host/sysfs.c
145
struct nvme_ns_ids *ids = &dev_to_ns_head(dev)->ids;
drivers/nvme/host/sysfs.c
150
if (uuid_is_null(&ids->uuid)) {
drivers/nvme/host/sysfs.c
153
return sysfs_emit(buf, "%pU\n", ids->nguid);
drivers/nvme/host/sysfs.c
155
return sysfs_emit(buf, "%pU\n", &ids->uuid);
drivers/nvme/host/sysfs.c
162
return sysfs_emit(buf, "%8ph\n", dev_to_ns_head(dev)->ids.eui64);
drivers/nvme/host/sysfs.c
176
return sysfs_emit(buf, "%u\n", dev_to_ns_head(dev)->ids.csi);
drivers/nvme/host/sysfs.c
274
struct nvme_ns_ids *ids = &dev_to_ns_head(dev)->ids;
drivers/nvme/host/sysfs.c
277
if (uuid_is_null(&ids->uuid) &&
drivers/nvme/host/sysfs.c
278
!memchr_inv(ids->nguid, 0, sizeof(ids->nguid)))
drivers/nvme/host/sysfs.c
282
if (!memchr_inv(ids->nguid, 0, sizeof(ids->nguid)))
drivers/nvme/host/sysfs.c
286
if (!memchr_inv(ids->eui64, 0, sizeof(ids->eui64)))
drivers/nvme/host/zns.c
184
if (ns->head->ids.csi != NVME_CSI_ZNS)
drivers/pci/hotplug/ibmphp_ebda.c
1101
static int ibmphp_probe(struct pci_dev *dev, const struct pci_device_id *ids)
drivers/pci/pci-driver.c
105
const struct pci_device_id *pci_match_id(const struct pci_device_id *ids,
drivers/pci/pci-driver.c
108
if (ids) {
drivers/pci/pci-driver.c
109
while (ids->vendor || ids->subvendor || ids->class_mask) {
drivers/pci/pci-driver.c
110
if (pci_match_one_device(ids, dev))
drivers/pci/pci-driver.c
111
return ids;
drivers/pci/pci-driver.c
112
ids++;
drivers/pci/pci-driver.c
140
const struct pci_device_id *found_id = NULL, *ids;
drivers/pci/pci-driver.c
161
for (ids = drv->id_table; (found_id = pci_match_id(ids, dev));
drivers/pci/pci-driver.c
162
ids = found_id + 1) {
drivers/pci/pci-driver.c
199
const struct pci_device_id *ids = pdrv->id_table;
drivers/pci/pci-driver.c
236
if (ids) {
drivers/pci/pci-driver.c
238
while (ids->vendor || ids->subvendor || ids->class_mask) {
drivers/pci/pci-driver.c
239
if (driver_data == ids->driver_data) {
drivers/pci/pci-driver.c
243
ids++;
drivers/pci/pci-stub.c
22
static char ids[1024] __initdata;
drivers/pci/pci-stub.c
24
module_param_string(ids, ids, sizeof(ids), 0);
drivers/pci/pci-stub.c
25
MODULE_PARM_DESC(ids, "Initial PCI IDs to add to the stub driver, format is "
drivers/pci/pci-stub.c
52
if (ids[0] == '\0')
drivers/pci/pci-stub.c
56
p = ids;
drivers/pci/search.c
456
int pci_dev_present(const struct pci_device_id *ids)
drivers/pci/search.c
460
while (ids->vendor || ids->subvendor || ids->class_mask) {
drivers/pci/search.c
461
found = pci_get_dev_by_id(ids, NULL);
drivers/pci/search.c
466
ids++;
drivers/pci/xen-pcifront.c
1065
.ids = xenpci_ids,
drivers/perf/xgene_pmu.c
1523
const struct acpi_device_id *ids,
drivers/perf/xgene_pmu.c
1529
for (id = ids; id->id[0] || id->cls; id++) {
drivers/pinctrl/renesas/sh_pfc.h
128
#define PINMUX_CFG_REG(name, r, r_width, f_width, ids) \
drivers/pinctrl/renesas/sh_pfc.h
131
BUILD_BUG_ON_ZERO(sizeof((const u16 []) { ids }) / sizeof(u16) != \
drivers/pinctrl/renesas/sh_pfc.h
133
.enum_ids = (const u16 [(r_width / f_width) << f_width]) { ids }
drivers/pinctrl/renesas/sh_pfc.h
148
#define PINMUX_CFG_REG_VAR(name, r, r_width, f_widths, ids) \
drivers/pinctrl/renesas/sh_pfc.h
151
SET_NR_ENUM_IDS(sizeof((const u16 []) { ids }) / sizeof(u16)) \
drivers/pinctrl/renesas/sh_pfc.h
152
.enum_ids = (const u16 []) { ids }
drivers/pinctrl/renesas/sh_pfc.h
198
#define PINMUX_DATA_REG(name, r, r_width, ids) \
drivers/pinctrl/renesas/sh_pfc.h
200
BUILD_BUG_ON_ZERO(sizeof((const u16 []) { ids }) / sizeof(u16) != \
drivers/pinctrl/renesas/sh_pfc.h
202
.enum_ids = (const u16 [r_width]) { ids }
drivers/pinctrl/renesas/sh_pfc.h
212
#define PINMUX_IRQ(ids...) { \
drivers/pinctrl/renesas/sh_pfc.h
213
.gpios = (const short []) { ids, -1 } \
drivers/pinctrl/renesas/sh_pfc.h
353
#define PINMUX_DATA(data_or_mark, ids...) data_or_mark, ids, 0
drivers/pnp/pnpacpi/core.c
200
list_for_each_entry(id, &device->pnp.ids, list) {
drivers/pnp/pnpacpi/core.c
262
list_for_each_entry(id, &device->pnp.ids, list) {
drivers/regulator/aat2870-regulator.c
104
#define AAT2870_LDO(ids) \
drivers/regulator/aat2870-regulator.c
107
.name = #ids, \
drivers/regulator/aat2870-regulator.c
108
.id = AAT2870_ID_##ids, \
drivers/regulator/max8907-regulator.c
46
#define REG_LDO(ids, supply, base, min, max, step) \
drivers/regulator/max8907-regulator.c
47
[MAX8907_##ids] = { \
drivers/regulator/max8907-regulator.c
48
.name = #ids, \
drivers/regulator/max8907-regulator.c
50
.id = MAX8907_##ids, \
drivers/regulator/max8907-regulator.c
63
#define REG_FIXED(ids, supply, voltage) \
drivers/regulator/max8907-regulator.c
64
[MAX8907_##ids] = { \
drivers/regulator/max8907-regulator.c
65
.name = #ids, \
drivers/regulator/max8907-regulator.c
67
.id = MAX8907_##ids, \
drivers/regulator/max8907-regulator.c
75
#define REG_OUT5V(ids, supply, base, voltage) \
drivers/regulator/max8907-regulator.c
76
[MAX8907_##ids] = { \
drivers/regulator/max8907-regulator.c
77
.name = #ids, \
drivers/regulator/max8907-regulator.c
79
.id = MAX8907_##ids, \
drivers/regulator/max8907-regulator.c
89
#define REG_BBAT(ids, supply, base, min, max, step) \
drivers/regulator/max8907-regulator.c
90
[MAX8907_##ids] = { \
drivers/regulator/max8907-regulator.c
91
.name = #ids, \
drivers/regulator/max8907-regulator.c
93
.id = MAX8907_##ids, \
drivers/regulator/stpmic1_regulator.c
198
#define REG_LDO(ids, base) { \
drivers/regulator/stpmic1_regulator.c
199
.name = #ids, \
drivers/regulator/stpmic1_regulator.c
200
.id = STPMIC1_##ids, \
drivers/regulator/stpmic1_regulator.c
207
.vsel_reg = ids##_ACTIVE_CR, \
drivers/regulator/stpmic1_regulator.c
209
.enable_reg = ids##_ACTIVE_CR, \
drivers/regulator/stpmic1_regulator.c
218
#define REG_LDO3(ids, base) { \
drivers/regulator/stpmic1_regulator.c
219
.name = #ids, \
drivers/regulator/stpmic1_regulator.c
220
.id = STPMIC1_##ids, \
drivers/regulator/stpmic1_regulator.c
242
#define REG_LDO4(ids, base) { \
drivers/regulator/stpmic1_regulator.c
243
.name = #ids, \
drivers/regulator/stpmic1_regulator.c
244
.id = STPMIC1_##ids, \
drivers/regulator/stpmic1_regulator.c
260
#define REG_BUCK(ids, base) { \
drivers/regulator/stpmic1_regulator.c
261
.name = #ids, \
drivers/regulator/stpmic1_regulator.c
262
.id = STPMIC1_##ids, \
drivers/regulator/stpmic1_regulator.c
269
.vsel_reg = ids##_ACTIVE_CR, \
drivers/regulator/stpmic1_regulator.c
271
.enable_reg = ids##_ACTIVE_CR, \
drivers/regulator/stpmic1_regulator.c
278
.pull_down_reg = ids##_PULL_DOWN_REG, \
drivers/regulator/stpmic1_regulator.c
279
.pull_down_mask = ids##_PULL_DOWN_MASK, \
drivers/regulator/stpmic1_regulator.c
283
#define REG_VREF_DDR(ids, base) { \
drivers/regulator/stpmic1_regulator.c
284
.name = #ids, \
drivers/regulator/stpmic1_regulator.c
285
.id = STPMIC1_##ids, \
drivers/regulator/stpmic1_regulator.c
300
#define REG_BOOST(ids, base) { \
drivers/regulator/stpmic1_regulator.c
301
.name = #ids, \
drivers/regulator/stpmic1_regulator.c
302
.id = STPMIC1_##ids, \
drivers/regulator/stpmic1_regulator.c
317
#define REG_VBUS_OTG(ids, base) { \
drivers/regulator/stpmic1_regulator.c
318
.name = #ids, \
drivers/regulator/stpmic1_regulator.c
319
.id = STPMIC1_##ids, \
drivers/regulator/stpmic1_regulator.c
337
#define REG_SW_OUT(ids, base) { \
drivers/regulator/stpmic1_regulator.c
338
.name = #ids, \
drivers/regulator/stpmic1_regulator.c
339
.id = STPMIC1_##ids, \
drivers/rpmsg/rpmsg_core.c
397
const struct rpmsg_device_id *ids = rpdrv->id_table;
drivers/rpmsg/rpmsg_core.c
405
if (ids)
drivers/rpmsg/rpmsg_core.c
406
for (i = 0; ids[i].name[0]; i++)
drivers/rpmsg/rpmsg_core.c
407
if (rpmsg_id_match(rpdev, &ids[i])) {
drivers/rpmsg/rpmsg_core.c
408
rpdev->id.driver_data = ids[i].driver_data;
drivers/s390/block/dasd_eckd.c
6860
.ids = dasd_eckd_ids,
drivers/s390/block/dasd_fba.c
64
.ids = dasd_fba_ids,
drivers/s390/char/con3215.c
820
.ids = raw3215_id,
drivers/s390/char/raw3270.c
1308
.ids = raw3270_id,
drivers/s390/char/tape_3490.c
790
.ids = tape_3490_ids,
drivers/s390/char/vmur.c
75
.ids = ur_ids,
drivers/s390/cio/device.c
64
const struct ccw_device_id *ids = cdrv->ids, *found;
drivers/s390/cio/device.c
66
if (!ids)
drivers/s390/cio/device.c
69
found = ccw_device_id_match(ids, &cdev->id);
drivers/s390/crypto/ap_bus.c
640
for (id = ap_drv->ids; id->match_flags; id++) {
drivers/s390/crypto/ap_bus.h
158
struct ap_device_id *ids;
drivers/s390/crypto/vfio_ap_drv.c
64
.ids = ap_queue_ids,
drivers/s390/crypto/zcrypt_cex4.c
661
.ids = zcrypt_cex4_card_ids,
drivers/s390/crypto/zcrypt_cex4.c
751
.ids = zcrypt_cex4_queue_ids,
drivers/s390/net/ctcm_main.c
1666
.ids = ctcm_ids,
drivers/s390/net/qeth_core_main.c
5189
.ids = qeth_ids,
drivers/s390/scsi/zfcp_ccw.c
283
.ids = zfcp_ccw_device_id,
drivers/s390/scsi/zfcp_scsi.c
724
struct fc_rport_identifiers ids;
drivers/s390/scsi/zfcp_scsi.c
730
ids.node_name = port->wwnn;
drivers/s390/scsi/zfcp_scsi.c
731
ids.port_name = port->wwpn;
drivers/s390/scsi/zfcp_scsi.c
732
ids.port_id = port->d_id;
drivers/s390/scsi/zfcp_scsi.c
733
ids.roles = FC_RPORT_ROLE_FCP_TARGET;
drivers/s390/scsi/zfcp_scsi.c
738
rport = fc_remote_port_add(port->adapter->scsi_host, 0, &ids);
drivers/s390/virtio/virtio_ccw.c
1469
.ids = virtio_ids,
drivers/scsi/bnx2fc/bnx2fc_fcoe.c
226
"r_ctl = 0x%x\n", rdata->ids.port_id,
drivers/scsi/bnx2fc/bnx2fc_tgt.c
270
tgt->rdata->ids.port_id, tgt->num_active_ios.counter);
drivers/scsi/bnx2fc/bnx2fc_tgt.c
391
rdata->ids.roles & FC_RPORT_ROLE_FCP_TARGET &&
drivers/scsi/bnx2fc/bnx2fc_tgt.c
392
!(rdata->ids.roles & FC_RPORT_ROLE_FCP_INITIATOR)) {
drivers/scsi/bnx2fc/bnx2fc_tgt.c
450
event, rdata->ids.port_id);
drivers/scsi/bnx2fc/bnx2fc_tgt.c
467
rdata->ids.port_id);
drivers/scsi/bnx2fc/bnx2fc_tgt.c
476
if (!(rdata->ids.roles & FC_RPORT_ROLE_FCP_TARGET)) {
drivers/scsi/bnx2fc/bnx2fc_tgt.c
526
port_id = rdata->ids.port_id;
drivers/scsi/bnx2fc/bnx2fc_tgt.c
589
if (rdata->ids.port_id == port_id) {
drivers/scsi/bnx2fc/bnx2fc_tgt.c
597
rdata->ids.port_id);
drivers/scsi/bnx2i/bnx2i.h
761
struct ep_handles ids;
drivers/scsi/bnx2i/bnx2i.h
762
#define ep_iscsi_cid ids.drv_iscsi_cid
drivers/scsi/bnx2i/bnx2i.h
763
#define ep_cid ids.fw_cid
drivers/scsi/bnx2i/bnx2i.h
764
#define ep_pg_cid ids.pg_cid
drivers/scsi/csiostor/csio_attr.c
101
ids.roles |= FC_RPORT_ROLE_FCP_TARGET;
drivers/scsi/csiostor/csio_attr.c
103
if (ids.roles != FC_RPORT_ROLE_UNKNOWN)
drivers/scsi/csiostor/csio_attr.c
104
fc_remote_port_rolechg(rport, ids.roles);
drivers/scsi/csiostor/csio_attr.c
109
rn->nport_id, ids.roles);
drivers/scsi/csiostor/csio_attr.c
63
struct fc_rport_identifiers ids;
drivers/scsi/csiostor/csio_attr.c
67
ids.node_name = wwn_to_u64(csio_rn_wwnn(rn));
drivers/scsi/csiostor/csio_attr.c
68
ids.port_name = wwn_to_u64(csio_rn_wwpn(rn));
drivers/scsi/csiostor/csio_attr.c
69
ids.port_id = rn->nport_id;
drivers/scsi/csiostor/csio_attr.c
70
ids.roles = FC_RPORT_ROLE_UNKNOWN;
drivers/scsi/csiostor/csio_attr.c
78
rn->rport = fc_remote_port_add(shost, 0, &ids);
drivers/scsi/csiostor/csio_attr.c
99
ids.roles |= FC_RPORT_ROLE_FCP_INITIATOR;
drivers/scsi/elx/libefc_sli/sli4.c
1373
bool send_abts, u32 ids, u32 mask, u16 tag, u16 cq_id)
drivers/scsi/elx/libefc_sli/sli4.c
1384
mask, ids);
drivers/scsi/elx/libefc_sli/sli4.c
1405
abort->t_tag = cpu_to_le32(ids);
drivers/scsi/elx/libefc_sli/sli4.h
4064
bool send_abts, u32 ids, u32 mask, u16 tag, u16 cq_id);
drivers/scsi/fcoe/fcoe_ctlr.c
2125
rdata->ids.port_id, event);
drivers/scsi/fcoe/fcoe_ctlr.c
2139
rdata->ids.port_id);
drivers/scsi/fcoe/fcoe_ctlr.c
2342
frport->rdata.ids.node_name =
drivers/scsi/fcoe/fcoe_ctlr.c
2350
frport->rdata.ids.port_id = ntoh24(vn->fd_fc_id);
drivers/scsi/fcoe/fcoe_ctlr.c
2351
frport->rdata.ids.port_name =
drivers/scsi/fcoe/fcoe_ctlr.c
2405
if (frport->rdata.ids.port_id != fip->port_id)
drivers/scsi/fcoe/fcoe_ctlr.c
2425
if (fip->lp->wwpn > frport->rdata.ids.port_name &&
drivers/scsi/fcoe/fcoe_ctlr.c
2456
if (frport->rdata.ids.port_id != fip->port_id)
drivers/scsi/fcoe/fcoe_ctlr.c
2487
struct fc_rport_identifiers *ids;
drivers/scsi/fcoe/fcoe_ctlr.c
2491
port_id = new->rdata.ids.port_id;
drivers/scsi/fcoe/fcoe_ctlr.c
2507
ids = &rdata->ids;
drivers/scsi/fcoe/fcoe_ctlr.c
2508
if ((ids->port_name != -1 &&
drivers/scsi/fcoe/fcoe_ctlr.c
2509
ids->port_name != new->rdata.ids.port_name) ||
drivers/scsi/fcoe/fcoe_ctlr.c
2510
(ids->node_name != -1 &&
drivers/scsi/fcoe/fcoe_ctlr.c
2511
ids->node_name != new->rdata.ids.node_name)) {
drivers/scsi/fcoe/fcoe_ctlr.c
2517
ids->port_name = new->rdata.ids.port_name;
drivers/scsi/fcoe/fcoe_ctlr.c
2518
ids->node_name = new->rdata.ids.node_name;
drivers/scsi/fcoe/fcoe_ctlr.c
2577
if (new->rdata.ids.port_id == fip->port_id) {
drivers/scsi/fcoe/fcoe_ctlr.c
2586
if (new->rdata.ids.port_id == fip->port_id) {
drivers/scsi/fcoe/fcoe_ctlr.c
2587
if (new->rdata.ids.port_name > fip->lp->wwpn) {
drivers/scsi/fcoe/fcoe_ctlr.c
2599
new->rdata.ids.port_id);
drivers/scsi/fcoe/fcoe_ctlr.c
2608
new->rdata.ids.port_id);
drivers/scsi/fcoe/fcoe_ctlr.c
2624
new->rdata.ids.port_id, fcoe_ctlr_state(fip->state));
drivers/scsi/fcoe/fcoe_ctlr.c
2648
rdata = fc_rport_lookup(lport, new->rdata.ids.port_id);
drivers/scsi/fcoe/fcoe_ctlr.c
2650
if (rdata->ids.node_name == new->rdata.ids.node_name &&
drivers/scsi/fcoe/fcoe_ctlr.c
2651
rdata->ids.port_name == new->rdata.ids.port_name) {
drivers/scsi/fcoe/fcoe_ctlr.c
2655
rdata->ids.port_id);
drivers/scsi/fcoe/fcoe_ctlr.c
2659
rdata->ids.port_id);
drivers/scsi/fcoe/fcoe_ctlr.c
2676
new->rdata.ids.port_id);
drivers/scsi/fcoe/fcoe_ctlr.c
2714
rdata->ids.port_name, rdata->ids.port_id);
drivers/scsi/fcoe/fcoe_ctlr.c
2862
frport->rdata.ids.node_name =
drivers/scsi/fnic/fnic_fcs.c
931
struct fc_rport_identifiers ids;
drivers/scsi/fnic/fnic_fcs.c
937
ids.node_name = tport->wwnn;
drivers/scsi/fnic/fnic_fcs.c
938
ids.port_name = tport->wwpn;
drivers/scsi/fnic/fnic_fcs.c
939
ids.port_id = tport->fcid;
drivers/scsi/fnic/fnic_fcs.c
940
ids.roles = FC_RPORT_ROLE_FCP_TARGET;
drivers/scsi/fnic/fnic_fcs.c
943
rport = fc_remote_port_add(fnic->host, 0, &ids);
drivers/scsi/ibmvscsi/ibmvfc.c
1382
fc_starget_port_name(starget) = tgt ? tgt->ids.node_name : 0;
drivers/scsi/ibmvscsi/ibmvfc.c
1397
fc_starget_port_name(starget) = tgt ? tgt->ids.port_name : 0;
drivers/scsi/ibmvscsi/ibmvfc.c
3250
if (crq->wwpn && cpu_to_be64(tgt->ids.port_name) != crq->wwpn)
drivers/scsi/ibmvscsi/ibmvfc.c
3252
if (crq->node_name && cpu_to_be64(tgt->ids.node_name) != crq->node_name)
drivers/scsi/ibmvscsi/ibmvfc.c
4053
tgt->ids.roles = 0;
drivers/scsi/ibmvscsi/ibmvfc.c
4055
tgt->ids.roles |= FC_PORT_ROLE_FCP_TARGET;
drivers/scsi/ibmvscsi/ibmvfc.c
4057
tgt->ids.roles |= FC_PORT_ROLE_FCP_INITIATOR;
drivers/scsi/ibmvscsi/ibmvfc.c
4168
if (tgt->ids.port_name &&
drivers/scsi/ibmvscsi/ibmvfc.c
4169
tgt->ids.port_name != wwn_to_u64(rsp->service_parms.port_name)) {
drivers/scsi/ibmvscsi/ibmvfc.c
4174
tgt->ids.node_name = wwn_to_u64(rsp->service_parms.node_name);
drivers/scsi/ibmvscsi/ibmvfc.c
4175
tgt->ids.port_name = wwn_to_u64(rsp->service_parms.port_name);
drivers/scsi/ibmvscsi/ibmvfc.c
4176
tgt->ids.port_id = tgt->scsi_id;
drivers/scsi/ibmvscsi/ibmvfc.c
4434
tgt->ids.node_name = wwn_to_u64(rsp->service_parms.node_name);
drivers/scsi/ibmvscsi/ibmvfc.c
4435
tgt->ids.port_name = wwn_to_u64(rsp->service_parms.port_name);
drivers/scsi/ibmvscsi/ibmvfc.c
4437
tgt->ids.port_id = tgt->scsi_id;
drivers/scsi/ibmvscsi/ibmvfc.c
4501
move->node_name = cpu_to_be64(tgt->ids.node_name);
drivers/scsi/ibmvscsi/ibmvfc.c
4522
if (wwn_to_u64((u8 *)&mad->fc_iu.response[2]) != tgt->ids.port_name)
drivers/scsi/ibmvscsi/ibmvfc.c
4524
if (wwn_to_u64((u8 *)&mad->fc_iu.response[4]) != tgt->ids.node_name)
drivers/scsi/ibmvscsi/ibmvfc.c
4835
query_tgt->wwpn = cpu_to_be64(tgt->ids.port_name);
drivers/scsi/ibmvscsi/ibmvfc.c
5515
rport = fc_remote_port_add(vhost->host, 0, &tgt->ids);
drivers/scsi/ibmvscsi/ibmvfc.c
6291
fc_remote_port_rolechg(rport, tgt->ids.roles);
drivers/scsi/ibmvscsi/ibmvfc.h
742
struct fc_rport_identifiers ids;
drivers/scsi/ibmvscsi/ibmvscsi.c
2231
struct srp_rport_identifiers ids;
drivers/scsi/ibmvscsi/ibmvscsi.c
2291
memcpy(ids.port_id, hostdata->madapter_info.partition_name,
drivers/scsi/ibmvscsi/ibmvscsi.c
2292
sizeof(ids.port_id));
drivers/scsi/ibmvscsi/ibmvscsi.c
2293
ids.roles = SRP_RPORT_ROLE_TARGET;
drivers/scsi/ibmvscsi/ibmvscsi.c
2294
rport = srp_rport_add(host, &ids);
drivers/scsi/libfc/fc_disc.c
384
struct fc_rport_identifiers ids;
drivers/scsi/libfc/fc_disc.c
428
ids.port_id = ntoh24(np->fp_fid);
drivers/scsi/libfc/fc_disc.c
429
ids.port_name = ntohll(np->fp_wwpn);
drivers/scsi/libfc/fc_disc.c
431
if (ids.port_id != lport->port_id &&
drivers/scsi/libfc/fc_disc.c
432
ids.port_name != lport->wwpn) {
drivers/scsi/libfc/fc_disc.c
433
rdata = fc_rport_create(lport, ids.port_id);
drivers/scsi/libfc/fc_disc.c
435
rdata->ids.port_name = ids.port_name;
drivers/scsi/libfc/fc_disc.c
440
"(%6.6x)\n", ids.port_id);
drivers/scsi/libfc/fc_disc.c
598
if (rdata->ids.port_name == -1)
drivers/scsi/libfc/fc_disc.c
599
rdata->ids.port_name = port_name;
drivers/scsi/libfc/fc_disc.c
600
else if (rdata->ids.port_name != port_name) {
drivers/scsi/libfc/fc_disc.c
603
rdata->ids.port_id, port_name);
drivers/scsi/libfc/fc_disc.c
607
new_rdata = fc_rport_create(lport, rdata->ids.port_id);
drivers/scsi/libfc/fc_disc.c
653
if (!lport->tt.elsct_send(lport, rdata->ids.port_id, fp, FC_NS_GPN_ID,
drivers/scsi/libfc/fc_libfc.h
53
FC_RPORT_ID_DBG((rdata)->local_port, (rdata)->ids.port_id, fmt, ##args)
drivers/scsi/libfc/fc_lport.c
176
rdata->ids.port_id);
drivers/scsi/libfc/fc_lport.c
192
"%d state", rdata->ids.port_id,
drivers/scsi/libfc/fc_lport.c
200
if (rdata->ids.port_id == FC_FID_DIR_SERV)
drivers/scsi/libfc/fc_lport.c
202
else if (rdata->ids.port_id == FC_FID_MGMT_SERV)
drivers/scsi/libfc/fc_lport.c
251
lport->ptp_rdata->ids.port_name = remote_wwpn;
drivers/scsi/libfc/fc_lport.c
252
lport->ptp_rdata->ids.node_name = remote_wwnn;
drivers/scsi/libfc/fc_rport.c
1015
rdata->ids.port_name = get_unaligned_be64(&plp->fl_wwpn);
drivers/scsi/libfc/fc_rport.c
1016
rdata->ids.node_name = get_unaligned_be64(&plp->fl_wwnn);
drivers/scsi/libfc/fc_rport.c
1052
if (rdata->ids.roles == FC_PORT_ROLE_UNKNOWN)
drivers/scsi/libfc/fc_rport.c
1054
if ((rdata->ids.roles & FC_PORT_ROLE_FCP_TARGET) &&
drivers/scsi/libfc/fc_rport.c
1057
if ((rdata->ids.roles & FC_PORT_ROLE_FCP_INITIATOR) &&
drivers/scsi/libfc/fc_rport.c
1097
if (!lport->tt.elsct_send(lport, rdata->ids.port_id, fp, ELS_PLOGI,
drivers/scsi/libfc/fc_rport.c
111
if (tmp_rdata->ids.port_id == port_id &&
drivers/scsi/libfc/fc_rport.c
1152
rdata->ids.roles = FC_RPORT_ROLE_UNKNOWN;
drivers/scsi/libfc/fc_rport.c
1212
rdata->ids.roles = roles;
drivers/scsi/libfc/fc_rport.c
1261
if (rdata->ids.port_id >= FC_FID_DOM_MGR) {
drivers/scsi/libfc/fc_rport.c
1294
fc_fill_fc_hdr(fp, FC_RCTL_ELS_REQ, rdata->ids.port_id,
drivers/scsi/libfc/fc_rport.c
1403
if (!lport->tt.elsct_send(lport, rdata->ids.port_id, fp, ELS_RTV,
drivers/scsi/libfc/fc_rport.c
147
rdata->ids.node_name = -1;
drivers/scsi/libfc/fc_rport.c
148
rdata->ids.port_name = -1;
drivers/scsi/libfc/fc_rport.c
1486
if (!lport->tt.elsct_send(lport, rdata->ids.port_id, fp, ELS_LOGO,
drivers/scsi/libfc/fc_rport.c
149
rdata->ids.port_id = port_id;
drivers/scsi/libfc/fc_rport.c
150
rdata->ids.roles = FC_RPORT_ROLE_UNKNOWN;
drivers/scsi/libfc/fc_rport.c
1536
ntoh24(adisc->adisc_port_id) != rdata->ids.port_id ||
drivers/scsi/libfc/fc_rport.c
1537
get_unaligned_be64(&adisc->adisc_wwpn) != rdata->ids.port_name ||
drivers/scsi/libfc/fc_rport.c
1538
get_unaligned_be64(&adisc->adisc_wwnn) != rdata->ids.node_name) {
drivers/scsi/libfc/fc_rport.c
1577
if (!lport->tt.elsct_send(lport, rdata->ids.port_id, fp, ELS_ADISC,
drivers/scsi/libfc/fc_rport.c
1879
rdata->ids.port_name = get_unaligned_be64(&pl->fl_wwpn);
drivers/scsi/libfc/fc_rport.c
1880
rdata->ids.node_name = get_unaligned_be64(&pl->fl_wwnn);
drivers/scsi/libfc/fc_rport.c
1902
if (rdata->ids.port_name < lport->wwpn) {
drivers/scsi/libfc/fc_rport.c
2206
rdata->ids.roles = FC_RPORT_ROLE_UNKNOWN;
drivers/scsi/libfc/fc_rport.c
2208
rdata->ids.roles |= FC_RPORT_ROLE_FCP_INITIATOR;
drivers/scsi/libfc/fc_rport.c
2210
rdata->ids.roles |= FC_RPORT_ROLE_FCP_TARGET;
drivers/scsi/libfc/fc_rport.c
267
struct fc_rport_identifiers ids;
drivers/scsi/libfc/fc_rport.c
281
ids = rdata->ids;
drivers/scsi/libfc/fc_rport.c
289
rport = fc_remote_port_add(lport->host, 0, &ids);
drivers/scsi/libfc/fc_rport.c
335
port_id = rdata->ids.port_id;
drivers/scsi/libfc/fc_rport.c
506
u32 port_id = rdata->ids.port_id;
drivers/scsi/libfc/fc_rport.c
797
if (rdata->ids.port_name < lport->wwpn)
drivers/scsi/libfc/fc_rport.c
840
if (!lport->tt.elsct_send(lport, rdata->ids.port_id, fp, ELS_FLOGI,
drivers/scsi/libfc/fc_rport.c
954
if (rdata->ids.port_name < lport->wwpn)
drivers/scsi/lpfc/lpfc_sli.c
6399
uint16_t *ids;
drivers/scsi/lpfc/lpfc_sli.c
6493
ids = phba->sli4_hba.rpi_ids;
drivers/scsi/lpfc/lpfc_sli.c
6513
ids = phba->vpi_ids;
drivers/scsi/lpfc/lpfc_sli.c
6536
ids = phba->sli4_hba.xri_ids;
drivers/scsi/lpfc/lpfc_sli.c
6558
ids = phba->sli4_hba.vfi_ids;
drivers/scsi/lpfc/lpfc_sli.c
6565
ids = NULL;
drivers/scsi/lpfc/lpfc_sli.c
6588
kfree(ids);
drivers/scsi/lpfc/lpfc_sli.c
6601
ids[j] = rsrc_id;
drivers/scsi/megaraid/megaraid_sas_base.c
4758
int ret = 0, ld_index = 0, ids = 0;
drivers/scsi/megaraid/megaraid_sas_base.c
4845
ids = ci->ldList[ld_index].ref.targetId;
drivers/scsi/megaraid/megaraid_sas_base.c
4846
instance->ld_ids[ids] = ci->ldList[ld_index].ref.targetId;
drivers/scsi/megaraid/megaraid_sas_base.c
4850
ld_index, ids);
drivers/scsi/megaraid/megaraid_sas_base.c
4875
int ret = 0, ld_index = 0, ids = 0;
drivers/scsi/megaraid/megaraid_sas_base.c
4963
ids = ci->targetId[ld_index];
drivers/scsi/megaraid/megaraid_sas_base.c
4964
instance->ld_ids[ids] = ci->targetId[ld_index];
drivers/scsi/qedf/qedf_debugfs.c
365
rdata->ids.port_id,
drivers/scsi/qedf/qedf_els.c
107
did = fcport->rdata->ids.port_id;
drivers/scsi/qedf/qedf_els.c
349
hton24(fh->fh_s_id, fcport->rdata->ids.port_id);
drivers/scsi/qedf/qedf_els.c
402
port_id = rdata->ids.port_id;
drivers/scsi/qedf/qedf_io.c
1634
fcport->rdata->ids.port_id, fcport->rport->scsi_target_id);
drivers/scsi/qedf/qedf_io.c
2210
refcount, fcport, fcport->rdata->ids.port_id);
drivers/scsi/qedf/qedf_io.c
2421
QEDF_ERR(NULL, "portid=%06x tm_flags =%s\n", rdata->ids.port_id,
drivers/scsi/qedf/qedf_io.c
2460
fcport, fcport->rdata->ids.port_id);
drivers/scsi/qedf/qedf_io.c
813
io_log->port_id = fcport->rdata->ids.port_id;
drivers/scsi/qedf/qedf_main.c
1036
if (rdata->ids.port_id == port_id) {
drivers/scsi/qedf/qedf_main.c
1327
"portid=%06x.\n", fcport->rdata->ids.port_id);
drivers/scsi/qedf/qedf_main.c
1332
"for portid=%06x.\n", fcport->rdata->ids.port_id);
drivers/scsi/qedf/qedf_main.c
1338
"fw_cid=%08x handle=%d.\n", fcport->rdata->ids.port_id,
drivers/scsi/qedf/qedf_main.c
1389
fcport->rdata->ids.port_id);
drivers/scsi/qedf/qedf_main.c
1400
"for portid=%06x.\n", fcport->rdata->ids.port_id);
drivers/scsi/qedf/qedf_main.c
1405
fcport->rdata->ids.port_id, total_sqe);
drivers/scsi/qedf/qedf_main.c
1433
"port_id=%06x.\n", fcport->rdata->ids.port_id);
drivers/scsi/qedf/qedf_main.c
1448
fcport->rdata->ids.port_id);
drivers/scsi/qedf/qedf_main.c
1479
"port_id = 0x%x\n", event, rdata->ids.port_id);
drivers/scsi/qedf/qedf_main.c
1495
"reached.\n", rdata->ids.port_id);
drivers/scsi/qedf/qedf_main.c
1506
rdata->ids.port_id);
drivers/scsi/qedf/qedf_main.c
1519
rdata->ids.port_id);
drivers/scsi/qedf/qedf_main.c
1528
if (!(rdata->ids.roles & FC_RPORT_ROLE_FCP_TARGET)) {
drivers/scsi/qedf/qedf_main.c
1547
rdata->ids.roles & FC_RPORT_ROLE_FCP_TARGET &&
drivers/scsi/qedf/qedf_main.c
1548
!(rdata->ids.roles & FC_RPORT_ROLE_FCP_INITIATOR)) {
drivers/scsi/qedf/qedf_main.c
1552
rdata->ids.port_id);
drivers/scsi/qedf/qedf_main.c
1579
port_id = rdata->ids.port_id;
drivers/scsi/qedf/qedf_main.c
1588
if (!(rdata->ids.roles & FC_RPORT_ROLE_FCP_TARGET)) {
drivers/scsi/qedf/qedf_main.c
756
rdata->ids.port_id);
drivers/scsi/qedf/qedf_main.c
769
io_req->sc_cmd, sc_cmd, rdata->ids.port_id);
drivers/scsi/qedf/qedf_main.c
779
refcount, rdata->ids.port_id);
drivers/scsi/qedf/qedf_main.c
791
io_req->xid, rdata->ids.port_id);
drivers/scsi/qedf/qedf_main.c
814
rdata->ids.port_id);
drivers/scsi/qedf/qedf_main.c
905
fcport, fcport->rdata->ids.port_id);
drivers/scsi/qla2xxx/qla_sup.c
520
uint32_t faddr, ids = 0;
drivers/scsi/qla2xxx/qla_sup.c
525
if (!qla24xx_read_flash_dword(ha, faddr, &ids)) {
drivers/scsi/qla2xxx/qla_sup.c
526
*man_id = LSB(ids);
drivers/scsi/qla2xxx/qla_sup.c
527
*flash_id = MSB(ids);
drivers/scsi/qla2xxx/qla_sup.c
531
if (ids != 0xDEADDEAD && (*man_id == 0 || *flash_id == 0)) {
drivers/scsi/qla2xxx/qla_sup.c
539
if (!qla24xx_read_flash_dword(ha, faddr, &ids)) {
drivers/scsi/qla2xxx/qla_sup.c
540
*man_id = LSB(ids);
drivers/scsi/qla2xxx/qla_sup.c
541
*flash_id = MSB(ids);
drivers/scsi/scsi_transport_fc.c
3090
struct fc_rport_identifiers *ids)
drivers/scsi/scsi_transport_fc.c
3110
memcpy(&rport->node_name, &ids->node_name, sizeof(rport->node_name));
drivers/scsi/scsi_transport_fc.c
3111
memcpy(&rport->port_name, &ids->port_name, sizeof(rport->port_name));
drivers/scsi/scsi_transport_fc.c
3112
rport->port_id = ids->port_id;
drivers/scsi/scsi_transport_fc.c
3113
rport->roles = ids->roles;
drivers/scsi/scsi_transport_fc.c
32
struct device *pdev, struct fc_vport_identifiers *ids,
drivers/scsi/scsi_transport_fc.c
3233
struct fc_rport_identifiers *ids)
drivers/scsi/scsi_transport_fc.c
3260
if (rport->port_name == ids->port_name)
drivers/scsi/scsi_transport_fc.c
3264
if (rport->node_name == ids->node_name)
drivers/scsi/scsi_transport_fc.c
3268
if (rport->port_id == ids->port_id)
drivers/scsi/scsi_transport_fc.c
3275
memcpy(&rport->node_name, &ids->node_name,
drivers/scsi/scsi_transport_fc.c
3277
memcpy(&rport->port_name, &ids->port_name,
drivers/scsi/scsi_transport_fc.c
3279
rport->port_id = ids->port_id;
drivers/scsi/scsi_transport_fc.c
3282
rport->roles = ids->roles;
drivers/scsi/scsi_transport_fc.c
3308
(!(ids->roles & FC_PORT_ROLE_FCP_TARGET)))
drivers/scsi/scsi_transport_fc.c
3364
if (rport->port_name == ids->port_name)
drivers/scsi/scsi_transport_fc.c
3368
if (rport->node_name == ids->node_name)
drivers/scsi/scsi_transport_fc.c
3372
if (rport->port_id == ids->port_id)
drivers/scsi/scsi_transport_fc.c
3386
memcpy(&rport->node_name, &ids->node_name,
drivers/scsi/scsi_transport_fc.c
3388
memcpy(&rport->port_name, &ids->port_name,
drivers/scsi/scsi_transport_fc.c
3390
rport->port_id = ids->port_id;
drivers/scsi/scsi_transport_fc.c
3399
fc_remote_port_rolechg(rport, ids->roles);
drivers/scsi/scsi_transport_fc.c
3407
rport = fc_remote_port_create(shost, channel, ids);
drivers/scsi/scsi_transport_fc.c
3884
struct fc_vport_identifiers *ids, struct fc_vport **ret_vport)
drivers/scsi/scsi_transport_fc.c
3908
vport->node_name = ids->node_name;
drivers/scsi/scsi_transport_fc.c
3909
vport->port_name = ids->port_name;
drivers/scsi/scsi_transport_fc.c
3910
vport->roles = ids->roles;
drivers/scsi/scsi_transport_fc.c
3911
vport->vport_type = ids->vport_type;
drivers/scsi/scsi_transport_fc.c
3949
error = fci->f->vport_create(vport, ids->disable);
drivers/scsi/scsi_transport_fc.c
4008
struct fc_vport_identifiers *ids)
drivers/scsi/scsi_transport_fc.c
4014
ids, &vport);
drivers/scsi/scsi_transport_srp.c
696
struct srp_rport_identifiers *ids)
drivers/scsi/scsi_transport_srp.c
714
memcpy(rport->port_id, ids->port_id, sizeof(rport->port_id));
drivers/scsi/scsi_transport_srp.c
715
rport->roles = ids->roles;
drivers/scsi/storvsc_drv.c
2099
struct fc_rport_identifiers ids = {
drivers/scsi/storvsc_drv.c
2105
stor_device->rport = fc_remote_port_add(host, 0, &ids);
drivers/scsi/xen-scsifront.c
1212
.ids = scsifront_ids,
drivers/soc/samsung/exynos-asv.h
17
unsigned int ids;
drivers/soc/samsung/exynos5422-asv.c
341
int hpm, ids, i;
drivers/soc/samsung/exynos5422-asv.c
361
ids = (pkgid_reg >> EXYNOS5422_IDS_OFFSET) & EXYNOS5422_IDS_MASK;
drivers/soc/samsung/exynos5422-asv.c
364
if (ids <= __asv_limits[i].ids)
drivers/target/tcm_fc/tfc_sess.c
215
ft_format_wwn(&initiatorname[0], TRANSPORT_IQN_LEN, rdata->ids.port_name);
drivers/target/tcm_fc/tfc_sess.c
379
sess = ft_sess_create(tport, rdata->ids.port_id, rdata);
drivers/target/tcm_fc/tfc_sess.c
390
sess->port_name = rdata->ids.port_name;
drivers/target/tcm_fc/tfc_sess.c
430
rdata->ids.port_id, rspp ? rspp->spp_flags : 0, ret);
drivers/target/tcm_fc/tfc_sess.c
463
sess = ft_sess_delete(tport, rdata->ids.port_id);
drivers/thermal/thermal_debugfs.c
194
char ids[IDSLENGTH];
drivers/thermal/thermal_debugfs.c
202
snprintf(ids, IDSLENGTH, "%d", id);
drivers/thermal/thermal_debugfs.c
204
thermal_dbg->d_top = debugfs_create_dir(ids, d);
drivers/thunderbolt/domain.c
52
const struct tb_service_id *ids;
drivers/thunderbolt/domain.c
63
for (ids = driver->id_table; ids->match_flags != 0; ids++) {
drivers/thunderbolt/domain.c
64
if (match_service_id(ids, svc))
drivers/thunderbolt/domain.c
65
return ids;
drivers/tty/hvc/hvc_xen.c
605
.ids = xencons_ids,
drivers/tty/serial/8250/8250_pci.c
643
const unsigned short *ids;
drivers/tty/serial/8250/8250_pci.c
674
const unsigned short *ids;
drivers/tty/serial/8250/8250_pci.c
678
ids = timedia_data[i].ids;
drivers/tty/serial/8250/8250_pci.c
679
for (j = 0; ids[j]; j++)
drivers/tty/serial/8250/8250_pci.c
680
if (dev->subsystem_device == ids[j])
drivers/uio/uio_aec.c
141
.id_table = ids,
drivers/uio/uio_aec.c
36
static const struct pci_device_id ids[] = {
drivers/uio/uio_aec.c
40
MODULE_DEVICE_TABLE(pci, ids);
drivers/usb/host/xen-hcd.c
1579
.ids = xenhcd_ids,
drivers/usb/misc/usb-ljca.c
161
const struct acpi_device_id *ids;
drivers/usb/misc/usb-ljca.c
437
if (acpi_match_device_ids(adev, wd->ids))
drivers/usb/misc/usb-ljca.c
485
wd.ids = ljca_gpio_hids;
drivers/usb/misc/usb-ljca.c
491
wd.ids = ljca_i2c_hids;
drivers/usb/misc/usb-ljca.c
495
wd.ids = ljca_spi_hids;
drivers/usb/typec/class.c
580
struct ida *ids;
drivers/usb/typec/class.c
583
ids = &to_typec_partner(dev)->mode_ids;
drivers/usb/typec/class.c
585
ids = &to_typec_plug(dev)->mode_ids;
drivers/usb/typec/class.c
587
ids = &to_typec_port(dev)->mode_ids;
drivers/usb/typec/class.c
589
return ida_alloc(ids, GFP_KERNEL);
drivers/usb/typec/class.c
594
struct ida *ids;
drivers/usb/typec/class.c
597
ids = &to_typec_partner(dev)->mode_ids;
drivers/usb/typec/class.c
599
ids = &to_typec_plug(dev)->mode_ids;
drivers/usb/typec/class.c
601
ids = &to_typec_port(dev)->mode_ids;
drivers/usb/typec/class.c
603
ida_free(ids, id);
drivers/vfio/pci/vfio_pci.c
242
if (ids[0] == '\0')
drivers/vfio/pci/vfio_pci.c
246
p = ids;
drivers/vfio/pci/vfio_pci.c
33
static char ids[1024] __initdata;
drivers/vfio/pci/vfio_pci.c
34
module_param_string(ids, ids, sizeof(ids), 0);
drivers/vfio/pci/vfio_pci.c
35
MODULE_PARM_DESC(ids, "Initial PCI IDs to add to the vfio driver, format is \"vendor:device[:subvendor[:subdevice[:class[:class_mask]]]]\" and multiple comma separated entries can be specified");
drivers/video/fbdev/xen-fbfront.c
666
.ids = xenfb_ids,
drivers/virtio/virtio.c
89
const struct virtio_device_id *ids;
drivers/virtio/virtio.c
91
ids = drv_to_virtio(_dr)->id_table;
drivers/virtio/virtio.c
92
for (i = 0; ids[i].device; i++)
drivers/virtio/virtio.c
93
if (virtio_id_match(dev, &ids[i]))
drivers/virtio/virtio_input.c
268
u.ids.bustype, &vi->idev->id.bustype);
drivers/virtio/virtio_input.c
270
u.ids.vendor, &vi->idev->id.vendor);
drivers/virtio/virtio_input.c
272
u.ids.product, &vi->idev->id.product);
drivers/virtio/virtio_input.c
274
u.ids.version, &vi->idev->id.version);
drivers/xen/pvcalls-back.c
1209
.ids = pvcalls_back_ids,
drivers/xen/pvcalls-front.c
1355
.ids = pvcalls_front_ids,
drivers/xen/xen-pciback/xenbus.c
734
.ids = xen_pcibk_ids,
drivers/xen/xen-scsiback.c
1862
.ids = scsiback_ids,
drivers/xen/xenbus/xenbus_probe.c
101
if (!drv->ids)
drivers/xen/xenbus/xenbus_probe.c
104
return match_device(drv->ids, to_xenbus_device(_dev)) != NULL;
drivers/xen/xenbus/xenbus_probe.c
286
id = match_device(drv->ids, dev);
drivers/xen/xenbus/xenbus_probe.c
376
drv->driver.name = drv->name ? drv->name : drv->ids[0].devicetype;
drivers/zorro/zorro-driver.c
125
const struct zorro_device_id *ids = zorro_drv->id_table;
drivers/zorro/zorro-driver.c
127
if (!ids)
drivers/zorro/zorro-driver.c
130
return !!zorro_match_device(ids, z);
drivers/zorro/zorro-driver.c
32
zorro_match_device(const struct zorro_device_id *ids,
drivers/zorro/zorro-driver.c
35
while (ids->id) {
drivers/zorro/zorro-driver.c
36
if (ids->id == ZORRO_WILDCARD || ids->id == z->id)
drivers/zorro/zorro-driver.c
37
return ids;
drivers/zorro/zorro-driver.c
38
ids++;
fs/squashfs/id.c
42
if (index >= msblk->ids)
fs/squashfs/squashfs_fs_sb.h
68
unsigned int ids;
fs/squashfs/super.c
296
msblk->ids = le16_to_cpu(sblk->no_ids);
fs/squashfs/super.c
308
TRACE("Number of ids %d\n", msblk->ids);
fs/squashfs/super.c
383
le64_to_cpu(sblk->id_table_start), next_table, msblk->ids);
include/acpi/acpi_bus.h
135
const struct acpi_device_id *ids;
include/acpi/acpi_bus.h
181
const struct acpi_device_id *ids; /* Supported Hardware IDs */
include/acpi/acpi_bus.h
263
struct list_head ids; /* _HID and _CIDs */
include/acpi/acpi_bus.h
690
const struct acpi_device_id *ids);
include/acpi/actypes.h
1173
struct acpi_pnp_device_id ids[]; /* ID array */
include/linux/acpi.h
744
const struct acpi_device_id *acpi_match_acpi_device(const struct acpi_device_id *ids,
include/linux/acpi.h
747
const struct acpi_device_id *acpi_match_device(const struct acpi_device_id *ids,
include/linux/acpi.h
984
const struct acpi_device_id *ids, const struct acpi_device *adev)
include/linux/acpi.h
990
const struct acpi_device_id *ids, const struct device *dev)
include/linux/adb.h
57
int adb_register(int default_id,int handler_id,struct adb_ids *ids,
include/linux/bpf.h
1523
int bpf_trampoline_multi_attach(struct bpf_prog *prog, u32 *ids,
include/linux/bpf.h
1640
static inline int bpf_trampoline_multi_attach(struct bpf_prog *prog, u32 *ids,
include/linux/btf.h
517
return bsearch(&id, set->ids, set->cnt, sizeof(u32), btf_id_cmp_func) != NULL;
include/linux/btf_ids.h
10
u32 ids[];
include/linux/crush/crush.h
176
__s32 *ids; /*!< values to use instead of items */
include/linux/iommu.h
1143
u32 ids[];
include/linux/iommu.h
1178
int iommu_fwspec_add_ids(struct device *dev, const u32 *ids, int num_ids);
include/linux/iommu.h
1489
static inline int iommu_fwspec_add_ids(struct device *dev, u32 *ids,
include/linux/iommu.h
1628
*stream_id = fwspec->ids[0] & 0xffff;
include/linux/ipc_namespace.h
32
struct ipc_ids ids[3];
include/linux/mtd/rawnand.h
1583
struct nand_flash_dev *ids);
include/linux/pci.h
1313
int pci_dev_present(const struct pci_device_id *ids);
include/linux/pci.h
1716
const struct pci_device_id *pci_match_id(const struct pci_device_id *ids,
include/linux/pci.h
2144
static inline int pci_dev_present(const struct pci_device_id *ids)
include/linux/pci.h
2226
static inline const struct pci_device_id *pci_match_id(const struct pci_device_id *ids,
include/linux/rseq.h
137
t->rseq.ids.cpu_id = RSEQ_CPU_ID_UNINITIALIZED;
include/linux/rseq_entry.h
14
unsigned long ids;
include/linux/rseq_entry.h
479
bool rseq_set_ids_get_csaddr(struct task_struct *t, struct rseq_ids *ids, u64 *csaddr)
include/linux/rseq_entry.h
489
if (cpu_id != t->rseq.ids.cpu_id)
include/linux/rseq_entry.h
495
if (uval != t->rseq.ids.node_id)
include/linux/rseq_entry.h
498
if (uval != t->rseq.ids.mm_cid)
include/linux/rseq_entry.h
502
unsafe_put_user(ids->cpu_id, &rseq->cpu_id_start, efault);
include/linux/rseq_entry.h
503
unsafe_put_user(ids->cpu_id, &rseq->cpu_id, efault);
include/linux/rseq_entry.h
504
unsafe_put_user(ids->node_id, &rseq->node_id, efault);
include/linux/rseq_entry.h
505
unsafe_put_user(ids->mm_cid, &rseq->mm_cid, efault);
include/linux/rseq_entry.h
516
t->rseq.ids = *ids;
include/linux/rseq_entry.h
517
rseq_stat_inc(rseq_stats.ids);
include/linux/rseq_entry.h
518
rseq_trace_update(t, ids);
include/linux/rseq_entry.h
532
struct rseq_ids *ids)
include/linux/rseq_entry.h
536
if (!rseq_set_ids_get_csaddr(t, ids, &csaddr))
include/linux/rseq_entry.h
58
static inline void rseq_trace_update(struct task_struct *t, struct rseq_ids *ids)
include/linux/rseq_entry.h
60
if (tracepoint_enabled(rseq_update) && ids)
include/linux/rseq_entry.h
639
struct rseq_ids ids = {
include/linux/rseq_entry.h
645
return rseq_update_usr(t, regs, &ids);
include/linux/rseq_entry.h
72
static inline void rseq_trace_update(struct task_struct *t, struct rseq_ids *ids) { }
include/linux/rseq_types.h
124
struct rseq_ids ids;
include/linux/sh_intc.h
39
#define INTC_GROUP(enum_id, ids...) { enum_id, { ids } }
include/linux/syscalls.h
1006
asmlinkage long sys_lsm_list_modules(u64 __user *ids, u32 __user *size, u32 flags);
include/net/cfg80211.h
10194
const u8 *ids, int n_ids,
include/net/cfg80211.h
10224
const u8 *ids, int n_ids, size_t offset)
include/net/cfg80211.h
10226
return ieee80211_ie_split_ric(ies, ielen, ids, n_ids, NULL, 0, offset);
include/net/mptcp.h
50
u8 ids[MPTCP_RM_IDS_MAX];
include/rdma/uverbs_ioctl.h
551
.u2.enum_def.ids = _enum_arr, \
include/rdma/uverbs_ioctl.h
89
const struct uverbs_attr_spec *ids;
include/scsi/libfc.h
200
struct fc_rport_identifiers ids;
include/scsi/scsi_transport_fc.h
846
int channel, struct fc_rport_identifiers *ids);
include/trace/events/rseq.h
24
__entry->cpu_id = t->rseq.ids.cpu_id;
include/trace/events/rseq.h
26
__entry->mm_cid = t->rseq.ids.mm_cid;
include/uapi/linux/bpf.h
1888
__aligned_u64 ids;
include/uapi/linux/netfilter_ipv6/ip6t_frag.h
8
__u32 ids[2]; /* Identification range */
include/uapi/linux/perf_event.h
570
__u32 ids[];
include/uapi/linux/virtio_input.h
66
struct virtio_input_devids ids;
include/xen/xenbus.h
111
const struct xenbus_device_id *ids;
ipc/ipc_sysctl.c
155
.data = &init_ipc_ns.ids[IPC_SEM_IDS].next_id,
ipc/ipc_sysctl.c
156
.maxlen = sizeof(init_ipc_ns.ids[IPC_SEM_IDS].next_id),
ipc/ipc_sysctl.c
164
.data = &init_ipc_ns.ids[IPC_MSG_IDS].next_id,
ipc/ipc_sysctl.c
165
.maxlen = sizeof(init_ipc_ns.ids[IPC_MSG_IDS].next_id),
ipc/ipc_sysctl.c
173
.data = &init_ipc_ns.ids[IPC_SHM_IDS].next_id,
ipc/ipc_sysctl.c
174
.maxlen = sizeof(init_ipc_ns.ids[IPC_SHM_IDS].next_id),
ipc/ipc_sysctl.c
214
if (((table->data == &ns->ids[IPC_SEM_IDS].next_id) ||
ipc/ipc_sysctl.c
215
(table->data == &ns->ids[IPC_MSG_IDS].next_id) ||
ipc/ipc_sysctl.c
216
(table->data == &ns->ids[IPC_SHM_IDS].next_id)) &&
ipc/ipc_sysctl.c
280
else if (tbl[i].data == &init_ipc_ns.ids[IPC_SEM_IDS].next_id)
ipc/ipc_sysctl.c
281
tbl[i].data = &ns->ids[IPC_SEM_IDS].next_id;
ipc/ipc_sysctl.c
283
else if (tbl[i].data == &init_ipc_ns.ids[IPC_MSG_IDS].next_id)
ipc/ipc_sysctl.c
284
tbl[i].data = &ns->ids[IPC_MSG_IDS].next_id;
ipc/ipc_sysctl.c
286
else if (tbl[i].data == &init_ipc_ns.ids[IPC_SHM_IDS].next_id)
ipc/ipc_sysctl.c
287
tbl[i].data = &ns->ids[IPC_SHM_IDS].next_id;
ipc/msg.c
100
#define msg_ids(ns) ((ns)->ids[IPC_MSG_IDS])
ipc/msg.c
1320
ipc_init_ids(&ns->ids[IPC_MSG_IDS]);
ipc/msg.c
1333
idr_destroy(&ns->ids[IPC_MSG_IDS].ipcs_idr);
ipc/msg.c
1334
rhashtable_destroy(&ns->ids[IPC_MSG_IDS].key_ht);
ipc/namespace.c
127
void free_ipcs(struct ipc_namespace *ns, struct ipc_ids *ids,
ipc/namespace.c
134
down_write(&ids->rwsem);
ipc/namespace.c
136
in_use = ids->in_use;
ipc/namespace.c
139
perm = idr_find(&ids->ipcs_idr, next_id);
ipc/namespace.c
147
up_write(&ids->rwsem);
ipc/sem.c
169
#define sem_ids(ns) ((ns)->ids[IPC_SEM_IDS])
ipc/sem.c
256
ipc_init_ids(&ns->ids[IPC_SEM_IDS]);
ipc/sem.c
263
idr_destroy(&ns->ids[IPC_SEM_IDS].ipcs_idr);
ipc/sem.c
264
rhashtable_destroy(&ns->ids[IPC_SEM_IDS].key_ht);
ipc/shm.c
144
idr_destroy(&ns->ids[IPC_SHM_IDS].ipcs_idr);
ipc/shm.c
145
rhashtable_destroy(&ns->ids[IPC_SHM_IDS].key_ht);
ipc/shm.c
97
#define shm_ids(ns) ((ns)->ids[IPC_SHM_IDS])
ipc/util.c
115
void ipc_init_ids(struct ipc_ids *ids)
ipc/util.c
117
ids->in_use = 0;
ipc/util.c
118
ids->seq = 0;
ipc/util.c
119
init_rwsem(&ids->rwsem);
ipc/util.c
120
rhashtable_init(&ids->key_ht, &ipc_kht_params);
ipc/util.c
121
idr_init(&ids->ipcs_idr);
ipc/util.c
122
ids->max_idx = -1;
ipc/util.c
123
ids->last_idx = -1;
ipc/util.c
125
ids->next_id = -1;
ipc/util.c
139
int ids, int (*show)(struct seq_file *, void *))
ipc/util.c
149
iface->ids = ids;
ipc/util.c
172
static struct kern_ipc_perm *ipc_findkey(struct ipc_ids *ids, key_t key)
ipc/util.c
176
ipcp = rhashtable_lookup_fast(&ids->key_ht, &key,
ipc/util.c
202
static inline int ipc_idr_alloc(struct ipc_ids *ids, struct kern_ipc_perm *new)
ipc/util.c
207
next_id = ids->next_id;
ipc/util.c
208
ids->next_id = -1;
ipc/util.c
226
max_idx = max(ids->in_use*3/2, ipc_min_cycle);
ipc/util.c
230
idx = idr_alloc_cyclic(&ids->ipcs_idr, NULL, 0, max_idx,
ipc/util.c
239
if (idx <= ids->last_idx) {
ipc/util.c
240
ids->seq++;
ipc/util.c
241
if (ids->seq >= ipcid_seq_max())
ipc/util.c
242
ids->seq = 0;
ipc/util.c
244
ids->last_idx = idx;
ipc/util.c
246
new->seq = ids->seq;
ipc/util.c
251
idr_replace(&ids->ipcs_idr, new, idx);
ipc/util.c
255
idx = idr_alloc(&ids->ipcs_idr, new, ipcid_to_idx(next_id),
ipc/util.c
278
int ipc_addid(struct ipc_ids *ids, struct kern_ipc_perm *new, int limit)
ipc/util.c
290
if (ids->in_use >= limit)
ipc/util.c
305
idx = ipc_idr_alloc(ids, new);
ipc/util.c
309
err = rhashtable_insert_fast(&ids->key_ht, &new->khtnode,
ipc/util.c
312
idr_remove(&ids->ipcs_idr, idx);
ipc/util.c
323
ids->in_use++;
ipc/util.c
324
if (idx > ids->max_idx)
ipc/util.c
325
ids->max_idx = idx;
ipc/util.c
339
static int ipcget_new(struct ipc_namespace *ns, struct ipc_ids *ids,
ipc/util.c
344
down_write(&ids->rwsem);
ipc/util.c
346
up_write(&ids->rwsem);
ipc/util.c
397
static int ipcget_public(struct ipc_namespace *ns, struct ipc_ids *ids,
ipc/util.c
408
down_write(&ids->rwsem);
ipc/util.c
409
ipcp = ipc_findkey(ids, params->key);
ipc/util.c
434
up_write(&ids->rwsem);
ipc/util.c
447
static void ipc_kht_remove(struct ipc_ids *ids, struct kern_ipc_perm *ipcp)
ipc/util.c
450
WARN_ON_ONCE(rhashtable_remove_fast(&ids->key_ht, &ipcp->khtnode,
ipc/util.c
467
static int ipc_search_maxidx(struct ipc_ids *ids, int limit)
ipc/util.c
483
if (idr_get_next(&ids->ipcs_idr, &tmpidx))
ipc/util.c
497
void ipc_rmid(struct ipc_ids *ids, struct kern_ipc_perm *ipcp)
ipc/util.c
501
WARN_ON_ONCE(idr_remove(&ids->ipcs_idr, idx) != ipcp);
ipc/util.c
502
ipc_kht_remove(ids, ipcp);
ipc/util.c
503
ids->in_use--;
ipc/util.c
506
if (unlikely(idx == ids->max_idx)) {
ipc/util.c
507
idx = ids->max_idx-1;
ipc/util.c
509
idx = ipc_search_maxidx(ids, idx);
ipc/util.c
510
ids->max_idx = idx;
ipc/util.c
522
void ipc_set_key_private(struct ipc_ids *ids, struct kern_ipc_perm *ipcp)
ipc/util.c
524
ipc_kht_remove(ids, ipcp);
ipc/util.c
626
struct kern_ipc_perm *ipc_obtain_object_idr(struct ipc_ids *ids, int id)
ipc/util.c
631
out = idr_find(&ids->ipcs_idr, idx);
ipc/util.c
647
struct kern_ipc_perm *ipc_obtain_object_check(struct ipc_ids *ids, int id)
ipc/util.c
649
struct kern_ipc_perm *out = ipc_obtain_object_idr(ids, id);
ipc/util.c
670
int ipcget(struct ipc_namespace *ns, struct ipc_ids *ids,
ipc/util.c
674
return ipcget_new(ns, ids, ops, params);
ipc/util.c
676
return ipcget_public(ns, ids, ops, params);
ipc/util.c
720
struct ipc_ids *ids, int id, int cmd,
ipc/util.c
727
ipcp = ipc_obtain_object_check(ids, id);
ipc/util.c
76
int ids;
ipc/util.c
797
static struct kern_ipc_perm *sysvipc_find_ipc(struct ipc_ids *ids, loff_t *pos)
ipc/util.c
805
ipc = idr_get_next(&ids->ipcs_idr, &tmpidx);
ipc/util.c
828
return sysvipc_find_ipc(&iter->ns->ids[iface->ids], pos);
ipc/util.c
839
struct ipc_ids *ids;
ipc/util.c
841
ids = &iter->ns->ids[iface->ids];
ipc/util.c
847
down_read(&ids->rwsem);
ipc/util.c
858
return sysvipc_find_ipc(ids, pos);
ipc/util.c
866
struct ipc_ids *ids;
ipc/util.c
872
ids = &iter->ns->ids[iface->ids];
ipc/util.c
874
up_read(&ids->rwsem);
ipc/util.h
114
void ipc_init_ids(struct ipc_ids *ids);
ipc/util.h
117
int ids, int (*show)(struct seq_file *, void *));
ipc/util.h
120
#define ipc_init_proc_interface(path, header, ids, show) do {} while (0)
ipc/util.h
152
static inline int ipc_get_maxidx(struct ipc_ids *ids)
ipc/util.h
154
if (ids->in_use == 0)
ipc/util.h
157
if (ids->in_use == ipc_mni)
ipc/util.h
160
return ids->max_idx;
ipc/util.h
176
struct kern_ipc_perm *ipc_obtain_object_idr(struct ipc_ids *ids, int id);
ipc/util.h
182
struct ipc_ids *ids, int id, int cmd,
ipc/util.h
242
struct kern_ipc_perm *ipc_obtain_object_check(struct ipc_ids *ids, int id);
ipc/util.h
243
int ipcget(struct ipc_namespace *ns, struct ipc_ids *ids,
ipc/util.h
245
void free_ipcs(struct ipc_namespace *ns, struct ipc_ids *ids,
kernel/bpf/btf.c
5803
new_aof = krealloc(aof, struct_size(new_aof, ids, aof->cnt + 1),
kernel/bpf/btf.c
5810
aof->ids[aof->cnt++] = id;
kernel/bpf/btf.c
5830
new_aof = krealloc(aof, struct_size(new_aof, ids, aof->cnt + 1),
kernel/bpf/btf.c
5837
aof->ids[aof->cnt++] = i;
kernel/bpf/btf.c
5844
sort(&aof->ids, aof->cnt, sizeof(aof->ids[0]), btf_id_cmp_func, NULL);
kernel/bpf/core.c
2845
u32 *ids;
kernel/bpf/core.c
2853
ids = kcalloc(cnt, sizeof(u32), GFP_USER | __GFP_NOWARN);
kernel/bpf/core.c
2854
if (!ids)
kernel/bpf/core.c
2856
nospc = bpf_prog_array_copy_core(array, ids, cnt);
kernel/bpf/core.c
2857
err = copy_to_user(prog_ids, ids, cnt * sizeof(u32));
kernel/bpf/core.c
2858
kfree(ids);
kernel/bpf/trampoline.c
1611
int bpf_trampoline_multi_attach(struct bpf_prog *prog, u32 *ids,
kernel/bpf/trampoline.c
1625
err = bpf_check_attach_btf_id_multi(btf, prog, ids[i], &tgt_info);
kernel/bpf/trampoline.c
1629
key = bpf_trampoline_compute_key(NULL, btf, ids[i]);
kernel/rseq.c
140
stats.ids += data_race(per_cpu(rseq_stats.ids, cpu));
kernel/rseq.c
157
seq_printf(m, "ids: %16lu\n", stats.ids);
kernel/rseq.c
265
struct rseq_ids ids;
kernel/rseq.c
294
ids.cpu_id = task_cpu(t);
kernel/rseq.c
295
ids.mm_cid = task_mm_cid(t);
kernel/rseq.c
301
ids.node_id = cpu_to_node(ids.cpu_id);
kernel/rseq.c
303
if (unlikely(!rseq_update_usr(t, regs, &ids))) {
kernel/trace/bpf_trace.c
2043
u32 *ids, prog_cnt, ids_len;
kernel/trace/bpf_trace.c
2056
ids = kcalloc(ids_len, sizeof(u32), GFP_USER | __GFP_NOWARN);
kernel/trace/bpf_trace.c
2057
if (!ids)
kernel/trace/bpf_trace.c
2068
ret = bpf_prog_array_copy_info(progs, ids, ids_len, &prog_cnt);
kernel/trace/bpf_trace.c
2072
copy_to_user(uquery->ids, ids, ids_len * sizeof(u32)))
kernel/trace/bpf_trace.c
2075
kfree(ids);
kernel/trace/bpf_trace.c
3750
u32 *id_a = a, *id_b = b, *ids;
kernel/trace/bpf_trace.c
3753
ids = data[0];
kernel/trace/bpf_trace.c
3757
cookie_a = cookies + (id_a - ids);
kernel/trace/bpf_trace.c
3758
cookie_b = cookies + (id_b - ids);
kernel/trace/bpf_trace.c
3764
static int check_dup_ids(u32 *ids, u64 *cookies, u32 cnt)
kernel/trace/bpf_trace.c
3766
void *data[2] = { ids, cookies };
kernel/trace/bpf_trace.c
3774
sort_r_nonatomic(ids, cnt, sizeof(ids[0]), ids_cmp_r, ids_swap_r, data);
kernel/trace/bpf_trace.c
3777
if (ids[i] == ids[i - 1]) {
kernel/trace/bpf_trace.c
3790
u32 cnt, *ids = NULL;
kernel/trace/bpf_trace.c
3796
uids = u64_to_user_ptr(attr->link_create.tracing_multi.ids);
kernel/trace/bpf_trace.c
3806
ids = kvmalloc_objs(*ids, cnt);
kernel/trace/bpf_trace.c
3807
if (!ids)
kernel/trace/bpf_trace.c
3810
if (copy_from_user(ids, uids, cnt * sizeof(*ids))) {
kernel/trace/bpf_trace.c
3828
err = check_dup_ids(ids, cookies, cnt);
kernel/trace/bpf_trace.c
3857
err = bpf_trampoline_multi_attach(prog, ids, link);
kernel/trace/bpf_trace.c
3858
kvfree(ids);
kernel/trace/bpf_trace.c
3868
kvfree(ids);
net/9p/trans_xen.c
571
.ids = xen_9pfs_front_ids,
net/ceph/crush/mapper.c
320
if (!arg || !arg->ids)
net/ceph/crush/mapper.c
323
return arg->ids;
net/ceph/crush/mapper.c
335
__s32 *ids = get_choose_arg_ids(bucket, arg);
net/ceph/crush/mapper.c
338
dprintk("weight 0x%x item %d\n", weights[i], ids[i]);
net/ceph/crush/mapper.c
340
u = crush_hash32_3(bucket->h.hash, x, ids[i], r);
net/ceph/osdmap.c
258
kfree(arg->ids);
net/ceph/osdmap.c
339
arg->ids = decode_array_32_alloc(p, end, &arg->ids_size);
net/ceph/osdmap.c
340
if (IS_ERR(arg->ids)) {
net/ceph/osdmap.c
341
ret = PTR_ERR(arg->ids);
net/ceph/osdmap.c
342
arg->ids = NULL;
net/ipv6/netfilter/ip6t_frag.c
64
id_match(fraginfo->ids[0], fraginfo->ids[1],
net/ipv6/netfilter/ip6t_frag.c
88
return id_match(fraginfo->ids[0], fraginfo->ids[1],
net/mptcp/options.c
1673
0, opts->rm_list.ids[0]);
net/mptcp/options.c
1678
id1 = opts->rm_list.ids[i];
net/mptcp/options.c
1679
id2 = i + 1 < opts->rm_list.nr ? opts->rm_list.ids[i + 1] : TCPOPT_NOP;
net/mptcp/options.c
1680
id3 = i + 2 < opts->rm_list.nr ? opts->rm_list.ids[i + 2] : TCPOPT_NOP;
net/mptcp/options.c
1681
id4 = i + 3 < opts->rm_list.nr ? opts->rm_list.ids[i + 3] : TCPOPT_NOP;
net/mptcp/options.c
305
mp_opt->rm_list.ids[i] = *ptr++;
net/mptcp/options.c
714
pr_debug("rm_list_ids[%d]=%d\n", i, opts->rm_list.ids[i]);
net/mptcp/pm.c
256
if (rm_list->ids[i] == id)
net/mptcp/pm.c
782
u8 rm_id = rm_list->ids[i];
net/mptcp/pm.c
842
mptcp_event_addr_removed(msk, rm_list->ids[i]);
net/mptcp/pm_kernel.c
1063
list.ids[list.nr++] = mptcp_endp_get_local_id(msk, addr);
net/mptcp/pm_kernel.c
1105
list.ids[0] = mptcp_endp_get_local_id(msk, addr);
net/mptcp/pm_kernel.c
1111
__mark_subflow_endp_available(msk, list.ids[0]);
net/mptcp/pm_kernel.c
1135
list.ids[list.nr++] = 0;
net/mptcp/pm_kernel.c
1240
slist.ids[slist.nr++] = mptcp_endp_get_local_id(msk, &entry->addr);
net/mptcp/pm_kernel.c
1243
alist.ids[alist.nr++] = mptcp_endp_get_local_id(msk, &entry->addr);
net/mptcp/pm_kernel.c
1472
list.ids[list.nr++] = mptcp_endp_get_local_id(msk, addr);
net/mptcp/pm_kernel.c
1476
__mark_subflow_endp_available(msk, list.ids[0]);
net/mptcp/pm_userspace.c
267
list.ids[list.nr++] = 0;
net/mptcp/pm_userspace.c
292
alist.ids[alist.nr++] = entry->addr.id;
net/openvswitch/datapath.c
1689
const struct nlattr *ids)
net/openvswitch/datapath.c
1693
if (!nla_len(ids) || nla_len(ids) % sizeof(u32))
net/openvswitch/datapath.c
1698
dp_nlsk_pids = kmalloc(sizeof(*dp_nlsk_pids) + nla_len(ids),
net/openvswitch/datapath.c
1703
dp_nlsk_pids->n_pids = nla_len(ids) / sizeof(u32);
net/openvswitch/datapath.c
1704
nla_memcpy(dp_nlsk_pids->pids, ids, nla_len(ids));
net/openvswitch/datapath.c
2439
struct nlattr *ids = a[OVS_VPORT_ATTR_UPCALL_PID];
net/openvswitch/datapath.c
2441
err = ovs_vport_set_upcall_portids(vport, ids);
net/openvswitch/vport.c
402
int ovs_vport_set_upcall_portids(struct vport *vport, const struct nlattr *ids)
net/openvswitch/vport.c
406
if (!nla_len(ids) || nla_len(ids) % sizeof(u32))
net/openvswitch/vport.c
409
if (nla_len(ids) / sizeof(u32) > nr_cpu_ids)
net/openvswitch/vport.c
414
vport_portids = kmalloc(sizeof(*vport_portids) + nla_len(ids),
net/openvswitch/vport.c
419
vport_portids->n_ids = nla_len(ids) / sizeof(u32);
net/openvswitch/vport.c
421
nla_memcpy(vport_portids->ids, ids, nla_len(ids));
net/openvswitch/vport.c
447
struct vport_portids *ids;
net/openvswitch/vport.c
449
ids = rcu_dereference_ovsl(vport->upcall_portids);
net/openvswitch/vport.c
453
ids->n_ids * sizeof(u32), (void *)ids->ids);
net/openvswitch/vport.c
455
return nla_put_u32(skb, OVS_VPORT_ATTR_UPCALL_PID, ids->ids[0]);
net/openvswitch/vport.c
472
struct vport_portids *ids;
net/openvswitch/vport.c
476
ids = rcu_dereference(vport->upcall_portids);
net/openvswitch/vport.c
479
if (ids->n_ids == 1)
net/openvswitch/vport.c
480
return ids->ids[0];
net/openvswitch/vport.c
483
ids_index = hash - ids->n_ids * reciprocal_divide(hash, ids->rn_ids);
net/openvswitch/vport.c
484
return ids->ids[ids_index];
net/openvswitch/vport.h
57
u32 ids[];
net/sctp/socket.c
7193
struct sctp_assoc_ids *ids;
net/sctp/socket.c
7207
ids_size = struct_size(ids, gaids_assoc_id, num);
net/sctp/socket.c
7212
ids = kmalloc(len, GFP_USER | __GFP_NOWARN);
net/sctp/socket.c
7213
if (unlikely(!ids))
net/sctp/socket.c
7216
ids->gaids_number_of_ids = num;
net/sctp/socket.c
7219
ids->gaids_assoc_id[num++] = asoc->assoc_id;
net/sctp/socket.c
7222
if (put_user(len, optlen) || copy_to_user(optval, ids, len)) {
net/sctp/socket.c
7223
kfree(ids);
net/sctp/socket.c
7227
kfree(ids);
net/wireless/util.c
2039
static bool ieee80211_id_in_list(const u8 *ids, int n_ids, u8 id, bool id_ext)
net/wireless/util.c
2044
if (WARN_ON(ids[n_ids - 1] == WLAN_EID_EXTENSION))
net/wireless/util.c
2049
if (ids[i] == WLAN_EID_EXTENSION) {
net/wireless/util.c
2050
if (id_ext && (ids[i + 1] == id))
net/wireless/util.c
2057
if (ids[i] == id && !id_ext)
net/wireless/util.c
2085
const u8 *ids, int n_ids,
net/wireless/util.c
2099
if (!ieee80211_id_in_list(ids, n_ids, ies[pos + ext],
security/lsm_syscalls.c
105
SYSCALL_DEFINE3(lsm_list_modules, u64 __user *, ids, u32 __user *, size,
security/lsm_syscalls.c
108
u32 total_size = lsm_active_cnt * sizeof(*ids);
security/lsm_syscalls.c
125
if (put_user(lsm_idlist[i]->id, ids++))
sound/pci/oxygen/oxygen.h
159
const struct pci_device_id *ids,
sound/pci/oxygen/oxygen_lib.c
236
oxygen_search_pci_id(struct oxygen *chip, const struct pci_device_id ids[])
sound/pci/oxygen/oxygen_lib.c
259
for (; ids->vendor; ++ids)
sound/pci/oxygen/oxygen_lib.c
260
if (ids->subdevice == subdevice &&
sound/pci/oxygen/oxygen_lib.c
261
ids->driver_data != BROKEN_EEPROM_DRIVER_DATA)
sound/pci/oxygen/oxygen_lib.c
262
return ids;
sound/pci/oxygen/oxygen_lib.c
577
const struct pci_device_id *ids,
sound/pci/oxygen/oxygen_lib.c
621
pci_id = oxygen_search_pci_id(chip, ids);
sound/pci/oxygen/oxygen_lib.c
703
const struct pci_device_id *ids,
sound/pci/oxygen/oxygen_lib.c
708
__oxygen_pci_probe(pci, index, id, owner, ids, get_model));
sound/soc/codecs/cs4234.c
740
uint8_t ids[3];
sound/soc/codecs/cs4234.c
791
ret = regmap_bulk_read(cs4234->regmap, CS4234_DEVID_AB, ids, ARRAY_SIZE(ids));
sound/soc/codecs/cs4234.c
797
devid = (ids[0] << 16) | (ids[1] << 8) | ids[2];
sound/soc/intel/atom/sst-atom-controls.c
1004
struct sst_ids *ids = w->priv;
sound/soc/intel/atom/sst-atom-controls.c
1008
ids->task_id, ids->location_id);
sound/soc/intel/atom/sst-atom-controls.c
1016
ids->location_id, SST_DEFAULT_MODULE_ID);
sound/soc/intel/atom/sst-atom-controls.c
1024
ids->task_id, 0, &cmd,
sound/soc/intel/atom/sst-atom-controls.c
1041
struct sst_ids *ids = w->priv;
sound/soc/intel/atom/sst-atom-controls.c
1050
ids->location_id, SST_DEFAULT_MODULE_ID);
sound/soc/intel/atom/sst-atom-controls.c
1057
cmd.param.part.cfg.format = ids->format; /* stereo/Mono */
sound/soc/intel/atom/sst-atom-controls.c
1343
struct sst_ids *ids = p->sink->priv;
sound/soc/intel/atom/sst-atom-controls.c
1348
sst_set_pipe_gain(ids, drv, mute);
sound/soc/intel/atom/sst-atom-controls.c
1359
struct sst_ids *ids = p->source->priv;
sound/soc/intel/atom/sst-atom-controls.c
1364
sst_set_pipe_gain(ids, drv, mute);
sound/soc/intel/atom/sst-atom-controls.c
1392
struct sst_ids *ids = w->priv;
sound/soc/intel/atom/sst-atom-controls.c
1404
list_add_tail(&module->node, &ids->gain_list);
sound/soc/intel/atom/sst-atom-controls.c
1410
list_add_tail(&module->node, &ids->algo_list);
sound/soc/intel/atom/sst-atom-controls.c
1487
struct sst_ids *ids)
sound/soc/intel/atom/sst-atom-controls.c
1490
unsigned int len = strlen(ids->parent_wname);
sound/soc/intel/atom/sst-atom-controls.c
1493
if (!strncmp(ids->parent_wname, w->name, len)) {
sound/soc/intel/atom/sst-atom-controls.c
1494
ids->parent_w = w;
sound/soc/intel/atom/sst-atom-controls.c
1511
struct sst_ids *ids = w->priv;
sound/soc/intel/atom/sst-atom-controls.c
1515
INIT_LIST_HEAD(&ids->algo_list);
sound/soc/intel/atom/sst-atom-controls.c
1516
INIT_LIST_HEAD(&ids->gain_list);
sound/soc/intel/atom/sst-atom-controls.c
1523
if (ids->parent_wname != NULL)
sound/soc/intel/atom/sst-atom-controls.c
1524
sst_fill_linked_widgets(component, ids);
sound/soc/intel/atom/sst-atom-controls.c
298
const char *pipe, struct sst_ids *ids)
sound/soc/intel/atom/sst-atom-controls.c
306
list_for_each_entry(algo, &ids->algo_list, node) {
sound/soc/intel/atom/sst-atom-controls.c
514
static int sst_set_pipe_gain(struct sst_ids *ids,
sound/soc/intel/atom/sst-atom-controls.c
522
struct sst_ids *ids = w->priv;
sound/soc/intel/atom/sst-atom-controls.c
525
sst_find_and_send_pipe_algo(drv, w->name, ids);
sound/soc/intel/atom/sst-atom-controls.c
526
sst_set_pipe_gain(ids, drv, 0);
sound/soc/intel/atom/sst-atom-controls.c
599
static int sst_set_pipe_gain(struct sst_ids *ids,
sound/soc/intel/atom/sst-atom-controls.c
607
list_for_each_entry(gain, &ids->gain_list, node) {
sound/soc/intel/atom/sst-atom-controls.c
628
struct sst_ids *ids = w->priv;
sound/soc/intel/atom/sst-atom-controls.c
674
ids->location_id, SST_DEFAULT_MODULE_ID);
sound/soc/intel/atom/sst-atom-controls.c
681
ids->task_id, 0, &cmd,
sound/soc/intel/avs/messages.c
895
int avs_ipc_probe_disconnect_points(struct avs_dev *adev, union avs_probe_point_id *ids,
sound/soc/intel/avs/messages.c
901
AVS_PROBE_POINTS_DISCONNECT, (u8 *)ids,
sound/soc/intel/avs/messages.c
902
array_size(sizeof(*ids), num_ids));
sound/soc/intel/avs/messages.h
1032
int avs_ipc_probe_disconnect_points(struct avs_dev *adev, union avs_probe_point_id *ids,
sound/soc/intel/avs/path.c
846
u32 *ids = mod->template->config_ids;
sound/soc/intel/avs/path.c
849
struct avs_tplg_init_config *config = &acomp->tplg->init_configs[ids[i]];
sound/soc/meson/aiu.c
176
const char * const *ids,
sound/soc/meson/aiu.c
188
clks[i].id = ids[i];
sound/xen/xen_snd_front.c
350
.ids = xen_drv_ids,
tools/bpf/bpftool/gen.c
2496
unsigned int *ids = NULL;
tools/bpf/bpftool/gen.c
2507
ids = calloc(n, sizeof(*ids));
tools/bpf/bpftool/gen.c
2508
if (!ids) {
tools/bpf/bpftool/gen.c
2565
ids[i] = new_id;
tools/bpf/bpftool/gen.c
2579
*type_id = ids[*type_id];
tools/bpf/bpftool/gen.c
2582
free(ids);
tools/bpf/bpftool/gen.c
2587
free(ids);
tools/bpf/resolve_btfids/main.c
771
qsort(set->ids, set->cnt, sizeof(set->ids[0]), cmp_id);
tools/include/linux/btf_ids.h
10
u32 ids[];
tools/include/uapi/linux/bpf.h
1888
__aligned_u64 ids;
tools/include/uapi/linux/perf_event.h
570
__u32 ids[];
tools/lib/bpf/bpf.c
852
attr.link_create.tracing_multi.ids = ptr_to_u64(OPTS_GET(opts, tracing_multi.ids, 0));
tools/lib/bpf/bpf.h
474
const __u32 *ids;
tools/lib/bpf/btf_dump.c
1358
decl_stack.ids = d->decl_stack + stack_start;
tools/lib/bpf/btf_dump.c
1378
id = decl_stack->ids[decl_stack->cnt - 1];
tools/lib/bpf/btf_dump.c
1404
id = decl_stack->ids[decl_stack->cnt - 1];
tools/lib/bpf/btf_dump.c
1440
id = decls->ids[--decls->cnt];
tools/lib/bpf/btf_dump.c
1528
next_id = decls->ids[decls->cnt - 1];
tools/lib/bpf/btf_dump.c
641
const __u32 *ids;
tools/lib/bpf/libbpf.c
12615
collect_btf_func_ids_by_glob(const struct btf *btf, const char *pattern, __u32 **ids)
tools/lib/bpf/libbpf.c
12639
err = libbpf_ensure_mem((void **) ids, &cap, sizeof(**ids), cnt + 1);
tools/lib/bpf/libbpf.c
12641
free(*ids);
tools/lib/bpf/libbpf.c
12644
(*ids)[cnt++] = type_id;
tools/lib/bpf/libbpf.c
12650
static int collect_func_ids_by_glob(const struct bpf_program *prog, const char *pattern, __u32 **ids)
tools/lib/bpf/libbpf.c
12681
err = collect_btf_func_ids_by_glob(btf, pattern, ids);
tools/lib/bpf/libbpf.c
12697
const __u32 *ids;
tools/lib/bpf/libbpf.c
12710
ids = OPTS_GET(opts, ids, NULL);
tools/lib/bpf/libbpf.c
12713
if (!!ids != !!cnt)
tools/lib/bpf/libbpf.c
12715
if (pattern && (ids || cookies))
tools/lib/bpf/libbpf.c
12717
if (!pattern && !ids)
tools/lib/bpf/libbpf.c
12726
ids = (const __u32 *) free_ids;
tools/lib/bpf/libbpf.c
12729
lopts.tracing_multi.ids = ids;
tools/lib/bpf/libbpf.h
732
const __u32 *ids;
tools/lib/perf/evlist.c
363
evsel->id[evsel->ids++] = id;
tools/lib/perf/evsel.c
554
evsel->ids = 0;
tools/lib/perf/include/internal/evsel.h
108
u32 ids;
tools/perf/builtin-inject.c
1383
for (j = 0; j < evsel->core.ids; j++) {
tools/perf/builtin-inject.c
1403
for (j = 0; j < evsel->core.ids; j++) {
tools/perf/builtin-inject.c
1456
id_array = calloc(evsel->core.ids, sizeof(*id_array));
tools/perf/builtin-inject.c
1460
vcpu_array = calloc(evsel->core.ids, sizeof(*vcpu_array));
tools/perf/builtin-inject.c
1464
for (i = 0; i < evsel->core.ids; i++) {
tools/perf/builtin-inject.c
1481
ret = perf_event__synthesize_attr(&inject->tool, &attr, evsel->core.ids,
tools/perf/builtin-inject.c
1486
for (i = 0; i < evsel->core.ids; i++) {
tools/perf/builtin-inject.c
1560
if (evsel->core.ids)
tools/perf/builtin-inject.c
237
u64 *ids;
tools/perf/builtin-inject.c
295
ids = (void *)&event->attr.attr + attr_size;
tools/perf/builtin-inject.c
305
ret = perf_event__synthesize_attr(tool, &attr, (u32)n_ids, ids,
tools/perf/builtin-record.c
1985
if (evsel->core.ids) {
tools/perf/tests/expr.c
137
TEST_ASSERT_VAL("find ids", hashmap__size(ctx->ids) == 3);
tools/perf/tests/expr.c
138
TEST_ASSERT_VAL("find ids", hashmap__find(ctx->ids, "BAR", &val_ptr));
tools/perf/tests/expr.c
139
TEST_ASSERT_VAL("find ids", hashmap__find(ctx->ids, "BAZ", &val_ptr));
tools/perf/tests/expr.c
140
TEST_ASSERT_VAL("find ids", hashmap__find(ctx->ids, "BOZO", &val_ptr));
tools/perf/tests/expr.c
147
TEST_ASSERT_VAL("find ids", hashmap__size(ctx->ids) == 2);
tools/perf/tests/expr.c
148
TEST_ASSERT_VAL("find ids", hashmap__find(ctx->ids, "EVENT1,param=3@", &val_ptr));
tools/perf/tests/expr.c
149
TEST_ASSERT_VAL("find ids", hashmap__find(ctx->ids, "EVENT2,param=3@", &val_ptr));
tools/perf/tests/expr.c
155
TEST_ASSERT_VAL("find ids", hashmap__size(ctx->ids) == 2);
tools/perf/tests/expr.c
156
TEST_ASSERT_VAL("find ids", hashmap__find(ctx->ids, "dash-event1", &val_ptr));
tools/perf/tests/expr.c
157
TEST_ASSERT_VAL("find ids", hashmap__find(ctx->ids, "dash-event2", &val_ptr));
tools/perf/tests/expr.c
169
TEST_ASSERT_VAL("find ids", hashmap__size(ctx->ids) == 1);
tools/perf/tests/expr.c
170
TEST_ASSERT_VAL("find ids", hashmap__find(ctx->ids,
tools/perf/tests/expr.c
178
TEST_ASSERT_VAL("find ids", hashmap__size(ctx->ids) == 1);
tools/perf/tests/expr.c
179
TEST_ASSERT_VAL("find ids", hashmap__find(ctx->ids,
tools/perf/tests/expr.c
189
TEST_ASSERT_VAL("find ids", hashmap__size(ctx->ids) == 0);
tools/perf/tests/expr.c
195
TEST_ASSERT_VAL("find ids", hashmap__size(ctx->ids) == 0);
tools/perf/tests/expr.c
199
TEST_ASSERT_VAL("find ids", hashmap__size(ctx->ids) == 0);
tools/perf/tests/expr.c
203
TEST_ASSERT_VAL("find ids", hashmap__size(ctx->ids) == 1);
tools/perf/tests/expr.c
204
TEST_ASSERT_VAL("find ids", hashmap__find(ctx->ids, "EVENT1", &val_ptr));
tools/perf/tests/expr.c
208
TEST_ASSERT_VAL("find ids", hashmap__size(ctx->ids) == 1);
tools/perf/tests/expr.c
209
TEST_ASSERT_VAL("find ids", hashmap__find(ctx->ids, "EVENT1", &val_ptr));
tools/perf/tests/expr.c
215
TEST_ASSERT_VAL("find ids", hashmap__size(ctx->ids) == 0);
tools/perf/tests/expr.c
219
TEST_ASSERT_VAL("find ids", hashmap__size(ctx->ids) == 0);
tools/perf/tests/expr.c
223
TEST_ASSERT_VAL("find ids", hashmap__size(ctx->ids) == 1);
tools/perf/tests/expr.c
224
TEST_ASSERT_VAL("find ids", hashmap__find(ctx->ids, "EVENT1", &val_ptr));
tools/perf/tests/expr.c
228
TEST_ASSERT_VAL("find ids", hashmap__size(ctx->ids) == 1);
tools/perf/tests/expr.c
229
TEST_ASSERT_VAL("find ids", hashmap__find(ctx->ids, "EVENT1", &val_ptr));
tools/perf/tests/expr.c
267
TEST_ASSERT_VAL("source count", hashmap__size(ctx->ids) == 1);
tools/perf/tests/expr.c
268
TEST_ASSERT_VAL("source count", hashmap__find(ctx->ids, "EVENT1", &val_ptr));
tools/perf/tests/pmu-events.c
1001
hashmap__for_each_entry(ctx->ids, cur, bkt)
tools/perf/tests/pmu-events.c
984
hashmap__for_each_entry(ctx->ids, cur, bkt)
tools/perf/tests/pmu-events.c
987
hashmap__for_each_entry(ctx->ids, cur, bkt) {
tools/perf/util/bpf-filter.c
240
u64 *ids = calloc(alloced, sizeof(*ids));
tools/perf/util/bpf-filter.c
242
if (ids == NULL)
tools/perf/util/bpf-filter.c
248
free(ids);
tools/perf/util/bpf-filter.c
261
tmp = realloc(ids, alloced * sizeof(*ids));
tools/perf/util/bpf-filter.c
265
ids = tmp;
tools/perf/util/bpf-filter.c
267
ids[num++] = key;
tools/perf/util/bpf-filter.c
274
bpf_map_delete_elem(fd, &ids[i]);
tools/perf/util/bpf-filter.c
276
free(ids);
tools/perf/util/expr.c
145
return ids__insert(ctx->ids, id);
tools/perf/util/expr.c
170
ret = hashmap__set(ctx->ids, id, data_ptr, &old_key, &old_data);
tools/perf/util/expr.c
217
ret = hashmap__set(ctx->ids, name, data_ptr, &old_key, &old_data);
tools/perf/util/expr.c
234
return hashmap__find(ctx->ids, id, data) ? 0 : -1;
tools/perf/util/expr.c
244
hashmap__for_each_entry(needles->ids, cur, bkt) {
tools/perf/util/expr.c
295
hashmap__delete(ctx->ids, id, &old_key, &old_val);
tools/perf/util/expr.c
308
ctx->ids = hashmap__new(key_hash, key_equal, NULL);
tools/perf/util/expr.c
309
if (IS_ERR(ctx->ids)) {
tools/perf/util/expr.c
322
hashmap__for_each_entry(ctx->ids, cur, bkt) {
tools/perf/util/expr.c
326
hashmap__clear(ctx->ids);
tools/perf/util/expr.c
338
hashmap__for_each_entry(ctx->ids, cur, bkt) {
tools/perf/util/expr.c
342
hashmap__free(ctx->ids);
tools/perf/util/expr.c
443
if (hashmap__find(ctx->ids, id, /*value=*/NULL))
tools/perf/util/expr.c
77
void ids__free(struct hashmap *ids)
tools/perf/util/expr.c
82
if (ids == NULL)
tools/perf/util/expr.c
85
hashmap__for_each_entry(ids, cur, bkt) {
tools/perf/util/expr.c
90
hashmap__free(ids);
tools/perf/util/expr.c
93
int ids__insert(struct hashmap *ids, const char *id)
tools/perf/util/expr.c
99
ret = hashmap__set(ids, id, data_ptr, &old_key, &old_data);
tools/perf/util/expr.h
16
struct hashmap *ids;
tools/perf/util/expr.h
23
void ids__free(struct hashmap *ids);
tools/perf/util/expr.h
24
int ids__insert(struct hashmap *ids, const char *id);
tools/perf/util/expr.h
54
struct expr_parse_ctx *ids);
tools/perf/util/expr.y
117
result.ids = NULL;
tools/perf/util/expr.y
125
result.ids = ids__new();
tools/perf/util/expr.y
126
if (!result.ids || ids__insert(result.ids, id)) {
tools/perf/util/expr.y
141
assert(LHS.ids == NULL); \
tools/perf/util/expr.y
142
assert(RHS.ids == NULL); \
tools/perf/util/expr.y
148
RESULT.ids = NULL; \
tools/perf/util/expr.y
159
ctx->ids = ids__union($1.ids, ctx->ids);
tools/perf/util/expr.y
174
$$.ids = $5.ids;
tools/perf/util/expr.y
184
$$.ids = $1.ids;
tools/perf/util/expr.y
193
$$.ids = NULL;
tools/perf/util/expr.y
211
$$.ids = NULL;
tools/perf/util/expr.y
219
$$.ids = NULL;
tools/perf/util/expr.y
225
$$.ids = NULL;
tools/perf/util/expr.y
233
$$.ids = NULL;
tools/perf/util/expr.y
241
$$.ids = NULL;
tools/perf/util/expr.y
250
$$.ids = NULL;
tools/perf/util/expr.y
263
$$.ids = NULL;
tools/perf/util/expr.y
270
$$.ids = NULL;
tools/perf/util/expr.y
279
$$.ids = NULL;
tools/perf/util/expr.y
292
$$.ids = NULL;
tools/perf/util/expr.y
310
$$.ids = NULL;
tools/perf/util/expr.y
315
$$.ids = NULL;
tools/perf/util/expr.y
32
struct hashmap *ids;
tools/perf/util/expr.y
330
$$.ids = NULL;
tools/perf/util/expr.y
345
$$.ids = NULL;
tools/perf/util/expr.y
351
$$.ids = NULL;
tools/perf/util/expr.y
360
$$.ids = $2.ids;
tools/perf/util/expr.y
370
$$.ids = NULL;
tools/perf/util/expr.y
379
$$.ids = NULL;
tools/perf/util/expr.y
387
$$.ids = NULL;
tools/perf/util/expr.y
41
} ids;
tools/perf/util/expr.y
56
%type <ids> expr if_expr
tools/perf/util/expr.y
57
%destructor { ids__free($$.ids); } <ids>
tools/perf/util/expr.y
81
static struct ids union_expr(struct ids ids1, struct ids ids2)
tools/perf/util/expr.y
83
struct ids result = {
tools/perf/util/expr.y
85
.ids = ids__union(ids1.ids, ids2.ids),
tools/perf/util/expr.y
96
static struct ids handle_id(struct expr_parse_ctx *ctx, char *id,
tools/perf/util/expr.y
99
struct ids result;
tools/perf/util/header.c
116
struct perf_file_section ids;
tools/perf/util/header.c
2314
evsel->core.ids = nr;
tools/perf/util/header.c
2357
if (evsel->core.ids) {
tools/perf/util/header.c
2359
for (j = 0, id = evsel->core.id; j < evsel->core.ids; j++, id++) {
tools/perf/util/header.c
4523
err = do_write(&ff, evsel->core.id, evsel->core.ids * sizeof(u64));
tools/perf/util/header.c
4529
attr_offset += evsel->core.ids * sizeof(u64);
tools/perf/util/header.c
4545
.ids = {
tools/perf/util/header.c
4547
.size = evsel->core.ids * sizeof(u64),
tools/perf/util/header.c
4620
data_offset += evsel->core.ids * sizeof(u64);
tools/perf/util/header.c
5042
ret = readn(fd, &f_attr->ids, sizeof(f_attr->ids));
tools/perf/util/header.c
5174
f_attr.ids.size = bswap_64(f_attr.ids.size);
tools/perf/util/header.c
5175
f_attr.ids.offset = bswap_64(f_attr.ids.offset);
tools/perf/util/header.c
5185
if (f_attr.ids.size % sizeof(u64)) {
tools/perf/util/header.c
5187
f_attr.ids.size, i);
tools/perf/util/header.c
5198
if (f_attr.ids.size / sizeof(u64) > MAX_IDS_PER_ATTR) {
tools/perf/util/header.c
5200
f_attr.ids.size, i);
tools/perf/util/header.c
5210
(f_attr.ids.offset > (u64)input_stat.st_size ||
tools/perf/util/header.c
5211
f_attr.ids.size > (u64)input_stat.st_size - f_attr.ids.offset)) {
tools/perf/util/header.c
5213
i, f_attr.ids.offset, f_attr.ids.size, (u64)input_stat.st_size);
tools/perf/util/header.c
5231
nr_ids = f_attr.ids.size / sizeof(u64);
tools/perf/util/header.c
5240
lseek(fd, f_attr.ids.offset, SEEK_SET);
tools/perf/util/header.c
5510
u64 *ids;
tools/perf/util/header.c
5608
ids = (void *)&event->attr.attr + attr_size;
tools/perf/util/header.c
5610
perf_evlist__id_add(&evlist->core, &evsel->core, 0, i, ids[i]);
tools/perf/util/header.c
636
nri = evsel->core.ids;
tools/perf/util/header.c
650
ret = do_write(ff, evsel->core.id, evsel->core.ids * sizeof(u64));
tools/perf/util/intel-bts.c
754
if (evsel->core.attr.type == bts->pmu_type && evsel->core.ids) {
tools/perf/util/intel-pt.c
3970
if (evsel->core.attr.type == pt->pmu_type && evsel->core.ids)
tools/perf/util/metricgroup.c
1230
hashmap__for_each_entry(m->pctx->ids, cur, bkt) {
tools/perf/util/metricgroup.c
1262
struct expr_parse_ctx *ids, const char *modifier,
tools/perf/util/metricgroup.c
1273
if (!metric_no_merge || hashmap__size(ids->ids) == 0) {
tools/perf/util/metricgroup.c
1295
ids__insert(ids->ids, tmp);
tools/perf/util/metricgroup.c
1299
if (!added_event && hashmap__size(ids->ids) == 0) {
tools/perf/util/metricgroup.c
1304
ids__insert(ids->ids, tmp);
tools/perf/util/metricgroup.c
1307
ret = metricgroup__build_event_string(&events, ids, modifier,
tools/perf/util/metricgroup.c
1347
if (hashmap__find(m->pctx->ids, metric_id, NULL))
tools/perf/util/metricgroup.c
1417
if (!ret && combined && hashmap__size(combined->ids)) {
tools/perf/util/metricgroup.c
1485
ret = setup_metric_events(fake_pmu ? "all" : m->pmu, m->pctx->ids,
tools/perf/util/metricgroup.c
290
static int setup_metric_events(const char *pmu, struct hashmap *ids,
tools/perf/util/metricgroup.c
302
ids_size = hashmap__size(ids);
tools/perf/util/metricgroup.c
330
if (hashmap__find(ids, metric_id, &val_ptr)) {
tools/perf/util/metricgroup.c
572
hashmap__for_each_entry(ctx->ids, cur, bkt) {
tools/perf/util/metricgroup.c
763
hashmap__for_each_entry(root_metric->pctx->ids, cur, bkt) {
tools/perf/util/metricgroup.c
990
left_count = hashmap__size(left->pctx->ids);
tools/perf/util/metricgroup.c
996
right_count = hashmap__size(right->pctx->ids);
tools/perf/util/session.c
2535
u64 ids[1];
tools/perf/util/session.c
2541
.attr_id.ids[0] = id,
tools/perf/util/synthetic-events.c
1881
nr += evsel->core.ids;
tools/perf/util/synthetic-events.c
1906
for (j = 0; j < evsel->core.ids; j++, i++) {
tools/perf/util/synthetic-events.c
2103
err = perf_event__synthesize_attr(tool, &evsel->core.attr, evsel->core.ids,
tools/perf/util/synthetic-events.c
2181
u32 ids, u64 *id, perf_event__handler_t process)
tools/perf/util/synthetic-events.c
2200
size += ids * sizeof(u64);
tools/perf/util/synthetic-events.c
2215
memcpy(perf_record_header_attr_id(ev), id, ids * sizeof(u64));
tools/perf/util/synthetic-events.h
48
int perf_event__synthesize_attr(const struct perf_tool *tool, struct perf_event_attr *attr, u32 ids, u64 *id, perf_event__handler_t process);
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
10
__u32 ids[5];
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
13
{ .ids = {}, .strs = {} },
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
14
{ .ids = {}, .strs = { "int" } },
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
15
{ .ids = {}, .strs = { "int64" } },
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
153
if (!ASSERT_EQ(*next_id, fields[id].ids[id_idx], "field_id_match"))
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
158
ASSERT_EQ(fields[id].ids[id_idx], 0, "field_id_cnt");
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
16
{ .ids = { 1 }, .strs = { "" } },
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
17
{ .ids = { 2, 1 }, .strs = { "" } },
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
18
{ .ids = { 3, 1 }, .strs = { "s1", "f1", "f2" } },
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
19
{ .ids = { 1, 5 }, .strs = { "u1", "f1", "f2" } },
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
20
{ .ids = {}, .strs = { "e1", "v1", "v2" } },
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
21
{ .ids = {}, .strs = { "fw1" } },
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
22
{ .ids = { 1 }, .strs = { "t" } },
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
23
{ .ids = { 2 }, .strs = { "" } },
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
24
{ .ids = { 1 }, .strs = { "" } },
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
25
{ .ids = { 3 }, .strs = { "" } },
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
26
{ .ids = { 1, 1, 3 }, .strs = { "", "p1", "p2" } },
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
27
{ .ids = { 13 }, .strs = { "func" } },
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
28
{ .ids = { 1 }, .strs = { "var1" } },
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
29
{ .ids = { 3 }, .strs = { "var2" } },
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
30
{ .ids = {}, .strs = { "float" } },
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
31
{ .ids = { 11 }, .strs = { "decltag" } },
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
32
{ .ids = { 6 }, .strs = { "typetag" } },
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
33
{ .ids = {}, .strs = { "e64", "eval1", "eval2", "eval3" } },
tools/testing/selftests/bpf/prog_tests/btf_field_iter.c
34
{ .ids = { 15, 16 }, .strs = { "datasec1" } }
tools/testing/selftests/bpf/prog_tests/resolve_btfids.c
150
if (test_symbols[j].id != test_set.ids[i])
tools/testing/selftests/bpf/prog_tests/resolve_btfids.c
158
test_set.ids[i]);
tools/testing/selftests/bpf/prog_tests/resolve_btfids.c
163
if (!ASSERT_LE(test_set.ids[i - 1], test_set.ids[i], "sort_check"))
tools/testing/selftests/bpf/prog_tests/tp_attach_query.c
124
if (CHECK(saved_prog_ids[j] != query->ids[j],
tools/testing/selftests/bpf/prog_tests/tp_attach_query.c
127
j, saved_prog_ids[j], query->ids[j]))
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
100
ids = calloc(funcs_cnt, sizeof(ids[0]));
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
101
if (!ids)
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
150
ids[idx] = type_id;
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
156
free(ids);
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
157
ids = NULL;
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
164
return ids;
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
243
__u32 *ids;
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
252
ids = get_ids(bpf_fentry_test, cnt, NULL);
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
253
if (!ASSERT_OK_PTR(ids, "get_ids"))
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
256
opts.ids = ids;
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
288
free(ids);
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
347
__u32 *ids;
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
355
ids = get_ids(bpf_testmod_fentry_test, cnt, "bpf_testmod");
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
356
if (!ASSERT_OK_PTR(ids, "get_ids"))
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
359
opts.ids = ids;
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
378
free(ids);
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
393
__u32 *ids, i;
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
405
ids = get_ids(funcs, cnt, NULL);
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
406
if (!ASSERT_OK_PTR(ids, "get_ids"))
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
409
opts.ids = ids;
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
412
free(ids);
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
512
__u32 ids[2] = {}, *ids2 = NULL;
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
527
.ids = ids,
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
538
.ids = NULL,
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
556
.ids = ids,
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
571
.ids = ids2,
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
581
ids[0] = ids2[0];
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
582
ids[1] = ids2[0];
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
585
.ids = ids,
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
610
__u32 *ids = NULL;
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
684
err = libbpf_ensure_mem((void **) &ids, &cap, sizeof(*ids), cnt + 1);
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
688
ids[cnt++] = type_id;
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
691
opts.ids = ids;
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
717
free(ids);
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
740
__u32 *ids = NULL;
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
754
ids = get_ids(bpf_fentry_test, cnt, NULL);
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
755
if (!ASSERT_OK_PTR(ids, "get_ids"))
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
762
ids[9] = 0;
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
764
opts.ids = ids;
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
784
free(ids);
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
84
__u32 *ids = NULL;
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
861
__u32 *ids = NULL;
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
896
ids = get_ids(bpf_fentry_test, cnt, NULL);
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
897
if (!ASSERT_OK_PTR(ids, "get_ids"))
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
900
opts.ids = ids;
tools/testing/selftests/bpf/prog_tests/tracing_multi.c
921
free(ids);
tools/testing/selftests/bpf/veristat.c
120
enum stat_id ids[ALL_STATS_CNT];
tools/testing/selftests/bpf/veristat.c
1365
if (env.output_spec.ids[i] == id)
tools/testing/selftests/bpf/veristat.c
2318
cmp = cmp_stat(s1, s2, env.sort_spec.ids[i],
tools/testing/selftests/bpf/veristat.c
2418
env.sort_spec.ids[i],
tools/testing/selftests/bpf/veristat.c
2456
int id = env.output_spec.ids[i];
tools/testing/selftests/bpf/veristat.c
2535
int id = env.output_spec.ids[i];
tools/testing/selftests/bpf/veristat.c
2720
err = parse_stat_value(next, specs->ids[col], st);
tools/testing/selftests/bpf/veristat.c
2779
int id = env.output_spec.ids[i];
tools/testing/selftests/bpf/veristat.c
2801
int id = env.output_spec.ids[i];
tools/testing/selftests/bpf/veristat.c
2847
int id = env.output_spec.ids[i], len;
tools/testing/selftests/bpf/veristat.c
3043
if (base_specs.ids[i] != comp_specs.ids[i]) {
tools/testing/selftests/bpf/veristat.c
3046
stat_defs[base_specs.ids[i]].names[0],
tools/testing/selftests/bpf/veristat.c
3047
stat_defs[comp_specs.ids[i]].names[0]);
tools/testing/selftests/bpf/veristat.c
743
.ids = {
tools/testing/selftests/bpf/veristat.c
794
.ids = {
tools/testing/selftests/bpf/veristat.c
805
.ids = {
tools/testing/selftests/bpf/veristat.c
814
.ids = {
tools/testing/selftests/bpf/veristat.c
934
if (specs->spec_cnt >= ARRAY_SIZE(specs->ids)) {
tools/testing/selftests/bpf/veristat.c
935
fprintf(stderr, "Can't specify more than %zd stats\n", ARRAY_SIZE(specs->ids));
tools/testing/selftests/bpf/veristat.c
950
specs->ids[specs->spec_cnt] = id;
tools/testing/selftests/lsm/common.h
25
static inline int lsm_list_modules(__u64 *ids, __u32 *size, __u32 flags)
tools/testing/selftests/lsm/common.h
27
return syscall(__NR_lsm_list_modules, ids, size, flags);
