games/adventure/save.c

129

for (p = save_array; p->address != NULL; p++)

games/adventure/save.c

130

sum = crc(p->address, p->width);

games/adventure/save.c

141

for (p = save_array; p->address != NULL; p++) {

games/adventure/save.c

142

for (s = p->address, i = 0; i < p->width; i++, s++)

games/adventure/save.c

144

fwrite(p->address, p->width, 1, out);

games/adventure/save.c

168

for (p = save_array; p->address != NULL; p++) {

games/adventure/save.c

169

fread(p->address, p->width, 1, in);

games/adventure/save.c

170

for (s = p->address, i = 0; i < p->width; i++, s++)

games/adventure/save.c

176

for (p = save_array; p->address != NULL; p++)

games/adventure/save.c

177

cksum = crc(p->address, p->width);

games/adventure/save.c

46

void *address;

lib/libarch/alpha/bwx.c

186

bwx_map_memory(u_int32_t address, u_int32_t size)

lib/libarch/alpha/bwx.c

195

mem_fd, bwx_mem_base + BWX_EV56_INT1 + address);

lib/libarch/alpha/bwx.c

202

mem_fd, bwx_mem_base + BWX_EV56_INT2 + address);

lib/libarch/alpha/bwx.c

210

mem_fd, bwx_mem_base + BWX_EV56_INT4 + address);

lib/libarch/alpha/io.c

100

map_memory(u_int32_t address, u_int32_t size)

lib/libarch/alpha/io.c

102

return ops->map_memory(address, size);

lib/libc/rpc/pmap_getmaps.c

58

pmap_getmaps(struct sockaddr_in *address)

lib/libc/rpc/pmap_getmaps.c

67

address->sin_port = htons(PMAPPORT);

lib/libc/rpc/pmap_getmaps.c

68

client = clnttcp_create(address, PMAPPROG,

lib/libc/rpc/pmap_getmaps.c

78

address->sin_port = 0;

lib/libc/rpc/pmap_getport.c

55

pmap_getport(struct sockaddr_in *address, u_long program, u_long version,

lib/libc/rpc/pmap_getport.c

63

address->sin_port = htons(PMAPPORT);

lib/libc/rpc/pmap_getport.c

64

client = clntudp_bufcreate(address, PMAPPROG,

lib/libc/rpc/pmap_getport.c

80

address->sin_port = 0;

lib/libcrypto/x509/x509_constraints.c

1104

memcpy(&name->address[0], bytes, len);

lib/libcrypto/x509/x509_constraints.c

1218

return x509_constraints_ipaddr(name->address, nlen,

lib/libcrypto/x509/x509_constraints.c

1219

constraint->address, clen);

lib/libcrypto/x509/x509_constraints.c

122

memcpy(new->address, name->address, sizeof(name->address));

lib/libcrypto/x509/x509_constraints.c

728

x509_constraints_ipaddr(uint8_t *address, size_t alen, uint8_t *constraint,

lib/libcrypto/x509/x509_constraints.c

739

if ((address[i] & mask[i]) != (constraint[i] & mask[i]))

lib/libcrypto/x509/x509_constraints.c

901

memcpy(vname->address, bytes, len);

lib/libcrypto/x509/x509_internal.h

51

uint8_t address[32]; /* Must hold ipv6 + mask */

lib/libz/zlib.h

86

typedef void (*free_func)(voidpf opaque, voidpf address);

regress/lib/libc/malloc/malloc_errs/malloc_errs.c

237

uintptr_t address;

regress/lib/libc/malloc/malloc_errs/malloc_errs.c

239

address = (uintptr_t)(void *)p;

regress/lib/libc/malloc/malloc_errs/malloc_errs.c

241

if (address / getpagesize() == (address + 32) / getpagesize())

regress/sbin/isakmpd/util/utiltest.c

50

int test_1 (char *address, char *port, int ok)

regress/sbin/isakmpd/util/utiltest.c

60

printf ("test_1 (\"%s\", \"%s\") ", address, port);

regress/sbin/isakmpd/util/utiltest.c

61

rv = text2sockaddr (address, port, &sa, 0, 0) == ok;

sbin/dhcp6leased/dhcp6leased.c

733

configure_address(struct imsg_configure_address *address)

sbin/dhcp6leased/dhcp6leased.c

741

if_name = if_indextoname(address->if_index, in6_addreq.ifra_name);

sbin/dhcp6leased/dhcp6leased.c

744

address->if_index);

sbin/dhcp6leased/dhcp6leased.c

748

memcpy(&in6_addreq.ifra_addr, &address->addr,

sbin/dhcp6leased/dhcp6leased.c

750

memcpy(&in6_addreq.ifra_prefixmask.sin6_addr, &address->mask,

sbin/dhcp6leased/dhcp6leased.c

758

in6_addreq.ifra_lifetime.ia6t_expire = t + address->vltime;

sbin/dhcp6leased/dhcp6leased.c

759

in6_addreq.ifra_lifetime.ia6t_vltime = address->vltime;

sbin/dhcp6leased/dhcp6leased.c

761

in6_addreq.ifra_lifetime.ia6t_preferred = t + address->pltime;

sbin/dhcp6leased/dhcp6leased.c

762

in6_addreq.ifra_lifetime.ia6t_pltime = address->pltime;

sbin/dhcp6leased/dhcp6leased.c

771

deconfigure_address(struct imsg_configure_address *address)

sbin/dhcp6leased/dhcp6leased.c

778

if_name = if_indextoname(address->if_index, in6_ridreq.ifr_name);

sbin/dhcp6leased/dhcp6leased.c

781

address->if_index);

sbin/dhcp6leased/dhcp6leased.c

785

memcpy(&in6_ridreq.ifr_addr, &address->addr,

sbin/dhcp6leased/engine.c

1536

struct imsg_configure_address address;

sbin/dhcp6leased/engine.c

1550

memset(&address, 0, sizeof(address));

sbin/dhcp6leased/engine.c

1552

address.if_index = if_index;

sbin/dhcp6leased/engine.c

1553

address.addr.sin6_family = AF_INET6;

sbin/dhcp6leased/engine.c

1554

address.addr.sin6_len = sizeof(address.addr);

sbin/dhcp6leased/engine.c

1555

address.addr.sin6_addr = pd->prefix;

sbin/dhcp6leased/engine.c

1558

address.addr.sin6_addr.s6_addr[i] |=

sbin/dhcp6leased/engine.c

1562

address.addr.sin6_addr.s6_addr[15] |= 1;

sbin/dhcp6leased/engine.c

1564

in6_prefixlen2mask(&address.mask, pd_conf->prefix_len);

sbin/dhcp6leased/engine.c

1568

&address.addr.sin6_addr, ntopbuf, INET6_ADDRSTRLEN),

sbin/dhcp6leased/engine.c

1571

address.vltime = pd->vltime;

sbin/dhcp6leased/engine.c

1572

address.pltime = pd->pltime;

sbin/dhcp6leased/engine.c

1575

engine_imsg_compose_main(IMSG_CONFIGURE_ADDRESS, 0, &address,

sbin/dhcp6leased/engine.c

1576

sizeof(address));

sbin/dhcp6leased/engine.c

1578

engine_imsg_compose_main(IMSG_DECONFIGURE_ADDRESS, 0, &address,

sbin/dhcp6leased/engine.c

1579

sizeof(address));

sbin/iked/iked.h

230

struct iked_addr address;

sbin/iked/ikev2.c

2556

(struct sockaddr_in *)&ikecfg->cfg.address.addr;

sbin/iked/ikev2.c

2577

in4 = (struct sockaddr_in *)&ikecfg->cfg.address.addr;

sbin/iked/ikev2.c

2578

mask4 = prefixlen2mask(ikecfg->cfg.address.addr_mask);

sbin/iked/ikev2.c

2591

in6 = (struct sockaddr_in6 *)&ikecfg->cfg.address.addr;

sbin/iked/ikev2.c

2605

(struct sockaddr_in6 *)&ikecfg->cfg.address.addr;

sbin/iked/ikev2.c

2613

if (ikecfg->cfg.address.addr_net)

sbin/iked/ikev2.c

2614

prefixlen = ikecfg->cfg.address.addr_mask;

sbin/iked/ikev2.c

7158

if (!ikecfg->cfg.address.addr_net)

sbin/iked/ikev2.c

7273

cfg4 = (struct sockaddr_in *)&ikecfg->cfg.address.addr;

sbin/iked/ikev2.c

7274

mask = prefixlen2mask(ikecfg->cfg.address.addr_mask);

sbin/iked/ikev2.c

7316

cfg6 = (struct sockaddr_in6 *)&ikecfg->cfg.address.addr;

sbin/iked/ikev2.c

7324

mask = (ikecfg->cfg.address.addr_mask >= 96)

sbin/iked/ikev2.c

7325

? prefixlen2mask(ikecfg->cfg.address.addr_mask - 96)

sbin/iked/ikev2.c

7380

addr.addr_mask = ikecfg->cfg.address.addr_mask;

sbin/iked/parse.y

1533

memcpy(&ipa->address, sa, sizeof(struct sockaddr_in6));

sbin/iked/parse.y

1535

memcpy(&ipa->address, sa, sizeof(struct sockaddr_in));

sbin/iked/parse.y

2431

memcpy(&n->address, sa_in, sizeof(*sa_in));

sbin/iked/parse.y

2436

memcpy(&n->address, sa_in6, sizeof(*sa_in6));

sbin/iked/parse.y

2557

in6 = (struct sockaddr_in6 *)&n->address;

sbin/iked/parse.y

2596

set_ipmask(struct ipsec_addr_wrap *address, int b)

sbin/iked/parse.y

2599

address->mask = address->af == AF_INET ? 32 : 128;

sbin/iked/parse.y

2601

address->mask = b;

sbin/iked/parse.y

2848

memcpy(&pol.pol_local.addr, &ipa->address,

sbin/iked/parse.y

2849

sizeof(ipa->address));

sbin/iked/parse.y

2857

memcpy(&pol.pol_peer.addr, &ipb->address,

sbin/iked/parse.y

2858

sizeof(ipb->address));

sbin/iked/parse.y

3122

memcpy(&cfg->cfg.address.addr, &ipa->address,

sbin/iked/parse.y

3123

sizeof(ipa->address));

sbin/iked/parse.y

3124

cfg->cfg.address.addr_mask = ipa->mask;

sbin/iked/parse.y

3125

cfg->cfg.address.addr_net = ipa->netaddress;

sbin/iked/parse.y

3126

cfg->cfg.address.addr_af = ipa->af;

sbin/iked/parse.y

3227

memcpy(&flow->flow_src.addr, &ipa->address,

sbin/iked/parse.y

3228

sizeof(ipa->address));

sbin/iked/parse.y

3234

memcpy(&flow->flow_dst.addr, &ipb->address,

sbin/iked/parse.y

3235

sizeof(ipb->address));

sbin/iked/parse.y

3243

memcpy(&flow->flow_prenat.addr, &ippn->address,

sbin/iked/parse.y

3244

sizeof(ippn->address));

sbin/iked/parse.y

338

struct sockaddr_storage address;

sbin/iked/print.c

234

cfg->cfg.address.addr_af, cpxfs),

sbin/iked/print.c

235

print_addr(&cfg->cfg.address.addr));

sbin/iked/radius.c

658

addr = &req->rr_cfg[req->rr_ncfg].cfg.address;

sbin/ipsecctl/ipsecctl.c

398

if (inet_ntop(ipa->af, &ipa->address, buf, sizeof(buf)) == NULL)

sbin/ipsecctl/ipsecctl.h

111

struct ipsec_addr address;

sbin/ipsecctl/parse.y

1712

memcpy(&ipa->address.v6,

sbin/ipsecctl/parse.y

1760

ipa->address.v4 = ina;

sbin/ipsecctl/parse.y

1799

memcpy(&ipa->address.v4,

sbin/ipsecctl/parse.y

1809

memcpy(&ipa->address.v6,

sbin/ipsecctl/parse.y

1901

memcpy(&n->address.v4, &((struct sockaddr_in *)

sbin/ipsecctl/parse.y

1909

memcpy(&n->address.v6, &((struct sockaddr_in6 *)

sbin/ipsecctl/parse.y

2032

if (IN6_IS_ADDR_LINKLOCAL(&n->address.v6)) {

sbin/ipsecctl/parse.y

2040

memcpy(&tmp16, &n->address.v6.s6_addr[2],

sbin/ipsecctl/parse.y

2045

n->address.v6.s6_addr[2] = 0;

sbin/ipsecctl/parse.y

2046

n->address.v6.s6_addr[3] = 0;

sbin/ipsecctl/parse.y

2066

set_ipmask(struct ipsec_addr_wrap *address, u_int8_t b)

sbin/ipsecctl/parse.y

2071

ipa = &address->mask;

sbin/ipsecctl/pfkdump.c

655

ipa->address.v4 = ((struct sockaddr_in *)sa)->sin_addr;

sbin/ipsecctl/pfkdump.c

659

ipa->address.v6 = ((struct sockaddr_in6 *)sa)->sin6_addr;

sbin/ipsecctl/pfkey.c

1004

&rule->src->address.v6,

sbin/ipsecctl/pfkey.c

1029

&rule->dst->address.v4,

sbin/ipsecctl/pfkey.c

1036

&rule->dst->address.v6,

sbin/ipsecctl/pfkey.c

116

((struct sockaddr_in *)&sdst)->sin_addr = dst->address.v4;

sbin/ipsecctl/pfkey.c

125

((struct sockaddr_in6 *)&sdst)->sin6_addr = dst->address.v6;

sbin/ipsecctl/pfkey.c

145

local->address.v4;

sbin/ipsecctl/pfkey.c

150

local->address.v6;

sbin/ipsecctl/pfkey.c

165

peer->address.v4;

sbin/ipsecctl/pfkey.c

170

peer->address.v6;

sbin/ipsecctl/pfkey.c

410

((struct sockaddr_in *)&ssrc)->sin_addr = src->address.v4;

sbin/ipsecctl/pfkey.c

414

((struct sockaddr_in6 *)&ssrc)->sin6_addr = src->address.v6;

sbin/ipsecctl/pfkey.c

426

((struct sockaddr_in *)&sdst)->sin_addr = dst->address.v4;

sbin/ipsecctl/pfkey.c

430

((struct sockaddr_in6 *)&sdst)->sin6_addr = dst->address.v6;

sbin/ipsecctl/pfkey.c

658

((struct sockaddr_in *)&sdst)->sin_addr = dst->address.v4;

sbin/ipsecctl/pfkey.c

662

((struct sockaddr_in6 *)&sdst)->sin6_addr = dst->address.v6;

sbin/ipsecctl/pfkey.c

674

((struct sockaddr_in *)&sdst2)->sin_addr = dst2->address.v4;

sbin/ipsecctl/pfkey.c

678

((struct sockaddr_in6 *)&sdst2)->sin6_addr = dst2->address.v6;

sbin/ipsecctl/pfkey.c

857

&rule->local->address.v4,

sbin/ipsecctl/pfkey.c

863

&rule->local->address.v6,

sbin/ipsecctl/pfkey.c

88

((struct sockaddr_in *)&ssrc)->sin_addr = src->address.v4;

sbin/ipsecctl/pfkey.c

885

&rule->peer->address.v4,

sbin/ipsecctl/pfkey.c

891

&rule->peer->address.v6,

sbin/ipsecctl/pfkey.c

97

((struct sockaddr_in6 *)&ssrc)->sin6_addr = src->address.v6;

sbin/ipsecctl/pfkey.c

997

&rule->src->address.v4,

sbin/isakmpd/ipsec.c

2041

char *type, *address, *netmask;

sbin/isakmpd/ipsec.c

2066

address = conf_get_str(section, "Address");

sbin/isakmpd/ipsec.c

2067

if (!address) {

sbin/isakmpd/ipsec.c

2072

if (text2sockaddr(address, NULL, addr, af, 0)) {

sbin/isakmpd/ipsec.c

2074

"section %s", address, section);

sbin/isakmpd/ipsec.c

2096

address = conf_get_str(section, "Network");

sbin/isakmpd/ipsec.c

2097

if (!address) {

sbin/isakmpd/ipsec.c

2102

if (text2sockaddr(address, NULL, addr, af, 0)) {

sbin/isakmpd/ipsec.c

2104

"network %s", section, address);

sbin/isakmpd/message.c

1927

char *address;

sbin/isakmpd/message.c

1931

if (sockaddr2text(dst, &address, 0)) {

sbin/isakmpd/message.c

1933

address = 0;

sbin/isakmpd/message.c

1948

"%s", address ? address : "<unknown>", htons(port),

sbin/isakmpd/message.c

1951

free(address);

sbin/isakmpd/util.c

192

text2sockaddr(char *address, char *port, struct sockaddr **sa, sa_family_t af,

sbin/isakmpd/util.c

198

char *np = address;

sbin/isakmpd/util.c

215

if (getaddrinfo(address, port, &hints, &ai)) {

sbin/isakmpd/util.c

221

if (!strcmp(address, "default")) {

sbin/isakmpd/util.c

352

sockaddr2text(struct sockaddr *sa, char **address, int zflag)

sbin/isakmpd/util.c

363

*address = strdup(buf);

sbin/isakmpd/util.c

364

if (!*address)

sbin/isakmpd/util.c

370

*address = malloc(addrlen);

sbin/isakmpd/util.c

371

if (!*address)

sbin/isakmpd/util.c

375

**address = '\0';

sbin/isakmpd/util.c

377

if (strlen(*address) > 12) {

sbin/isakmpd/util.c

378

free(*address);

sbin/isakmpd/util.c

384

free(*address);

sbin/isakmpd/util.c

387

snprintf(*address + strlen(*address),

sbin/isakmpd/util.c

388

addrlen - strlen(*address), "%03ld", val);

sbin/isakmpd/util.c

390

strlcat(*address, ".", addrlen);

sbin/isakmpd/util.c

401

*address = malloc(addrlen);

sbin/isakmpd/util.c

402

if (!*address)

sbin/isakmpd/util.c

406

snprintf((*address) + j, addrlen - j,

sbin/isakmpd/util.c

411

(*address)[j] =

sbin/isakmpd/util.c

418

*address = strdup("<error>");

sbin/isakmpd/util.c

419

if (!*address)

sbin/isakmpd/virtual.c

329

struct conf_list_node *address;

sbin/isakmpd/virtual.c

482

for (address = TAILQ_FIRST(&listen_on->fields); address;

sbin/isakmpd/virtual.c

483

address = TAILQ_NEXT(address, link)) {

sbin/isakmpd/virtual.c

484

if (text2sockaddr(address->field, 0, &addr, 0, 0)) {

sbin/isakmpd/virtual.c

487

address->field);

sbin/isakmpd/virtual.c

506

if (!address)

sbin/pdisk/file_media.c

105

write_block(int fd, uint64_t sector, void *address)

sbin/pdisk/file_media.c

109

off = pwrite(fd, address, DEV_BSIZE, sector * DEV_BSIZE);

sbin/pdisk/file_media.c

86

read_block(int fd, uint64_t sector, void *address)

sbin/pdisk/file_media.c

90

off = pread(fd, address, DEV_BSIZE, sector * DEV_BSIZE);

sbin/pdisk/partition_map.c

451

uint32_t base, length, address;

sbin/pdisk/partition_map.c

473

address = entry->disk_address;

sbin/pdisk/partition_map.c

476

entry = create_entry(map, address, "" , kFreeType, base, length);

sbin/slaacd/engine.c

2148

struct imsg_configure_address address;

sbin/slaacd/engine.c

2153

address.if_index = addr_proposal->if_index;

sbin/slaacd/engine.c

2154

memcpy(&address.addr, &addr_proposal->addr, sizeof(address.addr));

sbin/slaacd/engine.c

2155

memcpy(&address.gw, &addr_proposal->from, sizeof(address.gw));

sbin/slaacd/engine.c

2156

memcpy(&address.mask, &addr_proposal->mask, sizeof(address.mask));

sbin/slaacd/engine.c

2157

address.vltime = addr_proposal->vltime;

sbin/slaacd/engine.c

2158

address.pltime = addr_proposal->pltime;

sbin/slaacd/engine.c

2159

address.temporary = addr_proposal->temporary;

sbin/slaacd/engine.c

2160

address.mtu = addr_proposal->mtu;

sbin/slaacd/engine.c

2162

engine_imsg_compose_main(IMSG_CONFIGURE_ADDRESS, 0, &address,

sbin/slaacd/engine.c

2163

sizeof(address));

sbin/slaacd/engine.c

2253

struct imsg_configure_address address;

sbin/slaacd/engine.c

2256

memset(&address, 0, sizeof(address));

sbin/slaacd/engine.c

2257

address.if_index = addr_proposal->if_index;

sbin/slaacd/engine.c

2258

memcpy(&address.addr, &addr_proposal->addr, sizeof(address.addr));

sbin/slaacd/engine.c

2260

engine_imsg_compose_main(IMSG_WITHDRAW_ADDRESS, 0, &address,

sbin/slaacd/engine.c

2261

sizeof(address));

sbin/slaacd/slaacd.c

474

struct imsg_configure_address address;

sbin/slaacd/slaacd.c

508

if (imsg_get_data(&imsg, &address,

sbin/slaacd/slaacd.c

509

sizeof(address)) == -1)

sbin/slaacd/slaacd.c

512

configure_interface(&address);

sbin/slaacd/slaacd.c

515

if (imsg_get_data(&imsg, &address,

sbin/slaacd/slaacd.c

516

sizeof(address)) == -1)

sbin/slaacd/slaacd.c

519

delete_address(&address);

sbin/slaacd/slaacd.c

638

configure_interface(struct imsg_configure_address *address)

sbin/slaacd/slaacd.c

647

if_name = if_indextoname(address->if_index, in6_addreq.ifra_name);

sbin/slaacd/slaacd.c

650

address->if_index);

sbin/slaacd/slaacd.c

654

memcpy(&in6_addreq.ifra_addr, &address->addr,

sbin/slaacd/slaacd.c

656

memcpy(&in6_addreq.ifra_dstaddr, &address->gw,

sbin/slaacd/slaacd.c

658

memcpy(&in6_addreq.ifra_prefixmask.sin6_addr, &address->mask,

sbin/slaacd/slaacd.c

666

in6_addreq.ifra_lifetime.ia6t_expire = t + address->vltime;

sbin/slaacd/slaacd.c

667

in6_addreq.ifra_lifetime.ia6t_vltime = address->vltime;

sbin/slaacd/slaacd.c

669

in6_addreq.ifra_lifetime.ia6t_preferred = t + address->pltime;

sbin/slaacd/slaacd.c

670

in6_addreq.ifra_lifetime.ia6t_pltime = address->pltime;

sbin/slaacd/slaacd.c

674

if (address->temporary)

sbin/slaacd/slaacd.c

682

if (address->mtu) {

sbin/slaacd/slaacd.c

687

ifr.ifr_mtu = address->mtu;

sbin/slaacd/slaacd.c

696

delete_address(struct imsg_configure_address *address)

sbin/slaacd/slaacd.c

704

if_name = if_indextoname(address->if_index, in6_ridreq.ifr_name);

sbin/slaacd/slaacd.c

707

address->if_index);

sbin/slaacd/slaacd.c

711

memcpy(&in6_ridreq.ifr_addr, &address->addr,

sbin/unwind/libunbound/sldns/str2wire.c

1795

struct in_addr address;

sbin/unwind/libunbound/sldns/str2wire.c

1796

if(inet_pton(AF_INET, (char*)str, &address) != 1)

sbin/unwind/libunbound/sldns/str2wire.c

1798

if(*len < sizeof(address))

sbin/unwind/libunbound/sldns/str2wire.c

1800

memmove(rd, &address, sizeof(address));

sbin/unwind/libunbound/sldns/str2wire.c

1801

*len = sizeof(address);

sbin/unwind/libunbound/sldns/str2wire.c

1808

uint8_t address[LDNS_IP6ADDRLEN + 1];

sbin/unwind/libunbound/sldns/str2wire.c

1809

if(inet_pton(AF_INET6, (char*)str, address) != 1)

sbin/unwind/libunbound/sldns/str2wire.c

1813

memmove(rd, address, LDNS_IP6ADDRLEN);

sys/arch/amd64/amd64/db_disasm.c

1037

struct i_addr address;

sys/arch/amd64/amd64/db_disasm.c

1052

loc = db_read_address(loc, short_addr, regmodrm, rex, &address);

sys/arch/amd64/amd64/db_disasm.c

1077

db_print_address(seg, BYTE, &address);

sys/arch/amd64/amd64/db_disasm.c

1143

struct i_addr address;

sys/arch/amd64/amd64/db_disasm.c

1251

loc = db_read_address(loc, short_addr, regmodrm, rex, &address);

sys/arch/amd64/amd64/db_disasm.c

1335

db_print_address(seg, size, &address);

sys/arch/amd64/amd64/db_disasm.c

1339

db_print_address(seg, size, &address);

sys/arch/amd64/amd64/db_disasm.c

1342

db_print_address(seg, WORD, &address);

sys/arch/amd64/amd64/db_disasm.c

1345

db_print_address(seg, BYTE, &address);

sys/arch/arm/arm/db_disasm.c

58

db_disasm_read_word(db_expr_t address)

sys/arch/arm/arm/db_disasm.c

61

return db_get_value(address, 4, 0);

sys/arch/arm/arm/db_disasm.c

65

db_disasm_printaddr(db_expr_t address)

sys/arch/arm/arm/db_disasm.c

68

db_printsym((vaddr_t)address, DB_STGY_ANY, db_printf);

sys/arch/arm/arm/disassem.c

285

static db_expr_t disassemble_readword(db_expr_t address);

sys/arch/arm/arm/disassem.c

286

static void disassemble_printaddr(db_expr_t address);

sys/arch/arm/arm/disassem.c

670

disassemble_readword(db_expr_t address)

sys/arch/arm/arm/disassem.c

672

return(*((u_int *)address));

sys/arch/arm/arm/disassem.c

676

disassemble_printaddr(db_expr_t address)

sys/arch/arm/arm/disassem.c

678

db_printf("0x%08lx", address);

sys/arch/arm/arm/disassem.c

686

disassemble(u_int address)

sys/arch/arm/arm/disassem.c

689

(void)disasm(&disassemble_di, address, 0);

sys/arch/arm/arm/stubs.c

104

bootconfig.dram[block].address;

sys/arch/arm/arm/stubs.c

185

addr = bootconfig.dram[block].address;

sys/arch/arm/arm/stubs.c

186

for (;addr < (bootconfig.dram[block].address

sys/arch/arm/include/cpufunc.h

309

void set_stackptr (u_int mode, u_int address);

sys/arch/arm64/arm64/db_disasm.c

41

db_disasm_readword(db_expr_t address)

sys/arch/arm64/arm64/db_disasm.c

43

return db_get_value(address, sizeof(uint32_t), false);

sys/arch/arm64/arm64/db_disasm.c

47

db_disasm_printaddr(db_expr_t address)

sys/arch/arm64/arm64/db_disasm.c

49

db_printf("%lx <", address);

sys/arch/arm64/arm64/db_disasm.c

50

db_printsym((vaddr_t)address, DB_STGY_ANY, db_printf);

sys/arch/arm64/dev/acpicpu.c

220

sc->sc_desired_perf.address,

sys/arch/arm64/dev/acpicpu.c

294

sc->sc_desired_perf.address_space_id, sc->sc_desired_perf.address,

sys/arch/arm64/dev/acpicpu.c

321

sc->sc_desired_perf.address_space_id, sc->sc_desired_perf.address,

sys/arch/arm64/stand/efiboot/efiacpi.c

107

uint64_t address;

sys/arch/arm64/stand/efiboot/efiacpi.c

717

reg[0] = htobe64(base_address->address);

sys/arch/armv7/include/bootconfig.h

49

u_int address;

sys/arch/hppa/include/disklabel.h

76

int address;

sys/arch/hppa/stand/libsa/lif.c

129

load.address);

sys/arch/hppa/stand/mkboot/mkboot.c

256

load.address = htobe32(loadpoint + sizeof(load));

sys/arch/i386/i386/db_disasm.c

1003

struct i_addr address;

sys/arch/i386/i386/db_disasm.c

1018

loc = db_read_address(loc, short_addr, regmodrm, &address);

sys/arch/i386/i386/db_disasm.c

1043

db_print_address(seg, BYTE, &address);

sys/arch/i386/i386/db_disasm.c

1106

struct i_addr address;

sys/arch/i386/i386/db_disasm.c

1180

loc = db_read_address(loc, short_addr, regmodrm, &address);

sys/arch/i386/i386/db_disasm.c

1253

db_print_address(seg, size, &address);

sys/arch/i386/i386/db_disasm.c

1257

db_print_address(seg, size, &address);

sys/arch/i386/i386/db_disasm.c

1260

db_print_address(seg, LONG, &address);

sys/arch/i386/i386/db_disasm.c

1263

db_print_address(seg, WORD, &address);

sys/arch/i386/i386/db_disasm.c

1266

db_print_address(seg, BYTE, &address);

sys/arch/loongson/include/pmon.h

113

uint64_t address;

sys/arch/loongson/loongson/machdep.c

393

fp = atop(entry.address);

sys/arch/loongson/loongson/machdep.c

394

lp = atop(entry.address + ((uint64_t)entry.size << 20));

sys/arch/macppc/dev/dbdma.h

125

#define DBDMA_BUILD(d, cmd, key, count, address, interrupt, wait, branch) { \

sys/arch/macppc/dev/dbdma.h

127

dbdma_st32(&(d)->d_address, address); \

sys/arch/octeon/dev/iobusvar.h

50

bus_addr_t address;

sys/arch/octeon/dev/octeon_iobus.c

240

aa.aa_addr = iobus_addrs[i].address;

sys/arch/octeon/include/octeonvar.h

339

octeon_xkphys_read_8(paddr_t address)

sys/arch/octeon/include/octeonvar.h

342

(volatile uint64_t *)(PHYS_TO_XKPHYS(address, CCA_NC));

sys/arch/octeon/include/octeonvar.h

348

octeon_xkphys_write_8(paddr_t address, uint64_t value)

sys/arch/octeon/include/octeonvar.h

350

*(volatile uint64_t *)(PHYS_TO_XKPHYS(address, CCA_NC)) = value;

sys/arch/octeon/include/octeonvar.h

368

if (((address >> 40) & 0xfffff) == (0x118)) {

sys/ddb/db_break.c

107

bkpt->address = addr;

sys/ddb/db_break.c

124

if (bkpt->address == addr) {

sys/ddb/db_break.c

143

if (bkpt->address == addr)

sys/ddb/db_break.c

159

db_get_value(bkpt->address, BKPT_SIZE, 0);

sys/ddb/db_break.c

160

db_put_value(bkpt->address, BKPT_SIZE,

sys/ddb/db_break.c

174

db_put_value(bkpt->address, BKPT_SIZE, bkpt->bkpt_inst);

sys/ddb/db_break.c

202

bkpt->address = addr;

sys/ddb/db_break.c

207

bkpt->bkpt_inst = db_get_value(bkpt->address, BKPT_SIZE, 0);

sys/ddb/db_break.c

208

db_put_value(bkpt->address, BKPT_SIZE, BKPT_SET(bkpt->bkpt_inst));

sys/ddb/db_break.c

215

db_put_value(bkpt->address, BKPT_SIZE, bkpt->bkpt_inst);

sys/ddb/db_break.c

235

db_printsym(bkpt->address, DB_STGY_PROC, db_printf);

sys/ddb/db_break.h

42

vaddr_t address; /* set here */

sys/ddb/db_command.c

924

db_write_cmd(db_expr_t address, int have_addr, db_expr_t count, char *modif)

sys/ddb/db_command.c

932

addr = (vaddr_t) address;

sys/ddb/db_dwarf.c

262

uint64_t address = 0, file = 1, line = 1, column = 0;

sys/ddb/db_dwarf.c

279

address += diff / line_range;

sys/ddb/db_dwarf.c

301

address = address32;

sys/ddb/db_dwarf.c

305

if (!read_u64(&extra, &address))

sys/ddb/db_dwarf.c

331

address += delta * min_insn_length;

sys/ddb/db_dwarf.c

356

address += (255 - opcode_base) / line_range;

sys/ddb/db_dwarf.c

371

if (address > pc) {

sys/ddb/db_run.c

106

&& !((db_taken_bkpt && db_taken_bkpt->address == pc) ||

sys/ddb/db_run.c

107

(db_not_taken_bkpt && db_not_taken_bkpt->address == pc))

sys/dev/acpi/acpi.c

1276

(sc->sc_fadt->pm_tmr_blk || sc->sc_fadt->x_pm_tmr_blk.address)) {

sys/dev/acpi/acpi.c

1546

sc->sc_fadt->sleep_status_reg.address,

sys/dev/acpi/acpi.c

1625

sc->sc_fadt->sleep_status_reg.address,

sys/dev/acpi/acpi.c

1642

sc->sc_fadt->sleep_control_reg.address,

sys/dev/acpi/acpi.c

1732

addr = fadt->x_pm1a_evt_blk.address;

sys/dev/acpi/acpi.c

1747

addr = fadt->x_pm1a_cnt_blk.address;

sys/dev/acpi/acpi.c

1759

addr = fadt->x_pm1b_evt_blk.address;

sys/dev/acpi/acpi.c

1774

addr = fadt->x_pm1b_cnt_blk.address;

sys/dev/acpi/acpi.c

1785

addr = fadt->x_pm2_cnt_blk.address;

sys/dev/acpi/acpi.c

1798

addr = fadt->x_pm_tmr_blk.address;

sys/dev/acpi/acpi.c

1811

addr = fadt->x_gpe0_blk.address;

sys/dev/acpi/acpi.c

1832

addr = fadt->x_gpe1_blk.address;

sys/dev/acpi/acpi.c

2082

!(fadt->flags & FADT_RESET_REG_SUP) || fadt->reset_reg.address == 0)

sys/dev/acpi/acpi.c

2097

fadt->reset_reg.address, reset_as, reset_len, &value);

sys/dev/acpi/acpi.c

234

acpi_gasio(struct acpi_softc *sc, int iodir, int iospace, uint64_t address,

sys/dev/acpi/acpi.c

245

iospace, address, (iodir == ACPI_IOWRITE) ? "write" : "read");

sys/dev/acpi/acpi.c

258

if (acpi_bus_space_map(iot, address, len, 0, &ioh) != 0) {

sys/dev/acpi/acpi.c

269

reg+address, *(uint8_t *)(pb+reg));

sys/dev/acpi/acpi.c

2741

base += gas->address;

sys/dev/acpi/acpi.c

275

reg+address, *(uint16_t *)(pb+reg));

sys/dev/acpi/acpi.c

292

reg+address, *(uint8_t *)(pb+reg));

sys/dev/acpi/acpi.c

298

reg+address, *(uint16_t *)(pb+reg));

sys/dev/acpi/acpi.c

324

if (ACPI_PCI_FN(address) == 0xffff && iodir == ACPI_IOREAD) {

sys/dev/acpi/acpi.c

329

pc = pci_lookup_segment(ACPI_PCI_SEG(address),

sys/dev/acpi/acpi.c

330

ACPI_PCI_BUS(address));

sys/dev/acpi/acpi.c

332

ACPI_PCI_BUS(address), ACPI_PCI_DEV(address),

sys/dev/acpi/acpi.c

333

ACPI_PCI_FN(address));

sys/dev/acpi/acpi.c

335

reg = ACPI_PCI_REG(address);

sys/dev/acpi/acpi.c

385

acpiec_read(sc->sc_ec, (uint8_t)address, len, buffer);

sys/dev/acpi/acpi.c

387

acpiec_write(sc->sc_ec, (uint8_t)address, len, buffer);

sys/dev/acpi/acpicmos.c

76

acpicmos_opreg_handler(void *cookie, int iodir, uint64_t address, int size,

sys/dev/acpi/acpicmos.c

80

if (size != 8 || address > 0xff)

sys/dev/acpi/acpicmos.c

84

*value = mc146818_read(NULL, address);

sys/dev/acpi/acpicmos.c

86

mc146818_write(NULL, address, *value);

sys/dev/acpi/acpicpu_x86.c

112

uint64_t address; /* or mwait hint */

sys/dev/acpi/acpicpu_x86.c

1126

sc->sc_pct.pct_status.grd_gas.address,

sys/dev/acpi/acpicpu_x86.c

1129

sc->sc_pct.pct_ctrl.grd_gas.address,

sys/dev/acpi/acpicpu_x86.c

1134

sc->sc_pct.pct_status.grd_gas.address, sc->sc_pct_stat_as,

sys/dev/acpi/acpicpu_x86.c

1144

sc->sc_pct.pct_ctrl.grd_gas.address, sc->sc_pct_ctrl_as,

sys/dev/acpi/acpicpu_x86.c

1150

sc->sc_pct.pct_status.grd_gas.address, sc->sc_pct_stat_as,

sys/dev/acpi/acpicpu_x86.c

1222

inb((u_short)best->address);

sys/dev/acpi/acpicpu_x86.c

1253

hints = (unsigned)best->address;

sys/dev/acpi/acpicpu_x86.c

1280

inb((u_short)best->address);

sys/dev/acpi/acpicpu_x86.c

1323

inb((u_short)best->address);

sys/dev/acpi/acpicpu_x86.c

1331

hints = (unsigned)best->address;

sys/dev/acpi/acpicpu_x86.c

1348

inb((u_short)best->address);

sys/dev/acpi/acpicpu_x86.c

345

int flags, int latency, int power, uint64_t address)

sys/dev/acpi/acpicpu_x86.c

350

state, latency, power, address);

sys/dev/acpi/acpicpu_x86.c

365

cx->address = address;

sys/dev/acpi/acpicpu_x86.c

416

addr = grd->grd_gas.address;

sys/dev/acpi/acpicpu_x86.c

426

addr = grd->grd_gas.address;

sys/dev/acpi/acpicpu_x86.c

441

addr = grd->grd_gas.address;

sys/dev/acpi/acpicpu_x86.c

606

show_addr = cx->address != 0;

sys/dev/acpi/acpicpu_x86.c

627

printf("@0x%llx", cx->address);

sys/dev/acpi/acpicpu_x86.c

814

sc->sc_pct.pct_status.grd_gas.address,

sys/dev/acpi/acpicpu_x86.c

914

sc->sc_pct.pct_ctrl.grd_gas.address);

sys/dev/acpi/acpicpu_x86.c

923

sc->sc_pct.pct_status.grd_gas.address);

sys/dev/acpi/acpidmar.c

1893

if (_bus_space_map(sc->sc_memt, dh->address, len, 0, &iommu->ioh) != 0) {

sys/dev/acpi/acpidmar.c

2658

de->drhd.address,

sys/dev/acpi/acpidmar.c

2916

uint64_t address;

sys/dev/acpi/acpidmar.c

2923

address = _get64(&evt->dw2);

sys/dev/acpi/acpidmar.c

2929

dmar_bdf(sid), address,

sys/dev/acpi/acpidmar.c

2938

dmar_bdf(sid), did, address,

sys/dev/acpi/acpidmar.c

2946

ivhd_showpage(iommu, sid, address);

sys/dev/acpi/acpidmar.c

2950

dmar_bdf(sid), address,

sys/dev/acpi/acpidmar.c

2958

dmar_bdf(sid), address,

sys/dev/acpi/acpidmar.c

2965

printf("illegal command addr=0x%.16llx\n", address);

sys/dev/acpi/acpidmar.c

2970

address, flag);

sys/dev/acpi/acpidmar.c

2975

dmar_bdf(sid), address);

sys/dev/acpi/acpidmar.c

2979

dmar_bdf(sid), address, flag);

sys/dev/acpi/acpidmar.c

3306

if (_bus_space_map(sc->sc_memt, ivhd->address, 0x80000, 0, &iommu->ioh) != 0) {

sys/dev/acpi/acpidmar.c

3327

printf(": AMD iommu%d at 0x%.8llx\n", iommu->id, ivhd->address);

sys/dev/acpi/acpidmar.c

3435

ext->address, ext->info,

sys/dev/acpi/acpidmar.c

3462

ivhd->address, ivhd->info,

sys/dev/acpi/acpiec.c

454

sc->sc_ec_sc = ecdt->ec_control.address;

sys/dev/acpi/acpiec.c

460

sc->sc_ec_data = ecdt->ec_data.address;

sys/dev/acpi/acpimadt.c

284

entry->madt_ioapic.address,

sys/dev/acpi/acpimadt.c

291

aaa.apic_address = entry->madt_ioapic.address;

sys/dev/acpi/acpireg.h

247

uint32_t address;

sys/dev/acpi/acpireg.h

552

uint64_t address;

sys/dev/acpi/acpireg.h

697

uint64_t address;

sys/dev/acpi/acpireg.h

713

uint64_t address;

sys/dev/acpi/acpireg.h

98

uint64_t address;

sys/dev/acpi/acpisectwo.c

81

acpisectwo_bat_opreg_handler(void *cookie, int iodir, uint64_t address,

sys/dev/acpi/acpisectwo.c

85

__func__, iodir, address, size));

sys/dev/acpi/acpitimer.c

84

psc->sc_fadt->x_pm_tmr_blk.address != 0)

sys/dev/acpi/ccpmic.c

225

uint8_t address;

sys/dev/acpi/ccpmic.c

234

ccpmic_thermal_opreg_handler(void *cookie, int iodir, uint64_t address,

sys/dev/acpi/ccpmic.c

248

if (address == ccpmic_thermal_regmap[i].address)

sys/dev/acpi/ccpmic.c

252

printf("%s: addr 0x%02llx\n", __func__, address);

sys/dev/acpi/ccpmic.c

276

ccpmic_power_opreg_handler(void *cookie, int iodir, uint64_t address,

sys/dev/acpi/ccpmic.c

288

if (address == ccpmic_power_regmap[i].address)

sys/dev/acpi/ccpmic.c

292

printf("%s: addr 0x%02llx\n", __func__, address);

sys/dev/acpi/chvgpio.c

410

chvgpio_opreg_handler(void *cookie, int iodir, uint64_t address, int size,

sys/dev/acpi/chvgpio.c

416

if (size != 4 || address > sc->sc_size - size)

sys/dev/acpi/chvgpio.c

420

*value = bus_space_read_4(sc->sc_memt, sc->sc_memh, address);

sys/dev/acpi/chvgpio.c

422

bus_space_write_4(sc->sc_memt, sc->sc_memh, address, *value);

sys/dev/acpi/com_acpi.c

167

base->address == sc->sc.sc_iobase)

sys/dev/acpi/dsdt.c

2300

aml_opreg_sysmem_handler(void *cookie, int iodir, uint64_t address, int size,

sys/dev/acpi/dsdt.c

2304

address, size, size, value);

sys/dev/acpi/dsdt.c

2308

aml_opreg_sysio_handler(void *cookie, int iodir, uint64_t address, int size,

sys/dev/acpi/dsdt.c

2312

address, size, size, value);

sys/dev/acpi/dsdt.c

2316

aml_opreg_pcicfg_handler(void *cookie, int iodir, uint64_t address, int size,

sys/dev/acpi/dsdt.c

2320

address, size, size, value);

sys/dev/acpi/dsdt.c

2324

aml_opreg_ec_handler(void *cookie, int iodir, uint64_t address, int size,

sys/dev/acpi/dsdt.c

2328

address, size, size, value);

sys/dev/acpi/dsdt.c

2439

acpi_genio(struct acpi_softc *sc, int iodir, int iospace, uint64_t address,

sys/dev/acpi/dsdt.c

2447

iospace, address, (iodir == ACPI_IOWRITE) ? "write" : "read");

sys/dev/acpi/dsdt.c

2458

address + reg, access_size, &value);

sys/dev/acpi/dsdt.c

2493

address + reg, access_size, &value);

sys/dev/acpi/intelpmc.c

186

entry->entry_trigger.address);

sys/dev/acpi/intelpmc.c

198

entry->residency_counter.address);

sys/dev/acpi/intelpmc.c

276

rdmsr_safe(sc->sc_counter[i].address, &sc->sc_lpit[i][0]);

sys/dev/acpi/intelpmc.c

280

sc->sc_counter[i].address,

sys/dev/acpi/intelpmc.c

319

rdmsr_safe(sc->sc_counter[i].address, &sc->sc_lpit[i][1]);

sys/dev/acpi/intelpmc.c

323

sc->sc_counter[i].address,

sys/dev/acpi/pluart_acpi.c

114

base->address == sc->sc_addr)

sys/dev/acpi/qcuart_acpi.c

108

base->address == sc->sc_addr)

sys/dev/acpi/tipmic.c

270

uint8_t address;

sys/dev/acpi/tipmic.c

299

tipmic_thermal_opreg_handler(void *cookie, int iodir, uint64_t address,

sys/dev/acpi/tipmic.c

314

if (address == tipmic_thermal_regmap[i].address)

sys/dev/acpi/tipmic.c

318

printf("%s: addr 0x%02llx\n", __func__, address);

sys/dev/acpi/tipmic.c

403

tipmic_power_opreg_handler(void *cookie, int iodir, uint64_t address,

sys/dev/acpi/tipmic.c

415

if (address == tipmic_power_regmap[i].address)

sys/dev/acpi/tipmic.c

419

printf("%s: addr 0x%02llx\n", __func__, address);

sys/dev/fdt/imxesdhc.c

167

uint32_t address;

sys/dev/fdt/imxesdhc.c

969

desc[seg].address = htole32(paddr);

sys/dev/fdt/qcdpc.c

330

buf[0] = msg->address >> 16;

sys/dev/fdt/qcdpc.c

333

buf[1] = msg->address >> 8;

sys/dev/fdt/qcdpc.c

334

buf[2] = msg->address >> 0;

sys/dev/ic/aic79xx.c

244

u_int address);

sys/dev/ic/aic79xx.c

8483

ahd_resolve_seqaddr(struct ahd_softc *ahd, u_int address)

sys/dev/ic/aic79xx.c

8494

for (i = 0; i < address;) {

sys/dev/ic/aic79xx.c

8501

end_addr = MIN(address, skip_addr);

sys/dev/ic/aic79xx.c

8508

return (address - address_offset);

sys/dev/ic/aic79xx.c

8540

fmt3_ins->address = ahd_resolve_seqaddr(ahd, fmt3_ins->address);

sys/dev/ic/aic79xx.c

8627

const char *name, u_int address, u_int value,

sys/dev/ic/aic79xx.h

1520

u_int address,

sys/dev/ic/aic7xxx.c

6274

u_int address;

sys/dev/ic/aic7xxx.c

6280

address = fmt3_ins->address;

sys/dev/ic/aic7xxx.c

6284

for (i = 0; i < address;) {

sys/dev/ic/aic7xxx.c

6291

end_addr = MIN(address, skip_addr);

sys/dev/ic/aic7xxx.c

6298

address -= address_offset;

sys/dev/ic/aic7xxx.c

6299

fmt3_ins->address = address;

sys/dev/ic/aic7xxx.c

6348

| (fmt3_ins->address << 16)

sys/dev/ic/aic7xxx.c

6372

const char *name, u_int address, u_int value,

sys/dev/ic/aic7xxxvar.h

1327

u_int address,

sys/dev/ic/anxdp.c

773

AUX_ADDR_7_0(dpmsg->address));

sys/dev/ic/anxdp.c

775

AUX_ADDR_15_8(dpmsg->address));

sys/dev/ic/anxdp.c

777

AUX_ADDR_19_16(dpmsg->address));

sys/dev/ic/bcm2835_vcprop.h

298

uint32_t address; /* alignment for request */

sys/dev/ic/bt8xx.h

344

unsigned int address;

sys/dev/ic/mfireg.h

515

} __packed address;

sys/dev/ic/mpi.c

1643

u_int32_t address;

sys/dev/ic/mpi.c

1656

address = MPI_CFG_SAS_DEV_ADDR_BUS | link->target;

sys/dev/ic/mpi.c

1659

address, &ehdr) != 0)

sys/dev/ic/mpi.c

1662

if (mpi_ecfg_page(sc, address, &ehdr, 1, &pg0, sizeof(pg0)) != 0)

sys/dev/ic/mpi.c

2759

u_int32_t address, int flags, void *p)

sys/dev/ic/mpi.c

2771

address, flags, MPI_PG_FMT);

sys/dev/ic/mpi.c

2795

htolem32(&cq->page_address, address);

sys/dev/ic/mpi.c

2851

mpi_req_cfg_page(struct mpi_softc *sc, u_int32_t address, int flags,

sys/dev/ic/mpi.c

2864

DEVNAME(sc), address, read, hdr->page_type);

sys/dev/ic/mpi.c

2896

htolem32(&cq->page_address, address);

sys/dev/ic/mpi.c

3086

u_int32_t address;

sys/dev/ic/mpi.c

3119

address = sc->sc_vol_list[id].vol_id |

sys/dev/ic/mpi.c

3122

address, 0, &hdr) != 0)

sys/dev/ic/mpi.c

3124

if (mpi_req_cfg_page(sc, address, 0, &hdr, 1, rpg0, len)) {

sys/dev/ic/mpi.c

3312

u_int32_t address;

sys/dev/ic/mpi.c

3336

address = physdisk->phys_disk_num;

sys/dev/ic/mpi.c

3337

if (mpi_cfg_header(sc, MPI_CONFIG_REQ_PAGE_TYPE_RAID_PD, 0, address,

sys/dev/ic/mpi.c

3340

if (mpi_cfg_page(sc, address, &hdr, 1, &pdpg0, sizeof pdpg0)) {

sys/dev/ic/mpi.c

569

u_int32_t address;

sys/dev/ic/mpi.c

584

address = link->target;

sys/dev/ic/mpi.c

588

address = (physdisk->phys_disk_bus << 8) |

sys/dev/ic/mpi.c

594

address, &hdr0) != 0) {

sys/dev/ic/mpi.c

601

address, &hdr1) != 0) {

sys/dev/ic/mpi.c

608

if (mpi_cfg_page(sc, address, &hdr0, 1, &pg0, sizeof(pg0)) != 0) {

sys/dev/ic/mpi.c

620

if (mpi_cfg_page(sc, address, &hdr1, 1, &pg1, sizeof(pg1)) != 0) {

sys/dev/ic/mpi.c

667

if (mpi_cfg_page(sc, address, &hdr1, 0, &pg1, sizeof(pg1)) != 0) {

sys/dev/ic/mpi.c

673

if (mpi_cfg_page(sc, address, &hdr1, 1, &pg1, sizeof(pg1)) != 0) {

sys/dev/ic/mpi.c

690

if (mpi_cfg_page(sc, address, &hdr0, 1, &pg0, sizeof(pg0)) != 0) {

sys/dev/ic/nvmereg.h

108

u_int64_t address;

sys/dev/ic/nvmereg.h

99

u_int64_t address;

sys/dev/ic/trm.c

1065

pseg->address +=

sys/dev/ic/trm.c

1167

pseg->address += TempSRBXferredLength;

sys/dev/ic/trm.c

2244

pSRB->SegmentX[0].address = pSRB->scsisensePhyAddr;

sys/dev/ic/trm.c

409

pSRB->SegmentX[i].address = pSRB->dmamapxfer->dm_segs[i].ds_addr;

sys/dev/ic/trm.h

45

u_int32_t address;

sys/dev/isa/gus.c

1829

convert_to_16bit(u_long address)

sys/dev/isa/gus.c

1833

old_address = address;

sys/dev/isa/gus.c

1834

address >>= 1;

sys/dev/isa/gus.c

1835

address &= 0x0001ffffL;

sys/dev/isa/gus.c

1836

address |= (old_address & 0x000c0000L);

sys/dev/isa/gus.c

1838

return (address);

sys/dev/isa/gus.c

1846

guspoke(bus_space_tag_t iot, bus_space_handle_t ioh2, long address,

sys/dev/isa/gus.c

1855

bus_space_write_2(iot, ioh2, GUS_DATA_LOW, (unsigned int) (address & 0xffff));

sys/dev/isa/gus.c

1857

bus_space_write_1(iot, ioh2, GUS_DATA_HIGH, (unsigned char) ((address >> 16) & 0xff));

sys/dev/isa/gus.c

1871

guspeek(bus_space_tag_t iot, bus_space_handle_t ioh2, u_long address)

sys/dev/isa/gus.c

1879

bus_space_write_2(iot, ioh2, GUS_DATA_LOW, (unsigned int) (address & 0xffff));

sys/dev/isa/gus.c

1881

bus_space_write_1(iot, ioh2, GUS_DATA_HIGH, (unsigned char) ((address >> 16) & 0xff));

sys/dev/microcode/aic7xxx/aicasm.c

328

u_int address;

sys/dev/microcode/aic7xxx/aicasm.c

340

address = f3_instr->address;

sys/dev/microcode/aic7xxx/aicasm.c

341

address += cur_instr->patch_label->info.linfo->address;

sys/dev/microcode/aic7xxx/aicasm.c

342

f3_instr->address = address;

sys/dev/microcode/aic7xxx/aicasm_gram.y

1019

$2->info.linfo->address = instruction_ptr;

sys/dev/microcode/aic7xxx/aicasm_gram.y

102

expression_t *immed, symbol_ref_t *address);

sys/dev/microcode/aic7xxx/aicasm_gram.y

1024

address:

sys/dev/microcode/aic7xxx/aicasm_gram.y

1333

jmp_jc_jnc_call address ';'

sys/dev/microcode/aic7xxx/aicasm_gram.y

1343

T_OR reg_symbol ',' immediate jmp_jc_jnc_call address ';'

sys/dev/microcode/aic7xxx/aicasm_gram.y

1350

T_TEST source ',' immediate_or_a jz_jnz address ';'

sys/dev/microcode/aic7xxx/aicasm_gram.y

1357

T_CMP source ',' immediate_or_a je_jne address ';'

sys/dev/microcode/aic7xxx/aicasm_gram.y

1364

T_MOV source jmp_jc_jnc_call address ';'

sys/dev/microcode/aic7xxx/aicasm_gram.y

1374

T_MVI immediate jmp_jc_jnc_call address ';'

sys/dev/microcode/aic7xxx/aicasm_gram.y

1629

f1_instr->destination = dest->symbol->info.rinfo->address

sys/dev/microcode/aic7xxx/aicasm_gram.y

1631

f1_instr->source = src->symbol->info.rinfo->address

sys/dev/microcode/aic7xxx/aicasm_gram.y

1702

f2_instr->destination = dest->symbol->info.rinfo->address

sys/dev/microcode/aic7xxx/aicasm_gram.y

1704

f2_instr->source = src->symbol->info.rinfo->address

sys/dev/microcode/aic7xxx/aicasm_gram.y

1745

expression_t *immed, symbol_ref_t *address)

sys/dev/microcode/aic7xxx/aicasm_gram.y

1760

if (address->symbol == NULL) {

sys/dev/microcode/aic7xxx/aicasm_gram.y

1762

addr = instruction_ptr + address->offset;

sys/dev/microcode/aic7xxx/aicasm_gram.y

1763

} else if (address->symbol->type == UNINITIALIZED) {

sys/dev/microcode/aic7xxx/aicasm_gram.y

1765

addr = address->offset;

sys/dev/microcode/aic7xxx/aicasm_gram.y

1766

instr->patch_label = address->symbol;

sys/dev/microcode/aic7xxx/aicasm_gram.y

1768

addr = address->symbol->info.linfo->address + address->offset;

sys/dev/microcode/aic7xxx/aicasm_gram.y

1770

f3_instr->address = addr;

sys/dev/microcode/aic7xxx/aicasm_gram.y

1771

f3_instr->source = src->symbol->info.rinfo->address

sys/dev/microcode/aic7xxx/aicasm_gram.y

207

%type <sym_ref> reg_symbol address destination source opt_source

sys/dev/microcode/aic7xxx/aicasm_gram.y

331

if (cur_symbol->info.rinfo->address == 0)

sys/dev/microcode/aic7xxx/aicasm_gram.y

332

cur_symbol->info.rinfo->address =

sys/dev/microcode/aic7xxx/aicasm_gram.y

366

cur_symbol->info.rinfo->address = $2;

sys/dev/microcode/aic7xxx/aicasm_gram.y

378

max_addr = scb_or_sram_symbol->info.rinfo->address

sys/dev/microcode/aic7xxx/aicasm_gram.y

380

sym_max_addr = cur_symbol->info.rinfo->address

sys/dev/microcode/aic7xxx/aicasm_gram.y

682

$$.value = symbol->info.rinfo->address;

sys/dev/microcode/aic7xxx/aicasm_gram.y

800

sram_or_scb_offset = cur_symbol->info.rinfo->address;

sys/dev/microcode/aic7xxx/aicasm_gram.y

831

sram_or_scb_offset = cur_symbol->info.rinfo->address;

sys/dev/microcode/aic7xxx/aicasm_insformat.h

86

address : 10,

sys/dev/microcode/aic7xxx/aicasm_insformat.h

92

address : 10,

sys/dev/microcode/aic7xxx/aicasm_symbol.c

259

|| (!field && (curnode->symbol->info.rinfo->address >

sys/dev/microcode/aic7xxx/aicasm_symbol.c

260

newnode->symbol->info.rinfo->address))) {

sys/dev/microcode/aic7xxx/aicasm_symbol.c

280

&& (cursymbol->info.rinfo->address >

sys/dev/microcode/aic7xxx/aicasm_symbol.c

281

symbol->info.rinfo->address))) {

sys/dev/microcode/aic7xxx/aicasm_symbol.c

415

regnode->symbol->info.rinfo->address);

sys/dev/microcode/aic7xxx/aicasm_symbol.c

433

regnode->symbol->info.rinfo->address);

sys/dev/microcode/aic7xxx/aicasm_symbol.c

602

value = curnode->symbol->info.rinfo->address;

sys/dev/microcode/aic7xxx/aicasm_symbol.c

611

value = parent->info.rinfo->address;

sys/dev/microcode/aic7xxx/aicasm_symbol.c

674

curnode->symbol->info.linfo->address);

sys/dev/microcode/aic7xxx/aicasm_symbol.h

103

int address;

sys/dev/microcode/aic7xxx/aicasm_symbol.h

78

u_int address;

sys/dev/pci/azalia.c

1223

err = azalia_set_command(codec->az, codec->address, nid, control,

sys/dev/pci/azalia.c

1318

if (az->codecs[az->codecno].address == addr)

sys/dev/pci/azalia.c

1535

addr = this->address;

sys/dev/pci/azalia.c

870

az->codecs[n].address = i;

sys/dev/pci/azalia.h

655

int address;

sys/dev/pci/bktr/bktr_core.c

2091

msp->function, msp->address);

sys/dev/pci/bktr/bktr_core.c

2100

msp->address, msp->data );

sys/dev/pci/cz.c

1542

u_int move, get, put, size, address;

sys/dev/pci/cz.c

1552

address = CZTTY_BUF_READ(sc, BUFCTL_TX_BUFADDR);

sys/dev/pci/cz.c

1569

address + put, tp->t_outq.c_cf, move);

sys/dev/pci/cz.c

1588

u_int get, put, size, address;

sys/dev/pci/cz.c

1594

address = CZTTY_BUF_READ(sc, BUFCTL_RX_BUFADDR);

sys/dev/pci/cz.c

1603

address + get);

sys/dev/pci/drm/amd/amdgpu/amdgpu_bios.c

217

pcireg_t address, mask;

sys/dev/pci/drm/amd/amdgpu/amdgpu_bios.c

224

address = pci_conf_read(adev->pc, adev->pa_tag, PCI_ROM_REG);

sys/dev/pci/drm/amd/amdgpu/amdgpu_bios.c

227

address |= PCI_ROM_ENABLE;

sys/dev/pci/drm/amd/amdgpu/amdgpu_bios.c

228

pci_conf_write(adev->pc, adev->pa_tag, PCI_ROM_REG, address);

sys/dev/pci/drm/amd/amdgpu/amdgpu_bios.c

233

rc = bus_space_map(adev->memt, PCI_ROM_ADDR(address), size, 0, &romh);

sys/dev/pci/drm/amd/amdgpu/amdgpu_device.c

7587

unsigned long flags, address, data;

sys/dev/pci/drm/amd/amdgpu/amdgpu_device.c

7590

address = adev->nbio.funcs->get_pcie_port_index_offset(adev);

sys/dev/pci/drm/amd/amdgpu/amdgpu_device.c

7594

WREG32(address, reg * 4);

sys/dev/pci/drm/amd/amdgpu/amdgpu_device.c

7595

(void)RREG32(address);

sys/dev/pci/drm/amd/amdgpu/amdgpu_device.c

7604

unsigned long flags, address, data;

sys/dev/pci/drm/amd/amdgpu/amdgpu_device.c

7606

address = adev->nbio.funcs->get_pcie_port_index_offset(adev);

sys/dev/pci/drm/amd/amdgpu/amdgpu_device.c

7610

WREG32(address, reg * 4);

sys/dev/pci/drm/amd/amdgpu/amdgpu_device.c

7611

(void)RREG32(address);

sys/dev/pci/drm/amd/amdgpu/amdgpu_mode.h

307

uint64_t address;

sys/dev/pci/drm/amd/amdgpu/amdgpu_psp.c

1781

memcpy(&ras_cmd->ras_in_message.address,

sys/dev/pci/drm/amd/amdgpu/amdgpu_psp.c

1782

in, sizeof(ras_cmd->ras_in_message.address));

sys/dev/pci/drm/amd/amdgpu/amdgpu_psp.c

1803

&ras_cmd->ras_out_message.address,

sys/dev/pci/drm/amd/amdgpu/amdgpu_psp.c

1804

sizeof(ras_cmd->ras_out_message.address));

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

1618

.address = info->address,

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

1642

block_info.address =

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

1644

block_info.address);

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

173

static int amdgpu_reserve_page_direct(struct amdgpu_device *adev, uint64_t address)

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

179

ret = amdgpu_ras_check_bad_page(adev, address);

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

183

address);

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

188

address);

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

198

amdgpu_umc_fill_error_record(&err_data, address, address, 0, 0);

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

216

uint64_t address, uint64_t flags)

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

228

if (amdgpu_virt_check_vf_critical_region(adev, address, &hit))

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

233

if ((address >= adev->gmc.mc_vram_size) ||

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

234

(address >= RAS_UMC_INJECT_ADDR_LIMIT))

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

238

address, page_pfns, ARRAY_SIZE(page_pfns));

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

2865

addr_in.ma.err_addr = bps->address;

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

2892

die_id = adev->umc.ras->get_die_id_from_pa(adev, bps->address,

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

2902

addr_in.ma.err_addr = bps->address;

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

2972

err_data->err_addr[i].address = bps[0].address;

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

2983

if (bps[0].address == 0) {

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

2988

&(bps[0].address), AMDGPU_NPS1_PARTITION_MODE))

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

3020

err_data->err_addr[i].address = bps->address;

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

3027

if (bps->address) {

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

3035

&(bps->address), AMDGPU_NPS1_PARTITION_MODE))

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

3082

if ((bps[i].address == bps[i + 1].address) &&

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

3209

if ((bps[i].address == bps[i + 1].address) &&

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

341

u64 address, value;

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

371

if (sscanf(str, "%*s 0x%llx", &address) != 1 &&

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

372

sscanf(str, "%*s %llu", &address) != 1)

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

376

data->inject.address = address;

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

380

if (sscanf(str, "%*s 0x%llx 0x%llx", &address, &value) != 2 &&

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

381

sscanf(str, "%*s %llu %llu", &address, &value) != 2)

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

385

data->inject.address = address;

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

408

&sub_block, &address, &value, &instance_mask) != 4 &&

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

410

&sub_block, &address, &value, &instance_mask) != 4 &&

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

412

&sub_block, &address, &value) != 3 &&

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

414

&sub_block, &address, &value) != 3)

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

417

data->inject.address = address;

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

572

ret = amdgpu_reserve_page_direct(adev, data.inject.address);

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

578

ret = amdgpu_check_address_validity(adev, data.inject.address, data.inject.value);

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

595

ret = amdgpu_ras_check_bad_page(adev, data.inject.address);

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

598

data.inject.address);

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.c

602

data.inject.address);

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.h

706

uint64_t address;

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras.h

713

uint64_t address;

sys/dev/pci/drm/amd/amdgpu/amdgpu_ras_eeprom.h

128

uint64_t address;

sys/dev/pci/drm/amd/amdgpu/amdgpu_trace.h

566

TP_PROTO(uint32_t address, uint32_t value),

sys/dev/pci/drm/amd/amdgpu/amdgpu_trace.h

567

TP_ARGS(address, value),

sys/dev/pci/drm/amd/amdgpu/amdgpu_trace.h

569

__field(uint32_t, address)

sys/dev/pci/drm/amd/amdgpu/amdgpu_trace.h

573

__entry->address = address;

sys/dev/pci/drm/amd/amdgpu/amdgpu_trace.h

577

__entry->address,

sys/dev/pci/drm/amd/amdgpu/amdgpu_umc.c

378

err_rec->address = err_addr;

sys/dev/pci/drm/amd/amdgpu/amdgpu_vram_mgr.c

407

uint64_t address, struct amdgpu_vram_block_info *info)

sys/dev/pci/drm/amd/amdgpu/amdgpu_vram_mgr.c

419

if ((start <= address) && (address < (start + size))) {

sys/dev/pci/drm/amd/amdgpu/amdgpu_vram_mgr.h

90

uint64_t address, struct amdgpu_vram_block_info *info);

sys/dev/pci/drm/amd/amdgpu/atombios_dp.c

140

tx_buf[0] = msg->address & 0xff;

sys/dev/pci/drm/amd/amdgpu/atombios_dp.c

141

tx_buf[1] = msg->address >> 8;

sys/dev/pci/drm/amd/amdgpu/atombios_dp.c

143

((msg->address >> 16) & 0xf);

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

100

unsigned long flags, address, data;

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

102

address = adev->nbio.funcs->get_pcie_index_offset(adev);

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

106

WREG32(address, lo_addr);

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

108

WREG32(address, hi_addr);

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

122

unsigned long flags, address, data;

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

124

address = adev->nbio.funcs->get_pcie_index_offset(adev);

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

128

WREG32(address, lo_addr);

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

130

WREG32(address, hi_addr);

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

140

unsigned long flags, address, data;

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

143

address = adev->nbio.funcs->get_pcie_index_offset(adev);

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

147

WREG32(address, lo_addr);

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

149

WREG32(address, hi_addr);

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

152

WREG32(address, lo_addr);

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

154

WREG32(address, hi_addr);

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

48

unsigned long flags, address, data;

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

51

address = adev->nbio.funcs->get_pcie_index_offset(adev);

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

55

WREG32(address, smnDF_PIE_AON_FabricIndirectConfigAccessAddress3);

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

58

WREG32(address, smnDF_PIE_AON_FabricIndirectConfigAccessDataLo3);

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

61

WREG32(address, smnDF_PIE_AON_FabricIndirectConfigAccessDataHi3);

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

72

unsigned long flags, address, data;

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

74

address = adev->nbio.funcs->get_pcie_index_offset(adev);

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

78

WREG32(address, smnDF_PIE_AON_FabricIndirectConfigAccessAddress3);

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

81

WREG32(address, smnDF_PIE_AON_FabricIndirectConfigAccessDataLo3);

sys/dev/pci/drm/amd/amdgpu/df_v3_6.c

84

WREG32(address, smnDF_PIE_AON_FabricIndirectConfigAccessDataHi3);

sys/dev/pci/drm/amd/amdgpu/gfx_v10_0.c

4477

static uint32_t wave_read_ind(struct amdgpu_device *adev, uint32_t wave, uint32_t address)

sys/dev/pci/drm/amd/amdgpu/gfx_v10_0.c

4481

(address << SQ_IND_INDEX__INDEX__SHIFT));

sys/dev/pci/drm/amd/amdgpu/gfx_v11_0.c

977

static uint32_t wave_read_ind(struct amdgpu_device *adev, uint32_t wave, uint32_t address)

sys/dev/pci/drm/amd/amdgpu/gfx_v11_0.c

981

(address << SQ_IND_INDEX__INDEX__SHIFT));

sys/dev/pci/drm/amd/amdgpu/gfx_v12_0.c

815

static uint32_t wave_read_ind(struct amdgpu_device *adev, uint32_t wave, uint32_t address)

sys/dev/pci/drm/amd/amdgpu/gfx_v12_0.c

819

(address << SQ_IND_INDEX__INDEX__SHIFT));

sys/dev/pci/drm/amd/amdgpu/gfx_v6_0.c

3009

static uint32_t wave_read_ind(struct amdgpu_device *adev, uint32_t simd, uint32_t wave, uint32_t address)

sys/dev/pci/drm/amd/amdgpu/gfx_v6_0.c

3014

(address << SQ_IND_INDEX__INDEX__SHIFT) |

sys/dev/pci/drm/amd/amdgpu/gfx_v7_0.c

4012

static uint32_t wave_read_ind(struct amdgpu_device *adev, uint32_t simd, uint32_t wave, uint32_t address)

sys/dev/pci/drm/amd/amdgpu/gfx_v7_0.c

4017

(address << SQ_IND_INDEX__INDEX__SHIFT) |

sys/dev/pci/drm/amd/amdgpu/gfx_v8_0.c

5155

static uint32_t wave_read_ind(struct amdgpu_device *adev, uint32_t simd, uint32_t wave, uint32_t address)

sys/dev/pci/drm/amd/amdgpu/gfx_v8_0.c

5160

(address << SQ_IND_INDEX__INDEX__SHIFT) |

sys/dev/pci/drm/amd/amdgpu/gfx_v9_0.c

1929

static uint32_t wave_read_ind(struct amdgpu_device *adev, uint32_t simd, uint32_t wave, uint32_t address)

sys/dev/pci/drm/amd/amdgpu/gfx_v9_0.c

1934

(address << SQ_IND_INDEX__INDEX__SHIFT) |

sys/dev/pci/drm/amd/amdgpu/gfx_v9_0.c

6765

block_info.address = info->address;

sys/dev/pci/drm/amd/amdgpu/gfx_v9_4_2.c

1816

static uint32_t wave_read_ind(struct amdgpu_device *adev, uint32_t simd, uint32_t wave, uint32_t address)

sys/dev/pci/drm/amd/amdgpu/gfx_v9_4_2.c

1821

(address << SQ_IND_INDEX__INDEX__SHIFT) |

sys/dev/pci/drm/amd/amdgpu/gfx_v9_4_3.c

716

static uint32_t wave_read_ind(struct amdgpu_device *adev, uint32_t xcc_id, uint32_t simd, uint32_t wave, uint32_t address)

sys/dev/pci/drm/amd/amdgpu/gfx_v9_4_3.c

721

(address << SQ_IND_INDEX__INDEX__SHIFT) |

sys/dev/pci/drm/amd/amdgpu/nv.c

280

unsigned long flags, address, data;

sys/dev/pci/drm/amd/amdgpu/nv.c

283

address = SOC15_REG_OFFSET(GC, 0, mmDIDT_IND_INDEX);

sys/dev/pci/drm/amd/amdgpu/nv.c

287

WREG32(address, (reg));

sys/dev/pci/drm/amd/amdgpu/nv.c

295

unsigned long flags, address, data;

sys/dev/pci/drm/amd/amdgpu/nv.c

297

address = SOC15_REG_OFFSET(GC, 0, mmDIDT_IND_INDEX);

sys/dev/pci/drm/amd/amdgpu/nv.c

301

WREG32(address, (reg));

sys/dev/pci/drm/amd/amdgpu/smu_v11_0_i2c.c

159

static void smu_v11_0_i2c_set_address(struct i2c_adapter *control, u16 address)

sys/dev/pci/drm/amd/amdgpu/smu_v11_0_i2c.c

168

WREG32_SOC15(SMUIO, 0, mmCKSVII2C_IC_TAR, address & 0x3FF);

sys/dev/pci/drm/amd/amdgpu/smu_v11_0_i2c.c

269

u16 address, u8 *data,

sys/dev/pci/drm/amd/amdgpu/smu_v11_0_i2c.c

280

address, numbytes);

sys/dev/pci/drm/amd/amdgpu/smu_v11_0_i2c.c

288

smu_v11_0_i2c_set_address(control, address);

sys/dev/pci/drm/amd/amdgpu/smu_v11_0_i2c.c

368

u16 address, u8 *data,

sys/dev/pci/drm/amd/amdgpu/smu_v11_0_i2c.c

378

smu_v11_0_i2c_set_address(control, address);

sys/dev/pci/drm/amd/amdgpu/smu_v11_0_i2c.c

431

(uint16_t)address, bytes_received);

sys/dev/pci/drm/amd/amdgpu/soc15.c

242

unsigned long flags, address, data;

sys/dev/pci/drm/amd/amdgpu/soc15.c

245

address = SOC15_REG_OFFSET(UVD, 0, mmUVD_CTX_INDEX);

sys/dev/pci/drm/amd/amdgpu/soc15.c

249

WREG32(address, ((reg) & 0x1ff));

sys/dev/pci/drm/amd/amdgpu/soc15.c

257

unsigned long flags, address, data;

sys/dev/pci/drm/amd/amdgpu/soc15.c

259

address = SOC15_REG_OFFSET(UVD, 0, mmUVD_CTX_INDEX);

sys/dev/pci/drm/amd/amdgpu/soc15.c

263

WREG32(address, ((reg) & 0x1ff));

sys/dev/pci/drm/amd/amdgpu/soc15.c

270

unsigned long flags, address, data;

sys/dev/pci/drm/amd/amdgpu/soc15.c

273

address = SOC15_REG_OFFSET(GC, 0, mmDIDT_IND_INDEX);

sys/dev/pci/drm/amd/amdgpu/soc15.c

277

WREG32(address, (reg));

sys/dev/pci/drm/amd/amdgpu/soc15.c

285

unsigned long flags, address, data;

sys/dev/pci/drm/amd/amdgpu/soc15.c

287

address = SOC15_REG_OFFSET(GC, 0, mmDIDT_IND_INDEX);

sys/dev/pci/drm/amd/amdgpu/soc15.c

291

WREG32(address, (reg));

sys/dev/pci/drm/amd/amdgpu/soc21.c

195

unsigned long flags, address, data;

sys/dev/pci/drm/amd/amdgpu/soc21.c

198

address = SOC15_REG_OFFSET(GC, 0, regDIDT_IND_INDEX);

sys/dev/pci/drm/amd/amdgpu/soc21.c

202

WREG32(address, (reg));

sys/dev/pci/drm/amd/amdgpu/soc21.c

210

unsigned long flags, address, data;

sys/dev/pci/drm/amd/amdgpu/soc21.c

212

address = SOC15_REG_OFFSET(GC, 0, regDIDT_IND_INDEX);

sys/dev/pci/drm/amd/amdgpu/soc21.c

216

WREG32(address, (reg));

sys/dev/pci/drm/amd/amdgpu/ta_ras_if.h

147

uint64_t address; // explicit address of error

sys/dev/pci/drm/amd/amdgpu/ta_ras_if.h

200

struct ta_ras_query_address_input address;

sys/dev/pci/drm/amd/amdgpu/ta_ras_if.h

207

struct ta_ras_query_address_output address;

sys/dev/pci/drm/amd/amdkfd/kfd_chardev.c

3072

args->set_node_address_watch.address,

sys/dev/pci/drm/amd/amdkfd/kfd_chardev.c

3393

phys_addr_t address;

sys/dev/pci/drm/amd/amdkfd/kfd_chardev.c

3401

address = dev->adev->rmmio_remap.bus_addr;

sys/dev/pci/drm/amd/amdkfd/kfd_chardev.c

3414

address, vma->vm_flags, PAGE_SIZE);

sys/dev/pci/drm/amd/amdkfd/kfd_chardev.c

3418

address >> PAGE_SHIFT,

sys/dev/pci/drm/amd/amdkfd/kfd_doorbell.c

109

phys_addr_t address;

sys/dev/pci/drm/amd/amdkfd/kfd_doorbell.c

124

address = kfd_get_process_doorbells(pdd);

sys/dev/pci/drm/amd/amdkfd/kfd_doorbell.c

125

if (!address)

sys/dev/pci/drm/amd/amdkfd/kfd_doorbell.c

137

(unsigned long long) vma->vm_start, address, vma->vm_flags,

sys/dev/pci/drm/amd/amdkfd/kfd_doorbell.c

143

address >> PAGE_SHIFT,

sys/dev/pci/drm/amd/amdkfd/kfd_migrate.c

938

unsigned long addr = vmf->address;

sys/dev/pci/drm/amd/amdkfd/kfd_smi_events.c

264

unsigned long address, bool write_fault,

sys/dev/pci/drm/amd/amdkfd/kfd_smi_events.c

269

address, node->id, write_fault ? 'W' : 'R'));

sys/dev/pci/drm/amd/amdkfd/kfd_smi_events.c

273

unsigned long address, bool migration)

sys/dev/pci/drm/amd/amdkfd/kfd_smi_events.c

277

pid, address, node->id, migration ? 'M' : 'U'));

sys/dev/pci/drm/amd/amdkfd/kfd_smi_events.c

339

unsigned long address, unsigned long last,

sys/dev/pci/drm/amd/amdkfd/kfd_smi_events.c

344

pid, address, last - address + 1, node->id, trigger));

sys/dev/pci/drm/amd/amdkfd/kfd_smi_events.h

36

unsigned long address, bool write_fault,

sys/dev/pci/drm/amd/amdkfd/kfd_smi_events.h

39

unsigned long address, bool migration);

sys/dev/pci/drm/amd/amdkfd/kfd_smi_events.h

54

unsigned long address, unsigned long last,

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

10470

wb_info->mcif_buf_params.luma_address[i] = afb->address;

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

10476

wb_info->mcif_warmup_params.start_address.quad_part = afb->address;

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

13159

void dm_write_reg_func(const struct dc_context *ctx, uint32_t address,

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

13163

if (address == 0) {

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

13171

cgs_write_register(ctx->cgs_device, address, value);

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

13172

trace_amdgpu_dc_wreg(&ctx->perf_trace->write_count, address, value);

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

13175

uint32_t dm_read_reg_func(const struct dc_context *ctx, uint32_t address,

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

13180

if (address == 0) {

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

13196

value = cgs_read_register(ctx->cgs_device, address);

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

13198

trace_amdgpu_dc_rreg(&ctx->perf_trace->read_count, address, value);

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

13232

payload->address, payload->length,

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

2430

static uint32_t amdgpu_dm_dmub_reg_read(void *ctx, uint32_t address)

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

2434

return dm_read_reg(adev->dm.dc->ctx, address);

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

2437

static void amdgpu_dm_dmub_reg_write(void *ctx, uint32_t address,

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

2442

return dm_write_reg(adev->dm.dc->ctx, address, value);

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

6041

struct dc_plane_address *address,

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

6140

&plane_info->dcc, address,

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

6175

&dc_plane_state->address,

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

8886

cmd.payloads[i].address = msgs[i].addr;

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

9580

uint64_t address = afb ? afb->address : 0;

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

9610

attributes.address.high_part = upper_32_bits(address);

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

9611

attributes.address.low_part = lower_32_bits(address);

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

9822

&bundle->flip_addrs[planes_count].address,

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

9903

bundle->flip_addrs[planes_count].address.grph.addr.high_part,

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm.c

9904

bundle->flip_addrs[planes_count].address.grph.addr.low_part);

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_hdcp.c

42

lp_write_i2c(void *handle, uint32_t address, const uint8_t *data, uint32_t size)

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_hdcp.c

45

struct i2c_payload i2c_payloads[] = {{true, address, size, (void *)data} };

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_hdcp.c

53

lp_read_i2c(void *handle, uint32_t address, uint8_t offset, uint8_t *data, uint32_t size)

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_hdcp.c

57

struct i2c_payload i2c_payloads[] = {{true, address, 1, &offset},

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_hdcp.c

58

{false, address, size, data} };

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_hdcp.c

66

lp_write_dpcd(void *handle, uint32_t address, const uint8_t *data, uint32_t size)

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_hdcp.c

70

return dm_helpers_dp_write_dpcd(link->ctx, link, address, data, size);

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_hdcp.c

74

lp_read_dpcd(void *handle, uint32_t address, uint8_t *data, uint32_t size)

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_hdcp.c

78

return dm_helpers_dp_read_dpcd(link->ctx, link, address, data, size);

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_helpers.c

570

uint32_t address,

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_helpers.c

580

return drm_dp_dpcd_read(&aconnector->dm_dp_aux.aux, address, data,

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_helpers.c

587

uint32_t address,

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_helpers.c

597

address, (uint8_t *)data, size) > 0;

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_helpers.c

623

msgs[i].addr = cmd->payloads[i].address;

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_mst_types.c

71

payload.address = msg->address;

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_mst_types.c

98

if (msg->address == DP_SIDEBAND_MSG_DOWN_REQ_BASE &&

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

1010

&plane_state->dcc, &plane_state->address,

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

1347

uint64_t address = afb ? afb->address : 0;

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

1378

attributes.address.high_part = upper_32_bits(address);

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

1379

attributes.address.low_part = lower_32_bits(address);

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

267

const struct dc_plane_address *address,

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

317

struct dc_plane_address *address)

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

327

uint64_t dcc_address = afb->address + afb->base.offsets[1];

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

350

address->grph.meta_addr.low_part = lower_32_bits(dcc_address);

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

351

address->grph.meta_addr.high_part = upper_32_bits(dcc_address);

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

354

ret = amdgpu_dm_plane_validate_dcc(adev, format, rotation, tiling_info, dcc, address, plane_size);

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

368

struct dc_plane_address *address)

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

394

ret = amdgpu_dm_plane_validate_dcc(adev, format, rotation, tiling_info, dcc, address, plane_size);

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

846

struct dc_plane_address *address,

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

855

memset(address, 0, sizeof(*address));

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

857

address->tmz_surface = tmz_surface;

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

860

uint64_t addr = afb->address + fb->offsets[0];

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

869

address->type = PLN_ADDR_TYPE_GRAPHICS;

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

870

address->grph.addr.low_part = lower_32_bits(addr);

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

871

address->grph.addr.high_part = upper_32_bits(addr);

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

873

uint64_t luma_addr = afb->address + fb->offsets[0];

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

874

uint64_t chroma_addr = afb->address + fb->offsets[1];

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

892

address->type = PLN_ADDR_TYPE_VIDEO_PROGRESSIVE;

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

893

address->video_progressive.luma_addr.low_part =

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

895

address->video_progressive.luma_addr.high_part =

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

897

address->video_progressive.chroma_addr.low_part =

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

899

address->video_progressive.chroma_addr.high_part =

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

907

address);

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

914

address);

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c

986

afb->address = amdgpu_bo_gpu_offset(rbo);

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.h

53

struct dc_plane_address *address,

sys/dev/pci/drm/amd/display/amdgpu_dm/amdgpu_dm_wb.c

133

afb->address = amdgpu_bo_gpu_offset(rbo);

sys/dev/pci/drm/amd/display/dc/core/dc.c

2821

if (u->flip_addr->address.tmz_surface != u->surface->address.tmz_surface) {

sys/dev/pci/drm/amd/display/dc/core/dc.c

3085

surface->address = srf_update->flip_addr->address;

sys/dev/pci/drm/amd/display/dc/core/dc.c

5062

srf_updates[i].flip_addr->address.tmz_surface != srf_updates[i].surface->address.tmz_surface) ||

sys/dev/pci/drm/amd/display/dc/core/dc.c

5904

cmd.dp_aux_access.aux_control.dpaux.address = payload->address;

sys/dev/pci/drm/amd/display/dc/core/dc_debug.c

71

update->flip_addr->address.type,

sys/dev/pci/drm/amd/display/dc/core/dc_debug.c

72

update->flip_addr->address.grph.addr.quad_part,

sys/dev/pci/drm/amd/display/dc/core/dc_debug.c

73

update->flip_addr->address.grph.meta_addr.quad_part,

sys/dev/pci/drm/amd/display/dc/core/dc_hw_sequencer.c

803

block_sequence[*num_steps].params.subvp_save_surf_addr.addr = &current_mpc_pipe->plane_state->address;

sys/dev/pci/drm/amd/display/dc/core/dc_stream.c

288

if (attributes->address.quad_part == 0) {

sys/dev/pci/drm/amd/display/dc/core/dc_stream.c

789

pipe_ctx->stream->dmdata_address = attr->address;

sys/dev/pci/drm/amd/display/dc/core/dc_surface.c

140

if (pipe_ctx->plane_state && flags.bits.address)

sys/dev/pci/drm/amd/display/dc/core/dc_surface.c

155

if (flags.bits.address)

sys/dev/pci/drm/amd/display/dc/dc.h

1419

struct dc_plane_address address;

sys/dev/pci/drm/amd/display/dc/dc.h

2602

struct dc_plane_address address;

sys/dev/pci/drm/amd/display/dc/dc_ddc_types.h

108

uint8_t address;

sys/dev/pci/drm/amd/display/dc/dc_ddc_types.h

193

uint32_t address;

sys/dev/pci/drm/amd/display/dc/dc_ddc_types.h

51

uint32_t address;

sys/dev/pci/drm/amd/display/dc/dc_ddc_types.h

90

uint32_t address;

sys/dev/pci/drm/amd/display/dc/dc_dmub_srv.c

1007

if (pipe_ctx->plane_state->address.type == PLN_ADDR_TYPE_VIDEO_PROGRESSIVE ||

sys/dev/pci/drm/amd/display/dc/dc_dmub_srv.c

1845

struct dc_plane_address *address;

sys/dev/pci/drm/amd/display/dc/dc_dmub_srv.c

1858

address = &plane_state->address;

sys/dev/pci/drm/amd/display/dc/dc_dmub_srv.c

1881

switch (address->type) {

sys/dev/pci/drm/amd/display/dc/dc_dmub_srv.c

1883

if (address->grph.addr.quad_part == 0) {

sys/dev/pci/drm/amd/display/dc/dc_dmub_srv.c

1889

address->grph.meta_addr.low_part;

sys/dev/pci/drm/amd/display/dc/dc_dmub_srv.c

1891

(uint16_t)address->grph.meta_addr.high_part;

sys/dev/pci/drm/amd/display/dc/dc_dmub_srv.c

1893

address->grph.addr.low_part;

sys/dev/pci/drm/amd/display/dc/dc_dmub_srv.c

1895

(uint16_t)address->grph.addr.high_part;

sys/dev/pci/drm/amd/display/dc/dc_dmub_srv.c

1898

if (address->video_progressive.luma_addr.quad_part == 0 ||

sys/dev/pci/drm/amd/display/dc/dc_dmub_srv.c

1899

address->video_progressive.chroma_addr.quad_part == 0) {

sys/dev/pci/drm/amd/display/dc/dc_dmub_srv.c

1905

address->video_progressive.luma_meta_addr.low_part;

sys/dev/pci/drm/amd/display/dc/dc_dmub_srv.c

1907

(uint16_t)address->video_progressive.luma_meta_addr.high_part;

sys/dev/pci/drm/amd/display/dc/dc_dmub_srv.c

1909

address->video_progressive.chroma_meta_addr.low_part;

sys/dev/pci/drm/amd/display/dc/dc_dmub_srv.c

1911

(uint16_t)address->video_progressive.chroma_meta_addr.high_part;

sys/dev/pci/drm/amd/display/dc/dc_dmub_srv.c

1913

address->video_progressive.luma_addr.low_part;

sys/dev/pci/drm/amd/display/dc/dc_dmub_srv.c

1915

(uint16_t)address->video_progressive.luma_addr.high_part;

sys/dev/pci/drm/amd/display/dc/dc_dmub_srv.c

1917

address->video_progressive.chroma_addr.low_part;

sys/dev/pci/drm/amd/display/dc/dc_dmub_srv.c

1919

(uint16_t)address->video_progressive.chroma_addr.high_part;

sys/dev/pci/drm/amd/display/dc/dc_fused_io.c

28

loc->address = op->address;

sys/dev/pci/drm/amd/display/dc/dc_fused_io.c

52

loc->address = op->address;

sys/dev/pci/drm/amd/display/dc/dc_hw_types.h

250

struct dc_plane_address address;

sys/dev/pci/drm/amd/display/dc/dc_hw_types.h

602

PHYSICAL_ADDRESS_LOC address;

sys/dev/pci/drm/amd/display/dc/dc_plane.h

33

uint32_t address : 1;

sys/dev/pci/drm/amd/display/dc/dc_stream.h

84

PHYSICAL_ADDRESS_LOC address;

sys/dev/pci/drm/amd/display/dc/dce/dce_aux.c

174

#define COMPOSE_AUX_SW_DATA_16_20(command, address) \

sys/dev/pci/drm/amd/display/dc/dce/dce_aux.c

175

((command) | ((0xF0000 & (address)) >> 16))

sys/dev/pci/drm/amd/display/dc/dce/dce_aux.c

177

#define COMPOSE_AUX_SW_DATA_8_15(address) \

sys/dev/pci/drm/amd/display/dc/dce/dce_aux.c

178

((0xFF00 & (address)) >> 8)

sys/dev/pci/drm/amd/display/dc/dce/dce_aux.c

180

#define COMPOSE_AUX_SW_DATA_0_7(address) \

sys/dev/pci/drm/amd/display/dc/dce/dce_aux.c

181

(0xFF & (address))

sys/dev/pci/drm/amd/display/dc/dce/dce_aux.c

246

AUX_SW_DATA, COMPOSE_AUX_SW_DATA_16_20(request->action, request->address));

sys/dev/pci/drm/amd/display/dc/dce/dce_aux.c

250

AUX_SW_DATA, COMPOSE_AUX_SW_DATA_8_15(request->address));

sys/dev/pci/drm/amd/display/dc/dce/dce_aux.c

253

AUX_SW_DATA, COMPOSE_AUX_SW_DATA_0_7(request->address));

sys/dev/pci/drm/amd/display/dc/dce/dce_aux.c

278

request->action, request->address, request->length, request->data);

sys/dev/pci/drm/amd/display/dc/dce/dce_aux.c

590

aux_req.address = payload->address;

sys/dev/pci/drm/amd/display/dc/dce/dce_aux.c

733

payload->address,

sys/dev/pci/drm/amd/display/dc/dce/dce_aux.c

759

payload->address,

sys/dev/pci/drm/amd/display/dc/dce/dce_i2c_hw.c

226

DC_I2C_DATA, request->address,

sys/dev/pci/drm/amd/display/dc/dce/dce_i2c_hw.c

233

DC_I2C_DATA, request->address);

sys/dev/pci/drm/amd/display/dc/dce/dce_i2c_hw.c

594

request.address = (uint8_t) ((payload->address << 1) | (payload->write ? 0 : 1));

sys/dev/pci/drm/amd/display/dc/dce/dce_i2c_hw.h

281

uint8_t address;

sys/dev/pci/drm/amd/display/dc/dce/dce_i2c_sw.c

253

uint8_t address,

sys/dev/pci/drm/amd/display/dc/dce/dce_i2c_sw.c

259

if (!write_byte_sw(ctx, ddc_handle, clock_delay_div_4, address))

sys/dev/pci/drm/amd/display/dc/dce/dce_i2c_sw.c

275

uint8_t address,

sys/dev/pci/drm/amd/display/dc/dce/dce_i2c_sw.c

281

if (!write_byte_sw(ctx, ddc_handle, clock_delay_div_4, address))

sys/dev/pci/drm/amd/display/dc/dce/dce_i2c_sw.c

413

req->address, req->length, req->data);

sys/dev/pci/drm/amd/display/dc/dce/dce_i2c_sw.c

418

req->address, req->length, req->data);

sys/dev/pci/drm/amd/display/dc/dce/dce_i2c_sw.c

454

request.address = (uint8_t) ((payload->address << 1) | (payload->write ? 0 : 1));

sys/dev/pci/drm/amd/display/dc/dce/dce_ipp.c

128

CURSOR_SURFACE_ADDRESS_HIGH, attributes->address.high_part);

sys/dev/pci/drm/amd/display/dc/dce/dce_ipp.c

131

CURSOR_SURFACE_ADDRESS, attributes->address.low_part);

sys/dev/pci/drm/amd/display/dc/dce/dce_mem_input.c

816

PHYSICAL_ADDRESS_LOC address)

sys/dev/pci/drm/amd/display/dc/dce/dce_mem_input.c

821

address.high_part);

sys/dev/pci/drm/amd/display/dc/dce/dce_mem_input.c

824

GRPH_SECONDARY_SURFACE_ADDRESS, address.low_part >> 8,

sys/dev/pci/drm/amd/display/dc/dce/dce_mem_input.c

830

PHYSICAL_ADDRESS_LOC address)

sys/dev/pci/drm/amd/display/dc/dce/dce_mem_input.c

835

address.high_part);

sys/dev/pci/drm/amd/display/dc/dce/dce_mem_input.c

839

address.low_part >> 8);

sys/dev/pci/drm/amd/display/dc/dce/dce_mem_input.c

858

const struct dc_plane_address *address,

sys/dev/pci/drm/amd/display/dc/dce/dce_mem_input.c

869

switch (address->type) {

sys/dev/pci/drm/amd/display/dc/dce/dce_mem_input.c

871

if (address->grph.addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/dce/dce_mem_input.c

873

program_pri_addr(dce_mi, address->grph.addr);

sys/dev/pci/drm/amd/display/dc/dce/dce_mem_input.c

876

if (address->grph_stereo.left_addr.quad_part == 0 ||

sys/dev/pci/drm/amd/display/dc/dce/dce_mem_input.c

877

address->grph_stereo.right_addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/dce/dce_mem_input.c

879

program_pri_addr(dce_mi, address->grph_stereo.left_addr);

sys/dev/pci/drm/amd/display/dc/dce/dce_mem_input.c

880

program_sec_addr(dce_mi, address->grph_stereo.right_addr);

sys/dev/pci/drm/amd/display/dc/dce/dce_mem_input.c

888

mem_input->request_address = *address;

sys/dev/pci/drm/amd/display/dc/dce/dce_mem_input.c

891

mem_input->current_address = *address;

sys/dev/pci/drm/amd/display/dc/dce110/dce110_mem_input_v.c

102

temp = address.high_part &

sys/dev/pci/drm/amd/display/dc/dce110/dce110_mem_input_v.c

115

temp = address.low_part >>

sys/dev/pci/drm/amd/display/dc/dce110/dce110_mem_input_v.c

488

const struct dc_plane_address *address,

sys/dev/pci/drm/amd/display/dc/dce110/dce110_mem_input_v.c

495

address);

sys/dev/pci/drm/amd/display/dc/dce110/dce110_mem_input_v.c

497

mem_input->request_address = *address;

sys/dev/pci/drm/amd/display/dc/dce110/dce110_mem_input_v.c

62

PHYSICAL_ADDRESS_LOC address)

sys/dev/pci/drm/amd/display/dc/dce110/dce110_mem_input_v.c

67

temp = address.high_part &

sys/dev/pci/drm/amd/display/dc/dce110/dce110_mem_input_v.c

80

temp = address.low_part >>

sys/dev/pci/drm/amd/display/dc/dce110/dce110_mem_input_v.c

96

PHYSICAL_ADDRESS_LOC address)

sys/dev/pci/drm/amd/display/dc/dce110/dce110_timing_generator.c

111

uint32_t address = CRTC_REG(mmCRTC_CONTROL);

sys/dev/pci/drm/amd/display/dc/dce110/dce110_timing_generator.c

113

regval = dm_read_reg(tg->ctx, address);

sys/dev/pci/drm/amd/display/dc/dce110/dce110_timing_generator.c

116

dm_write_reg(tg->ctx, address, regval);

sys/dev/pci/drm/amd/display/dc/dce110/dce110_timing_generator.c

1223

uint32_t address = DCP_REG(mmDCP_GSL_CONTROL);

sys/dev/pci/drm/amd/display/dc/dce110/dce110_timing_generator.c

1226

value = dm_read_reg(tg->ctx, address);

sys/dev/pci/drm/amd/display/dc/dce110/dce110_timing_generator.c

1296

dm_write_reg(tg->ctx, address, value);

sys/dev/pci/drm/amd/display/dc/dce110/dce110_timing_generator.c

1299

address = CRTC_REG(mmCRTC_GSL_CONTROL);

sys/dev/pci/drm/amd/display/dc/dce110/dce110_timing_generator.c

1301

value = dm_read_reg(tg->ctx, address);

sys/dev/pci/drm/amd/display/dc/dce110/dce110_timing_generator.c

1312

dm_write_reg(tg->ctx, address, value);

sys/dev/pci/drm/amd/display/dc/dce110/dce110_timing_generator.c

1324

uint32_t address = DCP_REG(mmDCP_GSL_CONTROL);

sys/dev/pci/drm/amd/display/dc/dce110/dce110_timing_generator.c

1365

dm_write_reg(tg->ctx, address, value);

sys/dev/pci/drm/amd/display/dc/dce110/dce110_timing_generator.c

1368

address = CRTC_REG(mmCRTC_GSL_CONTROL);

sys/dev/pci/drm/amd/display/dc/dce110/dce110_timing_generator.c

1381

dm_write_reg(tg->ctx, address, value);

sys/dev/pci/drm/amd/display/dc/dce110/dce110_timing_generator_v.c

595

uint32_t address = mmCRTC_CONTROL;

sys/dev/pci/drm/amd/display/dc/dce110/dce110_timing_generator_v.c

597

regval = dm_read_reg(tg->ctx, address);

sys/dev/pci/drm/amd/display/dc/dce110/dce110_timing_generator_v.c

600

dm_write_reg(tg->ctx, address, regval);

sys/dev/pci/drm/amd/display/dc/dm_event_log.h

34

#define EVENT_LOG_AUX_REQ(ddc, type, action, address, len, data)

sys/dev/pci/drm/amd/display/dc/dm_helpers.h

137

uint32_t address,

sys/dev/pci/drm/amd/display/dc/dm_helpers.h

147

uint32_t address,

sys/dev/pci/drm/amd/display/dc/dm_services.h

56

uint32_t dm_read_reg_func(const struct dc_context *ctx, uint32_t address,

sys/dev/pci/drm/amd/display/dc/dm_services.h

62

void dm_write_reg_func(const struct dc_context *ctx, uint32_t address,

sys/dev/pci/drm/amd/display/dc/dm_services.h

65

#define dm_read_reg(ctx, address) \

sys/dev/pci/drm/amd/display/dc/dm_services.h

66

dm_read_reg_func(ctx, address, __func__)

sys/dev/pci/drm/amd/display/dc/dm_services.h

68

#define dm_write_reg(ctx, address, value) \

sys/dev/pci/drm/amd/display/dc/dm_services.h

69

dm_write_reg_func(ctx, address, value, __func__)

sys/dev/pci/drm/amd/display/dc/dml/dcn20/dcn20_fpu.c

1538

(res_ctx->pipe_ctx[i].plane_state->address.type == PLN_ADDR_TYPE_VIDEO_PROGRESSIVE ||

sys/dev/pci/drm/amd/display/dc/dml/dcn32/dcn32_fpu.c

635

!pipe->plane_state->address.tmz_surface &&

sys/dev/pci/drm/amd/display/dc/dml2/dml21/dml21_utils.c

295

memcpy(&phantom_plane->address, &main_plane->address, sizeof(phantom_plane->address));

sys/dev/pci/drm/amd/display/dc/dml2/dml2_mall_phantom.c

755

memcpy(&phantom_plane->address, &curr_pipe->plane_state->address, sizeof(phantom_plane->address));

sys/dev/pci/drm/amd/display/dc/hdcp/hdcp_msg.c

148

i2c_payloads[0].address = hdcp_i2c_addr_link_secondary;

sys/dev/pci/drm/amd/display/dc/hdcp/hdcp_msg.c

149

i2c_payloads[1].address = hdcp_i2c_addr_link_secondary;

sys/dev/pci/drm/amd/display/dc/hdcp/hdcp_msg.c

153

i2c_payloads[0].address = hdcp_i2c_addr_link_primary;

sys/dev/pci/drm/amd/display/dc/hdcp/hdcp_msg.c

154

i2c_payloads[1].address = hdcp_i2c_addr_link_primary;

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

1177

CURSOR_SURFACE_ADDRESS_HIGH, attr->address.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

1179

CURSOR_SURFACE_ADDRESS, attr->address.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

1223

if (hubp->curs_attr.address.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

351

const struct dc_plane_address *address,

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

362

if (address->type == PLN_ADDR_TYPE_GRPH_STEREO) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

379

switch (address->type) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

388

if (address->grph.addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

392

PRIMARY_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

393

PRIMARY_META_SURFACE_TMZ, address->tmz_surface);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

395

if (address->grph.meta_addr.quad_part != 0) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

398

address->grph.meta_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

402

address->grph.meta_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

407

address->grph.addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

411

address->grph.addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

414

if (address->video_progressive.luma_addr.quad_part == 0

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

415

|| address->video_progressive.chroma_addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

419

PRIMARY_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

420

PRIMARY_SURFACE_TMZ_C, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

421

PRIMARY_META_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

422

PRIMARY_META_SURFACE_TMZ_C, address->tmz_surface);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

424

if (address->video_progressive.luma_meta_addr.quad_part != 0) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

427

address->video_progressive.chroma_meta_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

431

address->video_progressive.chroma_meta_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

435

address->video_progressive.luma_meta_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

439

address->video_progressive.luma_meta_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

444

address->video_progressive.chroma_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

448

address->video_progressive.chroma_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

452

address->video_progressive.luma_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

456

address->video_progressive.luma_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

459

if (address->grph_stereo.left_addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

461

if (address->grph_stereo.right_addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

465

PRIMARY_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

466

PRIMARY_SURFACE_TMZ_C, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

467

PRIMARY_META_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

468

PRIMARY_META_SURFACE_TMZ_C, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

469

SECONDARY_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

470

SECONDARY_SURFACE_TMZ_C, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

471

SECONDARY_META_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

472

SECONDARY_META_SURFACE_TMZ_C, address->tmz_surface);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

474

if (address->grph_stereo.right_meta_addr.quad_part != 0) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

478

address->grph_stereo.right_meta_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

482

address->grph_stereo.right_meta_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

484

if (address->grph_stereo.left_meta_addr.quad_part != 0) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

488

address->grph_stereo.left_meta_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

492

address->grph_stereo.left_meta_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

497

address->grph_stereo.right_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

501

address->grph_stereo.right_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

505

address->grph_stereo.left_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

509

address->grph_stereo.left_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.c

516

hubp->request_address = *address;

sys/dev/pci/drm/amd/display/dc/hubp/dcn10/dcn10_hubp.h

777

const struct dc_plane_address *address,

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

1013

if (hubp->curs_attr.address.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

617

CURSOR_SURFACE_ADDRESS_HIGH, attr->address.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

619

CURSOR_SURFACE_ADDRESS, attr->address.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

637

hubp->att.SURFACE_ADDR_HIGH = attr->address.high_part;

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

638

hubp->att.SURFACE_ADDR = attr->address.low_part;

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

676

REG_WRITE(DMDATA_ADDRESS_LOW, attr->address.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

678

DMDATA_ADDRESS_HIGH, attr->address.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

728

const struct dc_plane_address *address,

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

739

VMID, address->vmid);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

747

switch (address->type) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

756

if (address->grph.addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

760

PRIMARY_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

761

PRIMARY_META_SURFACE_TMZ, address->tmz_surface);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

763

if (address->grph.meta_addr.quad_part != 0) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

766

address->grph.meta_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

770

address->grph.meta_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

775

address->grph.addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

779

address->grph.addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

782

if (address->video_progressive.luma_addr.quad_part == 0

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

783

|| address->video_progressive.chroma_addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

787

PRIMARY_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

788

PRIMARY_SURFACE_TMZ_C, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

789

PRIMARY_META_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

790

PRIMARY_META_SURFACE_TMZ_C, address->tmz_surface);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

792

if (address->video_progressive.luma_meta_addr.quad_part != 0) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

795

address->video_progressive.chroma_meta_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

799

address->video_progressive.chroma_meta_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

803

address->video_progressive.luma_meta_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

807

address->video_progressive.luma_meta_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

812

address->video_progressive.chroma_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

816

address->video_progressive.chroma_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

820

address->video_progressive.luma_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

824

address->video_progressive.luma_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

827

if (address->grph_stereo.left_addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

829

if (address->grph_stereo.right_addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

833

PRIMARY_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

834

PRIMARY_SURFACE_TMZ_C, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

835

PRIMARY_META_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

836

PRIMARY_META_SURFACE_TMZ_C, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

837

SECONDARY_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

838

SECONDARY_SURFACE_TMZ_C, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

839

SECONDARY_META_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

840

SECONDARY_META_SURFACE_TMZ_C, address->tmz_surface);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

842

if (address->grph_stereo.right_meta_addr.quad_part != 0) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

846

address->grph_stereo.right_meta_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

850

address->grph_stereo.right_meta_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

852

if (address->grph_stereo.left_meta_addr.quad_part != 0) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

856

address->grph_stereo.left_meta_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

860

address->grph_stereo.left_meta_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

865

address->grph_stereo.right_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

869

address->grph_stereo.right_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

873

address->grph_stereo.left_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

877

address->grph_stereo.left_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.c

884

hubp->request_address = *address;

sys/dev/pci/drm/amd/display/dc/hubp/dcn20/dcn20_hubp.h

361

const struct dc_plane_address *address,

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

700

const struct dc_plane_address *address,

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

705

flip_regs.vmid = address->vmid;

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

707

switch (address->type) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

709

if (address->grph.addr.quad_part == 0) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

714

if (address->grph.meta_addr.quad_part != 0) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

716

address->grph.meta_addr.low_part;

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

718

address->grph.meta_addr.high_part;

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

722

address->grph.addr.low_part;

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

724

address->grph.addr.high_part;

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

727

if (address->video_progressive.luma_addr.quad_part == 0

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

728

|| address->video_progressive.chroma_addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

731

if (address->video_progressive.luma_meta_addr.quad_part != 0) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

733

address->video_progressive.luma_meta_addr.low_part;

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

735

address->video_progressive.luma_meta_addr.high_part;

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

738

address->video_progressive.chroma_meta_addr.low_part;

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

740

address->video_progressive.chroma_meta_addr.high_part;

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

744

address->video_progressive.luma_addr.low_part;

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

746

address->video_progressive.luma_addr.high_part;

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

749

address->video_progressive.chroma_addr.low_part;

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

752

address->video_progressive.chroma_addr.high_part;

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

756

if (address->grph_stereo.left_addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

758

if (address->grph_stereo.right_addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

763

if (address->grph_stereo.right_meta_addr.quad_part != 0) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

765

address->grph_stereo.right_meta_addr.low_part;

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

767

address->grph_stereo.right_meta_addr.high_part;

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

770

if (address->grph_stereo.left_meta_addr.quad_part != 0) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

772

address->grph_stereo.left_meta_addr.low_part;

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

774

address->grph_stereo.left_meta_addr.high_part;

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

778

address->grph_stereo.left_addr.low_part;

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

780

address->grph_stereo.left_addr.high_part;

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

783

address->grph_stereo.right_addr.low_part;

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

785

address->grph_stereo.right_addr.high_part;

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

793

flip_regs.tmz_surface = address->tmz_surface;

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

796

if (hubp->ctx->dc->debug.enable_dmcub_surface_flip && address->type == PLN_ADDR_TYPE_VIDEO_PROGRESSIVE)

sys/dev/pci/drm/amd/display/dc/hubp/dcn21/dcn21_hubp.c

801

hubp->request_address = *address;

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

108

if (address->grph.addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

112

PRIMARY_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

113

PRIMARY_META_SURFACE_TMZ, address->tmz_surface);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

115

if (address->grph.meta_addr.quad_part != 0) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

118

address->grph.meta_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

122

address->grph.meta_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

127

address->grph.addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

131

address->grph.addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

134

if (address->video_progressive.luma_addr.quad_part == 0

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

135

|| address->video_progressive.chroma_addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

139

PRIMARY_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

140

PRIMARY_SURFACE_TMZ_C, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

141

PRIMARY_META_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

142

PRIMARY_META_SURFACE_TMZ_C, address->tmz_surface);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

144

if (address->video_progressive.luma_meta_addr.quad_part != 0) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

147

address->video_progressive.chroma_meta_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

151

address->video_progressive.chroma_meta_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

155

address->video_progressive.luma_meta_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

159

address->video_progressive.luma_meta_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

164

address->video_progressive.chroma_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

168

address->video_progressive.chroma_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

172

address->video_progressive.luma_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

176

address->video_progressive.luma_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

179

if (address->grph_stereo.left_addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

181

if (address->grph_stereo.right_addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

185

PRIMARY_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

186

PRIMARY_SURFACE_TMZ_C, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

187

PRIMARY_META_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

188

PRIMARY_META_SURFACE_TMZ_C, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

189

SECONDARY_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

190

SECONDARY_SURFACE_TMZ_C, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

191

SECONDARY_META_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

192

SECONDARY_META_SURFACE_TMZ_C, address->tmz_surface);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

194

if (address->grph_stereo.right_meta_addr.quad_part != 0) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

198

address->grph_stereo.right_alpha_meta_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

202

address->grph_stereo.right_alpha_meta_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

206

address->grph_stereo.right_meta_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

210

address->grph_stereo.right_meta_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

212

if (address->grph_stereo.left_meta_addr.quad_part != 0) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

216

address->grph_stereo.left_alpha_meta_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

220

address->grph_stereo.left_alpha_meta_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

224

address->grph_stereo.left_meta_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

228

address->grph_stereo.left_meta_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

233

address->grph_stereo.right_alpha_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

237

address->grph_stereo.right_alpha_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

241

address->grph_stereo.right_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

245

address->grph_stereo.right_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

249

address->grph_stereo.left_alpha_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

253

address->grph_stereo.left_alpha_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

257

address->grph_stereo.left_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

261

address->grph_stereo.left_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

264

if (address->rgbea.addr.quad_part == 0

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

265

|| address->rgbea.alpha_addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

269

PRIMARY_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

270

PRIMARY_SURFACE_TMZ_C, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

271

PRIMARY_META_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

272

PRIMARY_META_SURFACE_TMZ_C, address->tmz_surface);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

274

if (address->rgbea.meta_addr.quad_part != 0) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

278

address->rgbea.alpha_meta_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

282

address->rgbea.alpha_meta_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

286

address->rgbea.meta_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

290

address->rgbea.meta_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

295

address->rgbea.alpha_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

299

address->rgbea.alpha_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

303

address->rgbea.addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

307

address->rgbea.addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

314

hubp->request_address = *address;

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

402

REG_WRITE(DMDATA_ADDRESS_LOW, attr->address.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

404

DMDATA_ADDRESS_HIGH, attr->address.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

70

const struct dc_plane_address *address,

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

82

VMID, address->vmid);

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

84

if (address->type == PLN_ADDR_TYPE_GRPH_STEREO) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.c

99

switch (address->type) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn30/dcn30_hubp.h

262

const struct dc_plane_address *address,

sys/dev/pci/drm/amd/display/dc/hubp/dcn32/dcn32_hubp.c

125

CURSOR_SURFACE_ADDRESS_HIGH, attr->address.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn32/dcn32_hubp.c

127

CURSOR_SURFACE_ADDRESS, attr->address.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

151

HUBP_3DLUT_ADDRESS_HIGH, cfg->address.lut3d.addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

153

HUBP_3DLUT_ADDRESS_LOW, cfg->address.lut3d.addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

411

const struct dc_plane_address *address,

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

423

VMID, address->vmid);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

425

if (address->type == PLN_ADDR_TYPE_GRPH_STEREO) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

44

const struct dc_plane_address address)

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

440

switch (address->type) {

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

442

if (address->grph.addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

446

PRIMARY_SURFACE_TMZ, address->tmz_surface);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

450

address->grph.addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

454

address->grph.addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

457

if (address->video_progressive.luma_addr.quad_part == 0

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

458

|| address->video_progressive.chroma_addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

462

PRIMARY_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

463

PRIMARY_SURFACE_TMZ_C, address->tmz_surface);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

467

address->video_progressive.chroma_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

471

address->video_progressive.chroma_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

475

address->video_progressive.luma_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

479

address->video_progressive.luma_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

48

REG_UPDATE(HUBP_3DLUT_ADDRESS_HIGH, HUBP_3DLUT_ADDRESS_HIGH, address.lut3d.addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

482

if (address->grph_stereo.left_addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

484

if (address->grph_stereo.right_addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

488

PRIMARY_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

489

PRIMARY_SURFACE_TMZ_C, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

49

REG_WRITE(HUBP_3DLUT_ADDRESS_LOW, address.lut3d.addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

490

SECONDARY_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

491

SECONDARY_SURFACE_TMZ_C, address->tmz_surface);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

495

address->grph_stereo.right_alpha_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

499

address->grph_stereo.right_alpha_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

503

address->grph_stereo.right_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

507

address->grph_stereo.right_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

511

address->grph_stereo.left_alpha_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

515

address->grph_stereo.left_alpha_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

519

address->grph_stereo.left_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

523

address->grph_stereo.left_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

526

if (address->rgbea.addr.quad_part == 0

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

527

|| address->rgbea.alpha_addr.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

531

PRIMARY_SURFACE_TMZ, address->tmz_surface,

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

532

PRIMARY_SURFACE_TMZ_C, address->tmz_surface);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

536

address->rgbea.alpha_addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

540

address->rgbea.alpha_addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

544

address->rgbea.addr.high_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

548

address->rgbea.addr.low_part);

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

555

hubp->request_address = *address;

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.c

762

if (hubp->curs_attr.address.quad_part == 0)

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.h

273

const struct dc_plane_address *address,

sys/dev/pci/drm/amd/display/dc/hubp/dcn401/dcn401_hubp.h

348

void hubp401_program_3dlut_fl_addr(struct hubp *hubp, const struct dc_plane_address address);

sys/dev/pci/drm/amd/display/dc/hwss/dce100/dce100_hwseq.c

169

&plane_state->address,

sys/dev/pci/drm/amd/display/dc/hwss/dce110/dce110_hwseq.c

2648

&plane_state->address,

sys/dev/pci/drm/amd/display/dc/hwss/dce110/dce110_hwseq.c

2651

plane_state->status.requested_address = plane_state->address;

sys/dev/pci/drm/amd/display/dc/hwss/dce110/dce110_hwseq.c

2996

pipe_ctx->plane_state->address.grph.addr.high_part,

sys/dev/pci/drm/amd/display/dc/hwss/dce110/dce110_hwseq.c

2997

pipe_ctx->plane_state->address.grph.addr.low_part,

sys/dev/pci/drm/amd/display/dc/hwss/dce110/dce110_hwseq.c

3151

if (pipe_ctx->plane_state->address.type

sys/dev/pci/drm/amd/display/dc/hwss/dce60/dce60_hwseq.c

351

pipe_ctx->plane_state->address.grph.addr.high_part,

sys/dev/pci/drm/amd/display/dc/hwss/dce60/dce60_hwseq.c

352

pipe_ctx->plane_state->address.grph.addr.low_part,

sys/dev/pci/drm/amd/display/dc/hwss/dcn10/dcn10_hwseq.c

1984

if (sec_split && plane_state->address.type == PLN_ADDR_TYPE_GRPH_STEREO &&

sys/dev/pci/drm/amd/display/dc/hwss/dcn10/dcn10_hwseq.c

1989

*addr = plane_state->address.grph_stereo.left_addr;

sys/dev/pci/drm/amd/display/dc/hwss/dcn10/dcn10_hwseq.c

1990

plane_state->address.grph_stereo.left_addr =

sys/dev/pci/drm/amd/display/dc/hwss/dcn10/dcn10_hwseq.c

1991

plane_state->address.grph_stereo.right_addr;

sys/dev/pci/drm/amd/display/dc/hwss/dcn10/dcn10_hwseq.c

1995

plane_state->address.type != PLN_ADDR_TYPE_GRPH_STEREO) {

sys/dev/pci/drm/amd/display/dc/hwss/dcn10/dcn10_hwseq.c

1996

plane_state->address.type = PLN_ADDR_TYPE_GRPH_STEREO;

sys/dev/pci/drm/amd/display/dc/hwss/dcn10/dcn10_hwseq.c

1997

plane_state->address.grph_stereo.right_addr =

sys/dev/pci/drm/amd/display/dc/hwss/dcn10/dcn10_hwseq.c

1998

plane_state->address.grph_stereo.left_addr;

sys/dev/pci/drm/amd/display/dc/hwss/dcn10/dcn10_hwseq.c

1999

plane_state->address.grph_stereo.right_meta_addr =

sys/dev/pci/drm/amd/display/dc/hwss/dcn10/dcn10_hwseq.c

2000

plane_state->address.grph_stereo.left_meta_addr;

sys/dev/pci/drm/amd/display/dc/hwss/dcn10/dcn10_hwseq.c

2019

&plane_state->address,

sys/dev/pci/drm/amd/display/dc/hwss/dcn10/dcn10_hwseq.c

2022

plane_state->status.requested_address = plane_state->address;

sys/dev/pci/drm/amd/display/dc/hwss/dcn10/dcn10_hwseq.c

2025

plane_state->status.current_address = plane_state->address;

sys/dev/pci/drm/amd/display/dc/hwss/dcn10/dcn10_hwseq.c

2028

pipe_ctx->plane_state->address.grph_stereo.left_addr = addr;

sys/dev/pci/drm/amd/display/dc/hwss/dcn10/dcn10_hwseq.c

3092

if (pipe_ctx->stream->cursor_attributes.address.quad_part != 0) {

sys/dev/pci/drm/amd/display/dc/hwss/dcn10/dcn10_hwseq.c

3744

if (pipe_ctx->plane_state->address.type

sys/dev/pci/drm/amd/display/dc/hwss/dcn10/dcn10_hwseq.c

4142

&plane_state->address,

sys/dev/pci/drm/amd/display/dc/hwss/dcn20/dcn20_hwseq.c

1803

pipe_ctx->stream->cursor_attributes.address.quad_part != 0) {

sys/dev/pci/drm/amd/display/dc/hwss/dcn20/dcn20_hwseq.c

1863

params.subvp_save_surf_addr.addr = &pipe_ctx->plane_state->address;

sys/dev/pci/drm/amd/display/dc/hwss/dcn20/dcn20_hwseq.c

2649

attr.address.quad_part =

sys/dev/pci/drm/amd/display/dc/hwss/dcn20/dcn20_hwseq.c

2707

if (sec_split && plane_state->address.type == PLN_ADDR_TYPE_GRPH_STEREO &&

sys/dev/pci/drm/amd/display/dc/hwss/dcn20/dcn20_hwseq.c

2712

*addr = plane_state->address.grph_stereo.left_addr;

sys/dev/pci/drm/amd/display/dc/hwss/dcn20/dcn20_hwseq.c

2713

plane_state->address.grph_stereo.left_addr =

sys/dev/pci/drm/amd/display/dc/hwss/dcn20/dcn20_hwseq.c

2714

plane_state->address.grph_stereo.right_addr;

sys/dev/pci/drm/amd/display/dc/hwss/dcn20/dcn20_hwseq.c

2719

plane_state->address.type != PLN_ADDR_TYPE_GRPH_STEREO) {

sys/dev/pci/drm/amd/display/dc/hwss/dcn20/dcn20_hwseq.c

2720

plane_state->address.type = PLN_ADDR_TYPE_GRPH_STEREO;

sys/dev/pci/drm/amd/display/dc/hwss/dcn20/dcn20_hwseq.c

2721

plane_state->address.grph_stereo.right_addr =

sys/dev/pci/drm/amd/display/dc/hwss/dcn20/dcn20_hwseq.c

2722

plane_state->address.grph_stereo.left_addr;

sys/dev/pci/drm/amd/display/dc/hwss/dcn20/dcn20_hwseq.c

2723

plane_state->address.grph_stereo.right_meta_addr =

sys/dev/pci/drm/amd/display/dc/hwss/dcn20/dcn20_hwseq.c

2724

plane_state->address.grph_stereo.left_meta_addr;

sys/dev/pci/drm/amd/display/dc/hwss/dcn20/dcn20_hwseq.c

2741

vm_helper_mark_vmid_used(dc->vm_helper, plane_state->address.vmid, pipe_ctx->plane_res.hubp->inst);

sys/dev/pci/drm/amd/display/dc/hwss/dcn20/dcn20_hwseq.c

2745

&plane_state->address,

sys/dev/pci/drm/amd/display/dc/hwss/dcn20/dcn20_hwseq.c

2748

plane_state->status.requested_address = plane_state->address;

sys/dev/pci/drm/amd/display/dc/hwss/dcn20/dcn20_hwseq.c

2751

plane_state->status.current_address = plane_state->address;

sys/dev/pci/drm/amd/display/dc/hwss/dcn20/dcn20_hwseq.c

2754

pipe_ctx->plane_state->address.grph_stereo.left_addr = addr;

sys/dev/pci/drm/amd/display/dc/hwss/dcn201/dcn201_hwseq.c

144

uma = plane_state->address;

sys/dev/pci/drm/amd/display/dc/hwss/dcn201/dcn201_hwseq.c

154

plane_state->status.requested_address = plane_state->address;

sys/dev/pci/drm/amd/display/dc/hwss/dcn201/dcn201_hwseq.c

157

plane_state->status.current_address = plane_state->address;

sys/dev/pci/drm/amd/display/dc/hwss/dcn201/dcn201_hwseq.c

160

pipe_ctx->plane_state->address.grph_stereo.left_addr = addr;

sys/dev/pci/drm/amd/display/dc/hwss/dcn201/dcn201_hwseq.c

560

gpu_addr_to_uma(pipe_ctx->stream->ctx->dc->hwseq, &attributes->address);

sys/dev/pci/drm/amd/display/dc/hwss/dcn201/dcn201_hwseq.c

579

attr.address.quad_part =

sys/dev/pci/drm/amd/display/dc/hwss/dcn201/dcn201_hwseq.c

63

if (sec_split && plane_state->address.type == PLN_ADDR_TYPE_GRPH_STEREO &&

sys/dev/pci/drm/amd/display/dc/hwss/dcn201/dcn201_hwseq.c

68

*addr = plane_state->address.grph_stereo.left_addr;

sys/dev/pci/drm/amd/display/dc/hwss/dcn201/dcn201_hwseq.c

69

plane_state->address.grph_stereo.left_addr =

sys/dev/pci/drm/amd/display/dc/hwss/dcn201/dcn201_hwseq.c

70

plane_state->address.grph_stereo.right_addr;

sys/dev/pci/drm/amd/display/dc/hwss/dcn201/dcn201_hwseq.c

74

plane_state->address.type != PLN_ADDR_TYPE_GRPH_STEREO) {

sys/dev/pci/drm/amd/display/dc/hwss/dcn201/dcn201_hwseq.c

75

plane_state->address.type = PLN_ADDR_TYPE_GRPH_STEREO;

sys/dev/pci/drm/amd/display/dc/hwss/dcn201/dcn201_hwseq.c

76

plane_state->address.grph_stereo.right_addr =

sys/dev/pci/drm/amd/display/dc/hwss/dcn201/dcn201_hwseq.c

77

plane_state->address.grph_stereo.left_addr;

sys/dev/pci/drm/amd/display/dc/hwss/dcn201/dcn201_hwseq.c

78

plane_state->address.grph_stereo.right_meta_addr =

sys/dev/pci/drm/amd/display/dc/hwss/dcn201/dcn201_hwseq.c

79

plane_state->address.grph_stereo.left_meta_addr;

sys/dev/pci/drm/amd/display/dc/hwss/dcn30/dcn30_hwseq.c

1058

cmd.mall.cursor_copy_src.quad_part = cursor_attr.address.quad_part;

sys/dev/pci/drm/amd/display/dc/hwss/dcn30/dcn30_hwseq.c

1060

(plane->address.grph.cursor_cache_addr.quad_part + 2047) & ~2047;

sys/dev/pci/drm/amd/display/dc/hwss/dcn30/dcn30_hwseq.c

1068

cursor_attr.address.quad_part = cmd.mall.cursor_copy_dst.quad_part;

sys/dev/pci/drm/amd/display/dc/hwss/dcn30/dcn30_hwseq.c

952

plane->address.grph.cursor_cache_addr.quad_part;

sys/dev/pci/drm/amd/display/dc/hwss/dcn30/dcn30_hwseq.c

970

plane->address.page_table_base.quad_part == 0 &&

sys/dev/pci/drm/amd/display/dc/hwss/dcn32/dcn32_hwseq.c

302

if (plane->address.type == PLN_ADDR_TYPE_GRPH_STEREO ||

sys/dev/pci/drm/amd/display/dc/hwss/dcn32/dcn32_hwseq.c

303

plane->address.tmz_surface) {

sys/dev/pci/drm/amd/display/dc/hwss/dcn32/dcn32_hwseq.c

707

pipe->plane_state->address.type != PLN_ADDR_TYPE_GRPH_STEREO &&

sys/dev/pci/drm/amd/display/dc/hwss/dcn32/dcn32_hwseq.c

708

!pipe->plane_state->address.tmz_surface ? 2 : 0,

sys/dev/pci/drm/amd/display/dc/hwss/dcn401/dcn401_hwseq.c

1321

if (plane->address.type == PLN_ADDR_TYPE_GRPH_STEREO ||

sys/dev/pci/drm/amd/display/dc/hwss/dcn401/dcn401_hwseq.c

1322

plane->address.tmz_surface) {

sys/dev/pci/drm/amd/display/dc/inc/hw/aux_engine.h

45

uint32_t address;

sys/dev/pci/drm/amd/display/dc/inc/hw/hubp.h

109

struct dc_plane_address address;

sys/dev/pci/drm/amd/display/dc/inc/hw/hubp.h

191

const struct dc_plane_address *address,

sys/dev/pci/drm/amd/display/dc/inc/hw/hubp.h

296

const struct dc_plane_address address);

sys/dev/pci/drm/amd/display/dc/inc/hw/mem_input.h

147

const struct dc_plane_address *address,

sys/dev/pci/drm/amd/display/dc/inc/link_service.h

178

uint32_t address,

sys/dev/pci/drm/amd/display/dc/link/link_detection.c

286

uint32_t address,

sys/dev/pci/drm/amd/display/dc/link/link_detection.c

294

.address = address,

sys/dev/pci/drm/amd/display/dc/link/link_detection.c

299

.address = address,

sys/dev/pci/drm/amd/display/dc/link/link_dpms.c

323

uint8_t address, uint8_t *buffer, uint32_t length)

sys/dev/pci/drm/amd/display/dc/link/link_dpms.c

335

payload.address = address;

sys/dev/pci/drm/amd/display/dc/link/protocols/link_ddc.c

294

current_payload.address = payload->address;

sys/dev/pci/drm/amd/display/dc/link/protocols/link_ddc.c

315

uint32_t address,

sys/dev/pci/drm/amd/display/dc/link/protocols/link_ddc.c

341

payload.address = address;

sys/dev/pci/drm/amd/display/dc/link/protocols/link_ddc.c

382

&payloads, address, write_size, write_buf, true);

sys/dev/pci/drm/amd/display/dc/link/protocols/link_ddc.c

385

&payloads, address, read_size, read_buf, false);

sys/dev/pci/drm/amd/display/dc/link/protocols/link_ddc.c

464

.address = link_get_fixed_vs_pe_retimer_write_address(ddc->link),

sys/dev/pci/drm/amd/display/dc/link/protocols/link_ddc.c

482

.address = link_get_fixed_vs_pe_retimer_read_address(ddc->link),

sys/dev/pci/drm/amd/display/dc/link/protocols/link_ddc.c

88

uint32_t address,

sys/dev/pci/drm/amd/display/dc/link/protocols/link_ddc.c

99

.address = address,

sys/dev/pci/drm/amd/display/dc/link/protocols/link_ddc.h

58

uint32_t address,

sys/dev/pci/drm/amd/display/dc/link/protocols/link_dpcd.c

111

static uint32_t dpcd_get_next_partition_size(const uint32_t address, const uint32_t size)

sys/dev/pci/drm/amd/display/dc/link/protocols/link_dpcd.c

113

const uint32_t end_address = END_ADDRESS(address, size);

sys/dev/pci/drm/amd/display/dc/link/protocols/link_dpcd.c

121

address, end_address))

sys/dev/pci/drm/amd/display/dc/link/protocols/link_dpcd.c

125

return ADDRESS_RANGE_SIZE(address, mandatory_dpcd_partitions[partition_iterator].end);

sys/dev/pci/drm/amd/display/dc/link/protocols/link_dpcd.c

199

uint32_t address,

sys/dev/pci/drm/amd/display/dc/link/protocols/link_dpcd.c

214

dpcd_extend_address_range(address, data, size, &extended_address, &extended_data, &extended_size);

sys/dev/pci/drm/amd/display/dc/link/protocols/link_dpcd.c

226

dpcd_reduce_address_range(extended_address, extended_data, extended_size, address, data, size);

sys/dev/pci/drm/amd/display/dc/link/protocols/link_dpcd.c

232

uint32_t address,

sys/dev/pci/drm/amd/display/dc/link/protocols/link_dpcd.c

241

partition_size = dpcd_get_next_partition_size(address, size);

sys/dev/pci/drm/amd/display/dc/link/protocols/link_dpcd.c

242

status = internal_link_write_dpcd(link, address, &data[data_index], partition_size);

sys/dev/pci/drm/amd/display/dc/link/protocols/link_dpcd.c

245

address += partition_size;

sys/dev/pci/drm/amd/display/dc/link/protocols/link_dpcd.c

46

uint32_t address,

sys/dev/pci/drm/amd/display/dc/link/protocols/link_dpcd.c

52

link, address, data, size)) {

sys/dev/pci/drm/amd/display/dc/link/protocols/link_dpcd.c

61

uint32_t address,

sys/dev/pci/drm/amd/display/dc/link/protocols/link_dpcd.c

67

link, address, data, size)) {

sys/dev/pci/drm/amd/display/dc/link/protocols/link_dpcd.h

33

uint32_t address,

sys/dev/pci/drm/amd/display/dc/link/protocols/link_dpcd.h

39

uint32_t address,

sys/dev/pci/drm/amd/display/dc/resource/dcn32/dcn32_resource.c

1658

memcpy(&phantom_plane->address, &curr_pipe->plane_state->address, sizeof(phantom_plane->address));

sys/dev/pci/drm/amd/display/dmub/dmub_srv.h

390

uint32_t (*reg_read)(void *ctx, uint32_t address);

sys/dev/pci/drm/amd/display/dmub/dmub_srv.h

397

void (*reg_write)(void *ctx, uint32_t address, uint32_t value);

sys/dev/pci/drm/amd/display/dmub/inc/dmub_cmd.h

2809

uint32_t address; /**< DP AUX address */

sys/dev/pci/drm/amd/display/dmub/inc/dmub_cmd.h

5884

uint8_t address;

sys/dev/pci/drm/amd/display/dmub/inc/dmub_cmd.h

5891

uint32_t address : 20;

sys/dev/pci/drm/amd/display/modules/inc/mod_hdcp.h

137

uint8_t address;

sys/dev/pci/drm/amd/display/modules/inc/mod_hdcp.h

144

uint32_t address;

sys/dev/pci/drm/amd/display/modules/inc/mod_hdcp.h

153

uint32_t address,

sys/dev/pci/drm/amd/display/modules/inc/mod_hdcp.h

158

uint32_t address,

sys/dev/pci/drm/amd/display/modules/inc/mod_hdcp.h

162

uint32_t address,

sys/dev/pci/drm/amd/display/modules/inc/mod_hdcp.h

166

uint32_t address,

sys/dev/pci/drm/amd/pm/legacy-dpm/si_dpm.c

5815

u32 address = si_pi->state_table_start +

sys/dev/pci/drm/amd/pm/legacy-dpm/si_dpm.c

5826

return amdgpu_si_copy_bytes_to_smc(adev, address, (u8 *)smc_state,

sys/dev/pci/drm/amd/pm/legacy-dpm/si_dpm.c

5837

u32 address = si_pi->state_table_start +

sys/dev/pci/drm/amd/pm/legacy-dpm/si_dpm.c

5846

ret = amdgpu_si_copy_bytes_to_smc(adev, address, (u8 *)smc_state,

sys/dev/pci/drm/amd/pm/legacy-dpm/si_dpm.c

6025

u16 address;

sys/dev/pci/drm/amd/pm/legacy-dpm/si_dpm.c

6028

table->mc_reg_address[i].s0 = si_check_s0_mc_reg_index(table->mc_reg_address[i].s1, &address) ?

sys/dev/pci/drm/amd/pm/legacy-dpm/si_dpm.c

6029

address : table->mc_reg_address[i].s1;

sys/dev/pci/drm/amd/pm/legacy-dpm/si_dpm.c

6120

mc_reg_table->address[i].s0 =

sys/dev/pci/drm/amd/pm/legacy-dpm/si_dpm.c

6122

mc_reg_table->address[i].s1 =

sys/dev/pci/drm/amd/pm/legacy-dpm/si_dpm.c

6221

u32 address = si_pi->mc_reg_table_start +

sys/dev/pci/drm/amd/pm/legacy-dpm/si_dpm.c

6230

return amdgpu_si_copy_bytes_to_smc(adev, address,

sys/dev/pci/drm/amd/pm/legacy-dpm/si_dpm.h

293

SMC_Evergreen_MCRegisterAddress address[SMC_EVERGREEN_MC_REGISTER_ARRAY_SIZE];

sys/dev/pci/drm/amd/pm/legacy-dpm/si_dpm.h

323

SMC_NIslands_MCRegisterAddress address[SMC_NISLANDS_MC_REGISTER_ARRAY_SIZE];

sys/dev/pci/drm/amd/pm/legacy-dpm/sislands_smc.h

313

SMC_SIslands_MCRegisterAddress address[SMC_SISLANDS_MC_REGISTER_ARRAY_SIZE];

sys/dev/pci/drm/amd/pm/powerplay/inc/smu71_discrete.h

369

SMU71_Discrete_MCRegisterAddress address[SMU71_DISCRETE_MC_REGISTER_ARRAY_SIZE];

sys/dev/pci/drm/amd/pm/powerplay/inc/smu72_discrete.h

372

SMU72_Discrete_MCRegisterAddress address[SMU72_DISCRETE_MC_REGISTER_ARRAY_SIZE];

sys/dev/pci/drm/amd/pm/powerplay/inc/smu7_discrete.h

429

SMU7_Discrete_MCRegisterAddress address[SMU7_DISCRETE_MC_REGISTER_ARRAY_SIZE];

sys/dev/pci/drm/amd/pm/powerplay/smumgr/ci_smumgr.c

1742

mc_reg_table->address[i].s0 =

sys/dev/pci/drm/amd/pm/powerplay/smumgr/ci_smumgr.c

1744

mc_reg_table->address[i].s1 =

sys/dev/pci/drm/amd/pm/powerplay/smumgr/ci_smumgr.c

1822

uint32_t address;

sys/dev/pci/drm/amd/pm/powerplay/smumgr/ci_smumgr.c

1836

address = smu_data->mc_reg_table_start + (uint32_t)offsetof(SMU7_Discrete_MCRegisters, data[0]);

sys/dev/pci/drm/amd/pm/powerplay/smumgr/ci_smumgr.c

1838

return ci_copy_bytes_to_smc(hwmgr, address,

sys/dev/pci/drm/amd/pm/powerplay/smumgr/ci_smumgr.c

2552

uint16_t address;

sys/dev/pci/drm/amd/pm/powerplay/smumgr/ci_smumgr.c

2556

ci_check_s0_mc_reg_index(table->mc_reg_address[i].s1, &address)

sys/dev/pci/drm/amd/pm/powerplay/smumgr/ci_smumgr.c

2557

? address : table->mc_reg_address[i].s1;

sys/dev/pci/drm/amd/pm/powerplay/smumgr/iceland_smumgr.c

1699

mc_reg_table->address[i].s0 =

sys/dev/pci/drm/amd/pm/powerplay/smumgr/iceland_smumgr.c

1701

mc_reg_table->address[i].s1 =

sys/dev/pci/drm/amd/pm/powerplay/smumgr/iceland_smumgr.c

1779

uint32_t address;

sys/dev/pci/drm/amd/pm/powerplay/smumgr/iceland_smumgr.c

1794

address = smu_data->smu7_data.mc_reg_table_start + (uint32_t)offsetof(SMU71_Discrete_MCRegisters, data[0]);

sys/dev/pci/drm/amd/pm/powerplay/smumgr/iceland_smumgr.c

1796

return smu7_copy_bytes_to_smc(hwmgr, address,

sys/dev/pci/drm/amd/pm/powerplay/smumgr/iceland_smumgr.c

2471

uint16_t address;

sys/dev/pci/drm/amd/pm/powerplay/smumgr/iceland_smumgr.c

2475

iceland_check_s0_mc_reg_index(table->mc_reg_address[i].s1, &address)

sys/dev/pci/drm/amd/pm/powerplay/smumgr/iceland_smumgr.c

2476

? address : table->mc_reg_address[i].s1;

sys/dev/pci/drm/amd/pm/powerplay/smumgr/tonga_smumgr.c

2077

mc_reg_table->address[i].s0 =

sys/dev/pci/drm/amd/pm/powerplay/smumgr/tonga_smumgr.c

2079

mc_reg_table->address[i].s1 =

sys/dev/pci/drm/amd/pm/powerplay/smumgr/tonga_smumgr.c

2158

uint32_t address;

sys/dev/pci/drm/amd/pm/powerplay/smumgr/tonga_smumgr.c

2173

address = smu_data->smu7_data.mc_reg_table_start +

sys/dev/pci/drm/amd/pm/powerplay/smumgr/tonga_smumgr.c

2177

hwmgr, address,

sys/dev/pci/drm/amd/pm/powerplay/smumgr/tonga_smumgr.c

2933

uint16_t address;

sys/dev/pci/drm/amd/pm/powerplay/smumgr/tonga_smumgr.c

2938

&address) ?

sys/dev/pci/drm/amd/pm/powerplay/smumgr/tonga_smumgr.c

2939

address :

sys/dev/pci/drm/amd/pm/swsmu/smu11/smu_v11_0.c

631

uint64_t address;

sys/dev/pci/drm/amd/pm/swsmu/smu11/smu_v11_0.c

637

address = (uintptr_t)memory_pool->cpu_addr;

sys/dev/pci/drm/amd/pm/swsmu/smu11/smu_v11_0.c

638

address_high = (uint32_t)upper_32_bits(address);

sys/dev/pci/drm/amd/pm/swsmu/smu11/smu_v11_0.c

639

address_low = (uint32_t)lower_32_bits(address);

sys/dev/pci/drm/amd/pm/swsmu/smu11/smu_v11_0.c

654

address = memory_pool->mc_address;

sys/dev/pci/drm/amd/pm/swsmu/smu11/smu_v11_0.c

655

address_high = (uint32_t)upper_32_bits(address);

sys/dev/pci/drm/amd/pm/swsmu/smu11/smu_v11_0.c

656

address_low = (uint32_t)lower_32_bits(address);

sys/dev/pci/drm/amd/pm/swsmu/smu13/smu_v13_0.c

693

uint64_t address;

sys/dev/pci/drm/amd/pm/swsmu/smu13/smu_v13_0.c

699

address = memory_pool->mc_address;

sys/dev/pci/drm/amd/pm/swsmu/smu13/smu_v13_0.c

700

address_high = (uint32_t)upper_32_bits(address);

sys/dev/pci/drm/amd/pm/swsmu/smu13/smu_v13_0.c

701

address_low = (uint32_t)lower_32_bits(address);

sys/dev/pci/drm/amd/pm/swsmu/smu14/smu_v14_0.c

677

uint64_t address;

sys/dev/pci/drm/amd/pm/swsmu/smu14/smu_v14_0.c

683

address = memory_pool->mc_address;

sys/dev/pci/drm/amd/pm/swsmu/smu14/smu_v14_0.c

684

address_high = (uint32_t)upper_32_bits(address);

sys/dev/pci/drm/amd/pm/swsmu/smu14/smu_v14_0.c

685

address_low = (uint32_t)lower_32_bits(address);

sys/dev/pci/drm/display/drm_dp_helper.c

2156

msg.address = msgs[i].addr;

sys/dev/pci/drm/display/drm_dp_helper.c

2842

const u8 dpcd[DP_RECEIVER_CAP_SIZE], int address,

sys/dev/pci/drm/display/drm_dp_helper.c

2856

address + offset,

sys/dev/pci/drm/display/drm_dp_helper.c

589

msg.address = offset;

sys/dev/pci/drm/display/drm_dp_tunnel.c

224

int address = DP_TUNNELING_BASE + offset;

sys/dev/pci/drm/display/drm_dp_tunnel.c

226

if (drm_dp_dpcd_read_data(aux, address, tunnel_reg_ptr(regs, address), len) < 0)

sys/dev/pci/drm/display/drm_dp_tunnel.c

235

static u8 tunnel_reg(const struct drm_dp_tunnel_regs *regs, int address)

sys/dev/pci/drm/display/drm_dp_tunnel.c

237

return *tunnel_reg_ptr(regs, address);

sys/dev/pci/drm/drm_pagemap.c

789

vmf->page, vmf->address,

sys/dev/pci/drm/i915/display/intel_dp_aux.c

462

txbuf[0] = (msg->request << 4) | ((msg->address >> 16) & 0xf);

sys/dev/pci/drm/i915/display/intel_dp_aux.c

463

txbuf[1] = (msg->address >> 8) & 0xff;

sys/dev/pci/drm/i915/display/intel_dp_aux.c

464

txbuf[2] = msg->address & 0xff;

sys/dev/pci/drm/i915/display/intel_dp_aux.c

476

msg->address == DP_AUX_HDCP_AKSV)

sys/dev/pci/drm/i915/gem/i915_gem_mman.c

394

page_offset = (vmf->address - area->vm_start) >> PAGE_SHIFT;

sys/dev/pci/drm/i915/gt/intel_gpu_commands.h

457

static inline u64 gen8_canonical_addr(u64 address)

sys/dev/pci/drm/i915/gt/intel_gpu_commands.h

459

return sign_extend64(address, GEN8_HIGH_ADDRESS_BIT);

sys/dev/pci/drm/i915/gt/intel_gpu_commands.h

462

static inline u64 gen8_noncanonical_addr(u64 address)

sys/dev/pci/drm/i915/gt/intel_gpu_commands.h

464

return address & GENMASK_ULL(GEN8_HIGH_ADDRESS_BIT, 0);

sys/dev/pci/drm/i915/gt/intel_gtt.h

533

static inline u32 i915_pte_index(u64 address, unsigned int pde_shift)

sys/dev/pci/drm/i915/gt/intel_gtt.h

537

return (address >> PAGE_SHIFT) & mask;

sys/dev/pci/drm/i915/gt/selftest_timeline.c

37

unsigned long address = (unsigned long)page_address(hwsp_page(tl));

sys/dev/pci/drm/i915/gt/selftest_timeline.c

39

return (address + offset_in_page(tl->hwsp_offset)) / TIMELINE_SEQNO_BYTES;

sys/dev/pci/drm/i915/gt/uc/intel_guc_ads.c

501

ads.reg_state_list[guc_class][engine->instance].address,

sys/dev/pci/drm/i915/gt/uc/intel_guc_ads.c

510

ads.reg_state_list[guc_class][engine->instance].address,

sys/dev/pci/drm/i915/gt/uc/intel_guc_fwif.h

385

u32 address;

sys/dev/pci/drm/i915/gvt/trace.h

326

TP_PROTO(int id, unsigned int address, unsigned int data),

sys/dev/pci/drm/i915/gvt/trace.h

328

TP_ARGS(id, address, data),

sys/dev/pci/drm/i915/gvt/trace.h

332

__field(unsigned int, address)

sys/dev/pci/drm/i915/gvt/trace.h

338

__entry->address = address;

sys/dev/pci/drm/i915/gvt/trace.h

343

__entry->id, __entry->address, __entry->data)

sys/dev/pci/drm/include/drm/display/drm_dp_helper.h

320

unsigned int address;

sys/dev/pci/drm/include/uapi/drm/drm.h

381

void __user *address; /**< Address of buffer */

sys/dev/pci/drm/include/uapi/drm/radeon_drm.h

780

unsigned int address;

sys/dev/pci/drm/include/uapi/drm/radeon_drm.h

786

unsigned int address;

sys/dev/pci/drm/include/uapi/linux/kfd_ioctl.h

1348

__u64 address;

sys/dev/pci/drm/radeon/atombios_dp.c

171

tx_buf[0] = msg->address & 0xff;

sys/dev/pci/drm/radeon/atombios_dp.c

172

tx_buf[1] = (msg->address >> 8) & 0xff;

sys/dev/pci/drm/radeon/atombios_dp.c

174

((msg->address >> 16) & 0xf);

sys/dev/pci/drm/radeon/btc_dpm.c

1951

u16 address;

sys/dev/pci/drm/radeon/btc_dpm.c

1955

btc_check_s0_mc_reg_index(table->mc_reg_address[i].s1, &address) ?

sys/dev/pci/drm/radeon/btc_dpm.c

1956

address : table->mc_reg_address[i].s1;

sys/dev/pci/drm/radeon/ci_dpm.c

4450

u16 address;

sys/dev/pci/drm/radeon/ci_dpm.c

4454

ci_check_s0_mc_reg_index(table->mc_reg_address[i].s1, &address) ?

sys/dev/pci/drm/radeon/ci_dpm.c

4455

address : table->mc_reg_address[i].s1;

sys/dev/pci/drm/radeon/ci_dpm.c

4646

mc_reg_table->address[i].s0 = cpu_to_be16(pi->mc_reg_table.mc_reg_address[j].s0);

sys/dev/pci/drm/radeon/ci_dpm.c

4647

mc_reg_table->address[i].s1 = cpu_to_be16(pi->mc_reg_table.mc_reg_address[j].s1);

sys/dev/pci/drm/radeon/cypress_dpm.c

873

u16 address = pi->state_table_start +

sys/dev/pci/drm/radeon/cypress_dpm.c

882

return rv770_copy_bytes_to_smc(rdev, address, (u8 *)&state,

sys/dev/pci/drm/radeon/cypress_dpm.c

893

u16 address;

sys/dev/pci/drm/radeon/cypress_dpm.c

897

address = eg_pi->mc_reg_table_start +

sys/dev/pci/drm/radeon/cypress_dpm.c

900

return rv770_copy_bytes_to_smc(rdev, address,

sys/dev/pci/drm/radeon/cypress_dpm.c

958

mc_reg_table->address[i].s0 =

sys/dev/pci/drm/radeon/cypress_dpm.c

960

mc_reg_table->address[i].s1 =

sys/dev/pci/drm/radeon/evergreen_smc.h

49

SMC_Evergreen_MCRegisterAddress address[SMC_EVERGREEN_MC_REGISTER_ARRAY_SIZE];

sys/dev/pci/drm/radeon/ni_dpm.c

2691

u16 address = pi->state_table_start +

sys/dev/pci/drm/radeon/ni_dpm.c

2706

ret = rv770_copy_bytes_to_smc(rdev, address, (u8 *)smc_state, state_size, pi->sram_end);

sys/dev/pci/drm/radeon/ni_dpm.c

2840

u16 address;

sys/dev/pci/drm/radeon/ni_dpm.c

2844

ni_check_s0_mc_reg_index(table->mc_reg_address[i].s1, &address) ?

sys/dev/pci/drm/radeon/ni_dpm.c

2845

address : table->mc_reg_address[i].s1;

sys/dev/pci/drm/radeon/ni_dpm.c

2935

mc_reg_table->address[i].s0 =

sys/dev/pci/drm/radeon/ni_dpm.c

2937

mc_reg_table->address[i].s1 =

sys/dev/pci/drm/radeon/ni_dpm.c

3034

u16 address;

sys/dev/pci/drm/radeon/ni_dpm.c

3040

address = eg_pi->mc_reg_table_start +

sys/dev/pci/drm/radeon/ni_dpm.c

3043

return rv770_copy_bytes_to_smc(rdev, address,

sys/dev/pci/drm/radeon/nislands_smc.h

266

SMC_NIslands_MCRegisterAddress address[SMC_NISLANDS_MC_REGISTER_ARRAY_SIZE];

sys/dev/pci/drm/radeon/radeon_bios.c

152

pcireg_t address, mask;

sys/dev/pci/drm/radeon/radeon_bios.c

159

address = pci_conf_read(rdev->pc, rdev->pa_tag, PCI_ROM_REG);

sys/dev/pci/drm/radeon/radeon_bios.c

162

address |= PCI_ROM_ENABLE;

sys/dev/pci/drm/radeon/radeon_bios.c

163

pci_conf_write(rdev->pc, rdev->pa_tag, PCI_ROM_REG, address);

sys/dev/pci/drm/radeon/radeon_bios.c

168

rc = bus_space_map(rdev->memt, PCI_ROM_ADDR(address), size, 0, &romh);

sys/dev/pci/drm/radeon/radeon_dp_auxch.c

120

byte = (msg->request << 4) | ((msg->address >> 16) & 0xf);

sys/dev/pci/drm/radeon/radeon_dp_auxch.c

124

byte = (msg->address >> 8) & 0xff;

sys/dev/pci/drm/radeon/radeon_dp_auxch.c

128

byte = msg->address & 0xff;

sys/dev/pci/drm/radeon/rv770_dpm.c

1387

u16 address = pi->state_table_start +

sys/dev/pci/drm/radeon/rv770_dpm.c

1396

return rv770_copy_bytes_to_smc(rdev, address, (const u8 *)&state,

sys/dev/pci/drm/radeon/si_dpm.c

5219

u32 address = si_pi->state_table_start +

sys/dev/pci/drm/radeon/si_dpm.c

5231

ret = si_copy_bytes_to_smc(rdev, address, (u8 *)smc_state,

sys/dev/pci/drm/radeon/si_dpm.c

5244

u32 address = si_pi->state_table_start +

sys/dev/pci/drm/radeon/si_dpm.c

5253

ret = si_copy_bytes_to_smc(rdev, address, (u8 *)smc_state,

sys/dev/pci/drm/radeon/si_dpm.c

5441

u16 address;

sys/dev/pci/drm/radeon/si_dpm.c

5444

table->mc_reg_address[i].s0 = si_check_s0_mc_reg_index(table->mc_reg_address[i].s1, &address) ?

sys/dev/pci/drm/radeon/si_dpm.c

5445

address : table->mc_reg_address[i].s1;

sys/dev/pci/drm/radeon/si_dpm.c

5536

mc_reg_table->address[i].s0 =

sys/dev/pci/drm/radeon/si_dpm.c

5538

mc_reg_table->address[i].s1 =

sys/dev/pci/drm/radeon/si_dpm.c

5637

u32 address = si_pi->mc_reg_table_start +

sys/dev/pci/drm/radeon/si_dpm.c

5647

return si_copy_bytes_to_smc(rdev, address,

sys/dev/pci/drm/radeon/sislands_smc.h

317

SMC_SIslands_MCRegisterAddress address[SMC_SISLANDS_MC_REGISTER_ARRAY_SIZE];

sys/dev/pci/drm/radeon/smu7_discrete.h

412

SMU7_Discrete_MCRegisterAddress address[SMU7_DISCRETE_MC_REGISTER_ARRAY_SIZE];

sys/dev/pci/drm/ttm/ttm_bo_vm.c

200

unsigned long address = vmf->address;

sys/dev/pci/drm/ttm/ttm_bo_vm.c

214

page_offset = ((address - vma->vm_start) >> PAGE_SHIFT) +

sys/dev/pci/drm/ttm/ttm_bo_vm.c

269

ret = vmf_insert_pfn_prot(vma, address, pfn, prot);

sys/dev/pci/drm/ttm/ttm_bo_vm.c

279

address += PAGE_SIZE;

sys/dev/pci/drm/ttm/ttm_bo_vm.c

300

unsigned long address;

sys/dev/pci/drm/ttm/ttm_bo_vm.c

316

for (address = vma->vm_start; address < vma->vm_end;

sys/dev/pci/drm/ttm/ttm_bo_vm.c

317

address += PAGE_SIZE)

sys/dev/pci/drm/ttm/ttm_bo_vm.c

318

ret = vmf_insert_pfn_prot(vma, address, pfn, prot);

sys/dev/pci/drm/ttm/ttm_bo_vm.c

500

unsigned long address = (unsigned long)vaddr;

sys/dev/pci/drm/ttm/ttm_bo_vm.c

515

page_offset = ((address - ufi->entry->start) >> PAGE_SHIFT) +

sys/dev/pci/drm/ttm/ttm_bo_vm.c

569

err = pmap_enter(ufi->orig_map->pmap, address,

sys/dev/pci/drm/ttm/ttm_bo_vm.c

581

address += PAGE_SIZE;

sys/dev/pci/if_bnxtreg.h

66327

uint32_t address;

sys/dev/pci/if_bwfm_pci.c

619

uint64_t address;

sys/dev/pci/if_bwfm_pci.c

635

address = BWFM_PCI_DMA_DVA(sc->sc_dma_idx_buf);

sys/dev/pci/if_bwfm_pci.c

637

htole32(address & 0xffffffff);

sys/dev/pci/if_bwfm_pci.c

639

htole32(address >> 32);

sys/dev/pci/if_bwfm_pci.c

643

address += sc->sc_max_submissionrings * idx_offset;

sys/dev/pci/if_bwfm_pci.c

645

htole32(address & 0xffffffff);

sys/dev/pci/if_bwfm_pci.c

647

htole32(address >> 32);

sys/dev/pci/if_bwfm_pci.c

651

address += sc->sc_max_submissionrings * idx_offset;

sys/dev/pci/if_bwfm_pci.c

653

htole32(address & 0xffffffff);

sys/dev/pci/if_bwfm_pci.c

655

htole32(address >> 32);

sys/dev/pci/if_bwfm_pci.c

659

address += sc->sc_max_completionrings * idx_offset;

sys/dev/pci/if_bwfm_pci.c

661

htole32(address & 0xffffffff);

sys/dev/pci/if_bwfm_pci.c

663

htole32(address >> 32);

sys/dev/pci/if_cas.c

190

pcireg_t address;

sys/dev/pci/if_cas.c

198

address = pci_conf_read(pa->pa_pc, pa->pa_tag, PCI_ROM_REG);

sys/dev/pci/if_cas.c

199

address |= PCI_ROM_ENABLE;

sys/dev/pci/if_cas.c

200

pci_conf_write(pa->pa_pc, pa->pa_tag, PCI_ROM_REG, address);

sys/dev/pci/if_cas.c

288

address = pci_conf_read(pa->pa_pc, pa->pa_tag, PCI_ROM_REG);

sys/dev/pci/if_cas.c

289

address &= ~PCI_ROM_ENABLE;

sys/dev/pci/if_cas.c

290

pci_conf_write(pa->pa_pc, pa->pa_tag, PCI_ROM_REG, address);

sys/dev/pci/if_em.c

1275

desc_array.descriptor[j].address);

sys/dev/pci/if_em.c

308

u_int32_t em_fill_descriptors(u_int64_t address, u_int32_t length,

sys/dev/pci/if_em.c

3394

em_fill_descriptors(u_int64_t address, u_int32_t length,

sys/dev/pci/if_em.c

3401

desc_array->descriptor[0].address = address;

sys/dev/pci/if_em.c

3406

safe_terminator = (u_int32_t)((((u_int32_t)address & 0x7) + (length & 0xF)) & 0xF);

sys/dev/pci/if_em.c

3413

desc_array->descriptor[0].address = address;

sys/dev/pci/if_em.c

3419

desc_array->descriptor[0].address = address;

sys/dev/pci/if_em.c

3421

desc_array->descriptor[1].address = address + (length - 4);

sys/dev/pci/if_em.h

304

u_int64_t address;

sys/dev/pci/if_em_hw.c

11047

em_read_invm_word_i210(struct em_hw *hw, uint16_t address, uint16_t *data)

sys/dev/pci/if_em_hw.c

11066

if (word_address == address) {

sys/dev/pci/if_gem_pci.c

130

pcireg_t address;

sys/dev/pci/if_gem_pci.c

138

address = pci_conf_read(pa->pa_pc, pa->pa_tag, PCI_ROM_REG);

sys/dev/pci/if_gem_pci.c

139

address |= PCI_ROM_ENABLE;

sys/dev/pci/if_gem_pci.c

140

pci_conf_write(pa->pa_pc, pa->pa_tag, PCI_ROM_REG, address);

sys/dev/pci/if_gem_pci.c

179

address = pci_conf_read(pa->pa_pc, pa->pa_tag, PCI_ROM_REG);

sys/dev/pci/if_gem_pci.c

180

address &= ~PCI_ROM_ENABLE;

sys/dev/pci/if_gem_pci.c

181

pci_conf_write(pa->pa_pc, pa->pa_tag, PCI_ROM_REG, address);

sys/dev/pci/if_nep.c

675

pcireg_t address;

sys/dev/pci/if_nep.c

684

address = pci_conf_read(pa->pa_pc, pa->pa_tag, PCI_ROM_REG);

sys/dev/pci/if_nep.c

685

address |= PCI_ROM_ENABLE;

sys/dev/pci/if_nep.c

686

pci_conf_write(pa->pa_pc, pa->pa_tag, PCI_ROM_REG, address);

sys/dev/pci/if_nep.c

783

address = pci_conf_read(pa->pa_pc, pa->pa_tag, PCI_ROM_REG);

sys/dev/pci/if_nep.c

784

address &= ~PCI_ROM_ENABLE;

sys/dev/pci/if_nep.c

785

pci_conf_write(pa->pa_pc, pa->pa_tag, PCI_ROM_REG, address);

sys/dev/pci/if_ngbe.c

2520

buffer.address = 0;

sys/dev/pci/if_ngbe.c

3349

buffer.address = 0;

sys/dev/pci/if_ngbereg.h

713

uint32_t address;

sys/dev/pci/igc_i225.c

726

uint32_t address)

sys/dev/pci/igc_i225.c

750

flswctl = address | opcode;

sys/dev/pci/igc_phy.c

862

__igc_access_xmdio_reg(struct igc_hw *hw, uint16_t address, uint8_t dev_addr,

sys/dev/pci/igc_phy.c

873

ret_val = hw->phy.ops.write_reg(hw, IGC_MMDAAD, address);

sys/dev/pci/ixgbe_type.h

3212

uint32_t address;

sys/dev/pci/ixgbe_type.h

3221

uint32_t address;

sys/dev/pci/ixgbe_type.h

3246

__be16 address;

sys/dev/pci/ixgbe_x550.c

1272

write_cmd.address = htobe16(reg_addr);

sys/dev/pci/ixgbe_x550.c

1304

hic.cmd.address = htobe16(reg_addr);

sys/dev/pci/ixgbe_x550.c

2948

buffer.address = htobe32(offset * 2);

sys/dev/pci/ixgbe_x550.c

3010

buffer.address = htobe32((offset + current_word) * 2);

sys/dev/pci/ixgbe_x550.c

3069

buffer.address = htobe32(offset * 2);

sys/dev/pci/mpii.c

2241

u_int32_t address, int flags, void *p)

sys/dev/pci/mpii.c

2253

address, flags, MPII_PG_FMT);

sys/dev/pci/mpii.c

2277

htolem32(&cq->page_address, address);

sys/dev/pci/mpii.c

2336

mpii_req_cfg_page(struct mpii_softc *sc, u_int32_t address, int flags,

sys/dev/pci/mpii.c

2349

"type: %x\n", DEVNAME(sc), address, read, hdr->page_type);

sys/dev/pci/mpii.c

2381

htolem32(&cq->page_address, address);

sys/dev/pci/mpii.c

908

uint32_t address;

sys/dev/pci/mpii.c

929

address = MPII_CFG_RAID_VOL_ADDR_HANDLE | dev->dev_handle;

sys/dev/pci/mpii.c

932

1, address, MPII_PG_POLL, &hdr) != 0)

sys/dev/pci/mpii.c

939

if (mpii_req_cfg_page(sc, address, MPII_PG_POLL, &hdr, 1,

sys/dev/pci/mpii.c

962

address = MPII_PGAD_SAS_DEVICE_FORM_HANDLE | (uint32_t)dev->dev_handle;

sys/dev/pci/mpii.c

963

if (mpii_req_cfg_page(sc, address, MPII_PG_EXTENDED,

sys/dev/pci/pci.c

524

pcireg_t address, csr;

sys/dev/pci/pci.c

558

address = pci_conf_read(pc, tag, reg);

sys/dev/pci/pci.c

561

pci_conf_write(pc, tag, reg, address);

sys/dev/pci/pci_map.c

101

pci_conf_write(pc, tag, reg, address);

sys/dev/pci/pci_map.c

106

if (PCI_MAPREG_TYPE(address) != PCI_MAPREG_TYPE_IO) {

sys/dev/pci/pci_map.c

121

*basep = PCI_MAPREG_IO_ADDR(address);

sys/dev/pci/pci_map.c

134

pcireg_t address, mask, address1 = 0, mask1 = 0xffffffff, csr;

sys/dev/pci/pci_map.c

169

address = pci_conf_read(pc, tag, reg);

sys/dev/pci/pci_map.c

172

pci_conf_write(pc, tag, reg, address);

sys/dev/pci/pci_map.c

183

if (PCI_MAPREG_TYPE(address) != PCI_MAPREG_TYPE_MEM) {

sys/dev/pci/pci_map.c

190

PCI_MAPREG_MEM_TYPE(address) != PCI_MAPREG_MEM_TYPE(type)) {

sys/dev/pci/pci_map.c

194

PCI_MAPREG_MEM_TYPE(address));

sys/dev/pci/pci_map.c

199

waddress = (u_int64_t)address1 << 32UL | address;

sys/dev/pci/pci_map.c

210

switch (PCI_MAPREG_MEM_TYPE(address)) {

sys/dev/pci/pci_map.c

240

*basep = PCI_MAPREG_MEM_ADDR(address);

sys/dev/pci/pci_map.c

251

PCI_MAPREG_MEM_PREFETCHABLE(address) ?

sys/dev/pci/pci_map.c

266

pcireg_t address, mask, csr;

sys/dev/pci/pci_map.c

274

address = pci_conf_read(pc, tag, reg);

sys/dev/pci/pci_map.c

277

pci_conf_write(pc, tag, reg, address);

sys/dev/pci/pci_map.c

286

*typep = _PCI_MAPREG_TYPEBITS(address);

sys/dev/pci/pci_map.c

69

pcireg_t address, mask, csr;

sys/dev/pci/pci_map.c

98

address = pci_conf_read(pc, tag, reg);

sys/dev/pci/sti_pci.c

123

pcireg_t address;

sys/dev/pci/sti_pci.c

126

address = pci_conf_read(spc->sc_pc, spc->sc_tag, PCI_ROM_REG);

sys/dev/pci/sti_pci.c

127

address |= PCI_ROM_ENABLE;

sys/dev/pci/sti_pci.c

128

pci_conf_write(spc->sc_pc, spc->sc_tag, PCI_ROM_REG, address);

sys/dev/pci/sti_pci.c

140

pcireg_t address;

sys/dev/pci/sti_pci.c

143

address = pci_conf_read(spc->sc_pc, spc->sc_tag, PCI_ROM_REG);

sys/dev/pci/sti_pci.c

144

address &= ~PCI_ROM_ENABLE;

sys/dev/pci/sti_pci.c

145

pci_conf_write(spc->sc_pc, spc->sc_tag, PCI_ROM_REG, address);

sys/dev/pci/sti_pci.c

229

pcireg_t address, mask;

sys/dev/pci/sti_pci.c

241

address = pci_conf_read(pa->pa_pc, pa->pa_tag, PCI_ROM_REG);

sys/dev/pci/sti_pci.c

244

address |= PCI_ROM_ENABLE;

sys/dev/pci/sti_pci.c

245

pci_conf_write(pa->pa_pc, pa->pa_tag, PCI_ROM_REG, address);

sys/dev/pci/sti_pci.c

253

rc = bus_space_map(pa->pa_memt, PCI_ROM_ADDR(address), romsize,

sys/dev/pci/sti_pci.c

355

rc = bus_space_map(pa->pa_memt, PCI_ROM_ADDR(address) + offs,

sys/dev/sdmmc/sdhc.c

1044

desc32[seg].address = htole32(paddr);

sys/dev/sdmmc/sdhcreg.h

261

uint32_t address;

sys/dev/usb/dwc2/dwc2.c

1028

uint8_t addr = dev->address;

sys/dev/usb/dwc2/dwc2.c

1061

UGETW(req->wIndex), UGETW(req->wLength), dev->address,

sys/dev/usb/dwc2/dwc2.c

211

dev->address = addr;

sys/dev/usb/dwc2/dwc2.c

364

uint8_t addr = dev->address;

sys/dev/usb/dwc2/dwc2_hcd.c

539

*hub_addr = dev->myhsport->parent->address;

sys/dev/usb/ehci.c

1360

u_int8_t addr = dev->address;

sys/dev/usb/ehci.c

1376

hshubaddr = dev->myhsport->parent->address;

sys/dev/usb/ehci.c

3480

EHCI_ITD_SET_DADDR(xfer->pipe->device->address)

sys/dev/usb/ehci.c

3516

EHCI_SITD_SET_ADDR(xfer->device->address) |

sys/dev/usb/ehci.c

3518

EHCI_SITD_SET_HUBA(hshub->address);

sys/dev/usb/ehci.c

624

dev->address = addr;

sys/dev/usb/ohci.c

1567

UGETW(req->wIndex), len, xfer->device->address,

sys/dev/usb/ohci.c

1903

pipe, pipe->device->address, ed->bEndpointAddress));

sys/dev/usb/ohci.c

1945

OHCI_ED_SET_FA(pipe->device->address) |

sys/dev/usb/ohci.c

2021

dev->address = addr;

sys/dev/usb/ohci.c

2755

OHCI_ED_SET_FA(xfer->device->address));

sys/dev/usb/uhci.c

1295

xfer->device->address,

sys/dev/usb/uhci.c

1530

int addr = xfer->device->address;

sys/dev/usb/uhci.c

1970

int addr = xfer->device->address;

sys/dev/usb/uhci.c

2330

int addr = pipe->device->address;

sys/dev/usb/uhci.c

2634

pipe, pipe->device->address, ed->bEndpointAddress));

sys/dev/usb/uhci.c

768

dev->address, pipe,

sys/dev/usb/usb.c

1021

uph->uph_devaddr = htole16(xfer->device->address);

sys/dev/usb/usb_subr.c

1074

dev->address = USB_START_ADDR;

sys/dev/usb/usb_subr.c

1201

dev->address = addr;

sys/dev/usb/usb_subr.c

1300

di->udi_addr = dev->address;

sys/dev/usb/usb_subr.c

1458

dev->bus->devices[dev->address] = NULL;

sys/dev/usb/usb_subr.c

320

snprintf(cp, base + len - cp, " addr %d", dev->address);

sys/dev/usb/usb_subr.c

727

__func__, dev->address, cdp->bConfigurationValue, cdp->bmAttributes,

sys/dev/usb/usb_subr.c

745

dev->bus->bdev.dv_xname, dev->address,

sys/dev/usb/usbdi.c

1033

usbd_get_endpoint_descriptor(struct usbd_interface *iface, u_int8_t address)

sys/dev/usb/usbdi.c

1040

if (ep->edesc->bEndpointAddress == address)

sys/dev/usb/usbdi.c

131

"power=%d langid=%d\n", dev->address, dev->config, dev->depth,

sys/dev/usb/usbdi.c

175

usbd_open_pipe(struct usbd_interface *iface, u_int8_t address, u_int8_t flags,

sys/dev/usb/usbdi.c

178

return (usbd_open_pipe_ival(iface, address, flags, pipe,

sys/dev/usb/usbdi.c

183

usbd_open_pipe_ival(struct usbd_interface *iface, u_int8_t address,

sys/dev/usb/usbdi.c

192

iface, address, flags));

sys/dev/usb/usbdi.c

198

if (ep->edesc->bEndpointAddress == address)

sys/dev/usb/usbdi.c

214

usbd_open_pipe_intr(struct usbd_interface *iface, u_int8_t address,

sys/dev/usb/usbdi.c

223

address, flags, len));

sys/dev/usb/usbdi.c

225

err = usbd_open_pipe_ival(iface, address, USBD_EXCLUSIVE_USE, &ipipe,

sys/dev/usb/usbdi.h

107

struct usbd_interface *iface, u_int8_t address);

sys/dev/usb/usbdi.h

117

usbd_status usbd_open_pipe_intr(struct usbd_interface *iface, u_int8_t address,

sys/dev/usb/usbdi.h

151

struct usbd_interface *iface, u_int8_t address);

sys/dev/usb/usbdi.h

89

usbd_status usbd_open_pipe(struct usbd_interface *iface, u_int8_t address,

sys/dev/usb/usbdivar.h

147

u_int8_t address; /* device address */

sys/dev/usb/xhci.c

1616

" (epAddr=0x%x)\n", __func__, pipe, dev->address, dev->depth,

sys/lib/libz/zlib.h

86

typedef void (*free_func)(voidpf opaque, voidpf address, uInt size);

sys/net/if_ppp.c

653

int protocol, address, control;

sys/net/if_ppp.c

679

address = PPP_ALLSTATIONS;

sys/net/if_ppp.c

686

address = PPP_ALLSTATIONS;

sys/net/if_ppp.c

693

address = PPP_ADDRESS(dst->sa_data);

sys/net/if_ppp.c

727

*cp++ = address;

sys/net/if_ppp.c

763

*mtod(m0, u_char *) = address;

sys/net/if_ppp.c

874

int address, control, protocol;

sys/net/if_ppp.c

891

address = PPP_ADDRESS(cp);

sys/net/if_ppp.c

927

cp[0] = address; /* header has moved */

sys/net/if_ppp.c

979

if (sc->sc_flags & SC_COMP_AC && address == PPP_ALLSTATIONS &&

sys/net/if_spppsubr.c

174

u_char address;

sys/net/if_spppsubr.c

482

ht.address = PPP_ALLSTATIONS;

sys/net/if_spppsubr.c

497

switch (ht.address) {

sys/net/if_spppsubr.c

511

ht.address, ht.control, ntohs(ht.protocol));

sys/net/if_spppsubr.c

567

ht.address, ht.control, ntohs(ht.protocol));

sys/scsi/cd.h

259

u_int8_t address[4];

sys/scsi/scsi_base.c

2818

scsi_show_mem(u_char *address, int num)

sys/scsi/scsi_base.c

2826

printf("%02x ", *address++);

sys/uvm/uvm_map.c

1566

uvm_map_lookup_entry(struct vm_map *map, vaddr_t address,

sys/uvm/uvm_map.c

1571

*entry = uvm_map_entrybyaddr(&map->addr, address);

sys/uvm/uvm_map.c

1573

(*entry)->start <= address && (*entry)->end > address;

usr.bin/dig/dighost.c

3102

dighost_received(sevent->n, &sevent->address, query);

usr.bin/dig/dighost.c

3283

!isc_sockaddr_compare(&sevent->address, &query->sockaddr,

usr.bin/dig/dighost.c

3305

isc_sockaddr_getport(&sevent->address)) {

usr.bin/dig/dighost.c

3306

isc_sockaddr_format(&sevent->address, buf1,

usr.bin/dig/dighost.c

3582

dighost_received(b->used, &sevent->address, query);

usr.bin/dig/dighost.c

3647

dighost_received(b->used, &sevent->address, query);

usr.bin/dig/dighost.c

466

inet_ntop(af, confdata->nameservers[i].address,

usr.bin/dig/dighost.c

606

if (inet_pton(af, addr, &confdata->nameservers[i].address) == 1) {

usr.bin/dig/lib/isc/include/isc/socket.h

109

struct sockaddr_storage address; /*%< source address */

usr.bin/dig/lib/isc/include/isc/socket.h

452

struct sockaddr_storage *address, struct in6_pktinfo *pktinfo,

usr.bin/dig/lib/isc/include/isc/socket.h

96

struct sockaddr_storage address; /*%< source address */

usr.bin/dig/lib/isc/unix/socket.c

1060

isc_sockaddr_format(&dev->address, addrbuf, sizeof(addrbuf));

usr.bin/dig/lib/isc/unix/socket.c

2045

struct sockaddr_storage *address, struct in6_pktinfo *pktinfo,

usr.bin/dig/lib/isc/unix/socket.c

2054

set_dev_address(address, sock, dev);

usr.bin/dig/lib/isc/unix/socket.c

2059

if (!isc_sockaddr_issitelocal(&dev->address) &&

usr.bin/dig/lib/isc/unix/socket.c

2060

!isc_sockaddr_islinklocal(&dev->address)) {

usr.bin/dig/lib/isc/unix/socket.c

2135

struct sockaddr_storage *address, struct in6_pktinfo *pktinfo,

usr.bin/dig/lib/isc/unix/socket.c

2166

return (socket_send(sock, dev, task, address, pktinfo, flags));

usr.bin/dig/lib/isc/unix/socket.c

242

socket_log(isc_socket_t *sock, struct sockaddr_storage *address,

usr.bin/dig/lib/isc/unix/socket.c

246

socket_log(isc_socket_t *sock, struct sockaddr_storage *address,

usr.bin/dig/lib/isc/unix/socket.c

261

if (address == NULL) {

usr.bin/dig/lib/isc/unix/socket.c

265

isc_sockaddr_format(address, peerbuf, sizeof(peerbuf));

usr.bin/dig/lib/isc/unix/socket.c

508

msg->msg_name = (void *)&dev->address;

usr.bin/dig/lib/isc/unix/socket.c

509

msg->msg_namelen = dev->address.ss_len;

usr.bin/dig/lib/isc/unix/socket.c

705

memset(&dev->address, 0, sizeof(dev->address));

usr.bin/dig/lib/isc/unix/socket.c

706

msg->msg_name = (void *)&dev->address;

usr.bin/dig/lib/isc/unix/socket.c

707

msg->msg_namelen = sizeof(dev->address);

usr.bin/dig/lib/isc/unix/socket.c

711

dev->address = sock->peer_address;

usr.bin/dig/lib/isc/unix/socket.c

771

set_dev_address(struct sockaddr_storage *address, isc_socket_t *sock,

usr.bin/dig/lib/isc/unix/socket.c

775

if (address != NULL)

usr.bin/dig/lib/isc/unix/socket.c

776

dev->address = *address;

usr.bin/dig/lib/isc/unix/socket.c

778

dev->address = sock->peer_address;

usr.bin/dig/lib/isc/unix/socket.c

780

INSIST(address == NULL);

usr.bin/dig/lib/isc/unix/socket.c

781

dev->address = sock->peer_address;

usr.bin/dig/lib/isc/unix/socket.c

913

dev->address.ss_len = msghdr.msg_namelen;

usr.bin/dig/lib/isc/unix/socket.c

914

if (isc_sockaddr_getport(&dev->address) == 0) {

usr.bin/dig/lib/isc/unix/socket.c

916

socket_log(sock, &dev->address, IOEVENT,

usr.bin/dig/lib/isc/unix/socket.c

923

socket_log(sock, &dev->address, IOEVENT,

usr.bin/dig/lib/lwres/include/lwres/lwres.h

95

unsigned char address[sizeof(struct in6_addr)];

usr.bin/dig/lib/lwres/lwconfig.c

195

lwres_addr_t address;

usr.bin/dig/lib/lwres/lwconfig.c

209

res = lwres_create_addr(word, &address, 1);

usr.bin/dig/lib/lwres/lwconfig.c

213

((address.family == LWRES_ADDRTYPE_V4 && use_ipv4) ||

usr.bin/dig/lib/lwres/lwconfig.c

214

(address.family == LWRES_ADDRTYPE_V6 && use_ipv6))) {

usr.bin/dig/lib/lwres/lwconfig.c

215

confdata->nameservers[confdata->nsnext++] = address;

usr.bin/dig/lib/lwres/lwconfig.c

323

memcpy(addr->address, &v4, sizeof(v4));

usr.bin/dig/lib/lwres/lwconfig.c

328

memcpy(addr->address, &v6, sizeof(v6));

usr.bin/gprof/lookup.c

41

nllookup(unsigned long address)

usr.bin/gprof/lookup.c

56

if ( nl[ middle ].value <= address && nl[ middle+1 ].value > address ) {

usr.bin/gprof/lookup.c

64

if ( nl[ middle ].value > address ) {

usr.bin/hexdump/display.c

126

(void)printf(pr->fmt, (int64_t)address);

usr.bin/hexdump/display.c

239

address += blocksize;

usr.bin/hexdump/display.c

257

eaddress = address + nread;

usr.bin/hexdump/display.c

281

address += blocksize;

usr.bin/hexdump/display.c

337

address += sb.st_size;

usr.bin/hexdump/display.c

342

address += skip;

usr.bin/hexdump/display.c

352

address += cnt;

usr.bin/hexdump/display.c

49

static off_t address; /* address/offset in stream */

usr.bin/hexdump/display.c

70

for (fs = fshead, savebp = bp, saveaddress = address; fs;

usr.bin/hexdump/display.c

71

fs = fs->nextfs, bp = savebp, address = saveaddress)

usr.bin/hexdump/display.c

76

for (pr = fu->nextpr; pr; address += pr->bcnt,

usr.bin/hexdump/display.c

78

if (eaddress && address >= eaddress &&

usr.bin/hexdump/display.c

96

if (!address)

usr.bin/hexdump/display.c

98

eaddress = address;

usr.bin/rsync/extern.h

160

char *address; /* --address */

usr.bin/rsync/main.c

440

opts.address = optarg;

usr.bin/rsync/socket.c

311

if (opts->address != NULL)

usr.bin/rsync/socket.c

312

if ((bsrc = inet_resolve(&sess, opts->address, &bsrcsz, 1)) ==

usr.bin/ssh/dns.c

187

verify_host_key_dns(const char *hostname, struct sockaddr *address,

usr.bin/ssh/monitor_wrap.c

985

ci.address = ssh_remote_ipaddr(ssh);

usr.bin/ssh/servconf.c

2609

ci->address = xstrdup(val);

usr.bin/ssh/servconf.c

807

ci->address ? ci->address : "(null)",

usr.bin/ssh/servconf.c

909

if (ci == NULL || (ci->test && ci->address == NULL)) {

usr.bin/ssh/servconf.c

916

if (ci->address == NULL)

usr.bin/ssh/servconf.c

918

switch (addr_match_list(ci->address, arg)) {

usr.bin/ssh/servconf.c

921

"%.100s' at line %d", ci->address, arg, line);

usr.bin/ssh/servconf.h

388

const char *address; /* remote address */

usr.sbin/acpidump/acpidump.c

95

u_int64_t address;

usr.sbin/bgpd/parse.y

1527

address : STRING {

usr.sbin/bgpd/parse.y

1586

addrspec : address {

usr.sbin/bgpd/parse.y

1868

| LOCALADDR address {

usr.sbin/bgpd/parse.y

2198

| REFLECTOR address {

usr.sbin/bgpd/parse.y

2546

| address {

usr.sbin/bgpd/parse.y

279

%type <v.addr> address

usr.sbin/bgpd/parse.y

2946

| NEXTHOP address {

usr.sbin/bgpd/parse.y

3313

| NEXTHOP address {

usr.sbin/bgpd/parse.y

679

rtr : RTR address {

usr.sbin/bgpd/parse.y

689

| RTR address {

usr.sbin/bgpd/parse.y

717

| LOCALADDR address {

usr.sbin/bgpd/parse.y

753

| ROUTERID address {

usr.sbin/bgpd/parse.y

784

| LISTEN ON address {

usr.sbin/bgpd/parse.y

798

| LISTEN ON address PORT port {

usr.sbin/dvmrpd/dvmrpd.h

169

struct in_addr address;

usr.sbin/dvmrpd/neighbor.c

362

nm.address.s_addr = nbr->addr.s_addr;

usr.sbin/dvmrpd/rde.c

316

srt_expire_nbr(nm.address, nm.ifindex);

usr.sbin/httpd/httpd.h

154

TAILQ_ENTRY(address) entry;

usr.sbin/httpd/httpd.h

156

TAILQ_HEAD(addresslist, address);

usr.sbin/httpd/parse.y

111

struct address *host_v4(const char *);

usr.sbin/httpd/parse.y

112

struct address *host_v6(const char *);

usr.sbin/httpd/parse.y

2217

struct address *

usr.sbin/httpd/parse.y

2222

struct address *h;

usr.sbin/httpd/parse.y

2241

struct address *

usr.sbin/httpd/parse.y

2246

struct address *h = NULL;

usr.sbin/httpd/parse.y

2282

struct address *h;

usr.sbin/httpd/parse.y

2353

struct address *h;

usr.sbin/httpd/parse.y

2423

struct address *h;

usr.sbin/httpd/parse.y

2619

struct address *h;

usr.sbin/npppctl/npppctl.c

391

switch (result->address.ss_family) {

usr.sbin/npppctl/npppctl.c

393

if (((struct sockaddr_in *)&result->address)->sin_addr.

usr.sbin/npppctl/parser.c

227

memcpy(&res.address, &sin4, sin4.sin_len);

usr.sbin/npppctl/parser.c

230

memcpy(&res.address, &sin6, sin6.sin6_len);

usr.sbin/npppctl/parser.h

44

struct sockaddr_storage address;

usr.sbin/npppd/npppd/npppd.h

145

struct sockaddr_storage address;

usr.sbin/npppd/npppd/npppd_auth.c

557

memcpy(&rad->server[i].peer, &server->address,

usr.sbin/npppd/npppd/npppd_auth.c

558

server->address.ss_len);

usr.sbin/npppd/npppd/npppd_auth.c

578

memcpy(&rad->server[i].peer, &server->address,

usr.sbin/npppd/npppd/npppd_auth.c

579

server->address.ss_len);

usr.sbin/npppd/npppd/parse.y

142

%type <v.address> address

usr.sbin/npppd/npppd/parse.y

143

%type <v.address> addressport

usr.sbin/npppd/npppd/parse.y

530

| RADIUS DAE CLIENT address SECRET STRING {

usr.sbin/npppd/npppd/parse.y

604

address : STRING {

usr.sbin/npppd/npppd/parse.y

635

addressport : address optport {

usr.sbin/npppd/npppd/parse.y

788

radopt : ADDRESS address optport SECRET STRING {

usr.sbin/npppd/npppd/parse.y

812

n->address = $2;

usr.sbin/npppd/npppd/parse.y

813

((struct sockaddr_in *)&n->address)->sin_port =

usr.sbin/npppd/npppd/parse.y

96

struct sockaddr_storage address;

usr.sbin/nsd/axfr.c

199

char address[128], proxy[128];

usr.sbin/nsd/axfr.c

200

addr2str(&q->client_addr, address, sizeof(address));

usr.sbin/nsd/axfr.c

205

address));

usr.sbin/nsd/axfr.c

220

char address[128], proxy[128];

usr.sbin/nsd/axfr.c

221

addr2str(&q->client_addr, address, sizeof(address));

usr.sbin/nsd/axfr.c

226

address, proxy,

usr.sbin/nsd/configparser.y

1306

ip->address = region_strdup(cfg_parser->opt->region, $1);

usr.sbin/nsd/metrics.c

270

if(!metrics_add_open(metrics, cfg, p->address, cfg->metrics_port, 1)) {

usr.sbin/nsd/nsd-checkconf.c

104

quote(ip->address); \

usr.sbin/nsd/nsd-checkconf.c

692

printf("\tip-address: %s", ip->address);

usr.sbin/nsd/nsd-checkconf.c

746

print_string_var("metrics-interface:", ip->address);

usr.sbin/nsd/nsd-checkconf.c

772

print_string_var("control-interface:", ip->address);

usr.sbin/nsd/nsd-checkconf.c

782

print_string_var("ip-address:", ip->address);

usr.sbin/nsd/nsd-control.c

252

svr = cfg->control_interface->address;

usr.sbin/nsd/nsd.c

298

server->first, ip->address);

usr.sbin/nsd/nsd.c

303

server->first, ip->address);

usr.sbin/nsd/nsd.c

312

server->first, server->last, ip->address);

usr.sbin/nsd/nsd.c

317

server->first, server->last, ip->address);

usr.sbin/nsd/nsd.c

501

setup_socket(&(*udp)[i], ip->address, udp_port, &ai);

usr.sbin/nsd/nsd.c

504

setup_socket(&(*tcp)[i], ip->address, tcp_port, &ai);

usr.sbin/nsd/nsd.c

518

ip->address);

usr.sbin/nsd/nsd.c

940

ip->address = region_strdup(

usr.sbin/nsd/options.c

3025

if(!cfg->control_interface->address) return 1;

usr.sbin/nsd/options.c

3026

if(cfg->control_interface->address[0] == 0) return 1;

usr.sbin/nsd/options.c

3027

return (cfg->control_interface->address[0] != '/');

usr.sbin/nsd/options.c

3122

resolve_ifa_name(addrs, ip_addr->address, &ip_addresses,

usr.sbin/nsd/options.c

3132

current->address = region_strdup(region,

usr.sbin/nsd/options.h

271

char* address;

usr.sbin/nsd/query.c

1389

char address[128], proxy[128];

usr.sbin/nsd/query.c

1390

addr2str(&q->client_addr, address, sizeof(address));

usr.sbin/nsd/query.c

1394

address, proxy,

usr.sbin/nsd/query.c

1433

char address[128];

usr.sbin/nsd/query.c

1434

addr2str(&q->client_addr, address, sizeof(address));

usr.sbin/nsd/query.c

1437

address,

usr.sbin/nsd/query.c

480

char address[128], proxy[128];

usr.sbin/nsd/query.c

481

addr2str(&query->client_addr, address, sizeof(address));

usr.sbin/nsd/query.c

485

address, proxy,

usr.sbin/nsd/query.c

538

char address[128];

usr.sbin/nsd/query.c

539

addr2str(&query->client_addr, address, sizeof(address));

usr.sbin/nsd/query.c

542

dname_to_string(query->qname, NULL), address,

usr.sbin/nsd/query.c

546

dname_to_string(query->qname, NULL), address));

usr.sbin/nsd/query.c

565

char address[128];

usr.sbin/nsd/query.c

566

addr2str(&query->client_addr, address, sizeof(address));

usr.sbin/nsd/query.c

569

address,

usr.sbin/nsd/rdata.c

2594

uint8_t address[16];

usr.sbin/nsd/rdata.c

2619

memset(address, 0, sizeof(address));

usr.sbin/nsd/rdata.c

2620

if(length > sizeof(address))

usr.sbin/nsd/rdata.c

2622

memmove(address, rdata + *offset + 4, length);

usr.sbin/nsd/rdata.c

2624

if (!inet_ntop(af, address, text_address, sizeof(text_address)))

usr.sbin/nsd/remote.c

306

if(o->address && o->address[0] != '/')

usr.sbin/nsd/remote.c

307

log_msg(LOG_WARNING, "control-interface %s is not using TLS, but plain transfer, because first control-interface in config file is a local socket (starts with a /).", o->address);

usr.sbin/nsd/remote.c

535

if(!add_open(rc, cfg, p->address, cfg->control_port, 1)) {

usr.sbin/nsd/rrl.c

360

char address[128];

usr.sbin/nsd/rrl.c

362

addr2str(&query->client_addr, address, sizeof(address));

usr.sbin/nsd/rrl.c

371

address, rrtype_to_string(query->qtype));

usr.sbin/nsd/rrl.c

396

char address[128];

usr.sbin/nsd/rrl.c

397

addr2str(&query->client_addr, address, sizeof(address));

usr.sbin/nsd/rrl.c

401

address, rrtype_to_string(query->qtype),

usr.sbin/nsd/simdzone/src/haswell/simd.h

37

static really_inline void simd_loadu_8x(simd_8x_t *simd, const void *address)

usr.sbin/nsd/simdzone/src/haswell/simd.h

39

simd->chunks[0] = _mm256_loadu_si256((const __m256i *)(address));

usr.sbin/nsd/simdzone/src/haswell/simd.h

43

static really_inline void simd_storeu_8x(void *address, simd_8x_t *simd)

usr.sbin/nsd/simdzone/src/haswell/simd.h

45

_mm256_storeu_si256((__m256i *)address, simd->chunks[0]);

usr.sbin/nsd/simdzone/src/haswell/simd.h

67

static really_inline void simd_loadu_8x16(simd_8x16_t *simd, const uint8_t *address)

usr.sbin/nsd/simdzone/src/haswell/simd.h

69

simd->chunks[0] = _mm_loadu_si128((const __m128i *)address);

usr.sbin/nsd/simdzone/src/haswell/simd.h

81

#define simd_loadu_8x32(simd, address) simd_loadu_8x(simd, address)

usr.sbin/nsd/simdzone/src/haswell/simd.h

82

#define simd_storeu_8x32(address, simd) simd_storeu_8x(address, simd)

usr.sbin/nsd/simdzone/src/haswell/simd.h

86

static really_inline void simd_loadu_8x64(simd_8x64_t *simd, const uint8_t *address)

usr.sbin/nsd/simdzone/src/haswell/simd.h

88

simd->chunks[0] = _mm256_loadu_si256((const __m256i *)(address));

usr.sbin/nsd/simdzone/src/haswell/simd.h

89

simd->chunks[1] = _mm256_loadu_si256((const __m256i *)(address+32));

usr.sbin/nsd/simdzone/src/westmere/ip4.h

176

uint32_t address = (uint32_t)_mm_cvtsi128_si32(_mm_packus_epi16(acc, acc));

usr.sbin/nsd/simdzone/src/westmere/ip4.h

178

memcpy(destination, &address, 4);

usr.sbin/nsd/simdzone/src/westmere/simd.h

35

static really_inline void simd_loadu_8x(simd_8x_t *simd, const uint8_t *address)

usr.sbin/nsd/simdzone/src/westmere/simd.h

37

simd->chunks[0] = _mm_loadu_si128((const __m128i *)address);

usr.sbin/nsd/simdzone/src/westmere/simd.h

41

static really_inline void simd_storeu_8x(uint8_t *address, const simd_8x_t *simd)

usr.sbin/nsd/simdzone/src/westmere/simd.h

43

_mm_storeu_si128((__m128i *)address, simd->chunks[0]);

usr.sbin/nsd/simdzone/src/westmere/simd.h

64

#define simd_loadu_8x16(simd, address) simd_loadu_8x(simd, address)

usr.sbin/nsd/simdzone/src/westmere/simd.h

68

static really_inline void simd_loadu_8x32(simd_8x32_t *simd, const char *address)

usr.sbin/nsd/simdzone/src/westmere/simd.h

70

simd->chunks[0] = _mm_loadu_si128((const __m128i *)(address));

usr.sbin/nsd/simdzone/src/westmere/simd.h

71

simd->chunks[1] = _mm_loadu_si128((const __m128i *)(address+16));

usr.sbin/nsd/simdzone/src/westmere/simd.h

75

static really_inline void simd_storeu_8x32(uint8_t *address, const simd_8x32_t *simd)

usr.sbin/nsd/simdzone/src/westmere/simd.h

77

_mm_storeu_si128((__m128i *)(address), simd->chunks[0]);

usr.sbin/nsd/simdzone/src/westmere/simd.h

78

_mm_storeu_si128((__m128i *)(address+16), simd->chunks[1]);

usr.sbin/nsd/simdzone/src/westmere/simd.h

93

static really_inline void simd_loadu_8x64(simd_8x64_t *simd, const uint8_t *address)

usr.sbin/nsd/simdzone/src/westmere/simd.h

95

simd->chunks[0] = _mm_loadu_si128((const __m128i *)(address));

usr.sbin/nsd/simdzone/src/westmere/simd.h

96

simd->chunks[1] = _mm_loadu_si128((const __m128i *)(address+16));

usr.sbin/nsd/simdzone/src/westmere/simd.h

97

simd->chunks[2] = _mm_loadu_si128((const __m128i *)(address+32));

usr.sbin/nsd/simdzone/src/westmere/simd.h

98

simd->chunks[3] = _mm_loadu_si128((const __m128i *)(address+48));

usr.sbin/ntpd/client.c

505

const char *address;

usr.sbin/ntpd/client.c

507

address = log_ntp_addr(peer->addr);

usr.sbin/ntpd/client.c

509

log_debug("%s %s: %s", operation, address, strerror(error));

usr.sbin/ntpd/client.c

513

log_warn("%s %s", operation, address);

usr.sbin/ntpd/parse.y

109

main : LISTEN ON address listen_opts {

usr.sbin/ntpd/parse.y

161

| SERVERS address server_opts {

usr.sbin/ntpd/parse.y

204

| SERVER address server_opts {

usr.sbin/ntpd/parse.y

333

address : STRING {

usr.sbin/ntpd/parse.y

342

urllist : urllist address {

usr.sbin/ntpd/parse.y

91

%type <v.addr> address url urllist

usr.sbin/pppd/cbcp.c

261

char address[256];

usr.sbin/pppd/cbcp.c

264

address[0] = 0;

usr.sbin/pppd/cbcp.c

290

memcpy(address, pckt, opt_len - 4);

usr.sbin/pppd/cbcp.c

291

address[opt_len - 4] = 0;

usr.sbin/pppd/cbcp.c

292

if (address[0])

usr.sbin/pppd/cbcp.c

293

syslog(LOG_DEBUG, "address: %s", address);

usr.sbin/pppd/cbcp.c

387

char address[256];

usr.sbin/pppd/cbcp.c

401

memcpy(address, pckt, opt_len - 4);

usr.sbin/pppd/cbcp.c

402

address[opt_len - 4] = 0;

usr.sbin/pppd/cbcp.c

403

if (address[0])

usr.sbin/pppd/cbcp.c

404

syslog(LOG_DEBUG, "peer will call: %s", address);

usr.sbin/relayd/config.c

142

struct address *virt;

usr.sbin/relayd/config.c

437

struct address *virt;

usr.sbin/relayd/config.c

501

struct address *virt;

usr.sbin/relayd/parse.y

129

struct address *host_ip(const char *);

usr.sbin/relayd/parse.y

197

%type <v.addr> address rulesrc ruledst addrprefix

usr.sbin/relayd/parse.y

1999

struct address *h;

usr.sbin/relayd/parse.y

2107

struct address *h;

usr.sbin/relayd/parse.y

2339

host : address {

usr.sbin/relayd/parse.y

2412

address : STRING {

usr.sbin/relayd/parse.y

2413

struct address *h;

usr.sbin/relayd/parse.y

2436

addrprefix : address '/' NUMBER {

usr.sbin/relayd/parse.y

2447

| address {

usr.sbin/relayd/parse.y

3228

struct address *

usr.sbin/relayd/parse.y

3232

struct address *h = NULL;

usr.sbin/relayd/parse.y

3257

struct address *h;

usr.sbin/relayd/parse.y

3316

struct address *h;

usr.sbin/relayd/parse.y

3385

struct address *h;

usr.sbin/relayd/parse.y

3447

struct address *h, *next;

usr.sbin/relayd/parse.y

3469

struct address *h;

usr.sbin/relayd/pfe_filter.c

339

struct address *address;

usr.sbin/relayd/pfe_filter.c

367

TAILQ_FOREACH(address, &rdr->virts, entry) {

usr.sbin/relayd/pfe_filter.c

389

if (address->ipproto == IPPROTO_TCP) {

usr.sbin/relayd/pfe_filter.c

408

rio.rule.af = address->ss.ss_family;

usr.sbin/relayd/pfe_filter.c

409

rio.rule.proto = address->ipproto;

usr.sbin/relayd/pfe_filter.c

412

rio.rule.dst.port_op = address->port.op;

usr.sbin/relayd/pfe_filter.c

413

rio.rule.dst.port[0] = address->port.val[0];

usr.sbin/relayd/pfe_filter.c

414

rio.rule.dst.port[1] = address->port.val[1];

usr.sbin/relayd/pfe_filter.c

427

if (strlen(address->ifname))

usr.sbin/relayd/pfe_filter.c

428

(void)strlcpy(rio.rule.ifname, address->ifname,

usr.sbin/relayd/pfe_filter.c

431

if (address->ss.ss_family == AF_INET) {

usr.sbin/relayd/pfe_filter.c

432

sain = (struct sockaddr_in *)&address->ss;

usr.sbin/relayd/pfe_filter.c

438

sain6 = (struct sockaddr_in6 *)&address->ss;

usr.sbin/relayd/pfe_filter.c

456

if (address->port.op == PF_OP_EQ ||

usr.sbin/relayd/relayd.h

365

TAILQ_ENTRY(address) entry;

usr.sbin/relayd/relayd.h

367

TAILQ_HEAD(addresslist, address);

usr.sbin/ripd/message.c

105

u_int32_t address, netmask, nexthop, metric;

usr.sbin/ripd/message.c

125

address = rr->address.s_addr;

usr.sbin/ripd/message.c

132

ibuf_add(buf, &address, sizeof(address));

usr.sbin/ripd/message.c

152

u_int32_t address, netmask, nexthop;

usr.sbin/ripd/message.c

193

address = entry->rr->address.s_addr;

usr.sbin/ripd/message.c

203

ibuf_add(buf, &address, sizeof(address));

usr.sbin/ripd/message.c

229

u_int32_t address, netmask, nexthop;

usr.sbin/ripd/message.c

274

address = entry->rr->address.s_addr;

usr.sbin/ripd/message.c

294

ibuf_add(buf, &address, sizeof(address));

usr.sbin/ripd/message.c

361

rr.address.s_addr = e->address;

usr.sbin/ripd/message.c

415

r.address.s_addr = e->address;

usr.sbin/ripd/rde.c

416

if ((rn = rt_find(e->address.s_addr, e->mask.s_addr)) == NULL) {

usr.sbin/ripd/rde.c

475

rr.address.s_addr = rn->prefix.s_addr;

usr.sbin/ripd/rde_rib.c

178

rn->prefix.s_addr = e->address.s_addr;

usr.sbin/ripd/rde_rib.c

223

rr.address = r->prefix;

usr.sbin/ripd/rde_rib.c

257

if ((rn = rt_find(rr->address.s_addr, rr->mask.s_addr)) == NULL)

usr.sbin/ripd/rip.h

59

u_int32_t address;

usr.sbin/ripd/ripd.h

192

struct in_addr address;

usr.sbin/rpki-client/ccr.c

1136

if (!ip_addr_parse(r->address, afi, fn, &vrp->addr)) {

usr.sbin/rpki-client/ccr.c

398

if (!ASN1_BIT_STRING_set1(ripa->address, vrp->addr.addr, num_bytes,

usr.sbin/rpki-client/roa.c

165

if (!ip_addr_parse(addr->address, afi, fn, &ipaddr)) {

usr.sbin/rpki-client/roa.c

58

ASN1_SIMPLE(ROAIPAddress, address, ASN1_BIT_STRING),

usr.sbin/rpki-client/rpki-asn1.h

284

ASN1_BIT_STRING *address;

usr.sbin/smtpd/lka.c

470

m_get_string(&m, &address);

usr.sbin/smtpd/lka.c

474

lka_report_smtp_tx_mail(direction, &tv, reqid, msgid, address, ok);

usr.sbin/smtpd/lka.c

483

m_get_string(&m, &address);

usr.sbin/smtpd/lka.c

487

lka_report_smtp_tx_rcpt(direction, &tv, reqid, msgid, address, ok);

usr.sbin/smtpd/lka.c

70

const char *address;

usr.sbin/smtpd/lka_filter.c

1521

lka_report_smtp_tx_mail(const char *direction, struct timeval *tv, uint64_t reqid, uint32_t msgid, const char *address, int ok)

usr.sbin/smtpd/lka_filter.c

1537

msgid, result, address);

usr.sbin/smtpd/lka_filter.c

1541

lka_report_smtp_tx_rcpt(const char *direction, struct timeval *tv, uint64_t reqid, uint32_t msgid, const char *address, int ok)

usr.sbin/smtpd/lka_filter.c

1557

msgid, result, address);

usr.sbin/smtpd/mta_session.c

1825

mta_report_tx_mail(struct mta_session *s, uint32_t msgid, const char *address, int ok)

usr.sbin/smtpd/mta_session.c

1830

report_smtp_tx_mail("smtp-out", s->id, msgid, address, ok);

usr.sbin/smtpd/mta_session.c

1834

mta_report_tx_rcpt(struct mta_session *s, uint32_t msgid, const char *address, int ok)

usr.sbin/smtpd/mta_session.c

1839

report_smtp_tx_rcpt("smtp-out", s->id, msgid, address, ok);

usr.sbin/smtpd/report_smtp.c

149

report_smtp_tx_mail(const char *direction, uint64_t qid, uint32_t msgid, const char *address, int ok)

usr.sbin/smtpd/report_smtp.c

160

m_add_string(p_lka, address);

usr.sbin/smtpd/report_smtp.c

166

report_smtp_tx_rcpt(const char *direction, uint64_t qid, uint32_t msgid, const char *address, int ok)

usr.sbin/smtpd/report_smtp.c

177

m_add_string(p_lka, address);

usr.sbin/smtpd/smtp_session.c

3012

smtp_report_tx_mail(struct smtp_session *s, uint32_t msgid, const char *address, int ok)

usr.sbin/smtpd/smtp_session.c

3020

if ((p = strchr(address, '<')) == NULL)

usr.sbin/smtpd/smtp_session.c

3031

smtp_report_tx_rcpt(struct smtp_session *s, uint32_t msgid, const char *address, int ok)

usr.sbin/smtpd/smtp_session.c

3039

if ((p = strchr(address, '<')) == NULL)

usr.sbin/smtpd/smtp_session.c

378

header_address_rewrite_buffer(char *buffer, const char *address, size_t len)

usr.sbin/smtpd/smtp_session.c

447

address_len = strlen(address);

usr.sbin/smtpd/smtp_session.c

452

(void)strlcpy(copy+insert_beg, address, sizeof (copy) - insert_beg);

usr.sbin/snmpd/parse.y

1805

struct address *h;

usr.sbin/snmpd/parse.y

2075

struct address *h;

usr.sbin/snmpd/parse.y

419

char *address[2], *port = $3;

usr.sbin/snmpd/parse.y

432

address[0] = "0.0.0.0";

usr.sbin/snmpd/parse.y

433

address[1] = "::";

usr.sbin/snmpd/parse.y

436

address[0] = $2;

usr.sbin/snmpd/parse.y

440

if ((nhosts = host(address[i], port, AF_UNSPEC,

usr.sbin/snmpd/snmpd.h

315

TAILQ_ENTRY(address) entry;

usr.sbin/snmpd/snmpd.h

317

TAILQ_HEAD(addresslist, address);

usr.sbin/snmpd/snmpe.c

124

struct address *h;

usr.sbin/snmpd/snmpe.c

152

snmpe_bind(struct address *addr)

usr.sbin/snmpd/snmpe.c

494

struct address *h = arg;

usr.sbin/snmpd/snmpe.c

51

int snmpe_bind(struct address *);

usr.sbin/snmpd/snmpe.c

671

struct address *h = arg;

usr.sbin/snmpd/snmpe.c

72

struct address *h;

usr.sbin/snmpd/snmpe.c

91

struct address *h;

usr.sbin/syslogd/syslogd.c

907

address_alloc(const char *name, const char *address, char ***host,

usr.sbin/syslogd/syslogd.c

913

if ((p = strdup(address)) == NULL)

usr.sbin/syslogd/syslogd.c

914

err(1, "%s address %s", name, address);

usr.sbin/syslogd/syslogd.c

916

err(1, "%s host %s", name, address);

usr.sbin/syslogd/syslogd.c

918

err(1, "%s port %s", name, address);

usr.sbin/syslogd/syslogd.c

920

errx(1, "bad %s address: %s", name, address);

usr.sbin/tcpdump/print-ppp.c

1402

uint8_t address, control;

usr.sbin/tcpdump/print-ppp.c

1407

if (l < sizeof(address) + sizeof(control))

usr.sbin/tcpdump/print-ppp.c

1410

address = p[0];

usr.sbin/tcpdump/print-ppp.c

1413

p += sizeof(address) + sizeof(control);

usr.sbin/tcpdump/print-ppp.c

1414

l -= sizeof(address) + sizeof(control);

usr.sbin/tcpdump/print-ppp.c

1415

length -= sizeof(address) + sizeof(control);

usr.sbin/tcpdump/print-ppp.c

1417

switch (address) {

usr.sbin/tcpdump/print-ppp.c

1420

printf("%02x %02x %u ", address, control, length);

usr.sbin/tcpdump/print-ppp.c

1431

printf("ppp address 0x%02x unknown", address);

usr.sbin/unbound/dnstap/unbound-dnstap-socket.c

527

static char* str_of_addr(ProtobufCBinaryData address)

usr.sbin/unbound/dnstap/unbound-dnstap-socket.c

531

if(address.len == 4) {

usr.sbin/unbound/dnstap/unbound-dnstap-socket.c

532

if(inet_ntop(AF_INET, address.data, buf, len)!=0)

usr.sbin/unbound/dnstap/unbound-dnstap-socket.c

534

} else if(address.len == 16) {

usr.sbin/unbound/dnstap/unbound-dnstap-socket.c

535

if(inet_ntop(AF_INET6, address.data, buf, len)!=0)

usr.sbin/unbound/sldns/str2wire.c

1795

struct in_addr address;

usr.sbin/unbound/sldns/str2wire.c

1796

if(inet_pton(AF_INET, (char*)str, &address) != 1)

usr.sbin/unbound/sldns/str2wire.c

1798

if(*len < sizeof(address))

usr.sbin/unbound/sldns/str2wire.c

1800

memmove(rd, &address, sizeof(address));

usr.sbin/unbound/sldns/str2wire.c

1801

*len = sizeof(address);

usr.sbin/unbound/sldns/str2wire.c

1808

uint8_t address[LDNS_IP6ADDRLEN + 1];

usr.sbin/unbound/sldns/str2wire.c

1809

if(inet_pton(AF_INET6, (char*)str, address) != 1)

usr.sbin/unbound/sldns/str2wire.c

1813

memmove(rd, address, LDNS_IP6ADDRLEN);

usr.sbin/vmd/fw_cfg.c

199

if (write_mem(fw->address,

usr.sbin/vmd/fw_cfg.c

206

if (write_mem(fw->address + len, NULL,

usr.sbin/vmd/fw_cfg.c

291

fw_dma.address = be64toh(fw_dma.address);

usr.sbin/vmd/fw_cfg.c

48

uint64_t address;

usr.sbin/ypserv/mkalias/mkalias.c

46

split_address(char *address, size_t len, char *user, char *host)

usr.sbin/ypserv/mkalias/mkalias.c

51

if (memchr(address, '@', len)) {

usr.sbin/ypserv/mkalias/mkalias.c

53

for (c = address; i < len; i++) {

usr.sbin/ypserv/mkalias/mkalias.c

65

if ((r = memrchr(address, '!', len))) {

usr.sbin/ypserv/mkalias/mkalias.c

67

for (c = address; i < len; i++) {

usr.sbin/ypserv/mkalias/mkalias.c

81

check_host(char *address, size_t len, char *host, int dflag, int uflag, int Eflag)

usr.sbin/ypserv/mkalias/mkalias.c

89

if ((dflag && memchr(address, '@', len)) ||

usr.sbin/ypserv/mkalias/mkalias.c

90

(uflag && memchr(address, '!', len)))