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

    基于GPU的數(shù)學(xué)形態(tài)學(xué)運算并行加速研究

    2011-10-09 09:44:04邢同舉
    電子設(shè)計工程 2011年19期
    關(guān)鍵詞:待處理形態(tài)學(xué)線程

    張 聰,邢同舉,羅 穎,張 靜,孫 強(qiáng)

    (電子科技大學(xué) 光電信息學(xué)院,四川 成都 610054)

    數(shù)學(xué)形態(tài)學(xué)的應(yīng)用幾乎遍及計算機(jī)圖形圖像處理的所有方面,包括圖像濾波、圖像分割分類、圖像測量、模式識別以及紋理分析與合成,其應(yīng)用還涉及遙感監(jiān)測、工業(yè)自動化檢測測量、生物醫(yī)學(xué)影像、圖像壓縮、軍事、航空航天等眾多領(lǐng)域。在運用數(shù)學(xué)形態(tài)學(xué)處理氣象預(yù)報、工程計算和模擬等問題時,需要對巨大數(shù)據(jù)量進(jìn)行多次重復(fù)計算,這些計算又必須在有限的時間內(nèi)完成,比如在幾秒或幾分鐘內(nèi)完成。這就對數(shù)學(xué)形態(tài)學(xué)在處理這些問題時的運算速度提出了較高的要求。在數(shù)學(xué)形態(tài)學(xué)中,腐蝕和膨脹是最基本的兩個運算,這兩種對偶運算好比形態(tài)學(xué)字母表中的字母,其他運算都可以根據(jù)這兩種運算表述[1],因此形態(tài)學(xué)處理速度決定于膨脹、腐蝕處理速度。

    人們通過在腐蝕、膨脹處理中采用改進(jìn)算法來提高其運算速度[2],但其速度也只能提高幾倍,這在某些大數(shù)據(jù)量、實時性要求較高的應(yīng)用中仍不能滿足需要。針對這種情況,文章中提出了通過圖形處理器(GPU)并行處理的方式對數(shù)學(xué)形態(tài)學(xué)運算進(jìn)行加速。實驗結(jié)果表明,通過GPU對數(shù)學(xué)形態(tài)學(xué)運算進(jìn)行加速,其運算速度可達(dá)到1~2個數(shù)量級的提高。

    1 膨脹腐蝕的基本理論

    正文內(nèi)容腐蝕運算:構(gòu)造一個結(jié)構(gòu)元素,結(jié)構(gòu)元素的原點定位于待處理的目標(biāo)元素上,結(jié)構(gòu)元素完全包含在目標(biāo)區(qū)域中時,則結(jié)構(gòu)元素的原點所對應(yīng)的目標(biāo)像素點被保留,負(fù)責(zé)被腐蝕掉,置為背景點。膨脹運算:構(gòu)造一個結(jié)構(gòu)元素,結(jié)構(gòu)元素的原點定位在待處理的目標(biāo)元素上,當(dāng)有目標(biāo)點被結(jié)構(gòu)元素覆蓋時該點被膨脹為目標(biāo)點。

    膨脹腐蝕運算中存在一些重要的運算性質(zhì),在設(shè)計算法時使用這些性質(zhì)往往能簡化處理過程和提高運算速度。對偶性便是其中的一個重要性質(zhì),對偶性可用下面公式來表示:(XΘB)C=XC⊕B;(X⊕B)C=XCΘB。 這兩個公式表明,圖像膨脹等價于該圖像的補(bǔ)被相同結(jié)構(gòu)元素腐蝕所得結(jié)果的補(bǔ),反之亦然[3]。在本文中討論主要集中在腐蝕運算的并行加速,而膨脹運算可以通過待處理圖像補(bǔ)的腐蝕運算求得。

    2 GPU簡介

    2.1 GPU硬件架構(gòu)

    與CPU相比,GPU有著很高的計算吞吐量,這主要在于GPU和CPU不同的設(shè)計理念。GPU最初設(shè)計就是為了圖形處理,由于圖像渲染的高度并行性,GPU設(shè)計者通過增加數(shù)學(xué)邏輯單元(ALU)和控制單元(Control)的方式提高處理能力和存儲器帶寬。這樣就在GPU硬件架構(gòu)中形成了眾多的流處理器,Nvidia GTX 280的架構(gòu)[4]如圖1所示。

    圖1中:Nvidia GTX 280中有30個完整前端流多處理器(SM),每個流多處理器包含8個流處理器(SP)。每個SP又可看成一個SIMD處理器。每個SM擁有獨立的完整前端,包括取指、譯碼、發(fā)射和執(zhí)行單元等,但每兩個SM共享一條存儲器流水線。SP不具有獨立的處理器核,它們有獨立的寄存器和指令指針,但沒有取指和調(diào)度單元構(gòu)成的完整前端。

    圖1 Nvidia GTX 280架構(gòu)Fig.1 Nvidia GTX 280 architecture

    2.2 CUDA軟件開發(fā)環(huán)境

    由于GPU具有很高的計算吞吐量,利用GPU進(jìn)行通用計算已經(jīng)引起了人們的關(guān)注[5-8]。CUDA架構(gòu)正是專門為了GPU通用計算而設(shè)計的一種全新模塊,它使得開發(fā)人員無需再過多地考慮嚴(yán)格的資源限制和編程限制。CUDA C是在CUDA GPU上的編程語言,CUDA C語言本質(zhì)上是對C的簡單擴(kuò)展,它的出現(xiàn)使得開發(fā)人員不需要學(xué)習(xí)計算機(jī)圖形學(xué)和著色語言,就可以編寫出高效的GPU并行程序。

    CUDA 編程模型[9]將 CPU 作為主機(jī)(Host),GPU 作為設(shè)備(Device)[10]。在這個模型中GPU和CPU協(xié)同工作,CPU上負(fù)責(zé)邏輯性較強(qiáng)的事務(wù)處理和串行計算,GPU則專注于執(zhí)行高度并行化處理任務(wù)。運行在GPU上的CUDA函數(shù)稱為內(nèi)核函數(shù)(kernel),一個完整的CUDA程序是由Host串行代碼和Device上的kernel函數(shù)共同組成的,如圖2所示。

    運行在設(shè)備上的kernel函數(shù)定義和普通C語言函數(shù)基本一致,當(dāng)需要被主機(jī)調(diào)用時,只需在函數(shù)定義前面加上__global__修飾符__global__void Copy(char*src, char*dst)。在主機(jī)調(diào)用kernel函數(shù)時,需要傳遞額外的參數(shù),如:Copy<<<blocksPerGrid, threadsPerBlock>>>(ptr_src, ptr_dst)。kernel函數(shù)是以線程網(wǎng)格(Grid)的形式組織的,每個Grid由若干個線程塊(block)組成,每個block由若干線程(thread)組成。調(diào)用kernel函數(shù)所需傳遞的額外參數(shù)blocksPerGrid和threadsPerBlock分別是Grid和block的維度設(shè)計。

    3 基于GPU的腐蝕運算加速實現(xiàn)

    圖像腐蝕采用(2n+1)×(2n+1)且系數(shù)全為 1的模板,即進(jìn)行n尺寸腐蝕。要確定某一像素點是否被腐蝕掉,只需將模板中心對準(zhǔn)當(dāng)前待處理像素點,查看被模板覆蓋的所有像素點,如果全為目標(biāo)點則當(dāng)前待處理像素點保留為目標(biāo)點,否則腐蝕掉。腐蝕可進(jìn)一步轉(zhuǎn)化為鄰域像素點灰度值求和的問題,每一個像素點都由被模板覆蓋所有像素點灰度值的和決定。由此,確定每一點是否被腐蝕掉,所要執(zhí)行的操作是相同的,只是所處理的數(shù)據(jù)不同而已。這是典型的單指令多數(shù)據(jù)問題,具有很好的并行性。

    圖2 CUDA編程模型Fig.2 CUDA programming structure

    3.1 實現(xiàn)時需要注意問題

    在GPU上編碼實現(xiàn)腐蝕運算時,為了正確地執(zhí)行和盡可能地提高執(zhí)行效率需要注意幾個問題:1)避免當(dāng)前處理的像素點被已處理像素點所干擾。在具體實現(xiàn)時,生成一幅和原圖同樣大小的新圖,每個線程將處理結(jié)果存放在這幅新圖中,而運算數(shù)據(jù)則從原圖中獲取;2)充分利用GPU硬件資源,盡可能為每個像素點都開辟一個線程,目前GPU每個block允許開辟的線程數(shù)量已達(dá)到1 024個,每個Grid允許每一維開辟的block數(shù)量為65 535。所以對幾乎所有的二值圖像,都能實現(xiàn)為每一個像素點開辟一個線程;3)腐蝕運算訪問內(nèi)存模式具有很強(qiáng)的空間局部性,GPU紋理緩存是專門為了加速這種訪問模式而設(shè)計的,在這種內(nèi)存訪問模式下,使用紋理內(nèi)存能減少內(nèi)存流量是性能得到提高。4)block維度設(shè)計時,每個block的線程數(shù)量應(yīng)該為64的倍數(shù)[11],這樣GPU的性能才能最大限度地提高。

    3.2 實現(xiàn)過程

    上面已經(jīng)提到CUDA編程模型是GPU和CPU協(xié)同工作的,所以GPU腐蝕運算的實現(xiàn)過程是CPU和GPU共同完成的。CPU負(fù)責(zé)內(nèi)存分配、Grid和block的維度設(shè)定、啟動在GPU上運行的kernel函數(shù)并向其傳遞參數(shù)、最后從GPU獲取處理結(jié)果。GPU負(fù)責(zé)大量并行運算,并將處理數(shù)據(jù)保存下來。其具體顯現(xiàn)步驟如下:

    1)讀取待處理圖像,根據(jù)圖像大小在device上開辟顯存devSrc,并將圖像數(shù)據(jù)復(fù)制到這塊顯存上,并將其綁定二維紋理內(nèi)存;

    2)在device開辟和devSrc同樣大小的顯存devDst,用于GPU保存處理結(jié)果。在host上開辟和devDst同樣大小的內(nèi)存hostDst,用于接收GPU處理的結(jié)果;

    3)根據(jù)待處理圖像大小,設(shè)計grid和block的維度。為了提高性能將 block 維度固定為 dim3 blockDim(16,16),則 grid的維度則根據(jù)圖像寬度width、高度height和block的維度設(shè)定,可設(shè)定為 dim3 gridDim( (width+15)/16,(height+15)/16);

    4)啟動kernel函數(shù),并將設(shè)定好的參數(shù)傳遞到kernel函數(shù)中;

    5)kernel函數(shù)執(zhí)行完畢,將處理結(jié)果傳回host。host保存并顯示結(jié)果。

    4 實驗結(jié)果及分析

    文章所采用實驗平臺為:Interl(R)Xeon(R)CPU 5160,主頻 2.99 GHz,Windows7操作系統(tǒng),顯卡為 GForce GTX 570。文章中所處理的為 1 024×1 024、7 350×5 700 的圖像。表格1為在對大小為1 024×1 024的圖像進(jìn)行不同尺寸腐蝕運算時,CPU串行腐蝕和GPU并行腐蝕所耗用時間對比。

    表1 在不同腐蝕尺寸下CPU和GPU腐蝕時間對比Tab.1 The comparison of the erosion time between CPU and GPU in different erosion sizes

    從表格1中可看出,隨著腐蝕尺寸的增大,即隨著運算時間復(fù)雜度的增加,CPU串行腐蝕運算所耗用時間大幅度增加,GPU并行腐蝕運算所耗用時間沒有大幅增加,GPU并行運算加速比越來越大。

    在圖3中,可以看到在對圖像進(jìn)行同一腐蝕尺寸的腐蝕處理時,GPU腐蝕處理大小為7 350×5 700的圖像比處理1 024×1 024的圖像加速比要高。當(dāng)腐蝕尺寸增加到6時,對于1 024×1 024的圖像加速比可達(dá)到 80左右,對于7 350×5 700的圖像加速比可達(dá)150左右。GPU并行運算之所以有這么高的加速效果,主要因為它有如此多的數(shù)學(xué)邏輯單元,所以能同時運行較多的線程。它通過大量線程的切換來隱藏訪存延遲,當(dāng)某個線程被阻塞了,馬上切換到其他線程進(jìn)行處理,所以當(dāng)待處理數(shù)據(jù)規(guī)模越大時,GPU資源就越能被充分利用,加速效果就更好。

    圖3 對不同大小圖片,GPU加速比隨著腐蝕尺寸的變化而變化Fig.3 In different size of images,the speedup of GPU changes when the erosion size changes

    5 結(jié) 論

    通過GPU并行處理的方式,使形態(tài)學(xué)運算速度大幅提高。實驗結(jié)果表明,隨著待處理數(shù)據(jù)規(guī)模的增加和處理復(fù)雜度的增加,GPU并行腐蝕運算的加速效果顯著增加。在本實驗平臺上GPU并行腐蝕運算可達(dá)到150倍的性能提升,目前,還未見任何優(yōu)化算法達(dá)到如此高的加速效果的報道。本文還在支持CUDA的較低檔的型號為GT220的顯卡上進(jìn)行了測試,在其上進(jìn)行并行腐蝕運算也可達(dá)到10倍以上的性能提升??梢?,在數(shù)學(xué)形態(tài)學(xué)運算時,同時考慮性能和成本兩方面,GPU相對于CPU都有絕對的優(yōu)勢[12]。所以,在涉及數(shù)學(xué)形態(tài)學(xué)運算的領(lǐng)域,GPU并行運算是一個必然趨勢。

    [1]Solille P.形態(tài)學(xué)圖像分析原理與應(yīng)用[M].北京:清華大學(xué)出版社,2008:47-48.

    [2]陸宗騏,朱煜.數(shù)學(xué)形態(tài)學(xué)腐蝕膨脹運算的快速算法[C]//第十三屆全國圖象圖形學(xué)學(xué)術(shù)會議,2006-11-06,2006:306-311.

    [3]孫即祥.圖像分析[M].北京:科學(xué)出版社,2005:183-184.

    [4]Garland M,Grand S L,Nickolls J,et al.Parallel computing experiences with CUDA[J].Micro,IEEE,2008,28(4):13-27.

    [5]Nickolls J,Dally W J.The GPU computing era[J].IEEE Micro,2010,30(2):56-69.

    [6]Hawick K A,Leist A,Playne D P.Parallel graph component labelling with GPUs and CUDA[J].Parallel Computing,2010,36(12):655-678.

    [7]Ufimtsev J S,Schulten K.GPU-accelerated molecular modeling coming of age[J].Journal of Molecular and Modelling,2010,29(2):116-125.

    [8]吳恩華,柳有權(quán).基于圖形處理器(GPU)的通用計算[J].計算機(jī)輔助設(shè)計與圖形學(xué)學(xué)報,2004, 16(5):601-612.

    WU En-hua,LIU You-quan.General purpose computation on GPU[J].Journal of Computer-aided Design& Computer Graphics, 2004, 16(5):601-612.

    [9]Harish P,Narayanan P J.Accelerating large graph algrithms on the GPU using CUDA[J].Computer Science,2007(4873):197-208.

    [10]NVIDIA Corporation,NVIDIA C 3.1,NVIDIA CUDAC Programming Guid Version 3.1[S].2010.

    [11]左顥睿,張啟衡,徐勇,等.基于GPU的快速Sobel邊緣檢測算法[J].光電工程,2009, 36(1):8-12.

    ZUO Hao-rui, ZHANG Qi-heng, XU Yong, et al.Fast sobel edge detection algorithm based on GPU[J].Opto-electronic Engineering, 2009, 36(1):8-12.

    [12]Seung I P,Ponce S P,HUANG Jing,et al.Low-cost,highspeed computer vision using NVIDIA's CUDA architecture[C]//2008 37th IEEE Applied Imagery Pattern Recognition Workshop,2008:1-7.

    猜你喜歡
    待處理形態(tài)學(xué)線程
    財產(chǎn)清查結(jié)果的賬務(wù)處理
    “待處理”事項在科學(xué)事業(yè)單位的核算探討
    會計之友(2018年4期)2018-02-02 22:05:21
    政府會計核算中待處理財產(chǎn)損溢賬戶應(yīng)用探究
    淺談linux多線程協(xié)作
    醫(yī)學(xué)微觀形態(tài)學(xué)在教學(xué)改革中的應(yīng)用分析
    無法收回的房租押金,應(yīng)怎樣進(jìn)行賬務(wù)處理
    數(shù)學(xué)形態(tài)學(xué)濾波器在轉(zhuǎn)子失衡識別中的應(yīng)用
    巨核細(xì)胞數(shù)量及形態(tài)學(xué)改變在四種類型MPN中的診斷價值
    一May-Hegglin異常家系細(xì)胞形態(tài)學(xué)觀察
    Linux線程實現(xiàn)技術(shù)研究
    狂野欧美白嫩少妇大欣赏| 久久精品久久久久久噜噜老黄| 99久久中文字幕三级久久日本| 观看美女的网站| 九色亚洲精品在线播放| 80岁老熟妇乱子伦牲交| 日本-黄色视频高清免费观看| 26uuu在线亚洲综合色| 中国国产av一级| 美女国产高潮福利片在线看| 精品人妻在线不人妻| 我的老师免费观看完整版| 成人国产av品久久久| 九九爱精品视频在线观看| 国产毛片在线视频| 国产熟女午夜一区二区三区 | 国产精品.久久久| 欧美日韩视频精品一区| 国产成人av激情在线播放 | 在线看a的网站| 日韩大片免费观看网站| 日韩亚洲欧美综合| 在线观看人妻少妇| 天天操日日干夜夜撸| 精品午夜福利在线看| 精品少妇内射三级| 十八禁高潮呻吟视频| 女人久久www免费人成看片| 亚洲天堂av无毛| 成人漫画全彩无遮挡| 97精品久久久久久久久久精品| 国产淫语在线视频| 国产成人精品无人区| 久久久久视频综合| 丝袜脚勾引网站| 国产色婷婷99| 久久久亚洲精品成人影院| 中文精品一卡2卡3卡4更新| 我要看黄色一级片免费的| 18禁观看日本| 国产一区有黄有色的免费视频| av专区在线播放| 波野结衣二区三区在线| 各种免费的搞黄视频| 最后的刺客免费高清国语| 丝瓜视频免费看黄片| www.av在线官网国产| 五月伊人婷婷丁香| 美女内射精品一级片tv| 国产在线一区二区三区精| 久久久国产精品麻豆| 国产极品粉嫩免费观看在线 | 蜜桃在线观看..| 国产黄色免费在线视频| 黑人欧美特级aaaaaa片| 欧美丝袜亚洲另类| 亚洲av二区三区四区| 人人妻人人澡人人看| 男男h啪啪无遮挡| 亚洲人成网站在线播| 国产在线免费精品| 国产国语露脸激情在线看| 久久韩国三级中文字幕| 欧美成人午夜免费资源| 插逼视频在线观看| 在线观看三级黄色| 国产成人aa在线观看| 热99久久久久精品小说推荐| 69精品国产乱码久久久| 亚洲综合精品二区| 久久久a久久爽久久v久久| 日本-黄色视频高清免费观看| 五月玫瑰六月丁香| a 毛片基地| 精品一区二区三卡| 国产永久视频网站| 制服人妻中文乱码| 亚洲美女搞黄在线观看| 久久99一区二区三区| 高清av免费在线| 曰老女人黄片| 亚洲人成网站在线观看播放| 日韩伦理黄色片| 国产精品久久久久久av不卡| 中文字幕久久专区| 91aial.com中文字幕在线观看| 久久人人爽av亚洲精品天堂| 欧美 日韩 精品 国产| 亚洲在久久综合| 观看av在线不卡| 99热这里只有精品一区| 久久久久久久大尺度免费视频| 久热这里只有精品99| 亚洲av中文av极速乱| 中文字幕最新亚洲高清| 超碰97精品在线观看| 成年人免费黄色播放视频| 精品久久久久久久久亚洲| 丝袜美足系列| 国产av一区二区精品久久| 免费人妻精品一区二区三区视频| 精品少妇内射三级| 青春草视频在线免费观看| 日韩人妻高清精品专区| 国产av国产精品国产| 蜜桃久久精品国产亚洲av| 大陆偷拍与自拍| 国产成人精品婷婷| 最近的中文字幕免费完整| 尾随美女入室| 成人国产av品久久久| 国产精品一区二区三区四区免费观看| 国产精品偷伦视频观看了| 夜夜看夜夜爽夜夜摸| 爱豆传媒免费全集在线观看| 天堂俺去俺来也www色官网| 国产成人freesex在线| 日韩精品有码人妻一区| 日韩亚洲欧美综合| 人人妻人人爽人人添夜夜欢视频| 日本vs欧美在线观看视频| 国产亚洲精品久久久com| 久久这里有精品视频免费| 超色免费av| 国产高清有码在线观看视频| videos熟女内射| 人成视频在线观看免费观看| 91在线精品国自产拍蜜月| 国产深夜福利视频在线观看| 亚洲精品乱码久久久久久按摩| 人人澡人人妻人| 国产欧美日韩一区二区三区在线 | 国产精品一区www在线观看| 久久亚洲国产成人精品v| 美女主播在线视频| 久久久久精品性色| 性高湖久久久久久久久免费观看| 有码 亚洲区| 热re99久久精品国产66热6| 少妇高潮的动态图| 国产一区亚洲一区在线观看| 婷婷色av中文字幕| 黑丝袜美女国产一区| 一级片'在线观看视频| 少妇 在线观看| 不卡视频在线观看欧美| 国产精品人妻久久久影院| 欧美xxxx性猛交bbbb| 99re6热这里在线精品视频| 精品久久久久久电影网| 久久久久国产精品人妻一区二区| 亚洲av二区三区四区| 777米奇影视久久| 国产精品国产三级国产专区5o| 亚洲中文av在线| 久久久久视频综合| 99热6这里只有精品| 看免费成人av毛片| 亚州av有码| 亚洲欧美日韩另类电影网站| 老司机影院毛片| 国产亚洲午夜精品一区二区久久| 国产一级毛片在线| 亚洲精品aⅴ在线观看| 亚洲av电影在线观看一区二区三区| 亚洲国产成人一精品久久久| 91久久精品电影网| 毛片一级片免费看久久久久| 亚洲精品一二三| 日韩中字成人| 在线 av 中文字幕| 欧美+日韩+精品| 99久久中文字幕三级久久日本| 亚洲精品第二区| 大香蕉久久网| 亚洲精品国产色婷婷电影| 国产欧美日韩一区二区三区在线 | 日本黄色片子视频| 亚洲欧美精品自产自拍| 亚洲欧美日韩卡通动漫| 男女无遮挡免费网站观看| 国产精品成人在线| 曰老女人黄片| 大陆偷拍与自拍| 亚洲精品国产色婷婷电影| 国产深夜福利视频在线观看| 免费高清在线观看视频在线观看| 一区二区三区乱码不卡18| 亚洲人成网站在线观看播放| 日韩大片免费观看网站| 国产亚洲一区二区精品| 精品国产一区二区三区久久久樱花| 免费久久久久久久精品成人欧美视频 | 日韩免费高清中文字幕av| 热99久久久久精品小说推荐| 日韩三级伦理在线观看| 免费黄网站久久成人精品| 中文天堂在线官网| av电影中文网址| 亚洲欧美成人精品一区二区| 午夜激情久久久久久久| 国产乱人偷精品视频| 亚洲精品乱码久久久久久按摩| av卡一久久| 成人午夜精彩视频在线观看| 国产精品国产三级国产av玫瑰| 国产精品国产三级国产专区5o| 国产高清不卡午夜福利| 日本爱情动作片www.在线观看| 国产色爽女视频免费观看| 18在线观看网站| 性色avwww在线观看| 日韩在线高清观看一区二区三区| av又黄又爽大尺度在线免费看| 啦啦啦啦在线视频资源| 国产精品 国内视频| 男男h啪啪无遮挡| 另类亚洲欧美激情| 亚洲美女视频黄频| 日韩一区二区三区影片| 人妻夜夜爽99麻豆av| av国产精品久久久久影院| 日本欧美视频一区| www.色视频.com| 人妻系列 视频| 99国产综合亚洲精品| 国产亚洲最大av| av黄色大香蕉| av福利片在线| 少妇 在线观看| 美女脱内裤让男人舔精品视频| 国产高清国产精品国产三级| 美女中出高潮动态图| 欧美bdsm另类| 国产69精品久久久久777片| 欧美xxⅹ黑人| 国产免费一区二区三区四区乱码| 日韩,欧美,国产一区二区三区| 一级a做视频免费观看| 高清毛片免费看| 91午夜精品亚洲一区二区三区| 精品卡一卡二卡四卡免费| 在线播放无遮挡| 成人国产av品久久久| 少妇丰满av| 狂野欧美激情性bbbbbb| 成人毛片60女人毛片免费| 国产成人a∨麻豆精品| 少妇被粗大的猛进出69影院 | 国产精品一区二区在线不卡| 亚洲丝袜综合中文字幕| 18禁裸乳无遮挡动漫免费视频| 国产一级毛片在线| 久久99蜜桃精品久久| 五月天丁香电影| 国产精品一区二区三区四区免费观看| 观看美女的网站| 亚洲精品久久成人aⅴ小说 | 国产乱人偷精品视频| 亚洲美女黄色视频免费看| 亚洲国产色片| 亚洲欧美一区二区三区黑人 | 午夜免费鲁丝| 99久久精品一区二区三区| 久久青草综合色| h视频一区二区三区| 精品一区二区免费观看| 18禁动态无遮挡网站| 亚洲精品日韩在线中文字幕| 美女国产高潮福利片在线看| 欧美xxⅹ黑人| 亚洲成人手机| 看十八女毛片水多多多| 国产高清有码在线观看视频| 久久久欧美国产精品| 七月丁香在线播放| 九九爱精品视频在线观看| av播播在线观看一区| 精品一区二区三区视频在线| 天堂中文最新版在线下载| 久久韩国三级中文字幕| 午夜福利,免费看| 色哟哟·www| 免费黄频网站在线观看国产| 国产成人免费观看mmmm| 国产乱人偷精品视频| 欧美人与性动交α欧美精品济南到 | 久久久午夜欧美精品| 亚洲av免费高清在线观看| 亚洲中文av在线| 免费大片18禁| 91精品一卡2卡3卡4卡| 一级片'在线观看视频| 极品少妇高潮喷水抽搐| 国产伦精品一区二区三区视频9| 国产无遮挡羞羞视频在线观看| 日韩人妻高清精品专区| 精品人妻熟女av久视频| 亚洲精品aⅴ在线观看| 性色avwww在线观看| 精品酒店卫生间| 国产日韩一区二区三区精品不卡 | 桃花免费在线播放| av黄色大香蕉| 只有这里有精品99| 18禁在线无遮挡免费观看视频| 久久精品熟女亚洲av麻豆精品| 亚洲美女视频黄频| 九九爱精品视频在线观看| 亚洲色图 男人天堂 中文字幕 | 国产爽快片一区二区三区| 22中文网久久字幕| 九色亚洲精品在线播放| 男女边摸边吃奶| 曰老女人黄片| 男的添女的下面高潮视频| 热99国产精品久久久久久7| 国产精品一区二区在线观看99| 午夜免费鲁丝| 亚洲性久久影院| 国产视频首页在线观看| 国产淫语在线视频| 夫妻午夜视频| 午夜视频国产福利| 国产视频首页在线观看| 亚洲欧美成人精品一区二区| 青春草亚洲视频在线观看| 日韩欧美一区视频在线观看| 一级毛片电影观看| 久久毛片免费看一区二区三区| 一边亲一边摸免费视频| 美女中出高潮动态图| 日韩中文字幕视频在线看片| 国产成人精品一,二区| 久久久久久久久大av| 中文字幕免费在线视频6| 哪个播放器可以免费观看大片| 国产视频内射| 久久99蜜桃精品久久| 秋霞在线观看毛片| 在线观看免费日韩欧美大片 | 亚洲欧洲国产日韩| 乱人伦中国视频| 日韩精品有码人妻一区| 99久久人妻综合| 99热国产这里只有精品6| 婷婷成人精品国产| 国产一区二区在线观看日韩| 午夜精品国产一区二区电影| 又大又黄又爽视频免费| 久久精品国产亚洲av天美| 国产国语露脸激情在线看| 特大巨黑吊av在线直播| 亚洲美女视频黄频| 中文字幕人妻熟人妻熟丝袜美| 亚洲国产av新网站| 国产乱人偷精品视频| 亚洲国产av影院在线观看| 黑人巨大精品欧美一区二区蜜桃 | 99久久综合免费| 久久精品人人爽人人爽视色| 国模一区二区三区四区视频| 99国产综合亚洲精品| 丰满少妇做爰视频| 免费观看在线日韩| 国产精品嫩草影院av在线观看| 亚洲欧美一区二区三区黑人 | 精品国产国语对白av| 国产精品一区二区在线观看99| 热re99久久国产66热| 久久精品人人爽人人爽视色| 性色avwww在线观看| 九九在线视频观看精品| 大香蕉97超碰在线| 91久久精品电影网| 日韩一区二区三区影片| 成人黄色视频免费在线看| 另类精品久久| 最黄视频免费看| 纯流量卡能插随身wifi吗| 日本午夜av视频| 纯流量卡能插随身wifi吗| 又大又黄又爽视频免费| 国产日韩欧美亚洲二区| 五月玫瑰六月丁香| 两个人免费观看高清视频| a级毛片免费高清观看在线播放| 国产精品人妻久久久久久| 在线观看国产h片| 国产成人一区二区在线| 黄色毛片三级朝国网站| 九九在线视频观看精品| 在线 av 中文字幕| 午夜日本视频在线| 美女视频免费永久观看网站| 成人国产麻豆网| 伊人久久国产一区二区| 精品久久蜜臀av无| 日韩一区二区视频免费看| 欧美国产精品一级二级三级| 伦精品一区二区三区| 91在线精品国自产拍蜜月| 五月开心婷婷网| 热re99久久国产66热| 99视频精品全部免费 在线| 一区二区三区乱码不卡18| 天堂中文最新版在线下载| 国产片特级美女逼逼视频| 亚洲av欧美aⅴ国产| 九色亚洲精品在线播放| av播播在线观看一区| 欧美成人精品欧美一级黄| 免费播放大片免费观看视频在线观看| 老女人水多毛片| 午夜激情久久久久久久| 91精品一卡2卡3卡4卡| 久久ye,这里只有精品| 又黄又爽又刺激的免费视频.| 欧美日韩视频精品一区| 少妇熟女欧美另类| 欧美精品一区二区大全| 女性被躁到高潮视频| 中文字幕人妻丝袜制服| 热re99久久国产66热| 久久久久久久久久成人| 午夜激情久久久久久久| 欧美成人午夜免费资源| 国产精品成人在线| 国产精品久久久久久精品电影小说| 色94色欧美一区二区| 91久久精品国产一区二区成人| 国产精品不卡视频一区二区| 夫妻午夜视频| 免费人成在线观看视频色| 亚洲国产欧美在线一区| 欧美精品高潮呻吟av久久| 精品国产一区二区久久| 欧美成人午夜免费资源| av福利片在线| 美女视频免费永久观看网站| 一区二区三区精品91| 日韩 亚洲 欧美在线| 两个人的视频大全免费| 最后的刺客免费高清国语| 国产一区二区三区综合在线观看 | 丰满迷人的少妇在线观看| 国产日韩欧美在线精品| 亚洲国产av新网站| 国产精品久久久久久久久免| 午夜福利视频在线观看免费| 国产黄频视频在线观看| 久久久久网色| 中文字幕人妻丝袜制服| 嫩草影院入口| av有码第一页| 日本爱情动作片www.在线观看| 尾随美女入室| 中文字幕最新亚洲高清| 熟女av电影| 天堂8中文在线网| 欧美国产精品一级二级三级| 午夜免费男女啪啪视频观看| 天美传媒精品一区二区| 九九在线视频观看精品| 亚洲欧美一区二区三区国产| 婷婷色综合大香蕉| 91成人精品电影| 国产精品欧美亚洲77777| 亚洲在久久综合| videossex国产| 人成视频在线观看免费观看| 亚洲精品456在线播放app| 日韩制服骚丝袜av| 日韩精品免费视频一区二区三区 | av卡一久久| 男女免费视频国产| 丰满饥渴人妻一区二区三| 视频区图区小说| 夜夜爽夜夜爽视频| 色视频在线一区二区三区| 成人亚洲欧美一区二区av| 久久久久精品性色| 五月伊人婷婷丁香| 免费少妇av软件| 黑人欧美特级aaaaaa片| 人体艺术视频欧美日本| 欧美xxxx性猛交bbbb| 3wmmmm亚洲av在线观看| 免费黄频网站在线观看国产| 久久午夜综合久久蜜桃| 国产男女超爽视频在线观看| 久久精品夜色国产| 又大又黄又爽视频免费| 一级毛片aaaaaa免费看小| 校园人妻丝袜中文字幕| 天堂中文最新版在线下载| 麻豆精品久久久久久蜜桃| 国产精品秋霞免费鲁丝片| 大又大粗又爽又黄少妇毛片口| 人人澡人人妻人| 99国产综合亚洲精品| 少妇人妻精品综合一区二区| 搡女人真爽免费视频火全软件| 国产淫语在线视频| av在线播放精品| 国产免费福利视频在线观看| 另类精品久久| 亚洲精品色激情综合| 国产伦理片在线播放av一区| 国语对白做爰xxxⅹ性视频网站| 视频在线观看一区二区三区| av线在线观看网站| a级毛片免费高清观看在线播放| 亚洲中文av在线| 国产精品久久久久久精品电影小说| 亚洲天堂av无毛| 国产成人精品一,二区| 9色porny在线观看| 中文字幕人妻丝袜制服| 啦啦啦啦在线视频资源| 一本色道久久久久久精品综合| 亚洲精品一二三| 午夜91福利影院| 亚洲av国产av综合av卡| 亚洲av在线观看美女高潮| 一级毛片电影观看| 免费av不卡在线播放| 亚洲欧美日韩另类电影网站| 少妇人妻久久综合中文| 欧美老熟妇乱子伦牲交| 亚洲精品国产av成人精品| 免费人妻精品一区二区三区视频| 老女人水多毛片| 18禁在线播放成人免费| 欧美三级亚洲精品| 丝袜在线中文字幕| av又黄又爽大尺度在线免费看| 亚洲久久久国产精品| 高清欧美精品videossex| 91aial.com中文字幕在线观看| 亚洲国产毛片av蜜桃av| 精品少妇久久久久久888优播| 亚洲欧美精品自产自拍| 欧美成人精品欧美一级黄| 大片电影免费在线观看免费| 精品酒店卫生间| 最近2019中文字幕mv第一页| 极品人妻少妇av视频| 亚洲欧美成人精品一区二区| 日韩免费高清中文字幕av| 亚洲美女黄色视频免费看| 在线观看一区二区三区激情| 91在线精品国自产拍蜜月| 我的老师免费观看完整版| 在线观看www视频免费| 91国产中文字幕| 亚洲国产成人一精品久久久| 一级毛片 在线播放| 80岁老熟妇乱子伦牲交| 国模一区二区三区四区视频| 日本与韩国留学比较| 久久久久久久亚洲中文字幕| 国产高清有码在线观看视频| 久久热精品热| 久久精品国产亚洲av天美| 国产高清国产精品国产三级| 中文字幕人妻丝袜制服| 飞空精品影院首页| 一级a做视频免费观看| 免费av不卡在线播放| 国产乱来视频区| 最近最新中文字幕免费大全7| 99国产精品免费福利视频| av女优亚洲男人天堂| 精品国产一区二区久久| 日韩成人伦理影院| 老司机亚洲免费影院| 久久精品久久久久久噜噜老黄| 少妇被粗大的猛进出69影院 | 国产乱来视频区| 国产一区亚洲一区在线观看| 国产精品一区二区三区四区免费观看| 97精品久久久久久久久久精品| 女人精品久久久久毛片| 一个人看视频在线观看www免费| 亚洲国产精品成人久久小说| 国产伦精品一区二区三区视频9| 中国美白少妇内射xxxbb| av不卡在线播放| 久久精品国产自在天天线| 亚洲人成网站在线观看播放| 春色校园在线视频观看| av福利片在线| 日韩在线高清观看一区二区三区| av不卡在线播放| 视频区图区小说| 亚洲国产精品999| 在线 av 中文字幕| 亚洲国产av新网站| 国产精品99久久久久久久久| av女优亚洲男人天堂| 日本vs欧美在线观看视频| 亚洲在久久综合| 狂野欧美激情性bbbbbb| 一本—道久久a久久精品蜜桃钙片| 欧美日本中文国产一区发布| 精品人妻熟女av久视频| 最近最新中文字幕免费大全7| 成年人免费黄色播放视频| 99热6这里只有精品| av又黄又爽大尺度在线免费看| 久久久久久久久久久免费av| 国产精品一二三区在线看| 欧美精品国产亚洲| 久久国产精品大桥未久av|