第7章 指针

1. 指针的概念

1.1 什么是指针

指针是一种变量,用于存储内存地址。它指向内存中的某个位置,可以通过指针访问或修改该位置的数据。指针的本质是内存地址的抽象,是C语言中直接操作内存的核心机制。

1.2 指针的底层实现与内存模型

1.2.1 指针的内存表示

  1. 物理地址与虚拟地址

    • 现代计算机使用虚拟内存系统,指针存储的是虚拟地址
    • 虚拟地址通过MMU(内存管理单元)转换为物理地址
    • 指针操作的是虚拟地址空间,与物理内存的映射由操作系统管理
  2. 指针大小与架构

    • 32位架构:指针大小为4字节,虚拟地址空间为4GB
    • 64位架构:指针大小为8字节,虚拟地址空间理论上为16EB
    • 指针大小与所指向的数据类型无关,只与架构有关
  3. 指针的位表示

    • 指针值是一个无符号整数,表示虚拟地址空间中的偏移量
    • 空指针(NULL)在所有架构中都表示为全0
    • 野指针是指向无效虚拟地址的指针,使用野指针会导致段错误

1.2.2 指针的内存布局

1
2
3
4
5
6
7
8
9
10
11
12
13
+---------------------+
| 指针变量p |
+---------------------+
| 内存地址: &p | ← 指针变量自身的地址
+---------------------+
| 值: 0x1000 | ← 指针指向的内存地址
+---------------------+

+---------------------+
| 内存地址: 0x1000 | ← 指针指向的位置
+---------------------+
| 值: 42 | ← 指针指向的数据
+---------------------+

1.3 指针的作用

  • 直接访问内存:通过指针可以直接访问和修改内存中的数据,绕过高级语言的抽象层
  • 传递大型数据:通过传递指针而不是整个数据,可以提高函数调用的效率,减少数据复制开销
  • 动态内存分配:用于管理动态分配的内存,实现灵活的内存使用策略
  • 实现数据结构:如链表、树、图等复杂数据结构,是构建高级数据结构的基础
  • 函数指针:用于实现回调函数、策略模式和运行时多态,是C语言实现灵活性的关键
  • 系统编程:在操作系统、驱动程序等底层代码中,指针是直接操作硬件和内存的必要工具
  • 嵌入式开发:在资源受限的环境中,指针可以实现高效的内存管理和硬件访问

1.4 指针与内存层次结构

  1. 内存层次与指针访问

    • 寄存器:最快的内存,指针操作的最终目标
    • L1/L2/L3缓存:指针访问的主要目标,影响程序性能
    • 主存:指针访问的默认目标,速度较慢
    • 磁盘/交换空间:最慢的存储,指针访问会导致严重性能问题
  2. 指针访问的性能影响

    • 局部性原理:指针的顺序访问模式有利于缓存利用
    • 缓存未命中:随机指针访问会导致缓存未命中,显著降低性能
    • 预取机制:现代CPU会根据指针访问模式预取数据,提高缓存命中率
  3. 指针优化的硬件支持

    • 地址计算单元(ACU):专门用于处理指针算术运算
    • 内存管理单元(MMU):加速虚拟地址到物理地址的转换
    • 缓存控制器:管理多级缓存,优化指针访问的性能

2. 指针的声明与初始化

2.1 指针声明

指针声明的基本语法:

1
类型 *指针变量名;

其中:

  • 类型 是指针指向的数据类型
  • * 表示这是一个指针变量
  • 指针变量名 是指针变量的名称

示例

1
2
3
4
5
6
7
int *p;         // 指向int类型的指针
char *str; // 指向char类型的指针
float *fp; // 指向float类型的指针
void *vp; // 通用指针(可指向任何类型)
const int *cp; // 指向常量int的指针,不能通过指针修改值
int *const pc; // 常量指针,指针本身不能改变
const int *const cpc; // 指向常量的常量指针

2.2 指针的类型系统

  1. 指针类型的组成

    • 基础类型:指针指向的数据类型
    • 修饰符:const、volatile等
    • 存储类别:static、extern等
  2. 指针类型的兼容性

    • 不同类型的指针之间不能直接赋值,需要显式转换
    • void * 可以与任何类型的指针相互转换(无需显式转换)
    • 指向常量的指针可以接收指向非常量的指针,但反之不行
  3. 指针类型的层级

    • 一级指针:type *
    • 二级指针:type **
    • 多级指针:type ***
    • 函数指针:return_type (*)(params)

2.3 指针初始化

指针可以通过以下方式初始化:

  1. 使用地址运算符 &
1
2
int num = 10;
int *p = # // p指向num的地址
  1. 使用NULL
1
int *p = NULL;    // 空指针
  1. 使用其他指针
1
2
int *p1 = #
int *p2 = p1; // p2指向与p1相同的地址
  1. 使用动态内存分配
1
int *p = (int *)malloc(sizeof(int));
  1. 使用复合字面量(C99及以上):
1
int *p = (int[]){1, 2, 3, 4, 5};
  1. 使用字符串字面量
1
const char *str = "Hello, world!";

2.4 指针的大小与内存对齐

2.4.1 指针的大小

指针的大小取决于系统的地址总线宽度:

  • 32位系统:4字节
  • 64位系统:8字节
  • 16位系统:2字节(如某些嵌入式系统)

示例

1
2
3
4
printf("Size of int*: %zu\n", sizeof(int *));
printf("Size of char*: %zu\n", sizeof(char *));
printf("Size of void*: %zu\n", sizeof(void *));
printf("Size of function pointer: %zu\n", sizeof(void (*)(void)));

2.4.2 指针的内存对齐

  1. 指针变量的对齐要求

    • 指针变量本身也需要内存对齐
    • 在32位系统上,指针变量对齐到4字节边界
    • 在64位系统上,指针变量对齐到8字节边界
  2. 对齐的影响

    • 对齐的指针变量访问速度更快
    • 未对齐的指针变量可能导致性能下降
    • 某些架构(如SPARC)不支持未对齐的内存访问
  3. 控制对齐

    • 使用 __attribute__((aligned(n))) 强制指定对齐要求
    • 使用 alignof 运算符获取类型的对齐要求

示例

1
2
3
4
5
// 强制指针变量对齐到16字节边界
int *__attribute__((aligned(16))) aligned_ptr;

// 获取指针类型的对齐要求
printf("Alignment of int*: %zu\n", alignof(int *));

2.5 高级指针初始化技术

  1. 使用设计ated initializer(C99及以上):
1
2
3
4
5
6
7
8
struct Point {
int x;
int y;
};

// 初始化指向结构体的指针
struct Point p = {.x = 10, .y = 20};
struct Point *pp = &p;
  1. 使用复合字面量初始化
1
2
3
4
5
// 直接初始化指向数组的指针
int (*arr_ptr)[5] = &(int[]){1, 2, 3, 4, 5};

// 初始化指向结构体的指针
struct Point *pp = &(struct Point){.x = 10, .y = 20};
  1. 使用内存分配函数
1
2
3
4
5
// 使用calloc初始化(自动清零)
int *p = (int *)calloc(5, sizeof(int));

// 使用realloc调整大小
int *q = (int *)realloc(p, 10 * sizeof(int));
  1. 使用内存映射
1
2
3
4
5
6
// 映射文件到内存(POSIX)
#include <sys/mman.h>
#include <fcntl.h>

int fd = open("file.txt", O_RDONLY);
void *mapped = mmap(NULL, file_size, PROT_READ, MAP_PRIVATE, fd, 0);

3. 指针的基本操作

3.1 解引用运算符 *

解引用运算符用于访问指针指向的内存中的值,其底层实现涉及内存地址的直接访问和类型系统的深度交互:

1
2
3
4
5
int num = 10;
int *p = &num;
printf("%d\n", *p); // 输出10
*p = 20; // 修改num的值为20
printf("%d\n", num); // 输出20

3.1.1 解引用的底层实现

  1. 汇编级实现

    • x86架构:mov eax, [ebx](读取)或 mov [ebx], eax(写入)
    • ARM架构:ldr r0, [r1](读取)或 str r0, [r1](写入)
    • RISC-V架构:lw a0, 0(a1)(读取)或 sw a0, 0(a1)(写入)
  2. 内存访问机制

    • 解引用操作触发内存访问周期,包括地址计算、TLB查找、缓存访问等
    • 对于对齐的内存访问,现代CPU可以在一个时钟周期内完成
    • 对于未对齐的内存访问,可能需要多个时钟周期,甚至在某些架构上导致异常
  3. 类型系统交互

    • 编译器根据指针类型确定内存访问的宽度:char* 对应1字节,int* 对应4字节,double* 对应8字节
    • 类型检查确保解引用操作的安全性,避免类型不匹配导致的未定义行为
    • 指针类型决定了指针算术的步长,进而影响解引用的位置

3.1.2 解引用的内存访问控制

  1. 内存保护

    • 解引用空指针(NULL)会触发段错误(SIGSEGV)
    • 解引用野指针可能导致内存访问冲突或数据损坏
    • 解引用指向已释放内存的指针(悬垂指针)会导致未定义行为
    • 解引用指向只读内存的指针(如字符串字面量)会导致段错误
  2. 内存权限

    • 内存页具有读、写、执行权限
    • 解引用操作需要相应的权限:读取需要读权限,写入需要写权限
    • 操作系统通过页表控制内存权限,违反权限会导致段错误
  3. 边界检查

    • C语言不自动进行边界检查,需要程序员手动确保
    • 越界解引用可能修改其他变量或数据结构,导致难以调试的错误
    • 内存安全工具(如AddressSanitizer)可以检测越界访问

3.1.3 解引用的性能考量

  1. 内存层次结构

    • 解引用操作的性能取决于内存层次结构:寄存器 > L1缓存 > L2缓存 > L3缓存 > 主存 > 交换空间
    • 寄存器访问:~1ns
    • L1缓存访问:~2-4ns
    • L2缓存访问:~10-20ns
    • L3缓存访问:~30-40ns
    • 主存访问:~100-300ns
    • 交换空间访问:~10ms+(10^7倍于寄存器)
  2. 缓存优化

    • 连续的解引用操作可能受益于CPU的预取机制
    • 频繁的随机解引用会导致缓存未命中,显著降低性能
    • 空间局部性:访问附近内存的解引用操作更容易命中缓存
    • 时间局部性:最近访问过的内存再次访问时更容易命中缓存
  3. 编译器优化

    • 编译器会尝试优化解引用操作,如缓存局部变量、重排序内存访问等
    • 使用 restrict 关键字可以帮助编译器优化解引用操作
    • 内联函数可以减少解引用的开销,特别是对于频繁访问的小函数

3.1.4 高级应用

  1. 类型惩罚(Type Punning)
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
// 使用联合体进行类型惩罚(标准合规)
union FloatInt {
float f;
int i;
};

void print_float_bits(float f) {
union FloatInt fi;
fi.f = f;
for (int i = 31; i >= 0; i--) {
printf("%d", (fi.i >> i) & 1);
}
printf("\n");
}

// 通过指针进行类型转换(可能违反严格别名规则)
void print_float_bits_ptr(float f) {
unsigned int *p = (unsigned int *)&f;
for (int i = 31; i >= 0; i--) {
printf("%d", (*p >> i) & 1);
}
printf("\n");
}

// 标准合规的类型惩罚(C99及以上)
void print_float_bits_std(float f) {
unsigned char bytes[sizeof(float)];
memcpy(bytes, &f, sizeof(float));
for (int i = sizeof(float) - 1; i >= 0; i--) {
for (int j = 7; j >= 0; j--) {
printf("%d", (bytes[i] >> j) & 1);
}
}
printf("\n");
}
  1. 内存映射与直接访问
1
2
3
4
5
6
7
8
9
10
11
// 映射硬件寄存器(嵌入式系统)
#define REG_BASE 0x40000000
#define REG_OFFSET 0x100

volatile uint32_t *reg = (volatile uint32_t *)(REG_BASE + REG_OFFSET);

// 读取寄存器
uint32_t value = *reg;

// 写入寄存器
*reg = 0x12345678;
  1. 自定义内存分配器
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
// 简单的内存分配器
void *memory_pool;
size_t pool_size;
size_t next_free;

void init_allocator(size_t size) {
memory_pool = malloc(size);
pool_size = size;
next_free = 0;
}

void *alloc(size_t size) {
if (next_free + size > pool_size) {
return NULL; // 内存不足
}
void *ptr = (char *)memory_pool + next_free;
next_free += size;
return ptr;
}

void free_all() {
next_free = 0; // 简单重置,不处理碎片
}

// 使用自定义分配器
void *data = alloc(sizeof(int) * 10);
if (data) {
int *array = (int *)data;
for (int i = 0; i < 10; i++) {
array[i] = i; // 解引用自定义分配的内存
}
}
  1. SIMD指令与指针解引用
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
// 使用SSE指令并行处理数据
#include <immintrin.h>

void vector_add(float *a, float *b, float *result, size_t size) {
size_t i;
// 对齐部分
for (i = 0; i < size - 3; i += 4) {
__m128 va = _mm_loadu_ps(&a[i]); // 解引用并加载到SSE寄存器
__m128 vb = _mm_loadu_ps(&b[i]); // 解引用并加载到SSE寄存器
__m128 vresult = _mm_add_ps(va, vb);
_mm_storeu_ps(&result[i], vresult); // 解引用并存储结果
}
// 剩余部分
for (; i < size; i++) {
result[i] = a[i] + b[i];
}
}

3.2 地址运算符 &

地址运算符用于获取变量的内存地址,是指针操作的基础:

1
2
3
int num = 10;
int *p = &num; // p存储num的地址
printf("%p\n", p); // 输出num的地址

注意事项

  • 不能对寄存器变量使用 & 运算符,因为寄存器变量不存储在内存中
  • 不能对临时值或表达式结果使用 & 运算符,因为它们没有持久的内存地址
  • 对于数组名,& 运算符返回整个数组的地址,类型为「指向数组的指针」

3.3 指针算术运算

指针算术运算是C语言中最强大也最容易出错的特性之一,其行为与指针指向的类型密切相关,涉及底层地址计算和类型系统的深度交互:

基本操作

  1. 指针加法p + n 表示指向p指向的位置之后n个元素的位置,实际地址偏移为 n * sizeof(*p)
  2. 指针减法p - n 表示指向p指向的位置之前n个元素的位置,实际地址偏移为 -n * sizeof(*p)
  3. 指针自增p++++p 表示指向下一个元素,等同于 p = p + 1
  4. 指针自减p----p 表示指向上一个元素,等同于 p = p - 1
  5. 指针比较:可以使用比较运算符(如 ==, <, >)比较两个指针,仅当它们指向同一数组或内存块时才有意义

示例

1
2
3
4
5
6
7
8
9
10
11
12
int arr[] = {10, 20, 30, 40, 50};
int *p = arr; // p指向arr[0]

printf("%d\n", *p); // 输出10
p++; // p指向arr[1],地址增加4字节(在32位系统上)
printf("%d\n", *p); // 输出20

p = arr + 2; // p指向arr[2],地址增加8字节
printf("%d\n", *p); // 输出30

int *q = arr + 4; // q指向arr[4]
printf("%zu\n", q - p); // 输出2(两个指针之间的元素个数)

底层实现

  1. 编译时缩放

    • 编译器根据指针类型自动计算地址偏移:p + n 被编译为 (char*)p + n * sizeof(*p)
    • 例如:int* 指针 p + 1 等价于 (char*)p + 4(32位系统)
    • 例如:double* 指针 p + 1 等价于 (char*)p + 8
  2. 汇编级实现

    • x86架构:lea eax, [ebx + ecx*4](带缩放的地址计算)
    • ARM架构:add r0, r1, r2, lsl #2(左移2位实现*4缩放)
    • RISC-V架构:add a0, a1, a2, sll #2(左移2位实现*4缩放)
  3. 类型安全

    • 不同类型的指针之间的算术运算会导致编译错误
    • 指针与整数的比较(除了0)会导致编译警告或错误

性能优化应用

  1. 循环优化

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    // 优化前:使用下标访问
    for (int i = 0; i < size; i++) {
    sum += arr[i];
    }

    // 优化后:使用指针递增
    for (int *p = arr, *end = arr + size; p < end; p++) {
    sum += *p;
    }

    // 进一步优化:使用寄存器变量存储指针(GCC扩展)
    for (register int *p = arr, *end = arr + size; p < end; p++) {
    sum += *p;
    }
  2. 内存局部性优化

    • 指针递增模式利用CPU缓存预取机制,提高缓存命中率
    • 避免随机内存访问,减少缓存未命中 penalty
  3. SIMD向量化

    • 连续的指针访问模式有利于编译器生成SIMD指令
    • 例如:使用AVX2指令并行处理多个元素

高级应用

  1. 数组遍历的边界检查优化

    1
    2
    3
    4
    5
    6
    7
    // 带边界检查的安全数组访问
    void* safe_array_access(void* base, size_t elem_size, size_t index, size_t size) {
    if (index >= size) {
    return NULL; // 越界
    }
    return (char*)base + index * elem_size;
    }
  2. 多维数组的指针算术

    1
    2
    3
    4
    5
    6
    // 二维数组访问的指针算术
    int arr[3][4];
    int *p = &arr[0][0];

    // 访问arr[i][j]
    int value = *(p + i * 4 + j);
  3. 内存块操作

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    17
    18
    19
    20
    21
    22
    // 内存块复制的指针实现
    void* mem_copy(void* dest, const void* src, size_t size) {
    char* d = (char*)dest;
    const char* s = (const char*)src;

    // 优化:按字长复制
    if (size >= sizeof(long)) {
    while (size >= sizeof(long)) {
    *(long*)d = *(const long*)s;
    d += sizeof(long);
    s += sizeof(long);
    size -= sizeof(long);
    }
    }

    // 复制剩余字节
    while (size-- > 0) {
    *d++ = *s++;
    }

    return dest;
    }

常见陷阱

  • 指针算术运算仅对指向数组或已分配内存块的指针有效
  • 对空指针或野指针进行算术运算会导致未定义行为
  • 指针运算可能会导致内存越界,应始终确保在有效范围内操作
  • 不同类型指针之间的转换可能会破坏类型安全和内存对齐

标准合规性

  • C标准规定,指针算术运算的结果必须指向同一数组对象的元素或数组末尾的下一个位置
  • 超出此范围的指针算术运算会导致未定义行为
  • 指针减法的结果类型是 ptrdiff_t,这是一个有符号整数类型

4. 指针与数组

4.1 数组名作为指针

在大多数情况下,数组名会发生「数组衰减」(Array Decay),被视为指向数组第一个元素的指针,这是C语言中最核心的概念之一:

1
2
3
4
5
6
int arr[] = {10, 20, 30};
int *p = arr; // 等价于 int *p = &arr[0];

printf("%d\n", *p); // 输出10
printf("%d\n", *(p+1)); // 输出20
printf("%d\n", *(p+2)); // 输出30

数组衰减的底层原理

  1. 编译时处理

    • 编译器在遇到数组名作为右值时,自动将其转换为指向第一个元素的指针
    • 这个转换是隐式的,发生在编译阶段,不会产生运行时开销
    • 转换后的指针类型为 type*,其中 type 是数组元素的类型
  2. 类型系统

    • 数组类型 type[size] 与指针类型 type* 是不同的类型
    • 数组类型包含大小信息,而指针类型不包含
    • 数组衰减是类型转换,不是类型等价

数组衰减的例外情况

  • 当数组名作为 sizeof 运算符的操作数时,返回整个数组的大小
  • 当数组名作为 & 运算符的操作数时,返回指向整个数组的指针,类型为 type (*)[size]
  • 当数组名作为字符串字面量初始化字符数组时
  • 当数组名作为 _Alignof 运算符的操作数时
  • 当数组名作为函数参数的初始化器时(C99及以上)

示例

1
2
3
4
5
6
7
8
9
10
11
int arr[5];
printf("sizeof(arr): %zu\n", sizeof(arr)); // 输出20(5*4)
printf("sizeof(&arr): %zu\n", sizeof(&arr)); // 输出8(指针大小,64位系统)

int (*p)[5] = &arr; // 指向整个数组的指针
printf("%p\n", (void*)arr); // 输出数组首元素地址
printf("%p\n", (void*)&arr); // 输出相同的地址,但类型不同

// 指向数组的指针的算术运算
p++; // 指针移动整个数组的大小,即20字节
printf("%p\n", (void*)p); // 输出arr首地址 + 20字节

高级应用

  1. 数组与指针的类型转换

    1
    2
    3
    4
    5
    6
    7
    8
    // 从指向元素的指针转换为指向数组的指针
    int arr[5];
    int *p = arr;
    int (*pa)[5] = (int (*)[5])p;

    // 从指向数组的指针转换为指向元素的指针
    int (*pa)[5] = &arr;
    int *p = (int*)pa;
  2. 变长数组的指针操作

    1
    2
    3
    4
    5
    6
    // C99变长数组
    void process_array(int n, int arr[n]) {
    // arr 衰减为 int*
    int (*pa)[n] = &arr; // 指向变长数组的指针
    // 操作...
    }
  3. 数组指针与多维数组

    1
    2
    3
    4
    5
    6
    // 多维数组的指针表示
    int arr[2][3] = {{1, 2, 3}, {4, 5, 6}};
    int (*p)[3] = arr; // 指向包含3个int的数组的指针

    printf("%d\n", *(*p)); // 输出1
    printf("%d\n", *(*(p+1)+1)); // 输出5

性能考量

  • 数组衰减不会产生运行时开销,是编译时的类型转换
  • 指向数组的指针(type (*)[size])在处理多维数组时比指针的指针(type**)更高效,因为它保持了内存的连续性
  • 编译器可以对数组指针的算术运算进行更多优化,因为它知道数组的大小

标准合规性

  • C标准明确规定了数组衰减的规则和例外情况
  • C99引入了变长数组(VLA),允许数组大小在运行时确定
  • C11将变长数组设为可选特性,但大多数编译器仍支持

4.2 指针访问数组元素

使用指针访问数组元素是C语言中最常见的优化技巧之一:

1
2
3
4
5
6
int arr[] = {10, 20, 30, 40, 50};
int *p = arr;

for (int i = 0; i < 5; i++) {
printf("%d ", *(p + i)); // 输出10 20 30 40 50
}

性能优化技巧

  • 使用指针递增而非下标访问,减少循环内的地址计算
  • 对于大型数组,考虑使用寄存器变量存储指针,进一步提高性能
  • 利用编译器的自动向量化优化,确保代码风格有利于SIMD指令生成

优化示例

1
2
3
4
5
6
7
8
9
// 优化前:使用下标访问
for (int i = 0; i < size; i++) {
sum += arr[i];
}

// 优化后:使用指针递增
for (int *p = arr, *end = arr + size; p < end; p++) {
sum += *p;
}

4.3 指针与多维数组

多维数组在内存中是线性存储的,指针操作需要理解其内存布局:

1
2
3
4
5
6
int arr[2][3] = {{1, 2, 3}, {4, 5, 6}};
int (*p)[3] = arr; // p是指向包含3个int元素的数组的指针

printf("%d\n", *(*p)); // 输出1
printf("%d\n", *(*p + 1)); // 输出2
printf("%d\n", *(*(p + 1))); // 输出4

内存布局:多维数组在内存中按行主序(Row-Major Order)存储,即先存储第一行的所有元素,再存储第二行的所有元素,以此类推。对于 int arr[2][3],内存布局为:1 2 3 4 5 6

高级应用

  • 动态分配多维数组:使用指向指针的指针或指向数组的指针
  • 数组切片:通过指针操作实现数组的子数组访问
  • 矩阵运算优化:利用指针算术提高矩阵运算性能

动态分配二维数组示例

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
// 方法1:使用指向指针的指针
int **create_2d_array(int rows, int cols) {
int **arr = (int **)malloc(rows * sizeof(int *));
if (arr) {
for (int i = 0; i < rows; i++) {
arr[i] = (int *)malloc(cols * sizeof(int));
}
}
return arr;
}

// 方法2:使用指向数组的指针(连续内存)
int (*create_2d_array_contiguous(int rows, int cols))[cols] {
int (*arr)[cols] = (int (*)[cols])malloc(rows * cols * sizeof(int));
return arr;
}

// 方法3:使用一维数组模拟二维数组
int *create_2d_array_flat(int rows, int cols) {
return (int *)malloc(rows * cols * sizeof(int));
}
// 访问方式:arr[i * cols + j]

性能比较

  • 方法1(指针数组):内存不连续,缓存局部性差,但可以轻松处理不规则矩阵
  • 方法2(指向数组的指针):内存连续,缓存局部性好,语法直观
  • 方法3(一维数组模拟):内存连续,缓存局部性最好,但访问语法较复杂

多维数组与指针的类型转换

  • arr:类型为 int[2][3],衰减为 int(*)[3]
  • arr[0]:类型为 int[3],衰减为 int*
  • &arr:类型为 int(*)[2][3]
  • &arr[0]:类型为 int(*)[3]
  • &arr[0][0]:类型为 int*

5. 指针与函数

5.1 指针作为函数参数

指针作为函数参数是C语言中实现「传引用」语义的唯一方式,允许函数修改调用者作用域中的变量,同时也是实现高效数据传递的关键技术:

1
2
3
4
5
6
7
8
9
10
11
12
void swap(int *a, int *b) {
int temp = *a;
*a = *b;
*b = temp;
}

int main() {
int x = 10, y = 20;
swap(&x, &y); // 传递x和y的地址
printf("x = %d, y = %d\n", x, y); // 输出x = 20, y = 10
return 0;
}

底层实现

  1. 参数传递机制

    • 指针参数通过值传递:函数接收指针的副本,而非指针指向的数据
    • 指针副本与原始指针指向同一内存地址,因此可以修改该地址的数据
    • 不同调用约定(cdecl、stdcall、fastcall)影响指针参数的传递方式(栈或寄存器)
  2. 汇编级实现

    • x86架构(cdecl):push ebx(传递指针)、mov eax, [ebx](读取数据)
    • ARM架构:mov r0, #address(传递地址)、ldr r1, [r0](读取数据)
    • RISC-V架构:mv a0, a1(传递地址)、lw a2, 0(a0)(读取数据)

指针参数的优势

  • 允许函数修改实参的值
  • 对于大型数据结构,传递指针比传递值更高效,减少了数据复制开销
  • 可以通过指针返回多个值
  • 支持动态大小的参数(如变长数组)

高级应用

  1. 输出参数

    1
    2
    3
    4
    5
    6
    7
    8
    // 计算平方根并返回结果和状态
    int sqrt_with_status(double x, double *result) {
    if (x < 0) {
    return -1; // 错误:负数
    }
    *result = sqrt(x);
    return 0; // 成功
    }
  2. 指针到指针

    1
    2
    3
    4
    5
    6
    7
    8
    // 在函数中分配内存并更新调用者的指针
    int allocate_array(int **arr, size_t size) {
    *arr = (int *)malloc(size * sizeof(int));
    if (!*arr) {
    return -1; // 分配失败
    }
    return 0; // 成功
    }
  3. 变长参数

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    // 简单的变长参数函数
    double average(int count, ...) {
    va_list args;
    double sum = 0.0;

    va_start(args, count);
    for (int i = 0; i < count; i++) {
    sum += va_arg(args, double);
    }
    va_end(args);

    return sum / count;
    }
  4. 泛型参数

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    // 泛型比较函数
    int compare(const void *a, const void *b, size_t size) {
    const unsigned char *pa = (const unsigned char *)a;
    const unsigned char *pb = (const unsigned char *)b;

    for (size_t i = 0; i < size; i++) {
    if (pa[i] != pb[i]) {
    return pa[i] - pb[i];
    }
    }
    return 0;
    }

性能优化策略

  1. 参数传递优化

    • 对于小型结构体(≤ 2个指针大小),考虑直接传递值而非指针
    • 对于大型结构体,传递指针以减少复制开销
    • 使用restrict关键字告诉编译器指针是唯一访问其指向内存的方式
  2. 内存访问优化

    • 按顺序访问指针指向的数据,利用CPU缓存预取
    • 避免指针别名,允许编译器进行更多优化
    • 使用局部变量缓存指针指向的值,减少重复解引用
  3. 调用约定选择

    • cdecl:默认约定,适用于大多数情况
    • fastcall:通过寄存器传递前几个参数,适用于频繁调用的小函数
    • stdcall:由被调用者清理栈,适用于Windows API

标准合规性

  • C标准规定指针参数的传递方式与其他类型相同(值传递)
  • C99引入了restrict关键字,用于指针参数的优化
  • C11增强了泛型编程支持,通过_Generic表达式

5.2 指针作为函数返回值

函数可以返回指针,这是C语言中实现资源管理、数据共享和复杂数据结构操作的重要机制,但需要谨慎处理内存管理和生命周期问题:

1
2
3
4
5
6
7
8
9
10
11
int *create_array(int size) {
int *arr = (int *)malloc(size * sizeof(int));
return arr;
}

int main() {
int *arr = create_array(5);
// 使用arr
free(arr);
return 0;
}

底层原理

  1. 返回值传递机制

    • 指针作为返回值时,通过函数的返回寄存器传递(如x86的EAX/RAX,ARM的R0,RISC-V的A0)
    • 传递的是指针的值(内存地址),而非指针指向的数据
    • 返回值的大小固定为指针大小(32位系统4字节,64位系统8字节)
  2. 内存生命周期

    • 静态存储期:全局变量和静态变量在程序整个运行期间存在
    • 自动存储期:局部变量在函数返回后被销毁
    • 动态存储期:通过malloc/free管理的内存,其生命周期由程序员控制

返回指针的注意事项

  • 避免返回局部变量的地址:局部变量在函数返回后会被销毁,返回其地址会导致悬垂指针
  • 正确管理动态内存:返回动态分配的内存时,调用者必须负责释放
  • 返回静态变量的地址:可以安全返回静态变量的地址,但要注意线程安全性
  • 返回全局变量的地址:可以安全返回全局变量的地址
  • 返回字符串字面量:字符串字面量存储在只读内存区域,返回其地址是安全的

高级内存管理策略

  1. 引用计数

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    17
    18
    19
    20
    21
    22
    23
    24
    25
    26
    27
    // 简单的引用计数实现
    typedef struct {
    void *data;
    int ref_count;
    } RefCounted;

    RefCounted *create_ref_counted(void *data) {
    RefCounted *rc = (RefCounted *)malloc(sizeof(RefCounted));
    if (rc) {
    rc->data = data;
    rc->ref_count = 1;
    }
    return rc;
    }

    void retain(RefCounted *rc) {
    if (rc) {
    rc->ref_count++;
    }
    }

    void release(RefCounted *rc) {
    if (rc && --rc->ref_count == 0) {
    free(rc->data);
    free(rc);
    }
    }
  2. 内存池

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    17
    18
    19
    20
    21
    22
    23
    24
    25
    26
    27
    28
    29
    // 内存池管理
    typedef struct {
    void *pool;
    size_t block_size;
    size_t count;
    } MemoryPool;

    MemoryPool *create_pool(size_t block_size, size_t count) {
    MemoryPool *mp = (MemoryPool *)malloc(sizeof(MemoryPool));
    if (mp) {
    mp->pool = malloc(block_size * count);
    if (!mp->pool) {
    free(mp);
    return NULL;
    }
    mp->block_size = block_size;
    mp->count = count;
    }
    return mp;
    }

    void *alloc_from_pool(MemoryPool *mp) {
    // 简化实现,实际需要管理空闲块
    static size_t next = 0;
    if (next < mp->count) {
    return (char *)mp->pool + next++ * mp->block_size;
    }
    return NULL;
    }

安全的指针返回模式

  1. 模式1:返回动态分配的内存(调用者负责释放)

    1
    2
    3
    4
    5
    6
    7
    8
    void *safe_malloc(size_t size) {
    void *ptr = malloc(size);
    if (!ptr) {
    fprintf(stderr, "Memory allocation failed\n");
    exit(EXIT_FAILURE);
    }
    return ptr;
    }
  2. 模式2:返回静态缓冲区(注意线程安全和重入问题)

    1
    2
    3
    4
    5
    6
    7
    // 线程安全版本
    char *get_current_time(char *buffer, size_t size) {
    time_t now = time(NULL);
    struct tm *tm_info = localtime(&now);
    strftime(buffer, size, "%Y-%m-%d %H:%M:%S", tm_info);
    return buffer;
    }
  3. 模式3:返回全局或静态变量的地址

    1
    2
    3
    4
    static int global_counter = 0;
    int *get_counter() {
    return &global_counter;
    }
  4. 模式4:返回函数内部静态数组

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    // 返回错误信息
    const char *get_error_message(int error_code) {
    static const char *messages[] = {
    "Success",
    "Invalid parameter",
    "Memory allocation failed",
    "File not found"
    };

    if (error_code < 0 || error_code >= sizeof(messages)/sizeof(messages[0])) {
    return "Unknown error";
    }
    return messages[error_code];
    }

性能优化考虑

  • 避免频繁的内存分配/释放:考虑使用内存池或对象池
  • 返回值优化(RVO):编译器可以优化返回值的复制,适用于小型结构体
  • 内联函数:对于返回指针的小型函数,考虑使用内联以减少函数调用开销
  • 缓存局部性:返回的数据应尽量在缓存中,减少缓存未命中

安全最佳实践

  • 始终检查返回的指针:调用返回指针的函数后,检查是否为NULL
  • 文档化内存所有权:明确说明谁负责释放返回的内存
  • 使用const修饰符:对于不需要修改的返回值,使用const修饰
  • 避免返回指向内部数据结构的指针:可能破坏封装性
  • 考虑使用智能指针模拟:在C++中使用智能指针,在C中可以使用类似的机制

标准合规性

  • C标准允许函数返回任何类型的指针,包括void*
  • C99和C11对返回指针的函数没有特殊限制
  • 注意:返回指向未初始化内存的指针会导致未定义行为

5.3 函数指针

函数指针是C语言中最强大的特性之一,允许将函数作为参数传递、存储在数据结构中,甚至动态选择要调用的函数,是实现回调机制、策略模式和运行时多态的基础:

1
2
3
4
5
6
7
8
9
10
int add(int a, int b) {
return a + b;
}

int main() {
int (*func_ptr)(int, int) = add; // func_ptr指向add函数
int result = func_ptr(5, 3); // 调用add函数
printf("Result: %d\n", result); // 输出8
return 0;
}

底层实现

  1. 内存表示

    • 函数指针存储函数在内存中的入口地址
    • 在大多数系统中,函数指针的大小与数据指针相同(32位系统4字节,64位系统8字节)
    • 函数指针指向代码段(.text section)中的可执行指令
  2. 汇编级实现

    • x86架构:call eax(通过寄存器间接调用)
    • ARM架构:blx r0(带链接的间接跳转)
    • RISC-V架构:jalr ra, 0(a0)(跳转到寄存器指定的地址)
  3. 调用约定

    • 函数指针调用遵循与直接函数调用相同的调用约定
    • 不同调用约定的函数指针类型是不兼容的

函数指针的语法

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
// 声明函数指针类型
typedef int (*Operation)(int, int);

// 使用typedef简化函数指针声明
Operation op = add;

// 函数指针数组
typedef int (*MathFunc)(int, int);
MathFunc operations[] = {add, subtract, multiply, divide};

// 函数指针作为结构体成员
typedef struct {
const char *name;
Operation op;
} OperationInfo;

高级应用

  1. 回调函数系统

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    17
    18
    19
    20
    21
    // 事件处理系统
    typedef struct {
    int event_type;
    void (*handler)(void *data);
    } EventHandler;

    // 注册事件处理器
    void register_handler(EventHandler *handlers, size_t *count, int event_type, void (*handler)(void *)) {
    handlers[*count].event_type = event_type;
    handlers[*count].handler = handler;
    (*count)++;
    }

    // 触发事件
    void trigger_event(EventHandler *handlers, size_t count, int event_type, void *data) {
    for (size_t i = 0; i < count; i++) {
    if (handlers[i].event_type == event_type) {
    handlers[i].handler(data);
    }
    }
    }
  2. 函数指针数组与命令模式

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    17
    18
    19
    20
    21
    22
    23
    // 命令处理系统
    typedef struct {
    const char *name;
    int (*execute)(int argc, char *argv[]);
    } Command;

    // 命令表
    Command commands[] = {
    {"help", help_command},
    {"exit", exit_command},
    {"list", list_command},
    {"create", create_command}
    };

    // 执行命令
    int execute_command(const char *name, int argc, char *argv[]) {
    for (size_t i = 0; i < sizeof(commands)/sizeof(commands[0]); i++) {
    if (strcmp(commands[i].name, name) == 0) {
    return commands[i].execute(argc, argv);
    }
    }
    return -1; // 命令未找到
    }
  3. 高级状态机实现

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    17
    18
    19
    20
    21
    22
    23
    24
    25
    26
    27
    28
    29
    30
    31
    32
    33
    // 带状态转换的状态机
    typedef enum { S_IDLE, S_READY, S_RUNNING, S_ERROR } State;
    typedef State (*StateHandler)(void *context);

    // 状态转换表
    typedef struct {
    State current;
    State next;
    StateHandler handler;
    } StateTransition;

    // 状态处理函数
    State handle_idle(void *context) {
    printf("Idle state\n");
    return S_READY; // 转换到READY状态
    }

    State handle_ready(void *context) {
    printf("Ready state\n");
    return S_RUNNING; // 转换到RUNNING状态
    }

    // 状态机运行
    void run_state_machine(State *current_state, StateTransition *transitions, size_t count, void *context) {
    while (1) {
    for (size_t i = 0; i < count; i++) {
    if (transitions[i].current == *current_state) {
    *current_state = transitions[i].handler(context);
    break;
    }
    }
    }
    }
  4. 动态库函数加载

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    17
    18
    19
    20
    21
    22
    23
    24
    25
    26
    // 动态加载库函数(POSIX)
    #include <dlfcn.h>

    int main() {
    void *handle = dlopen("./libmath.so", RTLD_LAZY);
    if (!handle) {
    fprintf(stderr, "%s\n", dlerror());
    return 1;
    }

    // 获取函数指针
    int (*add)(int, int) = dlsym(handle, "add");
    const char *error = dlerror();
    if (error) {
    fprintf(stderr, "%s\n", error);
    dlclose(handle);
    return 1;
    }

    // 调用函数
    printf("5 + 3 = %d\n", add(5, 3));

    // 关闭库
    dlclose(handle);
    return 0;
    }
  5. 性能优化:函数内联与函数指针

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    // 条件内联
    #ifdef ENABLE_INLINE
    #define MATH_OP(op, a, b) ((op) == '+' ? (a) + (b) : \
    (op) == '-' ? (a) - (b) : \
    (op) == '*' ? (a) * (b) : \
    (op) == '/' ? (a) / (b) : 0)
    #else
    // 使用函数指针
    typedef int (*MathOp)(int, int);
    int apply_op(MathOp op, int a, int b) {
    return op(a, b);
    }
    #endif

性能优化策略

  1. 内联与函数指针权衡

    • 直接函数调用可以被内联,性能更高
    • 函数指针调用通常不能被内联,但提供了更大的灵活性
    • 对于性能关键路径,考虑使用模板或宏替代函数指针
  2. 分支预测

    • 函数指针调用可能导致分支预测失败
    • 对于频繁调用的函数指针,考虑使用分支表或计算跳转
  3. 缓存局部性

    • 相关的函数应放在一起,提高指令缓存命中率
    • 避免在热路径中使用指向不同内存区域的函数指针
  4. 编译时优化

    • 使用__attribute__((hot))标记频繁调用的函数
    • 启用链接时优化(LTO)以提高函数指针调用的性能

安全最佳实践

  1. 函数指针验证

    • 在调用函数指针前检查是否为NULL
    • 对于动态获取的函数指针,验证其有效性
  2. 类型安全

    • 使用typedef定义函数指针类型,提高类型安全性
    • 避免强制转换不同类型的函数指针
  3. 边界检查

    • 对于函数指针数组,确保索引在有效范围内
    • 避免越界访问导致的未定义行为
  4. 内存保护

    • 函数指针应指向有效的函数代码,避免指向数据或未初始化内存
    • 考虑使用常量函数指针防止意外修改

标准合规性

  • C标准允许函数指针的声明、赋值和调用
  • C99和C11对函数指针的使用没有特殊限制
  • 注意:函数指针与数据指针的转换是实现定义的,可能不兼容

6. 指针与字符串

6.1 字符串字面量与指针

字符串是C语言中最常见的数据结构之一,其底层实现与指针密切相关。深入理解字符串与指针的关系对于编写高效、安全的字符串处理代码至关重要。

6.1.1 字符串字面量的内存布局

  1. 存储区域

    • 字符串字面量存储在程序的只读数据段(.rodata section)中
    • 尝试修改字符串字面量会导致段错误(SIGSEGV)
    • 编译器会对相同的字符串字面量进行合并,减少内存使用
  2. 内存表示

    • 字符串字面量以空字符(’\0’)结尾
    • 例如:”Hello” 在内存中表示为 ‘H’,’e’,’l’,’l’,’o’,’\0’
    • 字符串字面量的类型为 const char[]
  3. 指针指向

    • 当字符串字面量赋值给指针时,指针指向其在只读数据段的地址
    • 例如:const char *str = "Hello";

6.1.2 字符串操作与指针算术

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
// 字符串长度计算
size_t string_length(const char *str) {
const char *p = str;
while (*p) {
p++;
}
return p - str;
}

// 字符串复制
char *string_copy(char *dest, const char *src) {
char *p = dest;
while (*src) {
*p++ = *src++;
}
*p = '\0';
return dest;
}

// 字符串比较
int string_compare(const char *s1, const char *s2) {
while (*s1 && *s1 == *s2) {
s1++;
s2++;
}
return *s1 - *s2;
}

6.1.3 高级字符串处理技术

  1. 字符串分割
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
66
67
68
69
70
71
72
73
74
75
76
// 字符串分割函数
char **split_string(const char *str, const char *delimiter, size_t *count) {
if (!str || !delimiter || !count) {
return NULL;
}

// 计算分割后的字符串数量
size_t num_tokens = 0;
const char *p = str;
size_t delim_len = strlen(delimiter);

while (*p) {
if (strncmp(p, delimiter, delim_len) == 0) {
num_tokens++;
p += delim_len;
} else {
p++;
}
}
num_tokens++;
*count = num_tokens;

// 分配内存
char **tokens = (char **)malloc(num_tokens * sizeof(char *));
if (!tokens) {
return NULL;
}

// 执行分割
p = str;
size_t token_index = 0;

while (*p && token_index < num_tokens) {
const char *start = p;
while (*p && strncmp(p, delimiter, delim_len) != 0) {
p++;
}

size_t token_len = p - start;
tokens[token_index] = (char *)malloc(token_len + 1);
if (!tokens[token_index]) {
// 释放已分配的内存
for (size_t i = 0; i < token_index; i++) {
free(tokens[i]);
}
free(tokens);
return NULL;
}

strncpy(tokens[token_index], start, token_len);
tokens[token_index][token_len] = '\0';
token_index++;

if (*p) {
p += delim_len;
}
}

return tokens;
}

// 使用示例
void split_example() {
const char *str = "apple,banana,orange,grape";
const char *delimiter = ",";
size_t count;

char **tokens = split_string(str, delimiter, &count);
if (tokens) {
for (size_t i = 0; i < count; i++) {
printf("Token %zu: %s\n", i, tokens[i]);
free(tokens[i]);
}
free(tokens);
}
}
  1. 字符串构建
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
66
67
68
69
70
71
72
73
74
75
76
77
78
79
80
81
82
83
84
85
86
87
88
89
90
91
92
93
94
95
96
97
98
99
100
101
102
103
104
105
106
107
108
109
110
111
112
113
114
115
116
117
118
119
120
121
122
123
124
125
126
127
128
// 动态字符串构建
typedef struct {
char *buffer;
size_t length;
size_t capacity;
} StringBuilder;

// 初始化字符串构建器
StringBuilder *sb_create(size_t initial_capacity) {
StringBuilder *sb = (StringBuilder *)malloc(sizeof(StringBuilder));
if (!sb) {
return NULL;
}

sb->capacity = initial_capacity > 0 ? initial_capacity : 16;
sb->buffer = (char *)malloc(sb->capacity);
if (!sb->buffer) {
free(sb);
return NULL;
}

sb->length = 0;
sb->buffer[0] = '\0';

return sb;
}

// 追加字符串
bool sb_append(StringBuilder *sb, const char *str) {
if (!sb || !str) {
return false;
}

size_t str_len = strlen(str);
size_t required = sb->length + str_len + 1;

// 检查容量
if (required > sb->capacity) {
size_t new_capacity = sb->capacity * 2;
while (new_capacity < required) {
new_capacity *= 2;
}

char *new_buffer = (char *)realloc(sb->buffer, new_capacity);
if (!new_buffer) {
return false;
}

sb->buffer = new_buffer;
sb->capacity = new_capacity;
}

// 追加字符串
strcpy(sb->buffer + sb->length, str);
sb->length += str_len;

return true;
}

// 追加字符
bool sb_append_char(StringBuilder *sb, char c) {
if (!sb) {
return false;
}

size_t required = sb->length + 2;

// 检查容量
if (required > sb->capacity) {
size_t new_capacity = sb->capacity * 2;
while (new_capacity < required) {
new_capacity *= 2;
}

char *new_buffer = (char *)realloc(sb->buffer, new_capacity);
if (!new_buffer) {
return false;
}

sb->buffer = new_buffer;
sb->capacity = new_capacity;
}

// 追加字符
sb->buffer[sb->length] = c;
sb->length++;
sb->buffer[sb->length] = '\0';

return true;
}

// 获取结果
char *sb_to_string(StringBuilder *sb) {
if (!sb) {
return NULL;
}

// 缩容到实际大小
char *result = (char *)realloc(sb->buffer, sb->length + 1);
if (!result) {
return sb->buffer; // 返回原始缓冲区
}

free(sb);
return result;
}

// 销毁字符串构建器
void sb_destroy(StringBuilder *sb) {
if (sb) {
free(sb->buffer);
free(sb);
}
}

// 使用示例
void string_builder_example() {
StringBuilder *sb = sb_create(32);
if (sb) {
sb_append(sb, "Hello");
sb_append_char(sb, ' ');
sb_append(sb, "world!");

char *result = sb_to_string(sb);
printf("Result: %s\n", result);
free(result);
}
}
  1. 字符串搜索
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
66
67
68
69
70
71
72
73
74
75
76
77
78
79
80
81
82
83
84
// KMP算法实现字符串搜索
int *compute_lps(const char *pattern, size_t pattern_len) {
int *lps = (int *)malloc(pattern_len * sizeof(int));
if (!lps) {
return NULL;
}

int len = 0; // 最长前缀后缀长度
lps[0] = 0; // lps[0] 始终为0

size_t i = 1;
while (i < pattern_len) {
if (pattern[i] == pattern[len]) {
len++;
lps[i] = len;
i++;
} else {
if (len != 0) {
len = lps[len - 1];
} else {
lps[i] = 0;
i++;
}
}
}

return lps;
}

// KMP字符串搜索
const char *kmp_search(const char *text, const char *pattern) {
if (!text || !pattern || *pattern == '\0') {
return NULL;
}

size_t text_len = strlen(text);
size_t pattern_len = strlen(pattern);

if (pattern_len > text_len) {
return NULL;
}

int *lps = compute_lps(pattern, pattern_len);
if (!lps) {
return NULL;
}

size_t i = 0; // text索引
size_t j = 0; // pattern索引

while (i < text_len) {
if (pattern[j] == text[i]) {
i++;
j++;
}

if (j == pattern_len) {
free(lps);
return text + i - j;
} else if (i < text_len && pattern[j] != text[i]) {
if (j != 0) {
j = lps[j - 1];
} else {
i++;
}
}
}

free(lps);
return NULL;
}

// 使用示例
void kmp_example() {
const char *text = "ABABDABACDABABCABAB";
const char *pattern = "ABABCABAB";

const char *result = kmp_search(text, pattern);
if (result) {
printf("Pattern found at position: %td\n", result - text);
} else {
printf("Pattern not found\n");
}
}

6.1.4 字符串与指针的性能优化

  1. 内存访问优化

    • 顺序访问字符串字符,利用CPU缓存预取机制
    • 避免随机访问字符串中的字符
    • 对于大型字符串,考虑使用内存映射(mmap)
  2. 指令级优化

    • 使用SIMD指令加速字符串操作(如SSE2/AVX2)
    • 利用编译器内置函数(如__builtin_strlen
    • 展开循环减少分支预测失败
  3. 算法选择

    • 对于短字符串,暴力搜索可能比KMP更快
    • 对于长字符串,使用高效的搜索算法(如Boyer-Moore)
    • 对于频繁的字符串操作,使用预分配的缓冲区
  4. 内存管理

    • 避免频繁的小内存分配(使用内存池)
    • 对于固定大小的字符串,使用栈分配
    • 对于动态字符串,使用指数级扩容策略

6.1.5 字符串处理的安全考量

  1. 缓冲区溢出防护

    • 使用strncpysnprintf等带长度限制的函数
    • 避免使用gets等不安全的函数
    • 始终检查目标缓冲区的大小
  2. 输入验证

    • 验证字符串输入的长度和内容
    • 处理特殊字符和转义序列
    • 防止注入攻击(如SQL注入、命令注入)
  3. 内存安全

    • 确保字符串操作不会越界
    • 正确释放动态分配的字符串内存
    • 避免使用已释放的字符串指针
  4. 编码处理

    • 正确处理多字节编码(如UTF-8)
    • 避免字符编码转换错误
    • 考虑国际化和本地化需求

6.2 指针与字符串的高级应用

  1. 字符串池
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
66
67
68
69
70
71
72
73
74
75
76
77
78
79
80
81
82
83
84
85
86
87
88
89
90
91
92
93
94
95
96
97
98
99
100
101
102
103
104
105
106
107
108
109
110
111
112
113
114
115
116
// 简单的字符串池实现
typedef struct StringPoolEntry {
char *string;
size_t length;
struct StringPoolEntry *next;
} StringPoolEntry;

typedef struct {
StringPoolEntry **buckets;
size_t bucket_count;
size_t size;
} StringPool;

// 哈希函数
static size_t string_hash(const char *str, size_t len) {
size_t hash = 5381;
for (size_t i = 0; i < len; i++) {
hash = ((hash << 5) + hash) + (unsigned char)str[i];
}
return hash;
}

// 创建字符串池
StringPool *pool_create(size_t bucket_count) {
StringPool *pool = (StringPool *)malloc(sizeof(StringPool));
if (!pool) {
return NULL;
}

pool->bucket_count = bucket_count > 0 ? bucket_count : 1024;
pool->buckets = (StringPoolEntry **)calloc(pool->bucket_count, sizeof(StringPoolEntry *));
if (!pool->buckets) {
free(pool);
return NULL;
}

pool->size = 0;
return pool;
}

// 插入字符串到池中(返回池中的字符串指针)
const char *pool_insert(StringPool *pool, const char *str) {
if (!pool || !str) {
return NULL;
}

size_t len = strlen(str);
size_t hash = string_hash(str, len);
size_t bucket = hash % pool->bucket_count;

// 查找是否已存在
StringPoolEntry *entry = pool->buckets[bucket];
while (entry) {
if (entry->length == len && strncmp(entry->string, str, len) == 0) {
return entry->string;
}
entry = entry->next;
}

// 创建新条目
entry = (StringPoolEntry *)malloc(sizeof(StringPoolEntry));
if (!entry) {
return NULL;
}

entry->string = (char *)malloc(len + 1);
if (!entry->string) {
free(entry);
return NULL;
}

strcpy(entry->string, str);
entry->length = len;
entry->next = pool->buckets[bucket];
pool->buckets[bucket] = entry;
pool->size++;

return entry->string;
}

// 销毁字符串池
void pool_destroy(StringPool *pool) {
if (!pool) {
return;
}

for (size_t i = 0; i < pool->bucket_count; i++) {
StringPoolEntry *entry = pool->buckets[i];
while (entry) {
StringPoolEntry *next = entry->next;
free(entry->string);
free(entry);
entry = next;
}
}

free(pool->buckets);
free(pool);
}

// 使用示例
void string_pool_example() {
StringPool *pool = pool_create(1024);
if (pool) {
const char *s1 = pool_insert(pool, "hello");
const char *s2 = pool_insert(pool, "world");
const char *s3 = pool_insert(pool, "hello"); // 应该返回与s1相同的指针

printf("s1: %s (address: %p)\n", s1, (void *)s1);
printf("s2: %s (address: %p)\n", s2, (void *)s2);
printf("s3: %s (address: %p)\n", s3, (void *)s3);
printf("s1 == s3: %d\n", s1 == s3);

pool_destroy(pool);
}
}
  1. 字符串视图
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
66
67
68
69
70
71
72
73
74
75
76
77
78
79
80
81
82
83
84
85
86
87
88
89
90
91
92
93
94
95
96
97
98
99
100
101
102
// 字符串视图(避免字符串复制)
typedef struct {
const char *data;
size_t length;
} StringView;

// 创建字符串视图
StringView sv_create(const char *str) {
StringView sv;
if (str) {
sv.data = str;
sv.length = strlen(str);
} else {
sv.data = NULL;
sv.length = 0;
}
return sv;
}

// 从字符串的指定位置创建视图
StringView sv_create_from_range(const char *str, size_t start, size_t length) {
StringView sv;
if (str) {
sv.data = str + start;
sv.length = length;
} else {
sv.data = NULL;
sv.length = 0;
}
return sv;
}

// 比较字符串视图
int sv_compare(StringView a, StringView b) {
if (!a.data || !b.data) {
return (!a.data) - (!b.data);
}

size_t min_len = a.length < b.length ? a.length : b.length;
int result = memcmp(a.data, b.data, min_len);

if (result == 0) {
return (int)(a.length - b.length);
}

return result;
}

// 检查字符串视图是否相等
bool sv_equal(StringView a, StringView b) {
return a.length == b.length && memcmp(a.data, b.data, a.length) == 0;
}

// 查找子字符串
ssize_t sv_find(StringView sv, char c) {
if (!sv.data) {
return -1;
}

for (size_t i = 0; i < sv.length; i++) {
if (sv.data[i] == c) {
return (ssize_t)i;
}
}

return -1;
}

// 字符串视图转C字符串
char *sv_to_string(StringView sv) {
if (!sv.data) {
return NULL;
}

char *str = (char *)malloc(sv.length + 1);
if (str) {
memcpy(str, sv.data, sv.length);
str[sv.length] = '\0';
}

return str;
}

// 使用示例
void string_view_example() {
const char *str = "Hello, world!";
StringView sv = sv_create(str);

printf("Length: %zu\n", sv.length);

// 创建子视图
StringView sv_sub = sv_create_from_range(str, 7, 5); // "world"
char *sub_str = sv_to_string(sv_sub);
printf("Substring: %s\n", sub_str);
free(sub_str);

// 查找字符
ssize_t pos = sv_find(sv, ',');
if (pos != -1) {
printf("Found ',' at position: %zd\n", pos);
}
}

7. 指针的高级应用

7.1 内存映射与直接内存访问

内存映射是一种将文件或设备内存映射到进程地址空间的技术,通过指针直接访问映射的内存区域,实现高效的I/O操作。

7.1.1 内存映射的底层实现

  1. 系统调用

    • POSIX系统:mmap()munmap()
    • Windows系统:CreateFileMapping()MapViewOfFile()
    • 内存映射由操作系统和硬件MMU共同实现
  2. 内存映射类型

    • 文件映射:将文件内容映射到内存
    • 匿名映射:创建未关联文件的内存映射
    • 共享映射:多个进程共享同一内存区域
    • 私有映射:进程私有,写时复制
  3. 内存映射的优势

    • 减少数据复制(避免内核空间到用户空间的复制)
    • 支持随机访问大文件
    • 简化文件I/O编程模型
    • 提高I/O性能,特别是对于大文件

7.1.2 内存映射的应用示例

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
// POSIX内存映射示例
#include <sys/mman.h>
#include <sys/stat.h>
#include <fcntl.h>
#include <unistd.h>

void mmap_example() {
int fd = open("large_file.txt", O_RDONLY);
if (fd == -1) {
perror("open");
return;
}

// 获取文件大小
struct stat sb;
if (fstat(fd, &sb) == -1) {
perror("fstat");
close(fd);
return;
}

// 映射文件到内存
void *addr = mmap(NULL, sb.st_size, PROT_READ, MAP_PRIVATE, fd, 0);
if (addr == MAP_FAILED) {
perror("mmap");
close(fd);
return;
}

// 通过指针访问映射的内存
char *data = (char *)addr;
for (size_t i = 0; i < sb.st_size; i++) {
// 处理数据...
if (i % 1000000 == 0) {
printf("Processing byte %zu\n", i);
}
}

// 解除映射
if (munmap(addr, sb.st_size) == -1) {
perror("munmap");
}

close(fd);
}

7.1.3 直接内存访问(DMA)

  1. DMA的原理

    • DMA允许外设直接访问系统内存,无需CPU干预
    • 通过指针操作DMA缓冲区,实现高效的数据传输
    • 适用于高速I/O设备(如网络适配器、磁盘控制器)
  2. DMA缓冲区管理

    • 物理内存连续:DMA需要物理上连续的内存
    • 内存对齐:缓冲区必须按设备要求对齐
    • 缓存一致性:确保CPU缓存与内存同步
  3. DMA的应用示例

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
66
67
68
69
70
// 嵌入式系统中的DMA示例
#define DMA_BUFFER_SIZE 4096
#define DMA_BASE_ADDR 0x40000000
#define DMA_CONTROL_REG 0x40001000
#define DMA_STATUS_REG 0x40001004
#define DMA_SOURCE_REG 0x40001008
#define DMA_DEST_REG 0x4000100C
#define DMA_LENGTH_REG 0x40001010

// 分配DMA缓冲区(物理连续且对齐)
void *allocate_dma_buffer(size_t size) {
// 实际实现依赖于平台
// 这里使用模拟的内存分配
static char dma_buffer[DMA_BUFFER_SIZE] __attribute__((aligned(16)));
return dma_buffer;
}

// 执行DMA传输
void dma_transfer(void *source, void *dest, size_t length) {
// 获取物理地址(实际实现依赖于平台)
uint32_t phys_source = (uint32_t)source;
uint32_t phys_dest = (uint32_t)dest;

// 配置DMA控制器
volatile uint32_t *control_reg = (volatile uint32_t *)(DMA_BASE_ADDR + DMA_CONTROL_REG);
volatile uint32_t *status_reg = (volatile uint32_t *)(DMA_BASE_ADDR + DMA_STATUS_REG);
volatile uint32_t *source_reg = (volatile uint32_t *)(DMA_BASE_ADDR + DMA_SOURCE_REG);
volatile uint32_t *dest_reg = (volatile uint32_t *)(DMA_BASE_ADDR + DMA_DEST_REG);
volatile uint32_t *length_reg = (volatile uint32_t *)(DMA_BASE_ADDR + DMA_LENGTH_REG);

// 等待前一次传输完成
while (*status_reg & 0x1);

// 设置传输参数
*source_reg = phys_source;
*dest_reg = phys_dest;
*length_reg = length;

// 启动传输
*control_reg = 0x1; // 启动位

// 等待传输完成
while (*status_reg & 0x1);

// 检查传输状态
if (*status_reg & 0x2) {
printf("DMA transfer error\n");
} else {
printf("DMA transfer completed successfully\n");
}
}

// 使用示例
void dma_example() {
void *source = allocate_dma_buffer(DMA_BUFFER_SIZE);
void *dest = allocate_dma_buffer(DMA_BUFFER_SIZE);

// 初始化源数据
memset(source, 0xAA, DMA_BUFFER_SIZE);

// 执行DMA传输
dma_transfer(source, dest, DMA_BUFFER_SIZE);

// 验证传输结果
if (memcmp(source, dest, DMA_BUFFER_SIZE) == 0) {
printf("Data transferred correctly\n");
} else {
printf("Data transfer failed\n");
}
}

7.2 指针与多线程编程

指针在多线程编程中扮演着重要角色,用于线程间通信、共享数据访问和同步原语的实现。

7.2.1 线程间共享数据

  1. 共享内存模型

    • 多个线程通过指针访问同一内存区域
    • 需要同步机制(如互斥锁、读写锁)保护共享数据
    • 避免数据竞争和不一致状态
  2. 线程局部存储

    • 使用__thread(GCC)或thread_local(C11)关键字
    • 每个线程拥有变量的独立副本
    • 避免线程间的竞争条件
  3. 原子操作

    • 使用原子指针操作(如atomic_compare_exchange
    • 无锁数据结构的实现基础
    • 提高并发性能

7.2.2 线程安全的数据结构

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
66
67
68
69
70
71
72
73
74
75
76
77
78
79
80
81
82
83
84
85
86
87
88
89
90
91
// 线程安全的单链表
#include <pthread.h>

typedef struct Node {
int data;
struct Node *next;
} Node;

typedef struct {
Node *head;
pthread_mutex_t mutex;
} ThreadSafeList;

// 初始化链表
void list_init(ThreadSafeList *list) {
list->head = NULL;
pthread_mutex_init(&list->mutex, NULL);
}

// 添加节点
void list_add(ThreadSafeList *list, int data) {
Node *new_node = (Node *)malloc(sizeof(Node));
if (!new_node) {
return;
}

new_node->data = data;

pthread_mutex_lock(&list->mutex);
new_node->next = list->head;
list->head = new_node;
pthread_mutex_unlock(&list->mutex);
}

// 查找节点
Node *list_find(ThreadSafeList *list, int data) {
pthread_mutex_lock(&list->mutex);

Node *current = list->head;
while (current) {
if (current->data == data) {
break;
}
current = current->next;
}

pthread_mutex_unlock(&list->mutex);
return current;
}

// 删除节点
bool list_remove(ThreadSafeList *list, int data) {
pthread_mutex_lock(&list->mutex);

Node *current = list->head;
Node *prev = NULL;

while (current) {
if (current->data == data) {
if (prev) {
prev->next = current->next;
} else {
list->head = current->next;
}
free(current);
pthread_mutex_unlock(&list->mutex);
return true;
}
prev = current;
current = current->next;
}

pthread_mutex_unlock(&list->mutex);
return false;
}

// 销毁链表
void list_destroy(ThreadSafeList *list) {
pthread_mutex_lock(&list->mutex);

Node *current = list->head;
while (current) {
Node *next = current->next;
free(current);
current = next;
}

list->head = NULL;
pthread_mutex_unlock(&list->mutex);
pthread_mutex_destroy(&list->mutex);
}

7.2.3 无锁数据结构

  1. 无锁设计原理

    • 使用原子指针操作实现线程安全
    • 避免传统锁的开销和竞争
    • 提高并发性能和可伸缩性
  2. 无锁栈实现

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
// 无锁栈
#include <stdatomic.h>

typedef struct Node {
int data;
struct Node *next;
} Node;

typedef struct {
Node *head;
} LockFreeStack;

// 初始化栈
void stack_init(LockFreeStack *stack) {
stack->head = NULL;
}

// 压栈
void stack_push(LockFreeStack *stack, int data) {
Node *new_node = (Node *)malloc(sizeof(Node));
if (!new_node) {
return;
}

new_node->data = data;

do {
new_node->next = stack->head;
} while (!atomic_compare_exchange_weak(
(atomic_uintptr_t *)&stack->head,
(uintptr_t *)&new_node->next,
(uintptr_t)new_node
));
}

// 出栈
bool stack_pop(LockFreeStack *stack, int *data) {
Node *old_head;

do {
old_head = stack->head;
if (!old_head) {
return false;
}
} while (!atomic_compare_exchange_weak(
(atomic_uintptr_t *)&stack->head,
(uintptr_t *)&old_head,
(uintptr_t)old_head->next
));

*data = old_head->data;
free(old_head);
return true;
}

// 销毁栈
void stack_destroy(LockFreeStack *stack) {
Node *current = stack->head;
while (current) {
Node *next = current->next;
free(current);
current = next;
}
stack->head = NULL;
}

7.3 指针与硬件编程

指针在硬件编程中用于直接访问硬件寄存器、内存映射I/O和设备内存,是嵌入式系统和系统编程的核心工具。

7.3.1 内存映射I/O

  1. MMIO的原理

    • 硬件寄存器映射到内存地址空间
    • 通过指针直接读写硬件寄存器
    • 无需系统调用,实现高效的硬件访问
  2. MMIO的实现

    • 使用volatile关键字确保编译器不优化内存访问
    • 按硬件要求进行内存对齐
    • 处理不同位宽的寄存器访问
  3. MMIO的应用示例

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
// 嵌入式系统中的GPIO控制
#define GPIO_BASE 0x40000000
#define GPIO_DIR 0x00
#define GPIO_OUT 0x04
#define GPIO_IN 0x08

// GPIO寄存器映射
typedef struct {
volatile uint32_t dir; // 方向寄存器
volatile uint32_t out; // 输出寄存器
volatile uint32_t in; // 输入寄存器
} GpioRegs;

#define GPIO ((GpioRegs *)GPIO_BASE)

// 初始化GPIO
void gpio_init() {
// 设置GPIO 0-7为输出
GPIO->dir |= 0xFF;
// 设置GPIO 8-15为输入
GPIO->dir &= ~0xFF00;
}

// 设置GPIO输出
void gpio_set(int pin, bool value) {
if (pin >= 0 && pin < 32) {
if (value) {
GPIO->out |= (1 << pin);
} else {
GPIO->out &= ~(1 << pin);
}
}
}

// 读取GPIO输入
bool gpio_get(int pin) {
if (pin >= 0 && pin < 32) {
return (GPIO->in & (1 << pin)) != 0;
}
return false;
}

// 切换GPIO状态
void gpio_toggle(int pin) {
if (pin >= 0 && pin < 32) {
GPIO->out ^= (1 << pin);
}
}

7.3.2 直接寄存器访问

  1. 寄存器映射

    • 使用结构体映射寄存器组
    • 位字段操作实现精细的寄存器控制
    • 内联汇编实现特殊寄存器访问
  2. 位操作技巧

    • 位设置:reg |= (1 << bit)
    • 位清除:reg &= ~(1 << bit)
    • 位切换:reg ^= (1 << bit)
    • 位测试:(reg & (1 << bit)) != 0
  3. 寄存器访问的安全考量

    • 避免未定义的寄存器访问
    • 处理寄存器访问的副作用
    • 确保寄存器操作的原子性

7.3.3 硬件中断处理

  1. 中断向量表

    • 指针数组存储中断处理函数地址
    • 中断控制器通过向量号索引中断处理函数
    • 实现高效的中断分发
  2. 中断处理函数

    • 使用函数指针注册中断处理程序
    • 中断上下文的特殊要求(如禁止嵌套中断)
    • 中断处理的性能优化
  3. 中断处理示例

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
// 中断处理示例
#define INTERRUPT_COUNT 256

// 中断处理函数类型
typedef void (*InterruptHandler)(void);

// 中断向量表
InterruptHandler interrupt_vector_table[INTERRUPT_COUNT];

// 注册中断处理函数
void register_interrupt_handler(int irq, InterruptHandler handler) {
if (irq >= 0 && irq < INTERRUPT_COUNT) {
interrupt_vector_table[irq] = handler;
}
}

// 中断分发器(由硬件调用)
void interrupt_dispatcher(int irq) {
if (irq >= 0 && irq < INTERRUPT_COUNT && interrupt_vector_table[irq]) {
interrupt_vector_table[irq]();
}
}

// 定时器中断处理函数
void timer_interrupt_handler() {
// 处理定时器中断
printf("Timer interrupt received\n");

// 清除中断标志
// ...
}

// UART中断处理函数
void uart_interrupt_handler() {
// 处理UART中断
printf("UART interrupt received\n");

// 清除中断标志
// ...
}

// 初始化中断系统
void init_interrupt_system() {
// 初始化中断向量表
for (int i = 0; i < INTERRUPT_COUNT; i++) {
interrupt_vector_table[i] = NULL;
}

// 注册中断处理函数
register_interrupt_handler(32, timer_interrupt_handler); // 定时器中断
register_interrupt_handler(33, uart_interrupt_handler); // UART中断

// 启用中断
// ...
}

8. 指针的性能优化

8.1 内存访问模式优化

  1. 局部性原理

    • 时间局部性:最近访问过的内存位置可能很快再次被访问
    • 空间局部性:访问某个内存位置时,其附近的位置也可能被访问
    • 利用局部性原理优化指针访问模式
  2. 缓存优化

    • 预取:提前加载即将访问的数据到缓存
    • 缓存阻塞:调整数据结构以提高缓存命中率
    • 缓存一致性:避免伪共享(false sharing)
  3. 内存访问模式

    • 顺序访问:最佳的内存访问模式,利用预取机制
    • 随机访问:最差的内存访问模式,导致大量缓存未命中
    • 步长访问:步长越小,缓存利用率越高

8.2 指针算术优化

  1. 编译时优化

    • 常量折叠:编译时计算常量指针表达式
    • 强度削弱:将乘法转换为移位操作
    • 循环不变量:将循环外的指针计算移到循环外
  2. 运行时优化

    • 指针递增:比下标访问更高效
    • 边界检查消除:编译器优化掉不必要的边界检查
    • 分支预测:优化指针条件判断
  3. SIMD向量化

    • 连续的指针访问模式有利于向量化
    • 使用SIMD指令并行处理数据
    • 提高数据处理吞吐量

8.3 内存分配优化

  1. 分配策略

    • 小内存:使用内存池或线程本地缓存
    • 大内存:直接使用mmap或类似机制
    • 频繁分配:使用对象池或 slab 分配器
  2. 内存池实现

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
// 简单的内存池
#define BLOCK_SIZE 16
#define POOL_SIZE 1024

typedef struct {
char memory[POOL_SIZE * BLOCK_SIZE];
bool free_blocks[POOL_SIZE];
int free_count;
} MemoryPool;

// 初始化内存池
void pool_init(MemoryPool *pool) {
for (int i = 0; i < POOL_SIZE; i++) {
pool->free_blocks[i] = true;
}
pool->free_count = POOL_SIZE;
}

// 分配内存
void *pool_alloc(MemoryPool *pool) {
if (pool->free_count == 0) {
return NULL;
}

for (int i = 0; i < POOL_SIZE; i++) {
if (pool->free_blocks[i]) {
pool->free_blocks[i] = false;
pool->free_count--;
return &pool->memory[i * BLOCK_SIZE];
}
}

return NULL;
}

// 释放内存
void pool_free(MemoryPool *pool, void *ptr) {
if (!ptr) {
return;
}

// 计算块索引
int index = ((char *)ptr - pool->memory) / BLOCK_SIZE;

if (index >= 0 && index < POOL_SIZE) {
pool->free_blocks[index] = true;
pool->free_count++;
}
}

// 检查内存池状态
void pool_status(MemoryPool *pool) {
printf("Memory pool status: %d free blocks of %d\n",
pool->free_count, POOL_SIZE);
}

8.4 指针别名优化

  1. 指针别名的影响

    • 编译器无法确定两个指针是否指向同一内存位置
    • 限制编译器的优化能力(如加载/存储优化)
    • 降低程序性能
  2. restrict关键字

    • 告诉编译器指针是唯一访问其指向内存的方式
    • 启用更积极的优化
    • 提高程序性能
  3. restrict的使用示例

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
// 使用restrict优化内存复制
void *memcpy_restrict(void *restrict dest, const void *restrict src, size_t size) {
char *d = (char *)dest;
const char *s = (const char *)src;

for (size_t i = 0; i < size; i++) {
d[i] = s[i];
}

return dest;
}

// 使用restrict优化矩阵乘法
void matrix_multiply(const float *restrict a, const float *restrict b,
float *restrict c, int n) {
for (int i = 0; i < n; i++) {
for (int j = 0; j < n; j++) {
float sum = 0.0f;
for (int k = 0; k < n; k++) {
sum += a[i * n + k] * b[k * n + j];
}
c[i * n + j] = sum;
}
}
}

8.5 性能分析与调优

  1. 性能分析工具

    • 硬件性能计数器:分析缓存未命中、分支预测失败等
    • profiling工具:如gprof、perf、VTune
    • 内存分析工具:如Valgrind、AddressSanitizer
  2. 调优策略

    • 识别性能瓶颈:找出最耗时的代码段
    • 优先优化热点路径:关注执行频率高的代码
    • 渐进式优化:小步改进,持续测试
  3. 案例分析

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
// 性能优化案例:矩阵乘法

// 原始实现
void matrix_multiply_naive(const float *a, const float *b, float *c, int n) {
for (int i = 0; i < n; i++) {
for (int j = 0; j < n; j++) {
c[i * n + j] = 0.0f;
for (int k = 0; k < n; k++) {
c[i * n + j] += a[i * n + k] * b[k * n + j];
}
}
}
}

// 优化1:缓存阻塞
void matrix_multiply_blocked(const float *a, const float *b, float *c, int n, int block_size) {
for (int i0 = 0; i0 < n; i0 += block_size) {
for (int j0 = 0; j0 < n; j0 += block_size) {
for (int k0 = 0; k0 < n; k0 += block_size) {
// 处理块
for (int i = i0; i < i0 + block_size && i < n; i++) {
for (int j = j0; j < j0 + block_size && j < n; j++) {
for (int k = k0; k < k0 + block_size && k < n; k++) {
c[i * n + j] += a[i * n + k] * b[k * n + j];
}
}
}
}
}
}
}

// 优化2:使用restrict和寄存器变量
void matrix_multiply_optimized(const float *restrict a, const float *restrict b,
float *restrict c, int n) {
for (int i = 0; i < n; i++) {
register int i_n = i * n;
for (int j = 0; j < n; j++) {
register float sum = 0.0f;
for (int k = 0; k < n; k++) {
sum += a[i_n + k] * b[k * n + j];
}
c[i_n + j] = sum;
}
}
}

9. 指针的安全编程

9.1 常见的指针错误

  1. 空指针解引用

    • 症状:段错误(SIGSEGV)
    • 原因:解引用值为NULL的指针
    • 预防:始终在解引用前检查指针是否为NULL
  2. 野指针

    • 症状:不可预测的行为,可能导致崩溃或数据损坏
    • 原因:使用未初始化的指针或指向已释放内存的指针
    • 预防:始终初始化指针,释放后将其置为NULL
  3. 缓冲区溢出

    • 症状:内存损坏,可能导致崩溃或安全漏洞
    • 原因:写入超出缓冲区边界的数据
    • 预防:使用带长度限制的函数,检查缓冲区大小
  4. 内存泄漏

    • 症状:内存使用量不断增加
    • 原因:分配内存后未释放
    • 预防:使用RAII模式(在C中模拟),使用智能指针
  5. 重复释放

    • 症状:未定义行为,可能导致崩溃
    • 原因:对同一内存块多次调用free
    • 预防:释放后将指针置为NULL,使用内存管理工具
  6. 指针类型错误

    • 症状:数据损坏,类型不匹配
    • 原因:错误的指针类型转换
    • 预防:使用正确的类型转换,避免强制转换

9.2 内存安全工具

  1. 静态分析工具

    • Clang Static Analyzer:检测潜在的内存错误
    • Coverity:全面的静态分析工具
    • PVS-Studio:检测C/C++代码中的错误
  2. 动态分析工具

    • Valgrind:内存调试和内存泄漏检测
    • AddressSanitizer:快速的内存错误检测器
    • LeakSanitizer:内存泄漏检测器
    • UndefinedBehaviorSanitizer:检测未定义行为
  3. 运行时保护

    • 栈保护:检测栈溢出攻击
    • 堆保护:检测堆溢出和使用-after-free
    • ASLR(地址空间布局随机化):增加攻击者的难度
    • DEP(数据执行保护):防止执行数据区域的代码

9.3 安全编码实践

  1. 防御性编程

    • 始终检查指针参数是否为NULL
    • 验证所有输入数据的有效性
    • 假设外部输入都是恶意的
  2. 内存管理最佳实践

    • 使用统一的内存分配和释放策略
    • 实现内存分配跟踪机制
    • 使用内存池减少碎片和提高性能
  3. 代码审查

    • 重点审查指针操作和内存管理代码
    • 使用代码审查工具辅助检查
    • 建立代码审查 checklist
  4. 测试策略

    • 单元测试:测试单个函数的指针操作
    • 集成测试:测试模块间的指针交互
    • 模糊测试:使用随机输入测试内存安全性
    • 压力测试:测试内存使用和性能

9.4 安全指针封装

  1. 智能指针模拟
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
// 简单的智能指针模拟
#define SMART_PTR(type, name) \
typedef struct { \
type *ptr; \
void (*destroy)(type *); \
} name; \
\
void name##_init(name *sp, type *p, void (*d)(type *)) { \
sp->ptr = p; \
sp->destroy = d; \
} \
\
type *name##_get(name *sp) { \
return sp->ptr; \
} \
\
void name##_reset(name *sp, type *p, void (*d)(type *)) { \
if (sp->ptr && sp->destroy) { \
sp->destroy(sp->ptr); \
} \
sp->ptr = p; \
sp->destroy = d; \
} \
\
void name##_destroy(name *sp) { \
if (sp->ptr && sp->destroy) { \
sp->destroy(sp->ptr); \
} \
sp->ptr = NULL; \
sp->destroy = NULL; \
}

// 使用示例
SMART_PTR(int, IntPtr);

void destroy_int(int *p) {
free(p);
}

void smart_ptr_example() {
IntPtr sp;
int *p = (int *)malloc(sizeof(int));
*p = 42;

IntPtr_init(&sp, p, destroy_int);
printf("Value: %d\n", *IntPtr_get(&sp));

// 自动释放内存
IntPtr_destroy(&sp);
}
  1. 安全数组
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
66
67
68
69
70
71
72
73
74
75
76
77
78
79
80
81
82
83
84
85
86
87
88
89
90
91
92
93
94
95
96
97
98
99
100
101
102
103
104
105
106
107
108
109
110
111
112
113
114
115
116
117
118
119
120
121
// 安全数组封装
typedef struct {
void *data;
size_t element_size;
size_t size;
size_t capacity;
} SafeArray;

// 初始化数组
SafeArray *sa_create(size_t element_size, size_t initial_capacity) {
SafeArray *sa = (SafeArray *)malloc(sizeof(SafeArray));
if (!sa) {
return NULL;
}

sa->element_size = element_size;
sa->capacity = initial_capacity > 0 ? initial_capacity : 8;
sa->size = 0;

sa->data = calloc(sa->capacity, element_size);
if (!sa->data) {
free(sa);
return NULL;
}

return sa;
}

// 获取元素
void *sa_get(const SafeArray *sa, size_t index) {
if (!sa || index >= sa->size) {
return NULL;
}
return (char *)sa->data + index * sa->element_size;
}

// 设置元素
bool sa_set(SafeArray *sa, size_t index, const void *value) {
if (!sa || !value || index >= sa->size) {
return false;
}
memcpy((char *)sa->data + index * sa->element_size, value, sa->element_size);
return true;
}

// 添加元素
bool sa_push(SafeArray *sa, const void *value) {
if (!sa || !value) {
return false;
}

// 检查容量
if (sa->size >= sa->capacity) {
size_t new_capacity = sa->capacity * 2;
void *new_data = realloc(sa->data, new_capacity * sa->element_size);
if (!new_data) {
return false;
}
sa->data = new_data;
sa->capacity = new_capacity;
}

// 添加元素
memcpy((char *)sa->data + sa->size * sa->element_size, value, sa->element_size);
sa->size++;
return true;
}

// 移除元素
bool sa_remove(SafeArray *sa, size_t index) {
if (!sa || index >= sa->size) {
return false;
}

// 移动元素
if (index < sa->size - 1) {
memmove((char *)sa->data + index * sa->element_size,
(char *)sa->data + (index + 1) * sa->element_size,
(sa->size - index - 1) * sa->element_size);
}

sa->size--;
return true;
}

// 获取大小
size_t sa_size(const SafeArray *sa) {
return sa ? sa->size : 0;
}

// 销毁数组
void sa_destroy(SafeArray *sa) {
if (sa) {
free(sa->data);
free(sa);
}
}

// 使用示例
void safe_array_example() {
SafeArray *sa = sa_create(sizeof(int), 4);
if (sa) {
int value = 10;
sa_push(sa, &value);

value = 20;
sa_push(sa, &value);

value = 30;
sa_push(sa, &value);

for (size_t i = 0; i < sa_size(sa); i++) {
int *p = (int *)sa_get(sa, i);
if (p) {
printf("Element %zu: %d\n", i, *p);
}
}

sa_destroy(sa);
}
}

10. 指针的未来发展

10.1 现代C语言中的指针特性

  1. C11/C17新特性

    • _Alignas_Alignof:更精细的内存对齐控制
    • thread_local:线程局部存储
    • _Generic:泛型选择表达式
    • 原子类型和操作:stdatomic.h
  2. C23新特性

    • nullptr:空指针常量
    • typeof:类型推断
    • 增强的边界检查
    • 改进的内存安全

10.2 指针与现代硬件

  1. 64位架构

    • 更大的地址空间:支持更大的内存和数据结构
    • 指针大小增加:从4字节到8字节
    • 新的寻址模式:如RIP相对寻址
  2. 多核与NUMA

    • 缓存一致性:指针访问需要考虑缓存一致性协议
    • NUMA优化:本地内存访问比远程内存访问更快
    • 并行编程:无锁数据结构和原子指针操作
  3. 异构计算

    • GPU编程:指针映射到设备内存
    • FPGA集成:硬件加速的指针操作
    • 内存层次结构:多级缓存和内存技术

10.3 指针的替代方案

  1. 引用类型

    • C++中的引用:提供更安全的指针语义
    • 自动解引用:简化代码
    • 不可为空:避免空指针错误
  2. 智能指针

    • C++中的std::unique_ptrstd::shared_ptr
    • 自动内存管理:减少内存泄漏
    • 引用计数:实现共享所有权
  3. 内存安全语言

    • Rust:所有权系统和借用检查器
    • Go:垃圾回收和安全指针
    • Java:引用类型和垃圾回收

10.4 指针的未来趋势

  1. 内存安全

    • 硬件支持的内存安全:如Intel MPX
    • 编译器增强:更严格的指针检查
    • 工具链改进:更好的静态和动态分析
  2. 性能优化

    • 硬件加速:专门的指针算术单元
    • 编译时优化:更智能的指针分析
    • 运行时优化:自适应的内存管理
  3. 编程模型

    • 混合编程:C与内存安全语言的结合
    • 领域特定语言:针对特定领域的指针抽象
    • 元编程:编译时指针操作优化
  4. 安全性与性能的平衡

    • 静态分析与运行时检查的结合
    • 硬件与软件的协同设计
    • 开发者工具与最佳实践的改进

总结

指针是C语言的核心特性,是实现高效、灵活、底层编程的关键。深入理解指针的底层实现、内存模型和操作机制,对于编写高质量的C代码至关重要。

本章节从以下几个方面全面探讨了指针的技术深度:

  1. 基础概念:指针的定义、内存表示、类型系统
  2. 基本操作:解引用、地址运算、指针算术
  3. 高级应用:函数指针、指针数组、多维数组
  4. 内存管理:动态内存分配、内存池、内存映射
  5. 性能优化:缓存优化、SIMD向量化、内存访问模式
  6. 安全编程:常见错误、内存安全工具、防御性编程
  7. 现代发展:C11/C17/C23新特性、硬件适配、替代方案

通过掌握这些知识,开发者可以:

  • 编写更高效、更安全的C代码
  • 更好地理解和优化程序性能
  • 解决复杂的系统编程和嵌入式开发问题
  • 为学习其他系统级语言和技术打下坚实基础

指针是一把双刃剑,既可以实现强大的功能,也可能导致严重的错误。只有通过深入学习和实践,才能真正掌握指针的精髓,发挥其最大潜力,同时避免其带来的风险。

  • 生命周期:程序整个运行期间都存在
  • 唯一性:相同的字符串字面量可能会被编译器优化为同一个内存地址
  • 类型const char[],但在C中允许隐式转换为char*(C++中不允许)
  • 大小:包含空字符,如"Hello"的大小为6字节

示例

1
2
3
4
5
6
7
8
9
10
11
12
13
const char *str1 = "Hello";
const char *str2 = "Hello"; // 可能与str1指向同一地址
printf("str1: %p\n", (void*)str1);
printf("str2: %p\n", (void*)str2);

// 危险:修改字符串字面量
char *str3 = "World"; // C中允许,但不推荐
// *str3 = 'w'; // 未定义行为,可能导致段错误

// 安全的字符串操作
char str4[] = "Hello"; // 存储在栈上,可修改
str4[0] = 'h'; // 合法操作
printf("%s\n", str4); // 输出hello

高级应用

  1. 字符串池化

    1
    2
    3
    4
    5
    6
    7
    // 字符串字面量池化示例
    const char *messages[] = {
    "Error: Invalid parameter",
    "Error: Memory allocation failed",
    "Error: File not found",
    "Error: Invalid parameter" // 与第一个字符串共享内存
    };
  2. 字符串哈希

    1
    2
    3
    4
    5
    6
    7
    8
    9
    // 简单的字符串哈希函数
    unsigned int string_hash(const char *str) {
    unsigned int hash = 5381;
    int c;
    while ((c = *str++)) {
    hash = ((hash << 5) + hash) + c; // hash * 33 + c
    }
    return hash;
    }
  3. 字符串视图

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    // 字符串视图结构(避免复制)
    typedef struct {
    const char *data;
    size_t length;
    } StringView;

    StringView make_string_view(const char *str) {
    StringView view;
    view.data = str;
    view.length = strlen(str);
    return view;
    }

性能考量

  • 字符串长度计算strlen() 是线性时间复杂度,避免在循环中重复调用
  • 字符串比较strcmp() 是线性时间复杂度,对长字符串可能影响性能
  • 内存分配:避免频繁分配和释放字符串内存,考虑使用内存池
  • 缓存局部性:连续的字符串操作有利于缓存利用

安全最佳实践

  • 始终使用const:对于字符串字面量,使用const char*类型
  • 避免修改:不要尝试修改字符串字面量
  • 边界检查:在字符串操作中始终进行边界检查
  • 使用安全函数:使用strncpy()snprintf()等带边界检查的函数
  • 编码处理:注意字符串的编码格式(ASCII、UTF-8等)

标准合规性

  • C标准规定字符串字面量的类型为char[],但建议视为const char[]
  • C99和C11允许使用宽字符串字面量(L"Hello"
  • C11引入了UTF-8字符串字面量(u8"Hello")和通用字符名

编码系统深度分析

  1. ASCII编码

    • 7位编码,共128个字符
    • 0-31为控制字符,32-126为可打印字符
    • 单字节表示,处理简单高效
  2. 扩展ASCII

    • 8位编码,共256个字符
    • 不同地区有不同的编码方案(如ISO-8859-1)
    • 仍为单字节编码,但字符集更大
  3. Unicode编码

    • UTF-8:变长编码,1-4字节,兼容ASCII
    • UTF-16:变长编码,2或4字节
    • UTF-32:定长编码,4字节
    • 支持全球所有字符
  4. C语言中的编码支持

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    // C11 Unicode支持
    #include <uchar.h>

    // UTF-8字符串
    const char *utf8_str = u8"Hello 世界";

    // UTF-16字符串
    const char16_t *utf16_str = u"Hello 世界";

    // UTF-32字符串
    const char32_t *utf32_str = U"Hello 世界";

字符串处理的性能优化

  1. 向量化字符串操作

    1
    2
    3
    4
    5
    6
    7
    8
    9
    // 使用SIMD指令优化字符串长度计算
    size_t vectorized_strlen(const char *str) {
    // 简化实现,实际需要使用SIMD指令
    const char *p = str;
    while (*p) {
    p++;
    }
    return p - str;
    }
  2. 字符串操作的内存对齐

    • 确保字符串操作的起始地址对齐到缓存行边界
    • 对于频繁访问的字符串,考虑使用对齐分配
  3. 字符串池

    • 对于重复出现的字符串,使用字符串池减少内存使用
    • 提高字符串比较的性能(通过指针比较)

6.2 指针操作字符串

使用指针操作字符串是C语言中最常见的字符串处理方式,也是许多字符串函数的实现基础,涉及底层内存操作和性能优化:

1
2
3
4
5
6
7
8
char str[] = "Hello";
char *p = str;

while (*p != '\0') {
printf("%c", *p);
p++;
}
printf("\n"); // 输出Hello

底层实现

  1. 字符串操作的汇编级实现

    • 字符串长度计算:使用repne scasb指令(x86)
    • 字符串复制:使用rep movsb指令(x86)
    • 字符串比较:使用repne cmpsb指令(x86)
    • 这些指令是硬件加速的,比软件实现更快
  2. 内存访问模式

    • 字符串操作通常是顺序内存访问,有利于CPU缓存预取
    • 连续的字符串操作可以利用SIMD指令并行处理
  3. 编译器优化

    • 现代编译器会自动将简单的字符串操作优化为硬件指令
    • 对于复杂的字符串操作,编译器可能会使用向量化技术

高级字符串操作实现

  1. 字符串长度计算

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    17
    18
    19
    20
    // 优化的strlen实现
    size_t optimized_strlen(const char *s) {
    const char *p = s;

    // 按字长处理,提高性能
    while ((uintptr_t)p % sizeof(long)) {
    if (!*p) return p - s;
    p++;
    }

    // 使用长整型比较,一次检查多个字节
    const long *lp = (const long *)p;
    while (*lp) lp++;

    // 回退到字节级检查
    p = (const char *)lp;
    while (*p) p++;

    return p - s;
    }
  2. 字符串复制

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    17
    18
    19
    20
    21
    22
    23
    24
    25
    26
    27
    28
    29
    30
    31
    32
    33
    34
    35
    36
    37
    // 高性能字符串复制
    char *fast_strcpy(char *dest, const char *src) {
    char *ret = dest;

    // 按字长复制(如果对齐)
    if (((uintptr_t)dest % sizeof(long) == 0) &&
    ((uintptr_t)src % sizeof(long) == 0)) {
    while (*(const long *)src) {
    *(long *)dest = *(const long *)src;
    dest += sizeof(long);
    src += sizeof(long);
    }
    }

    // 复制剩余字节
    while ((*dest++ = *src++));

    return ret;
    }

    // 安全的字符串复制(带边界检查)
    char *safe_strncpy(char *dest, const char *src, size_t n) {
    char *p = dest;
    size_t i = 0;

    while (i < n && (*p++ = *src++) != '\0') {
    i++;
    }

    // 填充剩余空间为\0
    while (i < n) {
    *p++ = '\0';
    i++;
    }

    return dest;
    }
  3. 字符串连接

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    // 高性能字符串连接
    char *fast_strcat(char *dest, const char *src) {
    char *p = dest;

    // 找到目标字符串末尾
    while (*p) p++;

    // 复制源字符串
    while ((*p++ = *src++));

    return dest;
    }
  4. 字符串比较

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    // 高性能字符串比较
    int fast_strcmp(const char *s1, const char *s2) {
    // 按字长比较
    while (*s1 && *s2 && *(const long *)s1 == *(const long *)s2) {
    s1 += sizeof(long);
    s2 += sizeof(long);
    }

    // 回退到字节级比较
    while (*s1 && *s2 && *s1 == *s2) {
    s1++;
    s2++;
    }

    return (unsigned char)*s1 - (unsigned char)*s2;
    }

高级字符串操作技巧

  1. 字符串反转

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    17
    18
    19
    20
    21
    22
    23
    24
    25
    26
    27
    28
    29
    void reverse_string(char *str) {
    if (!str) return;

    char *start = str;
    char *end = str + strlen(str) - 1;
    char temp;

    while (start < end) {
    temp = *start;
    *start++ = *end;
    *end-- = temp;
    }
    }

    // 优化版:不使用strlen
    void reverse_string_optimized(char *str) {
    if (!str) return;

    char *end = str;
    while (*end) end++;
    end--; // 指向最后一个字符

    char temp;
    while (str < end) {
    temp = *str;
    *str++ = *end;
    *end-- = temp;
    }
    }
  2. 字符串分割

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    17
    18
    19
    20
    21
    22
    23
    24
    25
    26
    27
    28
    29
    30
    31
    32
    33
    34
    35
    36
    37
    38
    39
    40
    41
    42
    43
    44
    45
    46
    47
    48
    49
    50
    51
    52
    53
    54
    55
    56
    57
    58
    59
    60
    61
    62
    63
    64
    65
    66
    67
    68
    69
    char **split_string(const char *str, const char *delimiter, int *count) {
    if (!str || !delimiter) return NULL;

    // 计算分割后的字符串数量
    int num_parts = 0;
    const char *p = str;
    size_t delimiter_len = strlen(delimiter);

    while ((p = strstr(p, delimiter)) != NULL) {
    num_parts++;
    p += delimiter_len;
    }
    num_parts++; // 最后一部分

    if (count) {
    *count = num_parts;
    }

    // 分配结果数组
    char **result = (char **)malloc(sizeof(char *) * num_parts);
    if (!result) return NULL;

    // 执行分割
    p = str;
    int i = 0;
    const char *next;

    while (i < num_parts - 1) {
    next = strstr(p, delimiter);
    size_t len = next - p;
    result[i] = (char *)malloc(len + 1);
    if (!result[i]) {
    // 清理已分配的内存
    for (int j = 0; j < i; j++) {
    free(result[j]);
    }
    free(result);
    return NULL;
    }
    strncpy(result[i], p, len);
    result[i][len] = '\0';
    p = next + delimiter_len;
    i++;
    }

    // 处理最后一部分
    size_t len = strlen(p);
    result[i] = (char *)malloc(len + 1);
    if (!result[i]) {
    // 清理已分配的内存
    for (int j = 0; j < i; j++) {
    free(result[j]);
    }
    free(result);
    return NULL;
    }
    strcpy(result[i], p);

    return result;
    }

    // 使用示例
    void free_split_result(char **result, int count) {
    if (!result) return;
    for (int i = 0; i < count; i++) {
    free(result[i]);
    }
    free(result);
    }
  3. 字符串格式化

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    17
    18
    19
    20
    21
    22
    23
    24
    25
    26
    27
    28
    29
    // 安全的字符串格式化(避免缓冲区溢出)
    int safe_sprintf(char *buffer, size_t size, const char *format, ...) {
    va_list args;
    va_start(args, format);
    int result = vsnprintf(buffer, size, format, args);
    va_end(args);
    return result;
    }

    // 动态字符串格式化
    char *dynamic_sprintf(const char *format, ...) {
    va_list args;
    va_start(args, format);

    // 计算所需缓冲区大小
    int size = vsnprintf(NULL, 0, format, args);
    va_end(args);

    // 分配内存
    char *buffer = (char *)malloc(size + 1);
    if (!buffer) return NULL;

    // 执行格式化
    va_start(args, format);
    vsnprintf(buffer, size + 1, format, args);
    va_end(args);

    return buffer;
    }
  4. 字符串搜索

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    17
    18
    19
    20
    21
    22
    23
    24
    25
    26
    27
    28
    29
    30
    // Boyer-Moore字符串搜索算法(高效)
    const char *boyer_moore_search(const char *haystack, size_t haystack_len,
    const char *needle, size_t needle_len) {
    if (needle_len == 0) return haystack;
    if (haystack_len < needle_len) return NULL;

    // 构建坏字符表
    size_t bad_char[256];
    for (size_t i = 0; i < 256; i++) {
    bad_char[i] = needle_len;
    }
    for (size_t i = 0; i < needle_len - 1; i++) {
    bad_char[(unsigned char)needle[i]] = needle_len - 1 - i;
    }

    // 搜索
    size_t i = 0;
    while (i <= haystack_len - needle_len) {
    size_t j = needle_len - 1;
    while (j >= 0 && haystack[i + j] == needle[j]) {
    j--;
    }
    if (j < 0) {
    return haystack + i; // 找到匹配
    }
    i += bad_char[(unsigned char)haystack[i + j]];
    }

    return NULL; // 未找到
    }

性能优化策略

  1. 内存对齐

    • 确保字符串操作的起始地址对齐到缓存行边界
    • 使用aligned_alloc分配对齐的内存
  2. 向量化

    • 使用SIMD指令(如SSE、AVX)加速字符串操作
    • 对于长字符串,向量化可以提供数倍的性能提升
  3. 缓存优化

    • 减少字符串操作中的缓存未命中
    • 对于频繁访问的字符串,考虑使用缓存
  4. 算法选择

    • 对于短字符串,使用简单的线性算法
    • 对于长字符串,使用更高效的算法(如Boyer-Moore)

安全最佳实践

  1. 边界检查

    • 始终检查字符串操作的边界
    • 使用带n后缀的函数(如strncpystrncat
  2. 输入验证

    • 验证所有用户输入的字符串
    • 检查字符串长度,避免缓冲区溢出
  3. 内存管理

    • 正确管理动态分配的字符串内存
    • 避免内存泄漏和双重释放
  4. 编码处理

    • 正确处理不同编码的字符串(ASCII、UTF-8等)
    • 避免字符集转换错误

标准库扩展

  1. POSIX扩展函数

    • strdup:复制字符串并分配内存
    • strndup:复制指定长度的字符串
    • strtok_r:可重入的字符串分割函数
  2. GNU扩展函数

    • asprintf:动态分配内存的字符串格式化
    • strcasestr:大小写不敏感的字符串搜索

字符串与指针的关系

  • 字符串本质上是字符数组,数组名衰减为指向第一个字符的指针
  • 字符串操作函数通常接受char*类型的参数
  • 指针算术是字符串操作的基础,如遍历、查找、复制等
  • 理解指针与字符串的关系是掌握C语言字符串处理的关键
  • 高级字符串处理技术依赖于对指针操作的深入理解

7. 复杂指针类型

7.1 指针的指针

指针的指针(Double Pointer)是指向指针的指针,常用于需要在函数中修改指针变量本身的场景,是实现多级间接寻址和动态数据结构的关键:

1
2
3
4
5
int num = 10;
int *p = &num;
int **pp = &p; // pp是指向p的指针

printf("%d\n", **pp); // 输出10

底层实现

  1. 内存布局

    • num:存储整数值 10(如地址 0x1000)
    • p:存储 num 的地址 0x1000(如地址 0x2000)
    • pp:存储 p 的地址 0x2000(如地址 0x3000)
  2. 访问机制

    • *pp 访问 p 的值(0x1000)
    • **pp 访问 num 的值(10)
  3. 类型系统

    • int** 类型表示指向 int* 类型的指针
    • 不同级别的指针类型是不兼容的

高级应用

  1. 函数中修改指针

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    17
    18
    19
    20
    21
    22
    23
    // 在函数中分配内存并更新调用者的指针
    int allocate_memory(int **ptr, size_t size) {
    *ptr = (int *)malloc(size * sizeof(int));
    if (!*ptr) {
    return -1; // 分配失败
    }
    return 0; // 成功
    }

    int main() {
    int *arr = NULL;
    size_t size = 5;

    if (allocate_memory(&arr, size) == 0) {
    // 使用arr
    for (size_t i = 0; i < size; i++) {
    arr[i] = i + 1;
    }

    free(arr);
    }
    return 0;
    }
  2. 动态二维数组

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    17
    18
    19
    20
    21
    22
    23
    24
    25
    26
    27
    28
    29
    30
    // 创建动态二维数组
    int **create_2d_array(size_t rows, size_t cols) {
    // 分配行指针数组
    int **arr = (int **)malloc(rows * sizeof(int *));
    if (!arr) return NULL;

    // 分配每一行的数据
    for (size_t i = 0; i < rows; i++) {
    arr[i] = (int *)malloc(cols * sizeof(int));
    if (!arr[i]) {
    // 清理已分配的内存
    for (size_t j = 0; j < i; j++) {
    free(arr[j]);
    }
    free(arr);
    return NULL;
    }
    }

    return arr;
    }

    void free_2d_array(int **arr, size_t rows) {
    if (!arr) return;

    for (size_t i = 0; i < rows; i++) {
    free(arr[i]);
    }
    free(arr);
    }
  3. 二维字符串数组

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    17
    18
    19
    20
    21
    22
    23
    // 二维字符串数组(指针的指针)
    const char **create_string_array(size_t size) {
    const char **arr = (const char **)malloc(size * sizeof(const char *));
    if (!arr) return NULL;

    // 初始化字符串
    for (size_t i = 0; i < size; i++) {
    char buffer[20];
    snprintf(buffer, sizeof(buffer), "String %zu", i + 1);
    arr[i] = strdup(buffer); // 复制字符串
    }

    return arr;
    }

    void free_string_array(const char **arr, size_t size) {
    if (!arr) return;

    for (size_t i = 0; i < size; i++) {
    free((void *)arr[i]);
    }
    free(arr);
    }
  4. 命令行参数处理

    1
    2
    3
    4
    5
    6
    7
    int main(int argc, char *argv[]) {
    // argv是指向指针的指针,指向命令行参数
    for (int i = 0; i < argc; i++) {
    printf("argv[%d]: %s\n", i, argv[i]);
    }
    return 0;
    }
  5. 链表的链表

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    17
    18
    19
    20
    21
    22
    23
    24
    25
    // 链表节点
    typedef struct Node {
    int data;
    struct Node *next;
    } Node;

    // 链表的链表(用于哈希表等)
    typedef struct {
    Node **buckets;
    size_t size;
    } HashTable;

    HashTable *create_hash_table(size_t size) {
    HashTable *table = (HashTable *)malloc(sizeof(HashTable));
    if (!table) return NULL;

    table->size = size;
    table->buckets = (Node **)calloc(size, sizeof(Node *));
    if (!table->buckets) {
    free(table);
    return NULL;
    }

    return table;
    }

性能优化策略

  1. 内存布局优化

    • 对于二维数组,考虑使用连续内存布局而非指针的指针
    • 连续内存布局具有更好的缓存局部性
  2. 缓存优化

    • 减少指针的指针带来的间接寻址
    • 对于频繁访问的数据,考虑使用局部变量缓存
  3. 内存分配优化

    • 对于动态二维数组,考虑一次性分配连续内存
    • 减少内存分配次数,提高性能

安全最佳实践

  1. 边界检查

    • 对于指针的指针数组,确保索引在有效范围内
    • 避免越界访问导致的未定义行为
  2. 内存管理

    • 正确管理多级指针的内存分配和释放
    • 避免内存泄漏和悬垂指针
  3. 类型安全

    • 使用typedef定义复杂指针类型,提高代码可读性
    • 避免强制转换不同级别的指针类型

标准合规性

  • C标准允许任意级别的指针间接寻址
  • C99和C11对指针的指针使用没有特殊限制
  • 注意:过度使用指针的指针可能会降低代码可读性,应谨慎使用

7.2 指向函数的指针

指向函数的指针是C语言中实现回调机制、多态行为和运行时函数选择的关键,是构建灵活可扩展系统的基础:

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
int (*operation)(int, int);

int add(int a, int b) {
return a + b;
}

int subtract(int a, int b) {
return a - b;
}

int main() {
operation = add;
printf("5 + 3 = %d\n", operation(5, 3)); // 输出8

operation = subtract;
printf("5 - 3 = %d\n", operation(5, 3)); // 输出2

return 0;
}

底层实现

  1. 内存表示

    • 函数指针存储函数在内存中的入口地址
    • 函数指针指向代码段(.text section)中的可执行指令
    • 不同调用约定的函数指针类型是不兼容的
  2. 调用机制

    • 函数指针调用与直接函数调用遵循相同的调用约定
    • 函数指针调用通常不能被内联,可能导致轻微的性能损失
  3. 类型系统

    • 函数指针类型包含返回类型和参数类型信息
    • 不同类型的函数指针是不兼容的

高级应用

  1. 函数指针数组与分发表

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    17
    18
    19
    20
    21
    22
    23
    24
    25
    26
    27
    28
    29
    30
    31
    32
    33
    34
    35
    36
    37
    38
    39
    40
    41
    42
    43
    44
       // 数学运算函数
    double add(double a, double b) { return a + b; }
    double subtract(double a, double b) { return a - b; }
    double multiply(double a, double b) { return a * b; }
    double divide(double a, double b) { return b != 0 ? a / b : 0; }

    // 函数指针数组(分发表)
    typedef double (*MathFunc)(double, double);
    MathFunc math_operations[] = {
    add,
    subtract,
    multiply,
    divide
    };

    // 操作符名称
    const char *operation_names[] = {
    "addition",
    "subtraction",
    "multiplication",
    "division"
    };

    // 操作符到函数的映射
    MathFunc get_operation(char op) {
    switch (op) {
    case '+': return add;
    case '-': return subtract;
    case '*': return multiply;
    case '/': return divide;
    default: return NULL;
    }
    }

    int main() {
    double a = 10.0, b = 5.0;

    for (size_t i = 0; i < sizeof(math_operations) / sizeof(math_operations[0]); i++) {
    double result = math_operations[i](a, b);
    printf("%s: %.2f\n", operation_names[i], result);
    }

    return 0;
    }
  2. 函数指针作为结构体成员

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    17
    18
    19
    20
    21
    22
    23
    24
    25
    26
    27
    28
    29
    30
    31
    32
    33
    34
    35
    36
    37
    38
    39
    40
    41
    42
    43
    44
    45
    46
    47
    48
    49
    50
    51
    52
    53
    54
    55
    56
    57
    58
    59
    60
    61
    62
    63
    64
    65
    66
    67
    68
    69
    70
    71
    72
       // 排序算法结构体
    typedef struct {
    const char *name;
    void (*sort)(int *, size_t);
    double (*benchmark)(int *, size_t); // 性能基准测试
    } SortAlgorithm;

    // 冒泡排序
    void bubble_sort(int *arr, size_t size) {
    for (size_t i = 0; i < size - 1; i++) {
    for (size_t j = 0; j < size - i - 1; j++) {
    if (arr[j] > arr[j + 1]) {
    int temp = arr[j];
    arr[j] = arr[j + 1];
    arr[j + 1] = temp;
    }
    }
    }
    }

    // 选择排序
    void selection_sort(int *arr, size_t size) {
    for (size_t i = 0; i < size - 1; i++) {
    size_t min_idx = i;
    for (size_t j = i + 1; j < size; j++) {
    if (arr[j] < arr[min_idx]) {
    min_idx = j;
    }
    }
    if (min_idx != i) {
    int temp = arr[i];
    arr[i] = arr[min_idx];
    arr[min_idx] = temp;
    }
    }
    }

    // 排序算法数组
    SortAlgorithm sort_algorithms[] = {
    {"Bubble Sort", bubble_sort, NULL},
    {"Selection Sort", selection_sort, NULL}
    };

    // 测试排序算法
    void test_sort_algorithm(SortAlgorithm algo, int *arr, size_t size) {
    int *test_arr = (int *)malloc(size * sizeof(int));
    if (!test_arr) return;

    memcpy(test_arr, arr, size * sizeof(int));

    printf("Testing %s:\n", algo.name);
    printf("Before: ");
    for (size_t i = 0; i < size; i++) {
    printf("%d ", test_arr[i]);
    }
    printf("\n");

    // 计时
    clock_t start = clock();
    algo.sort(test_arr, size);
    clock_t end = clock();
    double time_taken = ((double)(end - start)) / CLOCKS_PER_SEC;

    printf("After: ");
    for (size_t i = 0; i < size; i++) {
    printf("%d ", test_arr[i]);
    }
    printf("\n");
    printf("Time taken: %.6f seconds\n\n", time_taken);

    free(test_arr);
    }
  3. 回调函数系统

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    17
    18
    19
    20
    21
    22
    23
    24
    25
    26
    27
    28
    29
    30
    31
    32
    33
    34
    35
    36
    37
    38
    39
    // 事件系统
    typedef enum {
    EVENT_KEY_PRESS,
    EVENT_MOUSE_CLICK,
    EVENT_TIMER,
    EVENT_NETWORK
    } EventType;

    typedef struct {
    EventType type;
    void *data;
    } Event;

    typedef void (*EventHandler)(Event *event);

    // 事件监听器
    typedef struct {
    EventType type;
    EventHandler handler;
    void *user_data;
    } EventListener;

    // 注册事件监听器
    void register_listener(EventListener *listeners, size_t *count,
    EventType type, EventHandler handler, void *user_data) {
    listeners[*count].type = type;
    listeners[*count].handler = handler;
    listeners[*count].user_data = user_data;
    (*count)++;
    }

    // 触发事件
    void trigger_event(EventListener *listeners, size_t count, Event *event) {
    for (size_t i = 0; i < count; i++) {
    if (listeners[i].type == event->type) {
    listeners[i].handler(event);
    }
    }
    }
  4. 状态机实现

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    17
    18
    19
    20
    21
    22
    23
    24
    25
    26
    27
    28
    29
    30
    31
    32
    33
    34
    35
    36
    37
    38
    39
    40
    41
    42
    43
    44
    45
    46
    47
    48
    // 状态机
    typedef enum {
    STATE_OFF,
    STATE_ON,
    STATE_STANDBY
    } State;

    typedef struct {
    State current_state;
    int counter;
    } StateMachineContext;

    typedef State (*StateHandler)(StateMachineContext *ctx);

    // 状态处理函数
    State handle_off(StateMachineContext *ctx) {
    printf("Entering OFF state\n");
    ctx->counter = 0;
    return STATE_STANDBY;
    }

    State handle_on(StateMachineContext *ctx) {
    printf("Entering ON state\n");
    ctx->counter++;
    if (ctx->counter >= 5) {
    return STATE_OFF;
    }
    return STATE_ON;
    }

    State handle_standby(StateMachineContext *ctx) {
    printf("Entering STANDBY state\n");
    return STATE_ON;
    }

    // 状态表
    StateHandler state_handlers[] = {
    handle_off,
    handle_on,
    handle_standby
    };

    // 运行状态机
    void run_state_machine(StateMachineContext *ctx, size_t iterations) {
    for (size_t i = 0; i < iterations; i++) {
    ctx->current_state = state_handlers[ctx->current_state](ctx);
    }
    }
  5. 动态库函数加载

    1
    2
    3
    4
    5
    6
    7
    8
    9
    10
    11
    12
    13
    14
    15
    16
    17
    18
    19
    20
    21
    22
    23
    24
    25
    26
    27
    28
    29
    30
    31
    32
    33
    // 动态加载插件
    typedef struct {
    void *handle;
    const char *name;
    int (*initialize)(void);
    void (*process)(void *data);
    void (*shutdown)(void);
    } Plugin;

    Plugin *load_plugin(const char *path) {
    Plugin *plugin = (Plugin *)malloc(sizeof(Plugin));
    if (!plugin) return NULL;

    // 加载动态库
    plugin->handle = dlopen(path, RTLD_LAZY);
    if (!plugin->handle) {
    free(plugin);
    return NULL;
    }

    // 获取函数指针
    plugin->initialize = dlsym(plugin->handle, "initialize");
    plugin->process = dlsym(plugin->handle, "process");
    plugin->shutdown = dlsym(plugin->handle, "shutdown");

    if (!plugin->initialize || !plugin->process || !plugin->shutdown) {
    dlclose(plugin->handle);
    free(plugin);
    return NULL;
    }

    return plugin;
    }

性能优化策略

  1. 内联与函数指针权衡

    • 对于性能关键路径,考虑使用宏或模板替代函数指针
    • 对于频繁调用的函数指针,考虑使用分支预测优化
  2. 缓存优化

    • 相关的函数应放在一起,提高指令缓存命中率
    • 避免在热路径中使用指向不同内存区域的函数指针
  3. 编译时优化

    • 使用__attribute__((hot))标记频繁调用的函数
    • 启用链接时优化(LTO)以提高函数指针调用的性能
  4. 分支预测

    • 函数指针调用可能导致分支预测失败
    • 对于固定模式的函数指针调用,考虑使用计算跳转

安全最佳实践

  1. 函数指针验证

    • 在调用函数指针前检查是否为NULL
    • 对于动态获取的函数指针,验证其有效性
  2. 类型安全

    • 使用typedef定义函数指针类型,提高类型安全性
    • 避免强制转换不同类型的函数指针
  3. 内存管理

    • 对于动态加载的函数指针,确保正确管理库的加载和卸载
    • 避免使用已卸载库中的函数指针
  4. 边界检查

    • 对于函数指针数组,确保索引在有效范围内
    • 避免越界访问导致的未定义行为

标准合规性

  • C标准允许函数指针的声明、赋值和调用
  • C99和C11对函数指针的使用没有特殊限制
  • 注意:函数指针与数据指针的转换是实现定义的,可能不兼容

7.3 指向结构体的指针

指向结构体的指针用于存储结构体的地址,是C语言中处理复杂数据结构的基础:

1
2
3
4
5
6
7
8
9
10
11
12
13
14
typedef struct {
int id;
char *name;
} Person;

int main() {
Person person = {1, "John"};
Person *p = &person;

printf("ID: %d\n", p->id); // 输出1
printf("Name: %s\n", p->name); // 输出John

return 0;
}

结构体指针的内存布局与对齐

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
// 结构体定义
typedef struct {
char c; // 1字节
int i; // 4字节
double d; // 8字节
} MyStruct;

int main() {
printf("Size of MyStruct: %zu\n", sizeof(MyStruct)); // 输出16(由于内存对齐)

MyStruct s = {'A', 42, 3.14};
MyStruct *p = &s;

printf("Offset of c: %zu\n", offsetof(MyStruct, c)); // 输出0
printf("Offset of i: %zu\n", offsetof(MyStruct, i)); // 输出4(对齐到4字节边界)
printf("Offset of d: %zu\n", offsetof(MyStruct, d)); // 输出8(对齐到8字节边界)

return 0;
}

内存对齐的原因

  • 性能优化:许多CPU架构访问对齐的内存地址比非对齐地址更快
  • 硬件要求:某些CPU架构不支持非对齐的内存访问,会导致硬件异常

高级应用

  1. 结构体指针与链表
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
// 单向链表节点
typedef struct Node {
int data;
struct Node *next;
} Node;

// 创建新节点
Node *create_node(int data) {
Node *node = (Node *)malloc(sizeof(Node));
if (!node) return NULL;

node->data = data;
node->next = NULL;
return node;
}

// 插入节点到链表头部
Node *insert_front(Node *head, int data) {
Node *new_node = create_node(data);
if (!new_node) return head;

new_node->next = head;
return new_node;
}

// 遍历链表
void traverse_list(Node *head) {
Node *current = head;
while (current) {
printf("%d ", current->data);
current = current->next;
}
printf("\n");
}

// 释放链表
void free_list(Node *head) {
Node *current = head;
while (current) {
Node *next = current->next;
free(current);
current = next;
}
}
  1. 结构体指针与二叉树
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
// 二叉树节点
typedef struct TreeNode {
int data;
struct TreeNode *left;
struct TreeNode *right;
} TreeNode;

// 创建新节点
TreeNode *create_tree_node(int data) {
TreeNode *node = (TreeNode *)malloc(sizeof(TreeNode));
if (!node) return NULL;

node->data = data;
node->left = NULL;
node->right = NULL;
return node;
}

// 插入节点到二叉搜索树
TreeNode *insert_bst(TreeNode *root, int data) {
if (!root) {
return create_tree_node(data);
}

if (data < root->data) {
root->left = insert_bst(root->left, data);
} else if (data > root->data) {
root->right = insert_bst(root->right, data);
}

return root;
}

// 中序遍历二叉搜索树
void inorder_traversal(TreeNode *root) {
if (root) {
inorder_traversal(root->left);
printf("%d ", root->data);
inorder_traversal(root->right);
}
}

// 释放二叉树
void free_tree(TreeNode *root) {
if (root) {
free_tree(root->left);
free_tree(root->right);
free(root);
}
}
  1. 结构体指针与内存池
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
// 内存池节点
typedef struct PoolNode {
struct PoolNode *next;
char data[0]; // 柔性数组成员
} PoolNode;

// 内存池
typedef struct {
PoolNode *free_list;
size_t block_size;
size_t alignment;
} MemoryPool;

// 初始化内存池
void pool_init(MemoryPool *pool, size_t block_size, size_t alignment) {
pool->free_list = NULL;
pool->block_size = block_size;
pool->alignment = alignment;
}

// 从内存池分配内存
void *pool_alloc(MemoryPool *pool) {
if (pool->free_list) {
// 从自由列表中获取内存块
PoolNode *node = pool->free_list;
pool->free_list = node->next;
return node->data;
}

// 分配新的内存块
size_t total_size = sizeof(PoolNode) + pool->block_size;
// 对齐内存分配
PoolNode *node = (PoolNode *)aligned_alloc(pool->alignment, total_size);
if (!node) return NULL;

return node->data;
}

// 释放内存到内存池
void pool_free(MemoryPool *pool, void *ptr) {
if (!ptr) return;

// 将内存块添加到自由列表
PoolNode *node = (PoolNode *)((char *)ptr - sizeof(PoolNode));
node->next = pool->free_list;
pool->free_list = node;
}

// 销毁内存池
void pool_destroy(MemoryPool *pool) {
PoolNode *current = pool->free_list;
while (current) {
PoolNode *next = current->next;
free(current);
current = next;
}
pool->free_list = NULL;
}

8. 指针的高级应用

8.1 动态内存分配

指针与动态内存分配密切相关:

1
2
3
4
5
6
7
8
9
10
11
12
13
int *arr = (int *)malloc(5 * sizeof(int));
if (arr) {
for (int i = 0; i < 5; i++) {
arr[i] = i + 1;
}

for (int i = 0; i < 5; i++) {
printf("%d ", arr[i]);
}
printf("\n");

free(arr);
}

8.2 内存模型

C语言中的内存分为以下几个区域:

  • 代码区:存储程序的可执行指令
  • 全局/静态区:存储全局变量和静态变量
  • 栈区:存储函数的局部变量和函数参数
  • 堆区:存储动态分配的内存

8.3 指针与内存管理

使用指针时需要注意内存管理:

  • 避免野指针:指针未初始化或已释放后仍被使用
  • 避免内存泄漏:动态分配的内存未释放
  • 避免悬垂指针:指针指向的内存已被释放
  • 避免指针越界:指针访问了超出分配范围的内存

9. 指针的最佳实践

9.1 指针使用规范

  1. 始终初始化指针:避免使用未初始化的指针
  2. 使用NULL表示空指针:便于检查指针是否有效
  3. 避免指针算术运算错误:确保指针运算在有效范围内
  4. 正确释放动态内存:避免内存泄漏
  5. 使用const修饰符:对于不需要修改的指针指向的数据,使用const修饰

9.2 指针与安全性

  1. 避免缓冲区溢出:确保指针操作不会超出缓冲区边界
  2. 使用安全的内存分配函数:如callocrealloc
  3. 定期检查指针有效性:在使用指针前检查其是否为NULL
  4. 避免使用全局指针:减少指针的作用域
  5. 使用智能指针:在C++中使用智能指针管理内存

10. 常见指针错误

10.1 野指针

未初始化的指针:

1
2
int *p;    // 野指针
*p = 10; // 未定义行为

10.2 悬垂指针

指针指向的内存已被释放:

1
2
3
int *p = (int *)malloc(sizeof(int));
free(p);
*p = 10; // 未定义行为

10.3 内存泄漏

动态分配的内存未释放:

1
2
3
4
void func() {
int *p = (int *)malloc(sizeof(int));
// 未释放p
}

10.4 指针越界

指针访问了超出分配范围的内存:

1
2
3
int *p = (int *)malloc(5 * sizeof(int));
p[10] = 10; // 未定义行为
free(p);

11. 指针与现代C语言

11.1 C99和C11中的指针特性

  • ** restrict关键字**:用于告诉编译器指针是唯一访问其指向内存的方式
  • ** _Alignas和_Alignof**:用于控制内存对齐
  • 泛型选择表达式:用于根据类型选择不同的代码路径

11.2 智能指针模拟

虽然C语言没有内置的智能指针,但可以通过宏和函数模拟:

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
typedef struct {
void *ptr;
void (*free_func)(void *);
} smart_ptr;

void smart_ptr_init(smart_ptr *sp, void *ptr, void (*free_func)(void *)) {
sp->ptr = ptr;
sp->free_func = free_func;
}

void smart_ptr_free(smart_ptr *sp) {
if (sp->ptr && sp->free_func) {
sp->free_func(sp->ptr);
sp->ptr = NULL;
}
}

12. 示例代码

12.1 指针基础示例

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
#include <stdio.h>

int main() {
int num = 10;
int *p = &num;

printf("Value of num: %d\n", num);
printf("Address of num: %p\n", &num);
printf("Value of p: %p\n", p);
printf("Value pointed by p: %d\n", *p);

*p = 20;
printf("Value of num after modification: %d\n", num);

return 0;
}

12.2 指针与数组示例

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
#include <stdio.h>

int main() {
int arr[] = {10, 20, 30, 40, 50};
int *p = arr;
int size = sizeof(arr) / sizeof(arr[0]);

printf("Array elements using pointer: ");
for (int i = 0; i < size; i++) {
printf("%d ", *(p + i));
}
printf("\n");

return 0;
}

12.3 指针与函数示例

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
#include <stdio.h>

void modify_value(int *ptr, int new_value) {
*ptr = new_value;
}

int main() {
int num = 10;
printf("Original value: %d\n", num);

modify_value(&num, 20);
printf("Modified value: %d\n", num);

return 0;
}

12.4 动态内存分配示例

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
#include <stdio.h>
#include <stdlib.h>

int main() {
int *arr = NULL;
int size;

printf("Enter size of array: ");
scanf("%d", &size);

arr = (int *)malloc(size * sizeof(int));
if (arr == NULL) {
printf("Memory allocation failed\n");
return 1;
}

printf("Enter %d elements: ", size);
for (int i = 0; i < size; i++) {
scanf("%d", &arr[i]);
}

printf("Array elements: ");
for (int i = 0; i < size; i++) {
printf("%d ", arr[i]);
}
printf("\n");

free(arr);

return 0;
}