Linux源碼閱讀筆記12-RCU案例分析

在之前的文章中我們已經了解了RCU機制的原理和Linux的內核源碼,這里我們要根據RCU機制寫一個demo來展示他應該如何使用。

RCU機制的原理

  • RCU(全稱為Read-Copy-Update),它記錄所有指向共享數據的指針的使用者,當要修改構想數據時,首先創建一個副本,并在副本中修改,所喲訪問線程都離開讀臨界區后,使用者的指針指向修改后的副本,并且刪除舊數據。

  • 他是一種在共享數據結構中實現高效讀取和低延遲寫入操作的技術。在Linux內核中,RCU是一種基于時間窗口的鎖機制,通過充分利用多核處理器和內存系統的特性,在保證并發性的同時提供高性能。

代碼示例

#include <linux/kernel.h>
#include <linux/module.h>
#include <linux/spinlock.h>
#include <linux/kthread.h>
#include <linux/delay.h>
#include <linux/slab.h>
#include <linux/init.h>struct RCUStruct {int a;struct rcu_head rcu;
};static struct RCUStruct* Global_pointer;static struct task_struct* RCURDThread1, *RCURDThread2, *RCUWTThread;static int RCURDThreadFunc1(void* argc) {struct RCUStruct* pointer = NULL;while(1) {msleep(5);rcu_read_lock();mdelay(10);pointer = rcu_dereference(Global_pointer);if(pointer)printk("%s : read a = %d\n", __func__, pointer->a);rcu_read_unlock();}return 0;
}static int RCURDThreadFunc2(void* argc) {struct RCUStruct* pointer = NULL;while(1) {msleep(5);rcu_read_lock();mdelay(10);pointer = rcu_dereference(Global_pointer);if(pointer)printk("%s : read a = %d\n", __func__, pointer->a);rcu_read_unlock();}return 0;
}static void MyRCUDel(struct rcu_head* rcuh) {struct RCUStruct* p = container_of(rcuh, struct RCUStruct, rcu);printk("%s : a = %d\n", __func__, p->a);kfree(p);
}static int RCUWTThreadFunc(void* argc) {struct RCUStruct* old_pointer;struct RCUStruct* new_pointer;int value = (unsigned long)argc;while(1) {msleep(10);new_pointer = kmalloc(sizeof(struct RCUStruct), GFP_KERNEL);old_pointer = Global_pointer;*new_pointer = *old_pointer;new_pointer->a = value;rcu_assign_pointer(Global_pointer, new_pointer);call_rcu(&old_pointer->rcu, MyRCUDel);printk("%s : write to new %d\n", __func__, value);value++;}return 0;
}static int __init RCUFuncInit(void) {int value = 2;printk("Prompt:Successfully initialized the kernel module.\n");Global_pointer = kzalloc(sizeof(struct RCUStruct), GFP_KERNEL);RCURDThread1 = kthread_run(RCURDThreadFunc1, NULL, "RCURD1");RCURDThread2 = kthread_run(RCURDThreadFunc2, NULL, "RCURD2");RCUWTThread = kthread_run(RCUWTThreadFunc, (void*)(unsigned long)value, "RCUWT");return 0;
}static void __exit RCUFuncExit(void) {printk("Prompt:Successfully uninstalled kernel module!\n");kthread_stop(RCURDThread1);kthread_stop(RCURDThread2);kthread_stop(RCUWTThread);if(Global_pointer)kfree(Global_pointer);
}module_init(RCUFuncInit);
module_exit(RCUFuncExit);
MODULE_LICENSE("GPL");
MODULE_AUTHOR("lenn louis");
  • Makefile
obj-m:=rcu.o	CURRENT_PAHT:=$(shell pwd) 
LINUX_KERNEL:=$(shell uname -r)   LINUX_KERNEL_PATH:=/usr/src/linux-headers-$(LINUX_KERNEL)
all:make -C $(LINUX_KERNEL_PATH) M=$(CURRENT_PAHT) modulesclean:make -C $(LINUX_KERNEL_PATH) M=$(CURRENT_PAHT) cleals

運行結果

本文來自互聯網用戶投稿,該文觀點僅代表作者本人,不代表本站立場。本站僅提供信息存儲空間服務,不擁有所有權,不承擔相關法律責任。
如若轉載,請注明出處:http://www.pswp.cn/web/39027.shtml
繁體地址,請注明出處:http://hk.pswp.cn/web/39027.shtml
英文地址,請注明出處:http://en.pswp.cn/web/39027.shtml

如若內容造成侵權/違法違規/事實不符,請聯系多彩編程網進行投訴反饋email:809451989@qq.com,一經查實,立即刪除!

相關文章

不要把面子太當回事

新手拍短視頻真人出鏡&#xff0c;會覺得拍視頻不自然怎么辦&#xff1f;感覺自己好傻。 其實不要把面子太當回事&#xff0c;堅持不把面子太當回事&#xff0c;反正剛開始也沒人看。這是真的事實&#xff0c;大家都非常忙&#xff0c;在你身上停留的時間就幾秒鐘。不要在腦海…

postgreSQL入門

PostgreSQL 教程 約束條件 not null, 不能為空 unique, 在所有數據中必須唯一 check, 字段設置條件 default, 字段默認值 primary(not null, unique), 主鍵, 不能為空且不能重復 數據庫操作 create database [name]; // 建立數據庫 drop database [name]; // 刪除數據庫 \c …

如何快速使用C語言操作sqlite3

itopen組織1、提供OpenHarmony優雅實用的小工具2、手把手適配riscv qemu linux的三方庫移植3、未來計劃riscv qemu ohos的三方庫移植 小程序開發4、一切擁抱開源&#xff0c;擁抱國產化 一、sqlite3庫介紹 sqlite3庫可從官網下載&#xff0c;當前版本為sqlite3 3.45.3ht…

systemctl命令使用

systemctl 作用&#xff1a;可以控制軟件&#xff08;服務&#xff09;的啟動、關閉、開機自啟動 系統內置服務均可被systemctl控制第三方軟件&#xff0c;如果自動注冊了可以被systemctl控制第三方軟件&#xff0c;如果沒有自動注冊&#xff0c;可以手動注冊 語法 systemct…

#### golang的append到底干了啥 ####

代碼1.0 package mainimport "fmt"func main() {a : make([]int64, 0, 0) // 改為 a : make([]int64, 0, 2) 時執行輸出也都一樣的println(fmt.Sprintf("a: %v", a))// 輸出&#xff1a;a: []solve(a)println(fmt.Sprintf("a: %v", a))// 輸出&…

企業出海如何應對國際差旅報銷的復雜性?

在全球化浪潮的推動下&#xff0c;越來越多的中國企業開始邁向國際市場。然而&#xff0c;企業在“走出去”的過程中不僅面臨新的商機&#xff0c;也需要克服諸多挑戰。尤其是國際差旅報銷的復雜性&#xff0c;成為出海企業必須解決的重要問題。 國際差旅報銷的四大挑戰 多元…

【分布式數據倉庫Hive】常見問題及解決辦法

目錄 一、啟動hive時發現log4j版本和hadoop的版本有沖突 解決辦法&#xff1a;刪除hive下高版本的slf4j 二、啟動hive報錯 Exception in thread "main" java.lang.NoSuchMethodError:com.google.common.base.Preconditions.checkArgument(ZLjava/lang/Object;)V …

postgres數據庫的流復制

1. 流復制和邏輯復制的差異 邏輯復制和流復制最直觀的不同是&#xff0c;邏輯復制支持表級別復制區分點事原理不同 邏輯日志是在wal日志產生的數據庫上&#xff0c;由邏輯解析模塊對wal日志進行初步的解析&#xff0c;解析結果是ReorderBufferChange&#xff08;理解為HeapTup…

干貨分享|如何將前端代理服務器(BFF)接入身份認證(3完結篇)

續集3 前篇文章在前面發布&#xff0c;同學們可以自行找一下。 本篇文章將繼續通過實例來詳細講解如何將前端代理服務器&#xff08;BFF&#xff09;接入身份認證。我們將使用一個示例應用來演示 BFF 與身份認證的集成過程。 3 在 Full BFF 中接入認證平臺 本小節將介紹如何…

Raylib 坐標系適應與GPU繪制參數

通過750 - 鼠標坐標&#xff0c;把原點在左上角的鼠標坐標變成左下角 實現輸入數據后的坐標系同GPU原點在左下角坐標相同&#xff0c; 比數組0&#xff0c;0對應左上角好&#xff0c; 此時實際上數組0&#xff0c;0對應左下角 #include <raylib.h> // 感受&#xff1a…

【SpringBoot配置文件讀取】無法讀取yaml文件中文字符

1. yaml配置文件 注意要將該文件編碼格式改為UTF-8 spring:application:name: 好好學習admin:name: 李斯age: 24books:- name: 數據結構desc: 數據書- name: 編譯原理desc: 編譯書2.配置實體類 Data設置get&#xff0c;set方法Component注冊為BeanConfigurationProperties(p…

開發者聊科學作息時間表

非常有幸對科學作息時間表app的開發者做一次采訪。 問&#xff1a;你對科學作息時間表app滿意么&#xff1f; 答&#xff1a;非常不滿意&#xff0c;我們的設想是讓他更智能&#xff0c;更多的提醒方式&#xff0c;更好的交互體驗。如果作為一個鬧鐘他是非常不合格的&#xff0…

輕松駕馭Python 3.11:Windows環境下的安裝與配置全攻略

引言 Python是一種功能強大且易于學習的編程語言&#xff0c;廣泛應用于Web開發、數據分析、人工智能和自動化等領域。為了在Windows中使用Python&#xff0c;首先需要安裝Python解釋器并進行環境配置。本文將詳細介紹如何在Windows中安裝Python 3.11并進行環境配置。 目錄 …

R可視化數據必要格式——長格式

一、引言 我們在對數據進行可視化時遇到最頭疼、最常見的問題是什么&#xff1f;數據問題。 因為我們往往不會從零自己編程進行可視化&#xff0c;往往是現有模板或積累&#xff0c;而正確的數據格式對應正確的圖形包要求&#xff0c;一定會正確出圖&#xff0c;所以只有一個問…

調試 hipcc 的llvm llc gpu目標代碼生成模塊

源碼&#xff1a; hello_vectorAdd.hip: __global__ void vectorAdd(const float *A, const float *B, float *C) {int i blockDim.x * blockIdx.x threadIdx.x;C[i] A[i] B[i] 0.0f; } Makefile: x.O1.s: hello_vectorAdd.hip../../local_amdgpu/bin/clang ./hello_vec…

力扣hot100-普通數組2

文章目錄 題目&#xff1a;輪轉數組方法1-使用額外的數組方法2-三次反轉數組 除自身以外數組的乘積方法1-用到了除法方法2-前后綴乘積法 題目&#xff1a;輪轉數組 原題鏈接&#xff1a;輪轉數組 方法1-使用額外的數組 方法1是自己寫出來的。方法2參考的別人的&#xff0c;…

通配符和正則表達式之間的關系

通配符和正則表達式&#xff08;正則&#xff09;都是用于匹配字符串的工具&#xff0c;但它們的復雜性和用途有所不同。下面是它們之間的主要關系和區別&#xff1a; 通配符 通配符主要用于簡單的模式匹配&#xff0c;常見于文件系統操作中&#xff0c;例如在命令行中查找文…

AttackGen:一款基于LLM的網絡安全事件響應測試工具

關于AttackGen AttackGen是一款功能強大的網絡安全事件響應測試工具&#xff0c;該工具利用了大語言模型和MITRE ATT&CK框架的強大功能&#xff0c;并且能夠根據研究人員選擇的威脅行為組織以及自己組織的詳細信息生成定制化的事件響應場景。 功能介紹 1、根據所選的威脅行…

【MindSpore學習打卡】應用實踐-計算機視覺-FCN圖像語義分割-基于MindSpore實現FCN-8s進行圖像語義分割的教程

圖像語義分割是計算機視覺領域中的一個重要任務&#xff0c;它旨在對圖像中的每個像素進行分類&#xff0c;從而實現對圖像內容的詳細理解。在眾多圖像語義分割算法中&#xff0c;全卷積網絡&#xff08;Fully Convolutional Networks, FCN&#xff09;因其端到端的訓練方式和高…

7.7、指針和函數

代碼 #include <iostream> using namespace std;//實現兩個數字進行交換 void swap01(int a, int b) {int temp a;a b;b temp;cout << "swap01a " << a << endl;cout << "swap01b " << b << endl; }void sw…