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

    基于CUDA的圖像預(yù)處理并行化研究

    2014-09-06 05:42:47,,,
    機(jī)械與電子 2014年7期
    關(guān)鍵詞:均衡化線程直方圖

    , ,,

    (哈爾濱工業(yè)大學(xué)機(jī)器人技術(shù)與系統(tǒng)國(guó)家重點(diǎn)實(shí)驗(yàn)室,黑龍江 哈爾濱 150001)

    基于CUDA的圖像預(yù)處理并行化研究

    占正鋒,李戈,張學(xué)賀,尹旭悅

    (哈爾濱工業(yè)大學(xué)機(jī)器人技術(shù)與系統(tǒng)國(guó)家重點(diǎn)實(shí)驗(yàn)室,黑龍江 哈爾濱 150001)

    為加快圖像預(yù)處理算法的執(zhí)行速度,提出了基于計(jì)算統(tǒng)一設(shè)備架構(gòu)(CUDA)的預(yù)處理算法來(lái)實(shí)現(xiàn)高速并行處理。分析了圖像灰度化、高斯濾波以及直方圖均衡化等預(yù)處理方法的原理,并對(duì)它們進(jìn)行并行化分析,從而將CUDA并行計(jì)算技術(shù)引入到圖像預(yù)處理算法。實(shí)驗(yàn)結(jié)果表明,此算法充分利用GPU的并行處理能力,與CPU串行處理方法相比,速度提高明顯,有效提高數(shù)據(jù)處理能力。

    圖像預(yù)處理;CUDA;并行處理

    0 引言

    一般情況下,成像系統(tǒng)獲取的圖像(即原始圖像)由于受到種種條件限制和隨機(jī)干擾,往往不能在視覺(jué)系統(tǒng)中直接使用,必須在視覺(jué)信息處理的早期階段對(duì)原始圖像進(jìn)行灰度變換、噪聲過(guò)濾等圖像預(yù)處理[1]。傳統(tǒng)的預(yù)處理算法,當(dāng)數(shù)據(jù)量較大時(shí),這種方法的效率不高,難以滿足實(shí)時(shí)性的要求。近年來(lái),基于圖像處理器(GPU)的大規(guī)模通用并行計(jì)算,為圖像處理算法的高效分析計(jì)算提供了可能。NVIDIA公司提出的計(jì)算統(tǒng)一設(shè)備構(gòu)架,是一種將GPU作為數(shù)據(jù)并行計(jì)算設(shè)備的軟硬件體系,其特點(diǎn)是將CPU作為主機(jī),GPU作為協(xié)處理器[2]。這個(gè)模型中,CPU和GPU協(xié)同工作,CPU負(fù)責(zé)邏輯性強(qiáng)的事務(wù)和串行計(jì)算任務(wù),而GPU處理高度線程化的并行計(jì)算任務(wù)[3]。

    在此,以GPU作為計(jì)算平臺(tái),對(duì)圖像預(yù)處理算法中的圖像灰度化、高斯濾波以及直方圖均衡化處理進(jìn)行并行化分析,并在CUDA上實(shí)現(xiàn)。

    1 圖像的灰度化并行

    將彩色圖像轉(zhuǎn)化成為灰度圖像的過(guò)程稱為圖像的灰度化處理。彩色圖像中的每個(gè)像素的顏色由R,G,B3個(gè)分量決定,而每個(gè)分量有255種值可取,這樣一個(gè)像素點(diǎn)可以有1 600多萬(wàn)(255×255×255)種顏色的變化范圍。而灰度圖像是R,G,B3個(gè)分量相同的一種特殊的彩色圖像,其一個(gè)像素點(diǎn)的變化范圍為255種,所以在數(shù)字圖像處理中,一般先將各種格式的圖像轉(zhuǎn)變成灰度圖像,以使后續(xù)圖像的計(jì)算量變得少一些。圖像的灰度化處理,一般而言,常用如下幾種方法:最大值法、平均法和加權(quán)平均法等[4]。這里采用加權(quán)平均法,分別賦予R,G,B不同的權(quán)值,然后取其加權(quán)后的平均值作為最后的灰度值。

    并行灰度轉(zhuǎn)換實(shí)現(xiàn)過(guò)程中,將每個(gè)像素3個(gè)通道的顏色值存放在線程寄存器內(nèi),1個(gè)block包含256個(gè)thread,則對(duì)于一幅尺寸為width × height的圖像,一共需要width × height/256個(gè)block,創(chuàng)建索引標(biāo)號(hào)為index=blockIdx.x×256+threadIdx.x。

    2 高斯濾波并行化

    高斯濾波(高斯平滑)是數(shù)字圖像處理和計(jì)算機(jī)視覺(jué)里面最常見(jiàn)的操作。高斯濾波器是根據(jù)高斯函數(shù)的形狀來(lái)選擇權(quán)值的線性平滑濾波器[5]。高斯平滑濾波器對(duì)去除服從正態(tài)分布的噪聲有很好的效果。對(duì)圖像來(lái)說(shuō),常用二維高斯函數(shù)表達(dá)式為:

    (1)

    σ為高斯濾波器的寬度。

    高斯濾波時(shí),在對(duì)整幅圖像進(jìn)行加權(quán)平均的過(guò)程中,每一個(gè)像素點(diǎn)的值,都由其本身和鄰域內(nèi)的其他像素值經(jīng)過(guò)加權(quán)平均后得到。高斯濾波的具體操作是:用1個(gè)模板(或稱卷積、掩模)掃描圖像中的每一個(gè)像素,用模板確定的鄰域內(nèi)像素的加權(quán)平均灰度值,去替代模板中心像素點(diǎn)的值。

    為了實(shí)現(xiàn)高斯濾波的快速運(yùn)行,根據(jù)高斯函數(shù)具有可分離性的特點(diǎn),提出了可進(jìn)行分離的高斯卷積的方法,把二維高斯卷積轉(zhuǎn)換成2個(gè)一維高斯卷積,將高斯模板放入GPU帶緩存的常量存儲(chǔ)器中。

    由高斯函數(shù)的性質(zhì)可知,高斯函數(shù)具有各向同性的特點(diǎn),二維高斯函數(shù)可進(jìn)行逐次卷積,一個(gè)沿水平方向,另一個(gè)沿垂直方向。即

    (2)

    在離散系統(tǒng)中,二維高斯卷積是靠n×n的高斯模板對(duì)整幅圖像進(jìn)行卷積的,每個(gè)圖像的像素都需要進(jìn)行n×n次的乘加操作,對(duì)于大小為m×m的圖像就需要m×m×n×n次乘加操作,同時(shí)還要用n×n個(gè)存儲(chǔ)空間來(lái)存儲(chǔ)模板。而將二維高斯函數(shù)進(jìn)行分離以后,把二維的n×n高斯模板分解成1 ×n的一維高斯模板,對(duì)圖像先進(jìn)行行卷積再進(jìn)行列卷積,對(duì)于大小為m×m的圖像一共只需要2 ×m×n×n次操作。可以看出,當(dāng)圖像很大時(shí),使用本文的方法進(jìn)行高斯卷積將提升運(yùn)算速度。以5×5的二維高斯模板為例,如圖1所示。將其分解后對(duì)應(yīng)的一維高斯模板如圖2所示。圖1所示的5×5二維高斯模板可分解為圖2的1×5一維模板和其轉(zhuǎn)置的乘積,這樣就將二維高斯平滑轉(zhuǎn)換成了2次的一維高斯平滑。

    在GPU上對(duì)高斯卷積進(jìn)行并行化的主要流程如圖3所示。

    圖1 5×5高斯模板

    圖2 1×5一維高斯模板

    圖3 GPU高斯卷積流程

    首先將圖像從主機(jī)端拷入到設(shè)備端,綁定紋理內(nèi)存。選擇綁定紋理內(nèi)存是由于以下原因:紋理內(nèi)存緩存在芯片上,能夠減少對(duì)內(nèi)存的請(qǐng)求并提供更高效的內(nèi)存帶寬,是專(zhuān)門(mén)為那些在內(nèi)存訪問(wèn)模式中存在大量空間局部性的圖形應(yīng)用程序而設(shè)計(jì)的,能在隨機(jī)存取的環(huán)境中,保持較高的性能;圖像在高斯濾波時(shí)要面臨邊界問(wèn)題,而圖像處理器程序并不擅長(zhǎng)條件判斷語(yǔ)句的執(zhí)行,紋理內(nèi)存能夠通過(guò)屬性設(shè)置,比較高效處理此類(lèi)問(wèn)題。

    高斯卷積模板在主機(jī)端計(jì)算完畢后,傳入設(shè)備端的常量存儲(chǔ)器。在行列2個(gè)維度上使用2個(gè)kernel函數(shù)進(jìn)行卷積。對(duì)行維度卷積時(shí),將Grid中的block按照二維地址排序,每個(gè)block負(fù)責(zé)處理1幅圖像的1行的部分?jǐn)?shù)據(jù),大小可以定為16×16,即每個(gè)block有256個(gè)thread,每個(gè)thread負(fù)責(zé)處理圖像的1個(gè)像素點(diǎn)的值,即每個(gè)線程把當(dāng)前的像素點(diǎn)和其周?chē)?個(gè)像素點(diǎn)進(jìn)行加權(quán)計(jì)算。同一個(gè)block中的線程在進(jìn)行計(jì)算時(shí),有很多數(shù)據(jù)是重復(fù)的,將它們放在block的共享存儲(chǔ)器中,這樣就可以加快運(yùn)算速度。行卷積任務(wù)分配如圖4所示。對(duì)列的卷積與行卷積類(lèi)似,這樣完成行列卷積后,就可以完成對(duì)整幅圖像的高斯二維卷積。

    圖4 行卷積任務(wù)分配

    3 直方圖均衡化技術(shù)并行化

    利用直方圖統(tǒng)計(jì)的結(jié)果,通過(guò)使圖像直方圖均衡的方法稱為直方圖均衡化[6]。直方圖均衡化處理是數(shù)字圖像處理中增強(qiáng)圖像的一種重要的方法。

    灰度直方圖的計(jì)算十分簡(jiǎn)單,依據(jù)定義,在離散形式下有以下公式成立:

    (3)

    nk為圖像中出現(xiàn)Sk級(jí)灰度的像素?cái)?shù);n為圖像像素總數(shù);nk/n為頻數(shù)。

    計(jì)算累積直方圖各項(xiàng):

    (4)

    取整擴(kuò)展:

    tk=int[(L-1)tk+0.5]

    (5)

    映射對(duì)應(yīng)關(guān)系:

    k?tk

    在CUDA上實(shí)現(xiàn)直方圖的均衡化需要進(jìn)行原子操作,而使用原子操作的方式是調(diào)用函數(shù)atomicAdd(addr,y)生成1個(gè)原子的操作序列。這個(gè)操作序列包括讀取地址addr處的地址,將y增加到這個(gè)值,以及將結(jié)果保存回地址addr。底層硬件將確保當(dāng)執(zhí)行這些操作時(shí),其他任何線程都不會(huì)讀取或?qū)懭氲刂穉ddr上的值,這樣就能確保得到預(yù)計(jì)的結(jié)果。

    將直方圖的計(jì)算分為2個(gè)階段。在第1階段中,每個(gè)并行線程塊將計(jì)算它所處理數(shù)據(jù)的直方圖。由于每個(gè)線程塊在執(zhí)行這個(gè)操作時(shí)都是相互獨(dú)立的,因此,可以在共享內(nèi)存中計(jì)算這些直方圖,這將避免每次將寫(xiě)入操作從芯片發(fā)送到DRAM。因?yàn)樵诰€程塊中的多個(gè)線程之間會(huì)處理相同值的數(shù)據(jù)元素,所以需要原子操作。在第1階段中,給每個(gè)block分配256個(gè)thread,同時(shí)分配1個(gè)共享內(nèi)存緩存區(qū)并進(jìn)行初始化,用來(lái)保存每個(gè)線程塊的臨時(shí)直方圖,即_shared_ unsigned int temp[256];temp[threadIdx.x]=0。由于隨后的步驟將包括讀取和修改這個(gè)緩沖區(qū),因此,需要調(diào)用_syncthreads(),來(lái)確保每個(gè)線程的寫(xiě)入操作在線程繼續(xù)前進(jìn)之前完成。

    在第2階段,要求將每個(gè)線程塊的臨時(shí)直方圖合并到全局緩沖區(qū)histo中。假設(shè)將輸入數(shù)據(jù)分為兩半,這樣就有2個(gè)線程查看不同部分的數(shù)據(jù),并計(jì)算得到2個(gè)獨(dú)立的直方圖。如果線程A在輸入數(shù)據(jù)中發(fā)現(xiàn)字節(jié)0xFC出現(xiàn)了20次,線程B發(fā)現(xiàn)字節(jié)0xFC出現(xiàn)了5次,那么字節(jié)0xFC在輸入數(shù)據(jù)中共出現(xiàn)了25次。同樣,最終直方圖的每個(gè)元素,只是線程A直方圖中相應(yīng)元素和線程B直方圖中相應(yīng)元素的加和。這個(gè)邏輯可以擴(kuò)展到任意數(shù)量的線程,因此,將每個(gè)線程塊的直方圖合并為單個(gè)最終的直方圖,就是將線程塊直方圖的每個(gè)元素都相加到最終直方圖相應(yīng)位置的元素上。這個(gè)操作需要自動(dòng)完成,即atomicAdd(&(histo[threadIdx.x]),temp[threadIdx.x])。由于使用了256個(gè)線程,并且直方圖中包含了256個(gè)元素,因此,每個(gè)線程將自動(dòng)把它計(jì)算得到的元素只增加到最終直方圖的元素上。本算法并不保證線程塊將按照何種順序?qū)⒏髯缘闹迪嗉拥阶罱K的直方圖中,但由于整數(shù)加法是可以交換的,無(wú)論哪種順序都會(huì)得到相同的結(jié)果。

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

    實(shí)驗(yàn)平臺(tái)采用Windows 7操作系統(tǒng),CPU為Intel Core i7-3770,主頻3.40 GHz,系統(tǒng)內(nèi)存為8 GB;GPU為GeForce GTX 570。

    4.1 圖像灰度化

    分別使用圖形尺寸為256×256,512×512,1 024×1 024的圖像,在GPU上測(cè)試其運(yùn)行速度,并且與預(yù)處理算法在CPU上運(yùn)行的速度進(jìn)行比較。實(shí)驗(yàn)效果如圖5和表1所示。

    圖5 灰度化效果

    表1 灰度化在GPU和CPU上運(yùn)行時(shí)間的比較

    圖像大小CPU/msGPU/ms加速比(CPU/GPU)256×2560.0930.0283.26512×5120.1870.0355.311024×10240.4360.0449.87

    4.2 高斯濾波

    對(duì)平滑尺度為1,模板尺寸為5×5的高斯濾波算法在GPU上進(jìn)行實(shí)驗(yàn),分別使用圖形尺寸為256 ×256,512×512,1 024×1 024的加椒鹽噪聲的圖像,在GPU上測(cè)試其運(yùn)行速度,并且與該算法在CPU上運(yùn)行的速度進(jìn)行比較。實(shí)驗(yàn)效果如圖6和表2所示。

    圖6 高斯濾波效果

    表2 高斯濾波在GPU和CPU上運(yùn)行時(shí)間的比較

    圖像大小CPU/msGPU/ms加速比(CPU/GPU)256×2560.7560.04915.21512×5122.3590.08228.631024×10246.7850.18536.65

    4.3 直方圖均衡化處理

    分別使用圖形尺寸為256×256,512×512,1 024×1 024的圖像,在GPU上測(cè)試其運(yùn)行速度,并且與該算法在CPU上運(yùn)行的速度進(jìn)行比較。實(shí)驗(yàn)效果如表3和圖7所示。

    表3 均衡化在GPU和CPU上的運(yùn)行時(shí)間的比較

    圖像大小CPU/msGPU/ms加速比(CPU/GPU)256×2560.1240.0158.23512×5120.3870.02515.721024×10240.8360.03324.96

    圖7 直方圖均衡化效果

    4.4 實(shí)驗(yàn)結(jié)果分析

    由表1~表3可以看出,圖像預(yù)處理算法在GPU上運(yùn)行的速度明顯高于在CPU上的速度,并且從圖像灰度化、直方圖均衡化以及高斯濾波這3種算法的對(duì)比來(lái)看,算法越復(fù)雜、并行程度越高和圖像的分辨率越高,這種加速效果會(huì)越明顯。

    5 結(jié)束語(yǔ)

    對(duì)傳統(tǒng)的圖像預(yù)處理算法中的圖像灰度化、高斯濾波以及直方圖均衡化處理進(jìn)行了并行化分析,并且使其在CUDA上實(shí)現(xiàn)。實(shí)驗(yàn)結(jié)果表明,預(yù)處理算法在GPU上運(yùn)行與其在CPU上運(yùn)行相比,明顯提高了其運(yùn)算速度。

    [1] 顏 瑞.基于 CUDA 的立體匹配及去隔行算法[D].杭州:浙江大學(xué),2010.

    [2] 鄒治海.GPU 架構(gòu)分析與功耗模型研究[D].上海:上海交通大學(xué),2011.

    [3] 張 舒,褚艷利.GPU高性能運(yùn)算之CUDA[M].北京:中國(guó)水利水電出版社,2009.

    [4] Sanders J, Kandrot E.CUDA by example:an introduction to general-purpose GPU programming[M].Addison-Wesley Educational Publishers Inc,2010.

    [5] 郭陸峰.雙目視覺(jué)系統(tǒng)關(guān)鍵技術(shù)研究[D].泉州:華僑大學(xué),2007.

    [6] Oon-Ee Ng,Ganapathy V.A novel modular framework for stereo vision[C]∥IEEE/ASME International Conference on Advanced Intelligent Mechatronics,2009:857-862.

    Parallel Study of Image Preprocessing Based on CUDA

    ZHANZhengfeng,LIGe,ZHANGXuehe,YINXuyue

    (State Key Laboratory of Robotics and System,Harbin Institute of Technology,Harbin 150001,China)

    To speed up the execution speed of image preprocessing algorithm,the paper proposes preprocessing algorithm base on Compute Unified Device Architecture (CUDA) to achieve high-speed parallel processing.It analyzes the principle of image gray,Gaussian filtering and histogram equalization preprocessing methods,and does parallel analysis,and then puts CUDA parallel computing technology into the image preprocessing algorithm. Experimental results show that the image preprocessing algorithm based on CUDA takes full advantage of parallel processing capabilities of GPU,compared with CPU serial processing method,significantly faster,improve data processing capability.

    image preprocessing;CUDA;parallel processing

    2014-03-10

    機(jī)器人技術(shù)與系統(tǒng)國(guó)家重點(diǎn)實(shí)驗(yàn)室(哈爾濱工業(yè)大學(xué))自主研究課題(SKLRS201302C)

    TP301.6;TP391

    A

    1001-2257(2014)07-0064-04

    占正鋒(1990-),男,福建福安人,碩士研究生,研究方向?yàn)闄C(jī)器人視覺(jué)。

    猜你喜歡
    均衡化線程直方圖
    統(tǒng)計(jì)頻率分布直方圖的備考全攻略
    符合差分隱私的流數(shù)據(jù)統(tǒng)計(jì)直方圖發(fā)布
    用直方圖控制畫(huà)面影調(diào)
    淺談linux多線程協(xié)作
    制度變遷是資源均衡化的關(guān)鍵
    基于直方圖平移和互補(bǔ)嵌入的可逆水印方案
    直方圖均衡化技術(shù)在矢量等值填充圖中的算法及實(shí)現(xiàn)
    Linux線程實(shí)現(xiàn)技術(shù)研究
    一種改進(jìn)的直方圖均衡化方法
    么移動(dòng)中間件線程池并發(fā)機(jī)制優(yōu)化改進(jìn)
    久久这里只有精品19| 如何舔出高潮| 中文字幕精品免费在线观看视频| 亚洲综合精品二区| 欧美人与性动交α欧美软件| 久久国内精品自在自线图片| av不卡在线播放| 不卡av一区二区三区| 色婷婷久久久亚洲欧美| 亚洲国产精品成人久久小说| 在线免费观看不下载黄p国产| 激情视频va一区二区三区| 亚洲图色成人| av在线app专区| 另类亚洲欧美激情| 免费人妻精品一区二区三区视频| 久久ye,这里只有精品| 亚洲精品日本国产第一区| 国产精品蜜桃在线观看| 国产一区二区激情短视频 | 一本大道久久a久久精品| 老熟女久久久| 国产av码专区亚洲av| 亚洲欧美成人综合另类久久久| xxxhd国产人妻xxx| 天天躁夜夜躁狠狠躁躁| 捣出白浆h1v1| 日韩精品有码人妻一区| 一级毛片我不卡| 中文字幕亚洲精品专区| 午夜福利在线免费观看网站| 一本色道久久久久久精品综合| 国产免费一区二区三区四区乱码| 91成人精品电影| 大香蕉久久网| 菩萨蛮人人尽说江南好唐韦庄| 久久国产亚洲av麻豆专区| 如何舔出高潮| 99re6热这里在线精品视频| av在线观看视频网站免费| 夫妻午夜视频| 三级国产精品片| 久热这里只有精品99| 久久人妻熟女aⅴ| 国产成人免费观看mmmm| 99久国产av精品国产电影| 极品少妇高潮喷水抽搐| 亚洲欧美精品自产自拍| 高清av免费在线| 在线 av 中文字幕| 午夜影院在线不卡| 国产福利在线免费观看视频| 亚洲欧洲精品一区二区精品久久久 | 国产一区二区在线观看av| 男男h啪啪无遮挡| 午夜精品国产一区二区电影| 黄色一级大片看看| 亚洲一级一片aⅴ在线观看| 丰满少妇做爰视频| 欧美97在线视频| 国产免费福利视频在线观看| 国产片内射在线| 亚洲五月色婷婷综合| 少妇被粗大的猛进出69影院| 18在线观看网站| av一本久久久久| 久久人人爽人人片av| 蜜桃在线观看..| 国产极品天堂在线| 啦啦啦在线免费观看视频4| 在线亚洲精品国产二区图片欧美| 欧美日韩综合久久久久久| 中国三级夫妇交换| 亚洲欧美一区二区三区国产| 国产精品二区激情视频| 亚洲国产av新网站| 国产精品久久久久成人av| tube8黄色片| 纵有疾风起免费观看全集完整版| 七月丁香在线播放| 国产精品三级大全| 亚洲av电影在线观看一区二区三区| 亚洲成国产人片在线观看| 日本色播在线视频| 少妇的丰满在线观看| 日本猛色少妇xxxxx猛交久久| 日本爱情动作片www.在线观看| videossex国产| 成年人午夜在线观看视频| 午夜激情av网站| 国产无遮挡羞羞视频在线观看| 国产在线一区二区三区精| videos熟女内射| 18+在线观看网站| 十八禁网站网址无遮挡| 99国产综合亚洲精品| 亚洲av国产av综合av卡| 亚洲国产av影院在线观看| 激情五月婷婷亚洲| 精品少妇内射三级| 黄色视频在线播放观看不卡| 飞空精品影院首页| 男女无遮挡免费网站观看| 欧美日本中文国产一区发布| 纵有疾风起免费观看全集完整版| 色婷婷av一区二区三区视频| 我的亚洲天堂| 黑人巨大精品欧美一区二区蜜桃| 成人毛片60女人毛片免费| 黑人猛操日本美女一级片| 亚洲精品第二区| 免费在线观看完整版高清| 日本av免费视频播放| 亚洲,一卡二卡三卡| 久久精品国产鲁丝片午夜精品| 精品国产露脸久久av麻豆| 久久久久视频综合| 丰满饥渴人妻一区二区三| 不卡视频在线观看欧美| 成年女人毛片免费观看观看9 | 女人精品久久久久毛片| 一边摸一边做爽爽视频免费| 91精品三级在线观看| 国产欧美日韩综合在线一区二区| 夜夜骑夜夜射夜夜干| 国产精品香港三级国产av潘金莲 | 黄频高清免费视频| 成人18禁高潮啪啪吃奶动态图| 亚洲成人一二三区av| 人人妻人人澡人人爽人人夜夜| 日韩大片免费观看网站| 天堂俺去俺来也www色官网| 亚洲国产日韩一区二区| 亚洲av男天堂| 亚洲精品成人av观看孕妇| 国产探花极品一区二区| 亚洲精品乱久久久久久| 青春草国产在线视频| 日本黄色日本黄色录像| 菩萨蛮人人尽说江南好唐韦庄| 欧美国产精品va在线观看不卡| 午夜免费男女啪啪视频观看| 一区二区av电影网| 日韩 亚洲 欧美在线| 捣出白浆h1v1| 久久久国产一区二区| 建设人人有责人人尽责人人享有的| 日韩,欧美,国产一区二区三区| 精品国产一区二区久久| 日韩 亚洲 欧美在线| 亚洲精品美女久久久久99蜜臀 | 黄片无遮挡物在线观看| 亚洲欧美清纯卡通| 在线精品无人区一区二区三| 午夜激情久久久久久久| 亚洲精品国产av蜜桃| 香蕉丝袜av| 午夜久久久在线观看| 精品国产超薄肉色丝袜足j| www.av在线官网国产| 成人国语在线视频| 另类精品久久| 国产成人精品久久二区二区91 | 日韩欧美精品免费久久| 蜜桃在线观看..| 视频区图区小说| 在线 av 中文字幕| 看十八女毛片水多多多| 欧美另类一区| 91成人精品电影| 亚洲精品日韩在线中文字幕| 亚洲欧美一区二区三区久久| 日韩在线高清观看一区二区三区| 色吧在线观看| 国产一级毛片在线| 伊人亚洲综合成人网| 午夜免费鲁丝| 秋霞伦理黄片| 久久久精品国产亚洲av高清涩受| 亚洲三区欧美一区| 久久人妻熟女aⅴ| 中国国产av一级| 欧美成人午夜免费资源| 天天躁夜夜躁狠狠久久av| 青青草视频在线视频观看| 亚洲av在线观看美女高潮| 国产女主播在线喷水免费视频网站| 国产综合精华液| 国产乱人偷精品视频| 老鸭窝网址在线观看| 最近中文字幕高清免费大全6| 丁香六月天网| 美女主播在线视频| 侵犯人妻中文字幕一二三四区| 黄色一级大片看看| 搡老乐熟女国产| 国产在线一区二区三区精| 日韩av不卡免费在线播放| 亚洲精品av麻豆狂野| 国产免费又黄又爽又色| 久久这里只有精品19| 狂野欧美激情性bbbbbb| 日本-黄色视频高清免费观看| 丰满迷人的少妇在线观看| 女人高潮潮喷娇喘18禁视频| 亚洲色图 男人天堂 中文字幕| 中文字幕精品免费在线观看视频| 五月开心婷婷网| 高清av免费在线| 国产欧美日韩一区二区三区在线| 国产黄色免费在线视频| 亚洲精品日本国产第一区| 亚洲精品美女久久av网站| 亚洲综合色网址| 亚洲精品在线美女| 成人毛片60女人毛片免费| 国产av国产精品国产| 美女中出高潮动态图| av免费观看日本| 亚洲国产色片| 丰满乱子伦码专区| 国产乱人偷精品视频| 亚洲精品久久久久久婷婷小说| 欧美日韩国产mv在线观看视频| 国产精品国产av在线观看| 日韩不卡一区二区三区视频在线| 最近的中文字幕免费完整| 老司机影院毛片| 久久影院123| 丁香六月天网| 日韩不卡一区二区三区视频在线| 免费看av在线观看网站| 亚洲精品自拍成人| 中文乱码字字幕精品一区二区三区| 成年人免费黄色播放视频| 自拍欧美九色日韩亚洲蝌蚪91| 老汉色∧v一级毛片| 大话2 男鬼变身卡| 丰满少妇做爰视频| kizo精华| 欧美国产精品一级二级三级| 国产亚洲精品第一综合不卡| 午夜av观看不卡| 天天躁日日躁夜夜躁夜夜| 午夜精品国产一区二区电影| 欧美日本中文国产一区发布| 国产麻豆69| 少妇猛男粗大的猛烈进出视频| 18禁动态无遮挡网站| 亚洲av欧美aⅴ国产| 毛片一级片免费看久久久久| 欧美变态另类bdsm刘玥| 欧美精品国产亚洲| av在线app专区| 中文欧美无线码| 亚洲四区av| 女人久久www免费人成看片| 伦理电影免费视频| 国产成人精品一,二区| 欧美日韩一级在线毛片| 亚洲成人一二三区av| 你懂的网址亚洲精品在线观看| 女人精品久久久久毛片| 色播在线永久视频| 国产无遮挡羞羞视频在线观看| 蜜桃在线观看..| 大香蕉久久成人网| 欧美日韩视频高清一区二区三区二| 麻豆精品久久久久久蜜桃| a级片在线免费高清观看视频| 亚洲av日韩在线播放| 少妇人妻 视频| 亚洲色图综合在线观看| 一级黄片播放器| 80岁老熟妇乱子伦牲交| 免费高清在线观看视频在线观看| 国产成人av激情在线播放| 18禁观看日本| 久久久久久久久久人人人人人人| 18禁裸乳无遮挡动漫免费视频| 国产精品嫩草影院av在线观看| 国产av一区二区精品久久| 一区二区三区精品91| 国产免费视频播放在线视频| 女人高潮潮喷娇喘18禁视频| 亚洲av日韩在线播放| 国产视频首页在线观看| 如何舔出高潮| 2022亚洲国产成人精品| 不卡av一区二区三区| 国产成人精品在线电影| 久久韩国三级中文字幕| 免费大片黄手机在线观看| 精品一区在线观看国产| av视频免费观看在线观看| 中文字幕色久视频| 午夜福利视频在线观看免费| 亚洲综合色惰| 九九爱精品视频在线观看| 在线观看免费日韩欧美大片| 一级黄片播放器| 边亲边吃奶的免费视频| 女性被躁到高潮视频| 国产欧美亚洲国产| 国产精品亚洲av一区麻豆 | 好男人视频免费观看在线| 亚洲第一青青草原| 在线观看国产h片| 亚洲伊人色综图| 满18在线观看网站| 国产精品免费大片| 一二三四在线观看免费中文在| 日韩欧美一区视频在线观看| 国产黄频视频在线观看| 少妇熟女欧美另类| 汤姆久久久久久久影院中文字幕| 最近的中文字幕免费完整| 亚洲一码二码三码区别大吗| 久久久久网色| 人成视频在线观看免费观看| www日本在线高清视频| 久久久久久久久久人人人人人人| 99九九在线精品视频| 久久久久国产网址| 一二三四中文在线观看免费高清| 伦理电影大哥的女人| 久久青草综合色| a级片在线免费高清观看视频| 亚洲欧洲日产国产| 考比视频在线观看| 男女国产视频网站| 少妇的逼水好多| 国产成人精品婷婷| 男人添女人高潮全过程视频| 国产一区亚洲一区在线观看| 新久久久久国产一级毛片| 日本wwww免费看| 欧美 日韩 精品 国产| 国产黄频视频在线观看| 热re99久久精品国产66热6| 汤姆久久久久久久影院中文字幕| 日韩中文字幕欧美一区二区 | 叶爱在线成人免费视频播放| 99九九在线精品视频| 90打野战视频偷拍视频| 大片免费播放器 马上看| 精品酒店卫生间| 国产av国产精品国产| 国产探花极品一区二区| 国精品久久久久久国模美| 久久久久精品人妻al黑| 黄色毛片三级朝国网站| 90打野战视频偷拍视频| av卡一久久| 国产在线免费精品| 一区二区三区四区激情视频| 国产一区二区激情短视频 | 满18在线观看网站| 国产精品熟女久久久久浪| 香蕉丝袜av| 亚洲综合精品二区| 满18在线观看网站| 日韩 亚洲 欧美在线| 国产精品 国内视频| 777久久人妻少妇嫩草av网站| 亚洲国产精品一区二区三区在线| 曰老女人黄片| 天天操日日干夜夜撸| 亚洲国产色片| 男的添女的下面高潮视频| 欧美日韩av久久| 交换朋友夫妻互换小说| 亚洲精品成人av观看孕妇| 2022亚洲国产成人精品| 亚洲成人一二三区av| 午夜av观看不卡| 国产精品久久久久久久久免| 人人妻人人澡人人看| 久久精品国产亚洲av天美| 亚洲国产av影院在线观看| 亚洲精品一区蜜桃| 99久久中文字幕三级久久日本| 高清在线视频一区二区三区| 成年女人毛片免费观看观看9 | 人人妻人人澡人人看| 久久久久久人妻| 精品国产一区二区久久| 国产亚洲av片在线观看秒播厂| 日日撸夜夜添| 欧美在线黄色| 黑人猛操日本美女一级片| 亚洲人成网站在线观看播放| 成人漫画全彩无遮挡| 精品一品国产午夜福利视频| 欧美bdsm另类| 久久午夜福利片| 久热这里只有精品99| 成人国产麻豆网| 久久精品国产综合久久久| 亚洲精品久久成人aⅴ小说| 久久免费观看电影| 美女xxoo啪啪120秒动态图| 亚洲图色成人| 日韩av不卡免费在线播放| 国产免费视频播放在线视频| 久久久精品免费免费高清| 搡女人真爽免费视频火全软件| 日韩一区二区三区影片| 国产免费现黄频在线看| 七月丁香在线播放| 久久久精品区二区三区| 亚洲欧美精品自产自拍| 黄色怎么调成土黄色| 美女中出高潮动态图| 亚洲欧洲国产日韩| 色婷婷久久久亚洲欧美| 中文字幕人妻丝袜一区二区 | 亚洲综合色惰| 国产无遮挡羞羞视频在线观看| 成人毛片a级毛片在线播放| 91精品国产国语对白视频| 亚洲视频免费观看视频| 爱豆传媒免费全集在线观看| 香蕉精品网在线| 亚洲精品视频女| 日本欧美国产在线视频| 亚洲经典国产精华液单| 在线观看美女被高潮喷水网站| 午夜免费观看性视频| 亚洲一级一片aⅴ在线观看| 纯流量卡能插随身wifi吗| 亚洲av国产av综合av卡| 欧美日韩av久久| 免费女性裸体啪啪无遮挡网站| 国产精品久久久久久av不卡| 人人妻人人爽人人添夜夜欢视频| 看免费av毛片| 老司机影院毛片| 热99国产精品久久久久久7| 日韩一本色道免费dvd| 啦啦啦啦在线视频资源| 亚洲欧洲国产日韩| 国产xxxxx性猛交| 亚洲精品国产色婷婷电影| 在线精品无人区一区二区三| 99九九在线精品视频| 亚洲一码二码三码区别大吗| 丰满饥渴人妻一区二区三| 99香蕉大伊视频| 伊人久久国产一区二区| 日韩av免费高清视频| 亚洲国产精品999| 久久97久久精品| 人体艺术视频欧美日本| 97人妻天天添夜夜摸| 久久99精品国语久久久| 韩国精品一区二区三区| 十八禁网站网址无遮挡| 少妇猛男粗大的猛烈进出视频| 国产乱来视频区| 国产精品偷伦视频观看了| 最近的中文字幕免费完整| 边亲边吃奶的免费视频| 97人妻天天添夜夜摸| 日韩av在线免费看完整版不卡| 下体分泌物呈黄色| 夫妻性生交免费视频一级片| 精品久久久精品久久久| 日韩熟女老妇一区二区性免费视频| 热re99久久国产66热| 夫妻性生交免费视频一级片| 午夜老司机福利剧场| 久久人妻熟女aⅴ| 高清欧美精品videossex| 精品人妻熟女毛片av久久网站| 久久97久久精品| 久久精品人人爽人人爽视色| 欧美精品av麻豆av| 国产精品不卡视频一区二区| 观看美女的网站| 久久久久精品人妻al黑| 国产1区2区3区精品| 90打野战视频偷拍视频| 美国免费a级毛片| 精品国产乱码久久久久久男人| 丝袜美足系列| 国产一区二区激情短视频 | 我要看黄色一级片免费的| 国产有黄有色有爽视频| 少妇猛男粗大的猛烈进出视频| 国产在线免费精品| 丝袜美足系列| 一级毛片黄色毛片免费观看视频| 欧美国产精品va在线观看不卡| 精品国产乱码久久久久久男人| 咕卡用的链子| 制服丝袜香蕉在线| 人妻少妇偷人精品九色| 人成视频在线观看免费观看| 亚洲精品成人av观看孕妇| 国产一区二区三区av在线| 久久久久久久国产电影| 日韩制服骚丝袜av| 欧美精品高潮呻吟av久久| 在线观看三级黄色| 久久毛片免费看一区二区三区| 欧美日韩视频高清一区二区三区二| 在线精品无人区一区二区三| 中文字幕av电影在线播放| 色网站视频免费| 日韩免费高清中文字幕av| 叶爱在线成人免费视频播放| 咕卡用的链子| 永久网站在线| 免费黄色在线免费观看| 国产 一区精品| av线在线观看网站| 桃花免费在线播放| 久久狼人影院| 91久久精品国产一区二区三区| 99国产精品免费福利视频| 嫩草影院入口| 国产精品.久久久| 成人影院久久| 中文字幕人妻丝袜一区二区 | 我要看黄色一级片免费的| av.在线天堂| 亚洲av免费高清在线观看| 欧美最新免费一区二区三区| 色播在线永久视频| 亚洲成人av在线免费| 春色校园在线视频观看| 亚洲第一区二区三区不卡| 在线 av 中文字幕| 男女啪啪激烈高潮av片| 国产日韩欧美视频二区| 亚洲精品久久久久久婷婷小说| 黄网站色视频无遮挡免费观看| freevideosex欧美| 啦啦啦啦在线视频资源| av免费观看日本| 纵有疾风起免费观看全集完整版| 欧美国产精品va在线观看不卡| 国产免费福利视频在线观看| av不卡在线播放| 亚洲精品aⅴ在线观看| 国产黄色视频一区二区在线观看| 亚洲激情五月婷婷啪啪| 亚洲精品在线美女| 精品国产乱码久久久久久小说| 精品99又大又爽又粗少妇毛片| 日韩不卡一区二区三区视频在线| 免费黄频网站在线观看国产| 9色porny在线观看| 寂寞人妻少妇视频99o| 国产精品久久久久久精品古装| 成年女人毛片免费观看观看9 | 三上悠亚av全集在线观看| 国产男女内射视频| 亚洲经典国产精华液单| 麻豆乱淫一区二区| 一级毛片 在线播放| 国产毛片在线视频| 老司机影院成人| 婷婷色综合大香蕉| 午夜福利一区二区在线看| 亚洲欧美一区二区三区久久| 国产精品成人在线| 亚洲三级黄色毛片| 国产成人a∨麻豆精品| 1024视频免费在线观看| av在线app专区| 我的亚洲天堂| 纵有疾风起免费观看全集完整版| www.自偷自拍.com| av天堂久久9| 亚洲第一区二区三区不卡| 女人被躁到高潮嗷嗷叫费观| 欧美国产精品一级二级三级| 国产av精品麻豆| 蜜桃国产av成人99| 午夜激情久久久久久久| av有码第一页| 韩国av在线不卡| av免费在线看不卡| 精品人妻熟女毛片av久久网站| 欧美 亚洲 国产 日韩一| 在线观看免费日韩欧美大片| 波多野结衣av一区二区av| 久久99热这里只频精品6学生| 久久久久久久久久久久大奶| 久久精品国产亚洲av天美| 制服人妻中文乱码| 精品国产一区二区三区久久久樱花| 超碰97精品在线观看| 啦啦啦在线观看免费高清www| videosex国产| 麻豆乱淫一区二区| 亚洲综合色网址| 国产精品一区二区在线观看99| 性色av一级| 欧美日韩亚洲国产一区二区在线观看 | 人人妻人人添人人爽欧美一区卜| 国产成人精品无人区| 老熟女久久久| 午夜免费鲁丝| 男女边摸边吃奶| 欧美av亚洲av综合av国产av | 欧美 日韩 精品 国产| 女人精品久久久久毛片| h视频一区二区三区| 久久鲁丝午夜福利片| 中文字幕av电影在线播放| 日本免费在线观看一区| 欧美精品亚洲一区二区|