• <tr id="yyy80"></tr>
  • <sup id="yyy80"></sup>
  • <tfoot id="yyy80"><noscript id="yyy80"></noscript></tfoot>
  • 99热精品在线国产_美女午夜性视频免费_国产精品国产高清国产av_av欧美777_自拍偷自拍亚洲精品老妇_亚洲熟女精品中文字幕_www日本黄色视频网_国产精品野战在线观看 ?

    基于CUDA 并行化的K-Means 聚類算法優(yōu)化?

    2019-07-31 09:54:44丁芙蓉張功萱
    關(guān)鍵詞:優(yōu)化策略實(shí)驗(yàn)

    丁芙蓉 張功萱

    (南京理工大學(xué)計(jì)算機(jī)科學(xué)與工程學(xué)院 南京 210094)

    1 引言

    聚類分析是一個(gè)將數(shù)據(jù)集中在某些方面相似的數(shù)據(jù)成員進(jìn)行分類組織的過(guò)程。一個(gè)聚類就是一些數(shù)據(jù)實(shí)例的集合,這個(gè)集合中的元素彼此相似,但它們都與其他聚類中的元素不同。K-Means是一種基于劃分的聚類算法,它通過(guò)隨機(jī)初始聚類中心,不斷地迭代調(diào)整聚類中心,得到最終的聚類結(jié)果[1]。K-Means 算法執(zhí)行簡(jiǎn)單,聚類效率高,目前已被廣泛地應(yīng)用于數(shù)據(jù)挖掘[2]、模式識(shí)別[3]、圖像處理[4]、氣象分析[5]等領(lǐng)域。

    在大數(shù)據(jù)背景下,數(shù)據(jù)具有規(guī)模巨大,高速產(chǎn)生,形式多樣的特點(diǎn),針對(duì)大規(guī)模,高維數(shù)據(jù),聚類在每次迭代過(guò)程中的計(jì)算量非常大,耗時(shí)嚴(yán)重[6]。在高性能計(jì)算領(lǐng)域,多核和眾核芯片的普及,計(jì)算設(shè)備的計(jì)算能力不斷提高,如何充分利用計(jì)算設(shè)備的計(jì)算能力來(lái)進(jìn)行數(shù)據(jù)分析成為研究的熱點(diǎn)[7]。GPU 上有幾十個(gè)甚至上百個(gè)計(jì)算核心,采用GPU并行化K-Means 聚類算法相比于串行的K-Means算法,能達(dá)到 2~75x 的加速比[8],大大地降低了算法的運(yùn)行時(shí)間。目前,在GPU 上進(jìn)行K-Means 聚類優(yōu)化多集中在初始聚類中心選擇方面,文獻(xiàn)[9]提出了初始多組聚類中心,迭代4 到5 次選擇最佳聚類中心的方法,文獻(xiàn)[10]提出了動(dòng)態(tài)調(diào)整聚類中心的策略。上述方法在優(yōu)化聚類中心的選擇后,算法的準(zhǔn)確率和性能得到了提升,但是在進(jìn)行聚類的迭代計(jì)算過(guò)程時(shí),使用CUDA 的同步計(jì)算模式,即將CPU 作為程序的控制端,GPU 作為加速部件,在GPU 進(jìn)行加速計(jì)算時(shí),作為主控端的CPU 陷入忙等狀態(tài),直到GPU 上的計(jì)算任務(wù)完成并返回。在多核普及的時(shí)代,這種方式大大浪費(fèi)了主機(jī)端CPU的計(jì)算資源,因此本文提出了基于CPU/GPU 異步計(jì)算的優(yōu)化方法,利用GPU 核函數(shù)和CPU 異步執(zhí)行的特點(diǎn),通過(guò)數(shù)據(jù)并行策略,將聚類過(guò)程進(jìn)一步并行化,減少了CPU 忙等,加速了K-Means 聚類算法的執(zhí)行。

    2 相關(guān)算法與技術(shù)

    2.1 K-Means聚類算法

    設(shè) 樣 本 數(shù) 據(jù) 集 為 D={xi|i=1,2,…n} ,C={ci|i=1,2,…k}表示聚類的k 個(gè)類別,其中ci是第i 個(gè)聚類的中心。用‖‖xi-cj表示從xi到第j個(gè)聚類中心的距離,定義d(x,C)2=K-Means 算法的目的就是找到一個(gè)包含k 個(gè)聚類中心的集合C ,使得誤差最小。

    K-Means聚類算法的步驟如下[11]:

    1)隨機(jī)選擇k 個(gè)樣本(c1,c2,…ck)作為初始聚類中心;

    2)將樣本數(shù)據(jù)集D 中各樣本按照最近距離原則指派給k 個(gè)聚類中心;

    4)判斷是否滿足收斂準(zhǔn)則,不滿足跳轉(zhuǎn)至步驟2),否則算法收斂,中止算法。

    2.2 CUDA程序設(shè)計(jì)模型

    CUDA 是由NIVIDA 公司推出的一種利用GPU進(jìn)行通用并行計(jì)算的整套解決方案,包括硬件支持、程序語(yǔ)言擴(kuò)展、編譯器、調(diào)試器等整套開發(fā)工具鏈。在CUDA 中,物理上的SM(Streaming Multiprocessor,流多處理器)和SP(Streaming Processor,流處理器)被映射為邏輯上的網(wǎng)格(grid)、塊(block)和線程(thread),同一個(gè)線程塊中的線程可以通過(guò)共享存儲(chǔ)器實(shí)現(xiàn)數(shù)據(jù)共享,一個(gè)塊中可以通過(guò)唯一的索引來(lái)控制塊內(nèi)的每個(gè)線程來(lái)完成并行計(jì)算[12]。一個(gè)典型的CUDA 應(yīng)用由兩部分組成:在主機(jī)CPU上執(zhí)行的host 端程序,負(fù)責(zé)數(shù)據(jù)傳輸,初始化和啟動(dòng)GPU;完全在GPU 上執(zhí)行的device 端程序(被成為kernal 函數(shù))。host 端與device 端之間的數(shù)據(jù)傳輸通過(guò) PCI Express 總線傳輸[13]。CUDA 程序員可以使用CUDA C,一種擴(kuò)展C 語(yǔ)言的編程語(yǔ)言來(lái)實(shí)現(xiàn)kernal 函數(shù)。在調(diào)用kernal 函數(shù)時(shí),會(huì)以多線程的方式在GPU上并行執(zhí)行。

    2.3 基于CUDA并行化的K-Means算法

    由2.1 節(jié)可知,K-Means 聚類算法的迭代過(guò)程主要由樣本指派和更新聚類中心兩個(gè)階段組成。第一階段樣本指派,通過(guò)計(jì)算各個(gè)樣本到聚類中心的距離,將樣本指派給距離最近的聚類中心,該階段具備典型的數(shù)據(jù)并行的特點(diǎn),各個(gè)樣本的最小距離可以相互獨(dú)立計(jì)算,適合于在GPU 上用多線程來(lái)加速計(jì)算,即將聚類空間中的每個(gè)樣本點(diǎn)對(duì)應(yīng)一個(gè)線程,負(fù)責(zé)該點(diǎn)的指派。聚類算法中計(jì)算量最大的一部分是樣本指派,通過(guò)并行設(shè)計(jì),可以提高算法的運(yùn)行速度。對(duì)于更新聚類中心階段,需要計(jì)算樣本坐標(biāo)累加和,計(jì)算新的聚類中心。若在GPU上用多線程來(lái)更新聚類中心,需要所有線程訪問(wèn)一個(gè)求和值,而GPU的block間缺少全局的同步性,計(jì)算累加和容易引起B(yǎng)ank 沖突。因此將數(shù)據(jù)傳回主機(jī)端,將其在用于較大可讀寫cache 的CPU 上進(jìn)行[14]。

    基于CUDA 并行化的K-Means 聚類算法的偽代碼如算法1[15]所示,首先初始化聚類中心,之后進(jìn)行迭代計(jì)算。算法的主體包含一個(gè)循環(huán),先將聚類中心拷貝到GPU上,然后在GPU上通過(guò)調(diào)用CUDA 的函數(shù)進(jìn)行樣本指派gpu_labeling(),樣本指派完成后,將樣本指派的結(jié)果通過(guò)cudaMemcpy()拷貝回CPU,此時(shí)的數(shù)據(jù)拷貝是同步的,只有第4 行GPU 上的kernal 函數(shù)執(zhí)行完畢才開始數(shù)據(jù)拷貝。樣本指派的結(jié)果拷貝完成后,在CPU上進(jìn)行聚類更新updateCentroids()。通過(guò)定義偏差率φ 來(lái)表示先后迭代中聚類中心發(fā)生變化的比例占全部樣本的比例,并針對(duì)偏差率定義閾值φ0,表示算法終止的條件。

    算法1:基于CUDA的并行K-Means聚類算法

    1)init(D,C)//D 表示聚類的輸入數(shù)據(jù)集,C 表示聚類中心

    2)while φ > φ0do

    3) cudaMemcpy(…)

    4) gpu_labeling<< <…> >>(D ,C)

    5) cudaMemcpy(…)

    6) updateCentroids(D ,C)

    7) compute φ

    8)end while

    3 基于CPU/GPU異步計(jì)算的并行化

    3.1 算法存在問(wèn)題

    經(jīng)典的基于CUDA 并行化的K-Means 算法的執(zhí)行過(guò)程如圖1。S1 表示迭代的第一階段,樣本指派gpu_labeling();S2 表示迭代的第二階段,更新聚類中心點(diǎn)updateCentriods()。 D 表示輸入的數(shù)據(jù)集,圖中的箭頭表示各個(gè)執(zhí)行階段間的數(shù)據(jù)依賴關(guān)系。執(zhí)行時(shí),必須滿足箭頭標(biāo)示的順序一致性。

    圖1 基于CUDA的并行K-Means執(zhí)行過(guò)程

    在理論上,對(duì)于數(shù)據(jù)規(guī)模為n,樣本維度為d ,聚類劃分個(gè)數(shù)為k 的K-Means聚類過(guò)程,樣本指派的運(yùn)行時(shí)間是O(n×k×d),而更新聚類中心的運(yùn)行時(shí)間是O((n+k)×d)。采用CUDA 并行化后,樣本指派的運(yùn)行時(shí)間是,其中 p 為計(jì)算單元的數(shù)量,與GPU 的性能有關(guān)。此時(shí),樣本指派/更新聚類中心的比率等于n ?k 。隨著聚類劃分個(gè)數(shù)k 的增加,樣本指派/更新聚類中心的比率會(huì)變大,即S1/S2 的比值增大。大部分時(shí)間在GPU 上進(jìn)行計(jì)算,CPU 處于忙等狀態(tài),浪費(fèi)了CPU 的計(jì)算資源。隨著多核CPU 的普及,原有的并行模式不能充分利用CPU端的計(jì)算能力,浪費(fèi)了CPU 的計(jì)算資源。本文利用GPU/CPU異步執(zhí)行的特點(diǎn),提出數(shù)據(jù)并行策略,將聚類數(shù)據(jù)集分配到 CPU 和 GPU 上,增加了 CPU 和 GPU 的數(shù)據(jù)通量,對(duì)傳統(tǒng)的并行算法做優(yōu)化,提高了聚類的效率。

    3.2 數(shù)據(jù)并行優(yōu)化策略

    由3.1節(jié)分析可知,當(dāng)k 增大時(shí),算法的主要時(shí)間開銷在樣本指派階段,即GPU 上執(zhí)行的計(jì)算任務(wù),此時(shí)CPU 處于忙等狀態(tài),浪費(fèi)了多核CPU 的計(jì)算資源。樣本指派的時(shí)間復(fù)雜度為通過(guò)減小在GPU 上的聚類數(shù)據(jù)量,可以減小樣本指派階段的執(zhí)行時(shí)間。因此,將聚類數(shù)據(jù)集進(jìn)行劃分,一部分?jǐn)?shù)據(jù)在GPU 上進(jìn)行樣本指派,另一部分?jǐn)?shù)據(jù)在CPU 上進(jìn)行樣本指派,通過(guò)數(shù)據(jù)并行的方式,GPU 上的運(yùn)算和CPU 上的運(yùn)算同時(shí)進(jìn)行。通過(guò)GPU 和CPU 的計(jì)算重疊,減小算法的執(zhí)行時(shí)間。利用數(shù)據(jù)并行策略對(duì)CUDA 并行化的K-Means聚類算法進(jìn)行優(yōu)化,在提高CPU的利用率的同時(shí)提高了算法的執(zhí)行效率。如圖3 所示,數(shù)據(jù)集分成了g 和c 兩個(gè)部分,在保證原來(lái)的數(shù)據(jù)依賴關(guān)系下,完成聚類。

    圖2 數(shù)據(jù)并行優(yōu)化的K-Means執(zhí)行過(guò)程

    基于數(shù)據(jù)并行策略的CUDA 并行化聚類方法,將輸入數(shù)據(jù)集劃分成兩個(gè)部分,利用CPU 和GPU異步執(zhí)行的特點(diǎn),分別在CPU 和GPU 上完成迭代過(guò)程中的樣本指派。然后再實(shí)現(xiàn)CPU 和GPU 的同步,在CPU 上合并兩個(gè)部分樣本指派的結(jié)果,重新計(jì)算聚類中心。

    算法2 給出了基于數(shù)據(jù)并行策略的CUDA 并行化K-means 聚類的迭代過(guò)程。首先將數(shù)據(jù)集分成兩個(gè)部分D1、D2,每次迭代調(diào)用GPU 核函數(shù)gpu_labeling()來(lái)對(duì)數(shù)據(jù)集 D1 完成樣本指派,調(diào)用CPU 函數(shù) cpu_labeling()來(lái)對(duì)數(shù)據(jù)集 D2 完成樣本指派。由于GPU 和CPU 是異步執(zhí)行的,這兩部分的計(jì)算重疊。通過(guò)gpu_finish 和cpu_finish 變量來(lái)表示GPU 和CPU 上的樣本指派是否完成,從而實(shí)現(xiàn)GPU和CPU的同步。然后再對(duì)數(shù)據(jù)集D 進(jìn)行更新聚類中心updateCentroids()。

    其中,GPU 和CPU 的異步執(zhí)行以及同步操作,我們總結(jié)如下:

    1)GPU 和 CPU 之間的數(shù)據(jù)傳輸使用 cudaMemcpyAsync 異步傳輸?shù)姆绞?,因?-8 行代碼的操作提交到GPU 后,控制權(quán)立即返回給host 端,此時(shí)第9 行代碼開始執(zhí)行。通過(guò)這種方式,實(shí)現(xiàn)了GPU 和CPU的異步執(zhí)行。

    2)GPU上的樣本指派完成后,插入一個(gè)流事件gpu_finish。調(diào)用cudaEventQuery 函數(shù),通過(guò)監(jiān)聽gpu_finish 來(lái)判斷GPU 上的樣本指派是否完成。CPU上樣本指派完成后,將cpu_finish置為1。通過(guò)gpu_finish 和 cpu_finish 來(lái) 實(shí) 現(xiàn) GPU 和 CPU 樣本指派完成后的同步。

    3)當(dāng)更新聚類中心updateCentroids()完成后,要置cpu_finish為0,進(jìn)行復(fù)位。

    算法2:數(shù)據(jù)并行策略優(yōu)化的算法

    1.Init(D,C)//D 表示聚類的輸入數(shù)據(jù)集,C 表示聚類中心

    2.cpu_finish=0

    3.cudaEvent_t gpu_finish

    4.while φ > φ0do

    5. cudaMemcpyAsync(…)

    6. gpu_labeling<< <……>> >(D1,C)

    7. cudaMemcpyAsync(…)

    8. cudaEventRecord(gpu_finish)

    9. while(cudaEventQuery(gpu_finish)== cudaError-NotReady)do

    10. if(cpu_finish)

    11. continue

    12. cpu_labeling( D2,C)

    13. cpu_finish=1

    14. end while

    15. updateCentroids(D ,C)

    16. cpu_finish=0

    17. compute φ

    18.end while

    4 實(shí)驗(yàn)與分析

    有很多文獻(xiàn)在GPU 上加速K-Means 算法,算法的執(zhí)行流程如算法1。因此本文的對(duì)比算法為算法1,實(shí)驗(yàn)的主要目的是分析算法的執(zhí)行時(shí)間和加速比。由于相同初始條件下,K-Means算法最終的聚類迭代次數(shù)相同,在進(jìn)行實(shí)驗(yàn)時(shí),確保算法1和算法2的初始聚類中心相同。

    4.1 實(shí)驗(yàn)環(huán)境

    為了驗(yàn)證算法的有效性,依據(jù)本文提出的數(shù)據(jù)并行優(yōu)化策略,利用CUDA C 語(yǔ)言,在GPU 上實(shí)現(xiàn)了算法1 和算法2。實(shí)驗(yàn)平臺(tái)為配有兩個(gè)Intel Xeon E5-2620 2.10GHz CPU,NIVIDIA Tesla C2050 GPU的服務(wù)器,采用64位Windows server 2012操作系統(tǒng)。主機(jī)端的英特爾至強(qiáng)處理器每個(gè)處理器有8 個(gè)物理核心,支持超線程技術(shù),在主機(jī)端每次可以最多可以支持32 個(gè)線程。NVIDIA Tesla C2050計(jì)算卡擁有448 個(gè)頻率為1.15GHz 的CUDA 核心,3 GB GDDR5 專用存儲(chǔ)器,存儲(chǔ)器接口384 位,存儲(chǔ)器帶寬144GB/s,通過(guò)PCIe×16 Gen2 接口與主機(jī)相連。

    4.2 真實(shí)數(shù)據(jù)集測(cè)試

    使用UCI 上的真實(shí)數(shù)據(jù)集Spambase 進(jìn)行聚類測(cè)試[16]。該數(shù)據(jù)集具有4601 個(gè)數(shù)據(jù)樣本,每個(gè)樣本具有57 個(gè)維度。實(shí)驗(yàn)中聚類的劃分個(gè)數(shù)k 分別為10、20 和50,進(jìn)行三組實(shí)驗(yàn),每組實(shí)驗(yàn)算法各運(yùn)行10 次,統(tǒng)計(jì)聚類過(guò)程中樣本指派/更新聚類中心的耗時(shí)比值S1/S2 平均值、聚類迭代過(guò)程的平均耗時(shí)和優(yōu)化后的算法的加速比。

    表1 Spambase數(shù)據(jù)集實(shí)驗(yàn)結(jié)果

    由實(shí)驗(yàn)可以看出,隨著k 的增加,S1/S2 的比值增大,即在GPU 上的計(jì)算耗時(shí)占比增大。利用數(shù)據(jù)并行策略,將聚類數(shù)據(jù)劃分一部分到主控端CPU上,充分利用多核CPU 的計(jì)算能力,能夠?yàn)樗惴铀佟?/p>

    4.3 人工生成數(shù)據(jù)集測(cè)試

    為了評(píng)估文本提出的數(shù)據(jù)并行策略在樣本維度增加和聚類劃分個(gè)數(shù)增加時(shí)算法的性能,采用人工生成的數(shù)據(jù)集進(jìn)行實(shí)驗(yàn)。實(shí)驗(yàn)數(shù)據(jù)集包括10、50 和100 維的100 000 個(gè)樣本,所有的樣本被指派到 10,50,100 個(gè)聚類中,一共進(jìn)行 9 組對(duì)比試驗(yàn)。每組實(shí)驗(yàn)算法各運(yùn)行10 次,統(tǒng)計(jì)聚類迭代過(guò)程的平均耗時(shí)作為評(píng)價(jià)指標(biāo)。實(shí)驗(yàn)結(jié)果如圖3。

    圖3 運(yùn)行時(shí)間對(duì)比

    圖4 顯示了9 組對(duì)比試驗(yàn),每組對(duì)比試驗(yàn)的加速比,即本文提出的數(shù)據(jù)并行的優(yōu)化策略相對(duì)于傳統(tǒng)的基于CUDA 并行化的K-Means 算法的加速比。本文的優(yōu)化方法能獲得31% ~38%的性能提升。從圖4 中可以看出,隨著數(shù)據(jù)維度和聚類劃分個(gè)數(shù)的增加,加速比基本保持不變。

    圖4 加速比比較

    5 結(jié)語(yǔ)

    本文研究基于CUDA 并行化的K-Means 聚類算法在CPU 和GPU 上的執(zhí)行特征,指出了聚類劃分個(gè)數(shù)對(duì)聚類在GPU 和CPU 上執(zhí)行時(shí)間比值的影響,從而提出了數(shù)據(jù)并行策略,對(duì)原有的基于GPU并行化的K-Means 聚類算法進(jìn)行優(yōu)化,利用GPU核函數(shù)與CPU 異步執(zhí)行的特征,通過(guò)將CPU 與GPU的計(jì)算重疊,減小了算法的執(zhí)行時(shí)間。實(shí)驗(yàn)證明,優(yōu)化的算法有很好的加速比。隨著CPU性能的提升,多核CPU 的普及,CPU 和GPU 異構(gòu)計(jì)算中,作為主機(jī)端的CPU計(jì)算性能不斷提升,本文在研究加速計(jì)算時(shí),在使用GPU 作為加速部件的同時(shí),進(jìn)一步挖掘了主機(jī)端CPU的計(jì)算能力,提高了算法的并行性。本文的下一步研究工作是深入研究CPU和CPU異步計(jì)算的模式,以提高其他聚類算法的并行化。

    猜你喜歡
    優(yōu)化策略實(shí)驗(yàn)
    記一次有趣的實(shí)驗(yàn)
    超限高層建筑結(jié)構(gòu)設(shè)計(jì)與優(yōu)化思考
    民用建筑防煙排煙設(shè)計(jì)優(yōu)化探討
    關(guān)于優(yōu)化消防安全告知承諾的一些思考
    一道優(yōu)化題的幾何解法
    例談未知角三角函數(shù)值的求解策略
    做個(gè)怪怪長(zhǎng)實(shí)驗(yàn)
    我說(shuō)你做講策略
    高中數(shù)學(xué)復(fù)習(xí)的具體策略
    NO與NO2相互轉(zhuǎn)化實(shí)驗(yàn)的改進(jìn)
    女人高潮潮喷娇喘18禁视频| 免费高清在线观看日韩| 18禁黄网站禁片午夜丰满| 久久人人爽av亚洲精品天堂| 亚洲va日本ⅴa欧美va伊人久久 | 最近最新中文字幕大全免费视频| 亚洲成国产人片在线观看| 淫妇啪啪啪对白视频 | 俄罗斯特黄特色一大片| 在线av久久热| 亚洲色图综合在线观看| 久久久久久久国产电影| 岛国毛片在线播放| 国产麻豆69| 欧美久久黑人一区二区| 国产无遮挡羞羞视频在线观看| 久久久精品免费免费高清| 男女免费视频国产| 国产精品免费大片| 一级a爱视频在线免费观看| 免费少妇av软件| 精品国产一区二区三区久久久樱花| 国产熟女午夜一区二区三区| 91精品国产国语对白视频| 不卡一级毛片| www.av在线官网国产| 国产一区二区三区av在线| 中国国产av一级| 国产精品免费视频内射| 欧美变态另类bdsm刘玥| 成人手机av| 精品一区在线观看国产| 亚洲精品在线美女| 一二三四社区在线视频社区8| 超色免费av| 亚洲精品中文字幕一二三四区 | 欧美日韩福利视频一区二区| 欧美黄色片欧美黄色片| a级片在线免费高清观看视频| 欧美精品亚洲一区二区| 黄色a级毛片大全视频| 亚洲免费av在线视频| 欧美精品人与动牲交sv欧美| 亚洲人成77777在线视频| 叶爱在线成人免费视频播放| 久久精品aⅴ一区二区三区四区| 欧美精品高潮呻吟av久久| 高清视频免费观看一区二区| 高清视频免费观看一区二区| 青春草视频在线免费观看| 日韩精品免费视频一区二区三区| 欧美+亚洲+日韩+国产| 国产深夜福利视频在线观看| 亚洲国产看品久久| 国产精品一区二区在线观看99| 亚洲精品日韩在线中文字幕| av超薄肉色丝袜交足视频| 国产成人av教育| 高清av免费在线| 成人黄色视频免费在线看| 精品国产乱码久久久久久男人| 久久狼人影院| 国产成人欧美| 不卡av一区二区三区| 人人澡人人妻人| 成人国语在线视频| 黄片大片在线免费观看| 精品国产一区二区三区久久久樱花| 久久毛片免费看一区二区三区| 999久久久国产精品视频| www日本在线高清视频| 精品一区二区三区av网在线观看 | 黄片小视频在线播放| 精品亚洲成国产av| 午夜两性在线视频| 久久精品国产综合久久久| 欧美少妇被猛烈插入视频| bbb黄色大片| 亚洲激情五月婷婷啪啪| 亚洲av日韩精品久久久久久密| 美女中出高潮动态图| 性色av一级| 黄色a级毛片大全视频| 国产精品偷伦视频观看了| 狠狠婷婷综合久久久久久88av| 久久中文看片网| 丝袜喷水一区| 欧美 日韩 精品 国产| 一边摸一边抽搐一进一出视频| 一级毛片女人18水好多| 欧美另类亚洲清纯唯美| 久久精品久久久久久噜噜老黄| 天天操日日干夜夜撸| 国产亚洲欧美在线一区二区| 成年动漫av网址| 日韩制服丝袜自拍偷拍| 一二三四在线观看免费中文在| 王馨瑶露胸无遮挡在线观看| 欧美久久黑人一区二区| 人妻久久中文字幕网| 免费在线观看黄色视频的| 中亚洲国语对白在线视频| 大陆偷拍与自拍| 免费在线观看完整版高清| 精品一区二区三卡| 亚洲av成人不卡在线观看播放网 | 麻豆乱淫一区二区| 人妻人人澡人人爽人人| 久久久久久久精品精品| √禁漫天堂资源中文www| 欧美黄色淫秽网站| 精品熟女少妇八av免费久了| 免费看十八禁软件| 在线看a的网站| 免费高清在线观看日韩| 精品少妇黑人巨大在线播放| 国产精品香港三级国产av潘金莲| 99久久人妻综合| 免费在线观看影片大全网站| 9热在线视频观看99| 天天躁日日躁夜夜躁夜夜| 亚洲色图综合在线观看| 欧美大码av| 熟女少妇亚洲综合色aaa.| 日韩一卡2卡3卡4卡2021年| 国产色视频综合| 电影成人av| 久久99一区二区三区| 亚洲人成77777在线视频| 日本黄色日本黄色录像| 亚洲精品一二三| 久久精品aⅴ一区二区三区四区| tube8黄色片| 韩国精品一区二区三区| 亚洲国产欧美日韩在线播放| 亚洲熟女毛片儿| 777久久人妻少妇嫩草av网站| 天天躁日日躁夜夜躁夜夜| 真人做人爱边吃奶动态| 50天的宝宝边吃奶边哭怎么回事| 久久久精品94久久精品| 婷婷丁香在线五月| 十分钟在线观看高清视频www| 别揉我奶头~嗯~啊~动态视频 | 欧美日韩精品网址| 国产精品熟女久久久久浪| netflix在线观看网站| 精品国内亚洲2022精品成人 | 国产精品1区2区在线观看. | 日韩视频在线欧美| 免费黄频网站在线观看国产| 999久久久国产精品视频| 成人av一区二区三区在线看 | av超薄肉色丝袜交足视频| 大型av网站在线播放| 中文字幕另类日韩欧美亚洲嫩草| 久久女婷五月综合色啪小说| 国产精品.久久久| 日韩三级视频一区二区三区| 亚洲男人天堂网一区| 他把我摸到了高潮在线观看 | 国产日韩欧美在线精品| 波多野结衣av一区二区av| 91成人精品电影| 午夜免费成人在线视频| 自线自在国产av| 自线自在国产av| 自线自在国产av| 国产深夜福利视频在线观看| 欧美+亚洲+日韩+国产| 嫩草影视91久久| 丝瓜视频免费看黄片| 女人被躁到高潮嗷嗷叫费观| 不卡一级毛片| 丝袜在线中文字幕| 免费在线观看影片大全网站| 美女视频免费永久观看网站| 老汉色∧v一级毛片| 性色av一级| 老汉色∧v一级毛片| 欧美变态另类bdsm刘玥| 波多野结衣一区麻豆| 国产免费视频播放在线视频| videos熟女内射| 俄罗斯特黄特色一大片| 99热网站在线观看| 高清欧美精品videossex| 亚洲精品一区蜜桃| 午夜福利,免费看| av福利片在线| 国产在视频线精品| 亚洲国产看品久久| 免费高清在线观看视频在线观看| 高潮久久久久久久久久久不卡| 蜜桃国产av成人99| 美女高潮到喷水免费观看| 女人精品久久久久毛片| 国产精品久久久久成人av| 精品人妻一区二区三区麻豆| 久久精品国产亚洲av高清一级| 国产精品免费大片| 欧美日韩精品网址| 国产精品久久久人人做人人爽| 亚洲精品日韩在线中文字幕| 久久精品熟女亚洲av麻豆精品| 欧美日韩亚洲综合一区二区三区_| 国产欧美日韩一区二区精品| 欧美黄色淫秽网站| 老司机影院成人| 青春草视频在线免费观看| 国产av又大| av国产精品久久久久影院| 成人国产一区最新在线观看| 国产亚洲欧美在线一区二区| 午夜老司机福利片| 亚洲 欧美一区二区三区| 女人被躁到高潮嗷嗷叫费观| 国产欧美亚洲国产| 少妇人妻久久综合中文| 亚洲欧美一区二区三区久久| 老司机深夜福利视频在线观看 | 久久精品成人免费网站| 青草久久国产| 国产精品秋霞免费鲁丝片| 成人国语在线视频| 亚洲国产中文字幕在线视频| 国产日韩一区二区三区精品不卡| 亚洲精品久久午夜乱码| 亚洲国产欧美网| 成年人午夜在线观看视频| 国产日韩欧美视频二区| 久久久久久久大尺度免费视频| 乱人伦中国视频| 青春草视频在线免费观看| 亚洲第一青青草原| 美女高潮到喷水免费观看| 免费观看av网站的网址| 亚洲精品日韩在线中文字幕| 别揉我奶头~嗯~啊~动态视频 | 中文字幕制服av| 亚洲成人免费av在线播放| 欧美+亚洲+日韩+国产| 另类精品久久| 狂野欧美激情性bbbbbb| 国产精品久久久久久精品电影小说| 韩国高清视频一区二区三区| 天天躁夜夜躁狠狠躁躁| 国产一区有黄有色的免费视频| 国产不卡av网站在线观看| 19禁男女啪啪无遮挡网站| 香蕉丝袜av| 亚洲一区二区三区欧美精品| 成年人黄色毛片网站| 国产区一区二久久| 亚洲国产欧美网| 亚洲少妇的诱惑av| 中文字幕人妻丝袜一区二区| 99精国产麻豆久久婷婷| 亚洲国产av新网站| 国产老妇伦熟女老妇高清| 在线观看免费视频网站a站| 最近最新免费中文字幕在线| 久久综合国产亚洲精品| 午夜视频精品福利| 中文字幕人妻丝袜制服| 亚洲欧洲日产国产| 啦啦啦啦在线视频资源| 91成年电影在线观看| 91麻豆av在线| 又紧又爽又黄一区二区| 国产在线观看jvid| 国产一区二区激情短视频 | 国产一级毛片在线| 午夜影院在线不卡| 国产在线视频一区二区| 亚洲国产精品一区二区三区在线| 国产精品偷伦视频观看了| 女人精品久久久久毛片| 成人18禁高潮啪啪吃奶动态图| 免费一级毛片在线播放高清视频 | av网站免费在线观看视频| av福利片在线| 欧美国产精品一级二级三级| 亚洲国产欧美网| 亚洲欧美激情在线| videos熟女内射| 日本精品一区二区三区蜜桃| 日本a在线网址| 久久久精品免费免费高清| 精品人妻在线不人妻| 亚洲av日韩精品久久久久久密| 最近最新免费中文字幕在线| 老司机午夜十八禁免费视频| 成人18禁高潮啪啪吃奶动态图| av电影中文网址| 成年av动漫网址| 国产精品av久久久久免费| 亚洲第一欧美日韩一区二区三区 | 国产日韩一区二区三区精品不卡| 精品一区二区三区av网在线观看 | 亚洲精华国产精华精| 最近最新免费中文字幕在线| 午夜福利在线观看吧| a在线观看视频网站| 国产av又大| 国产亚洲午夜精品一区二区久久| 国产成人免费无遮挡视频| 又紧又爽又黄一区二区| 午夜福利视频在线观看免费| 精品人妻熟女毛片av久久网站| 亚洲成av片中文字幕在线观看| 男女下面插进去视频免费观看| 99久久国产精品久久久| 久久影院123| 老司机影院成人| 国产在线一区二区三区精| 国产不卡av网站在线观看| 精品免费久久久久久久清纯 | 欧美日韩黄片免| 久久亚洲精品不卡| 精品国产一区二区三区久久久樱花| tocl精华| 黑人猛操日本美女一级片| 夜夜骑夜夜射夜夜干| 国产无遮挡羞羞视频在线观看| 午夜免费观看性视频| 亚洲av电影在线进入| 丝袜人妻中文字幕| 两人在一起打扑克的视频| 久久久久久久精品精品| 精品少妇一区二区三区视频日本电影| 欧美精品高潮呻吟av久久| 亚洲精品国产精品久久久不卡| 亚洲av国产av综合av卡| 成年女人毛片免费观看观看9 | 欧美午夜高清在线| www.999成人在线观看| 亚洲一区二区三区欧美精品| 成人国语在线视频| 大片免费播放器 马上看| 伊人久久大香线蕉亚洲五| 亚洲成人国产一区在线观看| 午夜福利在线观看吧| www.熟女人妻精品国产| 亚洲午夜精品一区,二区,三区| 成年av动漫网址| 午夜福利免费观看在线| 99久久国产精品久久久| 精品国内亚洲2022精品成人 | 国产在线观看jvid| 日韩熟女老妇一区二区性免费视频| 日本猛色少妇xxxxx猛交久久| 黄色视频在线播放观看不卡| 亚洲精品国产精品久久久不卡| 桃花免费在线播放| a级毛片黄视频| 免费少妇av软件| 欧美日韩亚洲综合一区二区三区_| 美女主播在线视频| svipshipincom国产片| 色婷婷久久久亚洲欧美| 午夜精品国产一区二区电影| 精品乱码久久久久久99久播| 高清黄色对白视频在线免费看| 女警被强在线播放| 成人18禁高潮啪啪吃奶动态图| 一级a爱视频在线免费观看| 美女中出高潮动态图| 亚洲七黄色美女视频| 各种免费的搞黄视频| 欧美日韩国产mv在线观看视频| 亚洲精品国产av蜜桃| 十八禁网站免费在线| 亚洲色图 男人天堂 中文字幕| 伦理电影免费视频| 一级黄色大片毛片| 欧美午夜高清在线| 国产黄色免费在线视频| 丰满人妻熟妇乱又伦精品不卡| 国产精品99久久99久久久不卡| 精品视频人人做人人爽| 永久免费av网站大全| 91麻豆av在线| 欧美激情久久久久久爽电影 | 最黄视频免费看| 国产av国产精品国产| 午夜视频精品福利| 亚洲精品国产精品久久久不卡| 99香蕉大伊视频| 黄色毛片三级朝国网站| 男人舔女人的私密视频| 99国产精品免费福利视频| 1024视频免费在线观看| 色综合欧美亚洲国产小说| 咕卡用的链子| 欧美老熟妇乱子伦牲交| 亚洲熟女精品中文字幕| 在线观看免费高清a一片| 亚洲第一av免费看| 国产福利在线免费观看视频| 国产亚洲午夜精品一区二区久久| 天天躁狠狠躁夜夜躁狠狠躁| 久久天躁狠狠躁夜夜2o2o| 久久久久精品国产欧美久久久 | 人妻一区二区av| bbb黄色大片| 超碰成人久久| 国产一卡二卡三卡精品| 一进一出抽搐动态| 亚洲欧美日韩高清在线视频 | 99九九在线精品视频| 亚洲精品在线美女| 成年人免费黄色播放视频| 亚洲一卡2卡3卡4卡5卡精品中文| 一区二区三区四区激情视频| 狠狠精品人妻久久久久久综合| 宅男免费午夜| 亚洲免费av在线视频| 亚洲国产精品成人久久小说| 久热这里只有精品99| 伊人亚洲综合成人网| 中文精品一卡2卡3卡4更新| 免费在线观看视频国产中文字幕亚洲 | 亚洲精品av麻豆狂野| 三上悠亚av全集在线观看| 成人免费观看视频高清| 久久亚洲精品不卡| 欧美日韩成人在线一区二区| 国产1区2区3区精品| 无遮挡黄片免费观看| 亚洲一区二区三区欧美精品| 一本大道久久a久久精品| 考比视频在线观看| 久久性视频一级片| 老司机深夜福利视频在线观看 | 婷婷丁香在线五月| 婷婷色av中文字幕| 性色av乱码一区二区三区2| 久久人妻福利社区极品人妻图片| 可以免费在线观看a视频的电影网站| 女人高潮潮喷娇喘18禁视频| 日本wwww免费看| 嫩草影视91久久| 日本一区二区免费在线视频| 国产精品一二三区在线看| 久久精品成人免费网站| 精品国产国语对白av| 久久久欧美国产精品| svipshipincom国产片| 乱人伦中国视频| 亚洲一区二区三区欧美精品| 黄色视频在线播放观看不卡| 久久亚洲精品不卡| 久久久久视频综合| 亚洲精品国产区一区二| 在线看a的网站| 亚洲 欧美一区二区三区| 日本欧美视频一区| 日本vs欧美在线观看视频| 国产视频一区二区在线看| 亚洲一码二码三码区别大吗| 黄片播放在线免费| 两个人免费观看高清视频| 国产成人一区二区三区免费视频网站| 亚洲精品在线美女| 国产成人精品久久二区二区91| 中文字幕av电影在线播放| 在线观看免费视频网站a站| 亚洲免费av在线视频| 久久久精品区二区三区| 一区二区三区精品91| netflix在线观看网站| 在线观看一区二区三区激情| 这个男人来自地球电影免费观看| 亚洲av片天天在线观看| 久久女婷五月综合色啪小说| xxxhd国产人妻xxx| 久久久精品免费免费高清| 极品人妻少妇av视频| 性色av一级| a在线观看视频网站| 欧美激情久久久久久爽电影 | 秋霞在线观看毛片| 男女免费视频国产| 淫妇啪啪啪对白视频 | 在线观看免费日韩欧美大片| 午夜激情av网站| 久久中文字幕一级| 欧美精品av麻豆av| 日韩视频在线欧美| 亚洲伊人久久精品综合| 亚洲国产欧美日韩在线播放| 中亚洲国语对白在线视频| 99久久99久久久精品蜜桃| 五月开心婷婷网| 国产成人免费无遮挡视频| 国产精品二区激情视频| 国产亚洲欧美精品永久| 新久久久久国产一级毛片| 国产黄色免费在线视频| 色播在线永久视频| 亚洲九九香蕉| 亚洲欧美一区二区三区久久| 黄色视频,在线免费观看| 精品国产国语对白av| 国产一区二区三区综合在线观看| 午夜久久久在线观看| 好男人电影高清在线观看| 一级片免费观看大全| 免费在线观看视频国产中文字幕亚洲 | 波多野结衣一区麻豆| 12—13女人毛片做爰片一| 99精品久久久久人妻精品| 丝袜在线中文字幕| 人人妻人人澡人人看| 午夜精品国产一区二区电影| 一区在线观看完整版| 女人被躁到高潮嗷嗷叫费观| 日本av免费视频播放| 水蜜桃什么品种好| 中国美女看黄片| 久热爱精品视频在线9| 欧美激情高清一区二区三区| 亚洲 欧美一区二区三区| 久久中文看片网| 91麻豆av在线| 久久毛片免费看一区二区三区| 爱豆传媒免费全集在线观看| 欧美+亚洲+日韩+国产| 桃红色精品国产亚洲av| 欧美精品啪啪一区二区三区 | 亚洲精品乱久久久久久| 男人舔女人的私密视频| 桃红色精品国产亚洲av| 手机成人av网站| 成年美女黄网站色视频大全免费| 热99国产精品久久久久久7| 母亲3免费完整高清在线观看| 精品国产超薄肉色丝袜足j| 又大又爽又粗| 精品国产超薄肉色丝袜足j| 久久香蕉激情| 亚洲少妇的诱惑av| 久久久久视频综合| 国产精品麻豆人妻色哟哟久久| 各种免费的搞黄视频| 性色av一级| 操出白浆在线播放| 精品亚洲成国产av| 大片电影免费在线观看免费| 美女中出高潮动态图| 国产一区二区 视频在线| 五月开心婷婷网| 高清欧美精品videossex| 亚洲av电影在线进入| 热re99久久国产66热| 黄片小视频在线播放| 脱女人内裤的视频| 天天添夜夜摸| 在线十欧美十亚洲十日本专区| 最近中文字幕2019免费版| 国产成人a∨麻豆精品| 最近中文字幕2019免费版| 国产精品一区二区精品视频观看| 免费人妻精品一区二区三区视频| 曰老女人黄片| 久久九九热精品免费| 欧美+亚洲+日韩+国产| 人妻久久中文字幕网| 久久av网站| 美女扒开内裤让男人捅视频| 男女床上黄色一级片免费看| 欧美精品av麻豆av| 国产三级黄色录像| 少妇猛男粗大的猛烈进出视频| 久久亚洲国产成人精品v| 久久国产精品人妻蜜桃| 亚洲精品美女久久久久99蜜臀| 日日夜夜操网爽| 人妻 亚洲 视频| 青青草视频在线视频观看| 久久女婷五月综合色啪小说| 老司机影院成人| 亚洲av欧美aⅴ国产| 国产精品免费视频内射| 老司机福利观看| 天天躁狠狠躁夜夜躁狠狠躁| 亚洲成国产人片在线观看| 丁香六月天网| 亚洲欧洲日产国产| 国产欧美日韩一区二区三 | 91九色精品人成在线观看| 精品国产乱码久久久久久男人| 国产精品久久久久成人av| 久久99一区二区三区| 水蜜桃什么品种好| 欧美亚洲 丝袜 人妻 在线| 亚洲熟女毛片儿| 亚洲av国产av综合av卡| 亚洲精品在线美女| 精品国产乱码久久久久久小说| 人人妻,人人澡人人爽秒播| 欧美黄色淫秽网站| 精品亚洲成a人片在线观看| 性少妇av在线| 久久精品熟女亚洲av麻豆精品| 精品国产乱子伦一区二区三区 | 不卡av一区二区三区| 欧美日韩成人在线一区二区| 亚洲伊人色综图| 多毛熟女@视频| 五月开心婷婷网| 亚洲午夜精品一区,二区,三区| 亚洲熟女精品中文字幕| 亚洲成人免费av在线播放|